Home
last modified time | relevance | path

Searched refs:CeedCallSycl (Results 1 – 10 of 10) sorted by relevance

/libCEED/backends/sycl-shared/
H A Dceed-sycl-shared-basis.sycl.cpp146 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedBasisDestroy_Sycl_shared()
147 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 …CeedCallSycl(ceed, impl->d_q_weight_1d = sycl::malloc_device<CeedScalar>(Q_1d, data->sycl_device, … in CeedBasisCreateTensorH1_Sycl_shared()
211 …CeedCallSycl(ceed, impl->d_interp_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_d… in CeedBasisCreateTensorH1_Sycl_shared()
215 …CeedCallSycl(ceed, impl->d_grad_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_dev… in CeedBasisCreateTensorH1_Sycl_shared()
219 CeedCallSycl(ceed, sycl::event::wait_and_throw(copy_events)); in CeedBasisCreateTensorH1_Sycl_shared()
231 …CeedCallSycl(ceed, impl->d_collo_grad_1d = sycl::malloc_device<CeedScalar>(cgrad_length, data->syc… in CeedBasisCreateTensorH1_Sycl_shared()
[all …]
/libCEED/backends/sycl-ref/
H A Dceed-sycl-restriction.sycl.cpp191 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedElemRestrictionApply_Sycl()
234 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedElemRestrictionDestroy_Sycl()
237 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 …CeedCallSycl(ceed, impl->d_l_vec_indices = sycl::malloc_device<CeedInt>(num_nodes, data->sycl_devi… in CeedElemRestrictionOffset_Sycl()
317 …CeedCallSycl(ceed, impl->d_t_offsets = sycl::malloc_device<CeedInt>(size_offsets, data->sycl_devic… in CeedElemRestrictionOffset_Sycl()
320 …CeedCallSycl(ceed, impl->d_t_indices = sycl::malloc_device<CeedInt>(size_indices, data->sycl_devic… in CeedElemRestrictionOffset_Sycl()
324 CeedCallSycl(ceed, sycl::event::wait_and_throw({copy_lvec, copy_offsets, copy_indices})); in CeedElemRestrictionOffset_Sycl()
[all …]
H A Dceed-sycl-ref-qfunctioncontext.sycl.cpp37 …CeedCallSycl(ceed, impl->d_data_owned = sycl::malloc_device(ctx_size, sycl_data->sycl_device, sycl… in CeedQFunctionContextSyncH2D_Sycl()
44 CeedCallSycl(ceed, copy_event.wait_and_throw()); in CeedQFunctionContextSyncH2D_Sycl()
78 CeedCallSycl(ceed, copy_event.wait_and_throw()); in CeedQFunctionContextSyncD2H_Sycl()
207 CeedCallSycl(ceed, sycl_data->sycl_queue.wait_and_throw()); in CeedQFunctionContextSetDataDevice_Sycl()
208 CeedCallSycl(ceed, sycl::free(impl->d_data_owned, sycl_data->sycl_context)); in CeedQFunctionContextSetDataDevice_Sycl()
217 …CeedCallSycl(ceed, impl->d_data_owned = sycl::malloc_device(ctx_size, sycl_data->sycl_device, sycl… in CeedQFunctionContextSetDataDevice_Sycl()
221 CeedCallSycl(ceed, copy_event.wait_and_throw()); in CeedQFunctionContextSetDataDevice_Sycl()
358 CeedCallSycl(ceed, sycl_data->sycl_queue.wait_and_throw()); in CeedQFunctionContextDestroy_Sycl()
359 CeedCallSycl(ceed, sycl::free(impl->d_data_owned, sycl_data->sycl_context)); in CeedQFunctionContextDestroy_Sycl()
H A Dceed-sycl-ref-basis.sycl.cpp524 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedBasisDestroy_Sycl()
526 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()
547 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedBasisDestroyNonTensor_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 …CeedCallSycl(ceed, impl->d_q_weight_1d = sycl::malloc_device<CeedScalar>(Q_1d, data->sycl_device, … in CeedBasisCreateTensorH1_Sycl()
598 …CeedCallSycl(ceed, impl->d_interp_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_d… in CeedBasisCreateTensorH1_Sycl()
[all …]
H A Dceed-sycl-vector.sycl.cpp58 …CeedCallSycl(ceed, impl->d_array_owned = sycl::malloc_device<CeedScalar>(length, data->sycl_device… in CeedVectorSyncH2D_Sycl()
66 …CeedCallSycl(ceed, data->sycl_queue.copy<CeedScalar>(impl->h_array, impl->d_array, length, e).wait… in CeedVectorSyncH2D_Sycl()
100 …CeedCallSycl(ceed, data->sycl_queue.copy<CeedScalar>(impl->d_array, impl->h_array, length, e).wait… in CeedVectorSyncD2H_Sycl()
220 …CeedCallSycl(ceed, impl->d_array_owned = sycl::malloc_device<CeedScalar>(length, data->sycl_device… in CeedVectorSetArrayDevice_Sycl()
224 …CeedCallSycl(ceed, data->sycl_queue.copy<CeedScalar>(array, impl->d_array_owned, length, e).wait_a… in CeedVectorSetArrayDevice_Sycl()
232 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedVectorSetArrayDevice_Sycl()
233 CeedCallSycl(ceed, sycl::free(impl->d_array_owned, data->sycl_context)); in CeedVectorSetArrayDevice_Sycl()
242 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedVectorSetArrayDevice_Sycl()
243 CeedCallSycl(ceed, sycl::free(impl->d_array_owned, data->sycl_context)); in CeedVectorSetArrayDevice_Sycl()
690 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedVectorDestroy_Sycl()
[all …]
H A Dceed-sycl-ref-operator.sycl.cpp84 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()
103 CeedCallSycl(ceed, sycl_data->sycl_queue.wait_and_throw()); in CeedOperatorDestroy_Sycl()
104 CeedCallSycl(ceed, sycl::free(impl->asmb->d_B_in, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
[all …]
/libCEED/backends/sycl-gen/
H A Dceed-sycl-gen-qfunction.sycl.cpp36 CeedCallSycl(ceed, data->sycl_queue.wait_and_throw()); in CeedQFunctionDestroy_Sycl_gen()
37 CeedCallSycl(ceed, sycl::free(impl->d_c, data->sycl_context)); in CeedQFunctionDestroy_Sycl_gen()
H A Dceed-sycl-gen-operator.sycl.cpp149 CeedCallSycl(ceed, ceed_Sycl->sycl_queue.submit([&](sycl::handler &cgh) { in CeedOperatorApplyAdd_Sycl_gen()
154 CeedCallSycl(ceed, ceed_Sycl->sycl_queue.wait_and_throw()); in CeedOperatorApplyAdd_Sycl_gen()
H A Dceed-sycl-gen-operator-build.sycl.cpp766 CeedCallSycl(ceed, sycl::event::wait_and_throw({copy_B, copy_G, copy_indices})); in CeedOperatorBuildKernel_Sycl_gen()
/libCEED/backends/sycl/
H A Dceed-sycl-common.hpp15 #define CeedCallSycl(ceed, ...) \ macro