Lines Matching refs:sycl_data

21   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
199 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedQFunctionContextSetDataDevice_Sycl()
203 if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedQFunctionContextSetDataDevice_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 …cl(ceed, impl->d_data_owned = sycl::malloc_device(ctx_size, sycl_data->sycl_device, sycl_data->syc… in CeedQFunctionContextSetDataDevice_Sycl()
220 sycl::event copy_event = sycl_data->sycl_queue.memcpy(impl->d_data, data, ctx_size, e); in CeedQFunctionContextSetDataDevice_Sycl()
350 Ceed_Sycl *sycl_data; in CeedQFunctionContextDestroy_Sycl() local
355 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedQFunctionContextDestroy_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()