39 static int CeedBasisApplyInterp_Sycl(sycl::queue &sycl_queue, const SyclModule_t &sycl_module, Ceed…  in CeedBasisApplyInterp_Sycl()  argument
45   const sycl::device &sycl_device         = sycl_queue.get_device();  in CeedBasisApplyInterp_Sycl()
54   if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()};  in CeedBasisApplyInterp_Sycl()
56   sycl_queue.submit([&](sycl::handler &cgh) {  in CeedBasisApplyInterp_Sycl()
142 static int CeedBasisApplyGrad_Sycl(sycl::queue &sycl_queue, const SyclModule_t &sycl_module, CeedIn…  in CeedBasisApplyGrad_Sycl()  argument
149   const sycl::device &sycl_device     = sycl_queue.get_device();  in CeedBasisApplyGrad_Sycl()
157   if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()};  in CeedBasisApplyGrad_Sycl()
159   sycl_queue.submit([&](sycl::handler &cgh) {  in CeedBasisApplyGrad_Sycl()
245 static int CeedBasisApplyWeight_Sycl(sycl::queue &sycl_queue, CeedInt num_elem, const CeedBasis_Syc…  in CeedBasisApplyWeight_Sycl()  argument
257   if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()};  in CeedBasisApplyWeight_Sycl()
259   sycl_queue.parallel_for<CeedBasisSyclWeight>(kernel_range, e, [=](sycl::item<3> work_item) {  in CeedBasisApplyWeight_Sycl()
294     if (!data->sycl_queue.is_in_order()) e = {data->sycl_queue.ext_oneapi_submit_barrier()};  in CeedBasisApply_Sycl()
295     data->sycl_queue.fill<CeedScalar>(d_v, 0, length, e);  in CeedBasisApply_Sycl()
302 …CeedCallBackend(CeedBasisApplyInterp_Sycl<true>(data->sycl_queue, *impl->sycl_module, num_elem, im…  in CeedBasisApply_Sycl()
304 …CeedCallBackend(CeedBasisApplyInterp_Sycl<false>(data->sycl_queue, *impl->sycl_module, num_elem, i…  in CeedBasisApply_Sycl()
309 …CeedCallBackend(CeedBasisApplyGrad_Sycl<true>(data->sycl_queue, *impl->sycl_module, num_elem, impl…  in CeedBasisApply_Sycl()
311 …CeedCallBackend(CeedBasisApplyGrad_Sycl<false>(data->sycl_queue, *impl->sycl_module, num_elem, imp…  in CeedBasisApply_Sycl()
316       CeedCallBackend(CeedBasisApplyWeight_Sycl(data->sycl_queue, num_elem, impl, d_v));  in CeedBasisApply_Sycl()
338 static int CeedBasisApplyNonTensorInterp_Sycl(sycl::queue &sycl_queue, CeedInt num_elem, CeedInt is…  in CeedBasisApplyNonTensorInterp_Sycl()  argument
357   if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()};  in CeedBasisApplyNonTensorInterp_Sycl()
359   sycl_queue.parallel_for<CeedBasisSyclInterpNT>(kernel_range, e, [=](sycl::id<2> indx) {  in CeedBasisApplyNonTensorInterp_Sycl()
379 static int CeedBasisApplyNonTensorGrad_Sycl(sycl::queue &sycl_queue, CeedInt num_elem, CeedInt is_t…  in CeedBasisApplyNonTensorGrad_Sycl()  argument
403   if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()};  in CeedBasisApplyNonTensorGrad_Sycl()
405   sycl_queue.parallel_for<CeedBasisSyclGradNT>(kernel_range, e, [=](sycl::id<2> indx) {  in CeedBasisApplyNonTensorGrad_Sycl()
435 static int CeedBasisApplyNonTensorWeight_Sycl(sycl::queue &sycl_queue, CeedInt num_elem, const Ceed…  in CeedBasisApplyNonTensorWeight_Sycl()  argument
443   if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()};  in CeedBasisApplyNonTensorWeight_Sycl()
445   sycl_queue.parallel_for<CeedBasisSyclWeightNT>(kernel_range, e, [=](sycl::id<2> indx) {  in CeedBasisApplyNonTensorWeight_Sycl()
479     sycl::event e = data->sycl_queue.ext_oneapi_submit_barrier();  in CeedBasisApplyNonTensor_Sycl()
480     data->sycl_queue.fill<CeedScalar>(d_v, 0, length, {e});  in CeedBasisApplyNonTensor_Sycl()
486 …CeedCallBackend(CeedBasisApplyNonTensorInterp_Sycl(data->sycl_queue, num_elem, is_transpose, impl,…  in CeedBasisApplyNonTensor_Sycl()
489 …CeedCallBackend(CeedBasisApplyNonTensorGrad_Sycl(data->sycl_queue, num_elem, is_transpose, impl, d…  in CeedBasisApplyNonTensor_Sycl()
493       CeedCallBackend(CeedBasisApplyNonTensorWeight_Sycl(data->sycl_queue, num_elem, impl, d_v));  in CeedBasisApplyNonTensor_Sycl()
524   CeedCallSycl(ceed, data->sycl_queue.wait_and_throw());  in CeedBasisDestroy_Sycl()
547   CeedCallSycl(ceed, data->sycl_queue.wait_and_throw());  in CeedBasisDestroyNonTensor_Sycl()
588   if (!data->sycl_queue.is_in_order()) e = {data->sycl_queue.ext_oneapi_submit_barrier()};  in CeedBasisCreateTensorH1_Sycl()
593 …sycl::event copy_weight = data->sycl_queue.copy<CeedScalar>(q_weight_1d, impl->d_q_weight_1d, Q_1d…  in CeedBasisCreateTensorH1_Sycl()
599 …sycl::event copy_interp = data->sycl_queue.copy<CeedScalar>(interp_1d, impl->d_interp_1d, interp_l…  in CeedBasisCreateTensorH1_Sycl()
603 …sycl::event copy_grad = data->sycl_queue.copy<CeedScalar>(grad_1d, impl->d_grad_1d, interp_length,…  in CeedBasisCreateTensorH1_Sycl()
651   if (!data->sycl_queue.is_in_order()) e = {data->sycl_queue.ext_oneapi_submit_barrier()};  in CeedBasisCreateH1_Sycl()
656 …sycl::event copy_weight = data->sycl_queue.copy<CeedScalar>(q_weight, impl->d_q_weight, num_qpts, …  in CeedBasisCreateH1_Sycl()
662 …sycl::event copy_interp = data->sycl_queue.copy<CeedScalar>(interp, impl->d_interp, interp_length,…  in CeedBasisCreateH1_Sycl()
667   sycl::event copy_grad = data->sycl_queue.copy<CeedScalar>(grad, impl->d_grad, grad_length, e);  in CeedBasisCreateH1_Sycl()