Home
last modified time | relevance | path

Searched refs:sycl_data (Results 1 – 4 of 4) sorted by relevance

/libCEED/backends/sycl-ref/
H A Dceed-sycl-ref-qfunctioncontext.sycl.cpp21 Ceed_Sycl *sycl_data; in CeedQFunctionContextSyncH2D_Sycl() local
27 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedQFunctionContextSyncH2D_Sycl()
37 …cl(ceed, impl->d_data_owned = sycl::malloc_device(ctx_size, sycl_data->sycl_device, sycl_data->syc… in CeedQFunctionContextSyncH2D_Sycl()
42 if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedQFunctionContextSyncH2D_Sycl()
43 sycl::event copy_event = sycl_data->sycl_queue.memcpy(impl->d_data, impl->h_data, ctx_size, e); in CeedQFunctionContextSyncH2D_Sycl()
54 Ceed_Sycl *sycl_data; in CeedQFunctionContextSyncD2H_Sycl() local
60 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedQFunctionContextSyncD2H_Sycl()
76 if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedQFunctionContextSyncD2H_Sycl()
77 sycl::event copy_event = sycl_data->sycl_queue.memcpy(impl->h_data, impl->d_data, ctx_size, e); in CeedQFunctionContextSyncD2H_Sycl()
194 Ceed_Sycl *sycl_data; in CeedQFunctionContextSetDataDevice_Sycl() local
[all …]
H A Dceed-sycl-ref-operator.sycl.cpp50 Ceed_Sycl *sycl_data; in CeedOperatorDestroy_Sycl() local
55 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedOperatorDestroy_Sycl()
84 CeedCallSycl(ceed, sycl_data->sycl_queue.wait_and_throw()); in CeedOperatorDestroy_Sycl()
85 CeedCallSycl(ceed, sycl::free(impl->diag->d_eval_mode_in, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
86 CeedCallSycl(ceed, sycl::free(impl->diag->d_eval_mode_out, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
87 CeedCallSycl(ceed, sycl::free(impl->diag->d_identity, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
88 CeedCallSycl(ceed, sycl::free(impl->diag->d_interp_in, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
89 CeedCallSycl(ceed, sycl::free(impl->diag->d_interp_out, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
90 CeedCallSycl(ceed, sycl::free(impl->diag->d_grad_in, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
91 CeedCallSycl(ceed, sycl::free(impl->diag->d_grad_out, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
[all …]
/libCEED/backends/sycl-gen/
H A Dceed-sycl-gen-operator.sycl.cpp211 Ceed_Sycl *sycl_data; in CeedOperatorCreate_Sycl_gen() local
215 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedOperatorCreate_Sycl_gen()
220 …impl->indices = sycl::malloc_device<FieldsInt_Sycl>(1, sycl_data->sycl_device, sycl_data->sycl_con… in CeedOperatorCreate_Sycl_gen()
221 impl->fields = sycl::malloc_host<Fields_Sycl>(1, sycl_data->sycl_context); in CeedOperatorCreate_Sycl_gen()
222 …impl->B = sycl::malloc_device<Fields_Sycl>(1, sycl_data->sycl_device, sycl_data->sycl_contex… in CeedOperatorCreate_Sycl_gen()
223 …impl->G = sycl::malloc_device<Fields_Sycl>(1, sycl_data->sycl_device, sycl_data->sycl_contex… in CeedOperatorCreate_Sycl_gen()
224 …impl->W = sycl::malloc_device<CeedScalar>(1, sycl_data->sycl_device, sycl_data->sycl_context… in CeedOperatorCreate_Sycl_gen()
H A Dceed-sycl-gen-operator-build.sycl.cpp63 Ceed_Sycl *sycl_data; in CeedOperatorBuildKernel_Sycl_gen() local
84 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedOperatorBuildKernel_Sycl_gen()
227 …std::vector allowed_sg_sizes = sycl_data->sycl_device.get_info<sycl::info::device::sub_group_size… in CeedOperatorBuildKernel_Sycl_gen()
760 if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorBuildKernel_Sycl_gen()
762 sycl::event copy_B = sycl_data->sycl_queue.copy<Fields_Sycl>(&h_B, impl->B, 1, e); in CeedOperatorBuildKernel_Sycl_gen()
763 sycl::event copy_G = sycl_data->sycl_queue.copy<Fields_Sycl>(&h_G, impl->G, 1, e); in CeedOperatorBuildKernel_Sycl_gen()
764 …sycl::event copy_indices = sycl_data->sycl_queue.copy<FieldsInt_Sycl>(&h_indices, impl->indices, 1… in CeedOperatorBuildKernel_Sycl_gen()