27 static int CeedElemRestrictionStridedNoTranspose_Sycl(sycl::queue &sycl_queue, const CeedElemRestri…  in CeedElemRestrictionStridedNoTranspose_Sycl()
35   sycl::range<1> kernel_range(num_elem * elem_size);  in CeedElemRestrictionStridedNoTranspose_Sycl()
37   std::vector<sycl::event> e;  in CeedElemRestrictionStridedNoTranspose_Sycl()
40   sycl_queue.parallel_for<CeedElemRestrSyclStridedNT>(kernel_range, e, [=](sycl::id<1> node) {  in CeedElemRestrictionStridedNoTranspose_Sycl()
54 static int CeedElemRestrictionOffsetNoTranspose_Sycl(sycl::queue &sycl_queue, const CeedElemRestric…  in CeedElemRestrictionOffsetNoTranspose_Sycl()
62   sycl::range<1> kernel_range(num_elem * elem_size);  in CeedElemRestrictionOffsetNoTranspose_Sycl()
64   std::vector<sycl::event> e;  in CeedElemRestrictionOffsetNoTranspose_Sycl()
67   sycl_queue.parallel_for<CeedElemRestrSyclOffsetNT>(kernel_range, e, [=](sycl::id<1> node) {  in CeedElemRestrictionOffsetNoTranspose_Sycl()
82 static int CeedElemRestrictionStridedTranspose_Sycl(sycl::queue &sycl_queue, const CeedElemRestrict…  in CeedElemRestrictionStridedTranspose_Sycl()
91   sycl::range<1> kernel_range(num_elem * elem_size);  in CeedElemRestrictionStridedTranspose_Sycl()
93   std::vector<sycl::event> e;  in CeedElemRestrictionStridedTranspose_Sycl()
96   sycl_queue.parallel_for<CeedElemRestrSyclStridedT>(kernel_range, e, [=](sycl::id<1> node) {  in CeedElemRestrictionStridedTranspose_Sycl()
110 static int CeedElemRestrictionOffsetTranspose_Sycl(sycl::queue &sycl_queue, const CeedElemRestricti…  in CeedElemRestrictionOffsetTranspose_Sycl()
121   sycl::range<1> kernel_range(num_nodes * num_comp);  in CeedElemRestrictionOffsetTranspose_Sycl()
123   std::vector<sycl::event> e;  in CeedElemRestrictionOffsetTranspose_Sycl()
126   sycl_queue.parallel_for<CeedElemRestrSyclOffsetT>(kernel_range, e, [=](sycl::id<1> id) {  in CeedElemRestrictionOffsetTranspose_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()
309   std::vector<sycl::event> e;  in CeedElemRestrictionOffset_Sycl()
314 …CeedCallSycl(ceed, impl->d_l_vec_indices = sycl::malloc_device<CeedInt>(num_nodes, data->sycl_devi…  in CeedElemRestrictionOffset_Sycl()
315 …sycl::event copy_lvec = data->sycl_queue.copy<CeedInt>(l_vec_indices, impl->d_l_vec_indices, num_n…  in CeedElemRestrictionOffset_Sycl()
317 …CeedCallSycl(ceed, impl->d_t_offsets = sycl::malloc_device<CeedInt>(size_offsets, data->sycl_devic…  in CeedElemRestrictionOffset_Sycl()
318 …sycl::event copy_offsets = data->sycl_queue.copy<CeedInt>(t_offsets, impl->d_t_offsets, size_offse…  in CeedElemRestrictionOffset_Sycl()
320 …CeedCallSycl(ceed, impl->d_t_indices = sycl::malloc_device<CeedInt>(size_indices, data->sycl_devic…  in CeedElemRestrictionOffset_Sycl()
321 …sycl::event copy_indices = data->sycl_queue.copy<CeedInt>(t_indices, impl->d_t_indices, size_indic…  in CeedElemRestrictionOffset_Sycl()
324   CeedCallSycl(ceed, sycl::event::wait_and_throw({copy_lvec, copy_offsets, copy_indices}));  in CeedElemRestrictionOffset_Sycl()
421 …CeedCallSycl(ceed, impl->d_offsets_owned = sycl::malloc_device<CeedInt>(size, data->sycl_device, d…  in CeedElemRestrictionCreate_Sycl()
424         sycl::event e          = data->sycl_queue.ext_oneapi_submit_barrier();  in CeedElemRestrictionCreate_Sycl()
425 …sycl::event copy_event = data->sycl_queue.copy<CeedInt>(impl->h_offsets, impl->d_offsets_owned, si…  in CeedElemRestrictionCreate_Sycl()
436 …CeedCallSycl(ceed, impl->d_offsets_owned = sycl::malloc_device<CeedInt>(size, data->sycl_device, d…  in CeedElemRestrictionCreate_Sycl()
439             sycl::event e          = data->sycl_queue.ext_oneapi_submit_barrier();  in CeedElemRestrictionCreate_Sycl()
440 …sycl::event copy_event = data->sycl_queue.copy<CeedInt>(offsets, impl->d_offsets_owned, size, {e});  in CeedElemRestrictionCreate_Sycl()
460         sycl::event e          = data->sycl_queue.ext_oneapi_submit_barrier();  in CeedElemRestrictionCreate_Sycl()
461 …sycl::event copy_event = data->sycl_queue.copy<CeedInt>(impl->d_offsets, impl->h_offsets_owned, el…  in CeedElemRestrictionCreate_Sycl()