Home
last modified time | relevance | path

Searched refs:sycl_context (Results 1 – 11 of 11) sorted by relevance

/libCEED/backends/sycl/
H A Dceed-sycl-common.sycl.cpp67 sycl::context sycl_context{sycl_device.get_platform().get_devices()}; in CeedInit_Sycl() local
68 …sycl::queue sycl_queue{sycl_context, sycl_device, sycl_async_handler, sycl::property::queue::in_… in CeedInit_Sycl()
73 data->sycl_context = sycl_context; in CeedInit_Sycl()
104 data->sycl_context = q->get_context(); in CeedSetStream_Sycl()
H A Dceed-sycl-compile.sycl.cpp86 static int CeedLoadModule_Sycl(Ceed ceed, const sycl::context &sycl_context, const sycl::device &sy… in CeedLoadModule_Sycl() argument
88 auto lz_context = sycl::get_native<sycl::backend::ext_oneapi_level_zero>(sycl_context); in CeedLoadModule_Sycl()
117 {lz_module, sycl::ext::oneapi::level_zero::ownership::transfer}, sycl_context)); in CeedLoadModule_Sycl()
134 …CeedCallBackend(CeedLoadModule_Sycl(ceed, data->sycl_context, data->sycl_device, il_binary, sycl_m… in CeedBuildModule_Sycl()
162 … data->sycl_context)); in CeedGetKernel_Sycl()
H A Dceed-sycl-common.hpp35 sycl::context sycl_context; member
/libCEED/backends/sycl-shared/
H A Dceed-sycl-shared-basis.sycl.cpp147 if (impl->d_q_weight_1d) CeedCallSycl(ceed, sycl::free(impl->d_q_weight_1d, data->sycl_context)); in CeedBasisDestroy_Sycl_shared()
148 CeedCallSycl(ceed, sycl::free(impl->d_interp_1d, data->sycl_context)); in CeedBasisDestroy_Sycl_shared()
149 CeedCallSycl(ceed, sycl::free(impl->d_grad_1d, data->sycl_context)); in CeedBasisDestroy_Sycl_shared()
150 CeedCallSycl(ceed, sycl::free(impl->d_collo_grad_1d, data->sycl_context)); in CeedBasisDestroy_Sycl_shared()
205 …mpl->d_q_weight_1d = sycl::malloc_device<CeedScalar>(Q_1d, data->sycl_device, data->sycl_context)); in CeedBasisCreateTensorH1_Sycl_shared()
211 …interp_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_device, data->sycl_context)); in CeedBasisCreateTensorH1_Sycl_shared()
215 …d_grad_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_device, data->sycl_context)); in CeedBasisCreateTensorH1_Sycl_shared()
231 …lo_grad_1d = sycl::malloc_device<CeedScalar>(cgrad_length, data->sycl_device, data->sycl_context)); in CeedBasisCreateTensorH1_Sycl_shared()
/libCEED/backends/sycl-gen/
H A Dceed-sycl-gen-operator.sycl.cpp220 …>indices = sycl::malloc_device<FieldsInt_Sycl>(1, sycl_data->sycl_device, sycl_data->sycl_context); in CeedOperatorCreate_Sycl_gen()
221 impl->fields = sycl::malloc_host<Fields_Sycl>(1, sycl_data->sycl_context); in CeedOperatorCreate_Sycl_gen()
222 …pl->B = sycl::malloc_device<Fields_Sycl>(1, sycl_data->sycl_device, sycl_data->sycl_context); in CeedOperatorCreate_Sycl_gen()
223 …pl->G = sycl::malloc_device<Fields_Sycl>(1, sycl_data->sycl_device, sycl_data->sycl_context); in CeedOperatorCreate_Sycl_gen()
224 …mpl->W = sycl::malloc_device<CeedScalar>(1, sycl_data->sycl_device, sycl_data->sycl_context); in CeedOperatorCreate_Sycl_gen()
H A Dceed-sycl-gen-qfunction.sycl.cpp37 CeedCallSycl(ceed, sycl::free(impl->d_c, data->sycl_context)); in CeedQFunctionDestroy_Sycl_gen()
/libCEED/backends/sycl-ref/
H A Dceed-sycl-restriction.sycl.cpp237 CeedCallSycl(ceed, sycl::free(impl->d_offsets_owned, data->sycl_context)); in CeedElemRestrictionDestroy_Sycl()
238 CeedCallSycl(ceed, sycl::free(impl->d_t_offsets, data->sycl_context)); in CeedElemRestrictionDestroy_Sycl()
239 CeedCallSycl(ceed, sycl::free(impl->d_t_indices, data->sycl_context)); in CeedElemRestrictionDestroy_Sycl()
240 CeedCallSycl(ceed, sycl::free(impl->d_l_vec_indices, data->sycl_context)); in CeedElemRestrictionDestroy_Sycl()
314 …>d_l_vec_indices = sycl::malloc_device<CeedInt>(num_nodes, data->sycl_device, data->sycl_context)); in CeedElemRestrictionOffset_Sycl()
317 …->d_t_offsets = sycl::malloc_device<CeedInt>(size_offsets, data->sycl_device, data->sycl_context)); in CeedElemRestrictionOffset_Sycl()
320 …->d_t_indices = sycl::malloc_device<CeedInt>(size_indices, data->sycl_device, data->sycl_context)); in CeedElemRestrictionOffset_Sycl()
421 …impl->d_offsets_owned = sycl::malloc_device<CeedInt>(size, data->sycl_device, data->sycl_context)); in CeedElemRestrictionCreate_Sycl()
436 …impl->d_offsets_owned = sycl::malloc_device<CeedInt>(size, data->sycl_device, data->sycl_context)); in CeedElemRestrictionCreate_Sycl()
H A Dceed-sycl-ref-basis.sycl.cpp526 if (impl->d_q_weight_1d) CeedCallSycl(ceed, sycl::free(impl->d_q_weight_1d, data->sycl_context)); in CeedBasisDestroy_Sycl()
527 CeedCallSycl(ceed, sycl::free(impl->d_interp_1d, data->sycl_context)); in CeedBasisDestroy_Sycl()
528 CeedCallSycl(ceed, sycl::free(impl->d_grad_1d, data->sycl_context)); in CeedBasisDestroy_Sycl()
549 if (impl->d_q_weight) CeedCallSycl(ceed, sycl::free(impl->d_q_weight, data->sycl_context)); in CeedBasisDestroyNonTensor_Sycl()
550 CeedCallSycl(ceed, sycl::free(impl->d_interp, data->sycl_context)); in CeedBasisDestroyNonTensor_Sycl()
551 CeedCallSycl(ceed, sycl::free(impl->d_grad, data->sycl_context)); in CeedBasisDestroyNonTensor_Sycl()
592 …mpl->d_q_weight_1d = sycl::malloc_device<CeedScalar>(Q_1d, data->sycl_device, data->sycl_context)); in CeedBasisCreateTensorH1_Sycl()
598 …interp_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_device, data->sycl_context)); in CeedBasisCreateTensorH1_Sycl()
602 …d_grad_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_device, data->sycl_context)); in CeedBasisCreateTensorH1_Sycl()
611 … input_bundle = sycl::get_kernel_bundle<sycl::bundle_state::input>(data->sycl_context, kernel_ids); in CeedBasisCreateTensorH1_Sycl()
[all …]
H A Dceed-sycl-ref-operator.sycl.cpp85 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()
104 CeedCallSycl(ceed, sycl::free(impl->asmb->d_B_in, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
105 CeedCallSycl(ceed, sycl::free(impl->asmb->d_B_out, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
778 …dentity = sycl::malloc_device<CeedScalar>(i_len, sycl_data->sycl_device, sycl_data->sycl_context)); in CeedOperatorAssembleDiagonalSetup_Sycl()
[all …]
H A Dceed-sycl-ref-qfunctioncontext.sycl.cpp37 …pl->d_data_owned = sycl::malloc_device(ctx_size, sycl_data->sycl_device, sycl_data->sycl_context)); in CeedQFunctionContextSyncH2D_Sycl()
208 CeedCallSycl(ceed, sycl::free(impl->d_data_owned, sycl_data->sycl_context)); in CeedQFunctionContextSetDataDevice_Sycl()
217 …pl->d_data_owned = sycl::malloc_device(ctx_size, sycl_data->sycl_device, sycl_data->sycl_context)); in CeedQFunctionContextSetDataDevice_Sycl()
359 CeedCallSycl(ceed, sycl::free(impl->d_data_owned, sycl_data->sycl_context)); in CeedQFunctionContextDestroy_Sycl()
H A Dceed-sycl-vector.sycl.cpp58 …l->d_array_owned = sycl::malloc_device<CeedScalar>(length, data->sycl_device, data->sycl_context)); in CeedVectorSyncH2D_Sycl()
220 …l->d_array_owned = sycl::malloc_device<CeedScalar>(length, data->sycl_device, data->sycl_context)); in CeedVectorSetArrayDevice_Sycl()
233 CeedCallSycl(ceed, sycl::free(impl->d_array_owned, data->sycl_context)); in CeedVectorSetArrayDevice_Sycl()
243 CeedCallSycl(ceed, sycl::free(impl->d_array_owned, data->sycl_context)); in CeedVectorSetArrayDevice_Sycl()
691 CeedCallSycl(ceed, sycl::free(impl->d_array_owned, data->sycl_context)); in CeedVectorDestroy_Sycl()
692 CeedCallSycl(ceed, sycl::free(impl->reduction_norm, data->sycl_context)); in CeedVectorDestroy_Sycl()
711 CeedCallSycl(ceed, impl->reduction_norm = sycl::malloc_host<CeedScalar>(1, data->sycl_context)); in CeedVectorCreate_Sycl()