Lines Matching refs:sycl_data

50   Ceed_Sycl         *sycl_data;  in CeedOperatorDestroy_Sycl()  local
55 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedOperatorDestroy_Sycl()
84 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()
105 CeedCallSycl(ceed, sycl::free(impl->asmb->d_B_out, sycl_data->sycl_context)); in CeedOperatorDestroy_Sycl()
636 Ceed_Sycl *sycl_data; in CeedOperatorAssembleDiagonalSetup_Sycl() local
738 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedOperatorAssembleDiagonalSetup_Sycl()
771 if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorAssembleDiagonalSetup_Sycl()
778 …, diag->d_identity = sycl::malloc_device<CeedScalar>(i_len, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
779 …sycl::event identity_copy = sycl_data->sycl_queue.copy<CeedScalar>(identity, diag->d_identity, i_l… in CeedOperatorAssembleDiagonalSetup_Sycl()
785 … diag->d_interp_in = sycl::malloc_device<CeedScalar>(i_len, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
786 …sycl::event interp_in_copy = sycl_data->sycl_queue.copy<CeedScalar>(interp_in, diag->d_interp_in, … in CeedOperatorAssembleDiagonalSetup_Sycl()
790 …diag->d_interp_out = sycl::malloc_device<CeedScalar>(i_len, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
791 …sycl::event interp_out_copy = sycl_data->sycl_queue.copy<CeedScalar>(interp_out, diag->d_interp_ou… in CeedOperatorAssembleDiagonalSetup_Sycl()
796 …d, diag->d_grad_in = sycl::malloc_device<CeedScalar>(g_len, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
797 …sycl::event grad_in_copy = sycl_data->sycl_queue.copy<CeedScalar>(grad_in, diag->d_grad_in, g_len,… in CeedOperatorAssembleDiagonalSetup_Sycl()
801 …, diag->d_grad_out = sycl::malloc_device<CeedScalar>(g_len, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
802 …sycl::event grad_out_copy = sycl_data->sycl_queue.copy<CeedScalar>(grad_out, diag->d_grad_out, g_l… in CeedOperatorAssembleDiagonalSetup_Sycl()
806 …de_in = sycl::malloc_device<CeedEvalMode>(num_eval_mode_in, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
807 …sycl::event eval_mode_in_copy = sycl_data->sycl_queue.copy<CeedEvalMode>(eval_mode_in, diag->d_eva… in CeedOperatorAssembleDiagonalSetup_Sycl()
810 …_out = sycl::malloc_device<CeedEvalMode>(num_eval_mode_out, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
811 …sycl::event eval_mode_out_copy = sycl_data->sycl_queue.copy<CeedEvalMode>(eval_mode_out, diag->d_e… in CeedOperatorAssembleDiagonalSetup_Sycl()
914 Ceed_Sycl *sycl_data; in CeedOperatorAssembleDiagonalCore_Sycl() local
922 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedOperatorAssembleDiagonalCore_Sycl()
964 …CeedCallBackend(CeedOperatorLinearDiagonal_Sycl(sycl_data->sycl_queue, is_point_block, num_elem, d… in CeedOperatorAssembleDiagonalCore_Sycl()
967 sycl_data->sycl_queue.wait_and_throw(); in CeedOperatorAssembleDiagonalCore_Sycl()
1107 Ceed_Sycl *sycl_data; in CeedOperatorAssembleSingleSetup_Sycl() local
1108 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedOperatorAssembleSingleSetup_Sycl()
1127 …, asmb->d_B_in = sycl::malloc_device<CeedScalar>(size_B_in, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleSingleSetup_Sycl()
1134 … if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorAssembleSingleSetup_Sycl()
1135sycl_data->sycl_queue.copy<CeedScalar>(interp_in, &asmb->d_B_in[mat_start], elem_size * num_qpts, … in CeedOperatorAssembleSingleSetup_Sycl()
1140 … if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorAssembleSingleSetup_Sycl()
1141sycl_data->sycl_queue.copy<CeedScalar>(grad_in, &asmb->d_B_in[mat_start], dim * elem_size * num_qp… in CeedOperatorAssembleSingleSetup_Sycl()
1159 …asmb->d_B_out = sycl::malloc_device<CeedScalar>(size_B_out, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleSingleSetup_Sycl()
1166 … if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorAssembleSingleSetup_Sycl()
1167sycl_data->sycl_queue.copy<CeedScalar>(interp_out, &asmb->d_B_out[mat_start], elem_size * num_qpts… in CeedOperatorAssembleSingleSetup_Sycl()
1172 … if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorAssembleSingleSetup_Sycl()
1173sycl_data->sycl_queue.copy<CeedScalar>(grad_out, &asmb->d_B_out[mat_start], dim * elem_size * num_… in CeedOperatorAssembleSingleSetup_Sycl()
1342 Ceed_Sycl *sycl_data; in CeedOperatorAssembleSingle_Sycl() local
1350 CeedCallBackend(CeedGetData(ceed, &sycl_data)); in CeedOperatorAssembleSingle_Sycl()
1368 …CeedCallBackend(CeedOperatorLinearAssemble_Sycl(sycl_data->sycl_queue, impl, qf_array, values_arra… in CeedOperatorAssembleSingle_Sycl()
1372 sycl_data->sycl_queue.wait_and_throw(); in CeedOperatorAssembleSingle_Sycl()