Lines Matching refs:sycl_queue
84 CeedCallSycl(ceed, sycl_data->sycl_queue.wait_and_throw()); in CeedOperatorDestroy_Sycl()
103 CeedCallSycl(ceed, sycl_data->sycl_queue.wait_and_throw()); in CeedOperatorDestroy_Sycl()
771 if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorAssembleDiagonalSetup_Sycl()
779 …sycl::event identity_copy = sycl_data->sycl_queue.copy<CeedScalar>(identity, diag->d_identity, i_l… in CeedOperatorAssembleDiagonalSetup_Sycl()
786 …sycl::event interp_in_copy = sycl_data->sycl_queue.copy<CeedScalar>(interp_in, diag->d_interp_in, … in CeedOperatorAssembleDiagonalSetup_Sycl()
791 …sycl::event interp_out_copy = sycl_data->sycl_queue.copy<CeedScalar>(interp_out, diag->d_interp_ou… 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()
802 …sycl::event grad_out_copy = sycl_data->sycl_queue.copy<CeedScalar>(grad_out, diag->d_grad_out, g_l… 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()
811 …sycl::event eval_mode_out_copy = sycl_data->sycl_queue.copy<CeedEvalMode>(eval_mode_out, diag->d_e… in CeedOperatorAssembleDiagonalSetup_Sycl()
832 static int CeedOperatorLinearDiagonal_Sycl(sycl::queue &sycl_queue, const bool is_point_block, cons… in CeedOperatorLinearDiagonal_Sycl() argument
851 if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorLinearDiagonal_Sycl()
853 sycl_queue.parallel_for<CeedOperatorSyclLinearDiagonal>(kernel_range, e, [=](sycl::id<1> idx) { in CeedOperatorLinearDiagonal_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()
1134 … if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorAssembleSingleSetup_Sycl()
1135 …sycl_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()
1141 …sycl_data->sycl_queue.copy<CeedScalar>(grad_in, &asmb->d_B_in[mat_start], dim * elem_size * num_qp… in CeedOperatorAssembleSingleSetup_Sycl()
1166 … if (!sycl_data->sycl_queue.is_in_order()) e = {sycl_data->sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorAssembleSingleSetup_Sycl()
1167 …sycl_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()
1173 …sycl_data->sycl_queue.copy<CeedScalar>(grad_out, &asmb->d_B_out[mat_start], dim * elem_size * num_… in CeedOperatorAssembleSingleSetup_Sycl()
1189 static int CeedOperatorLinearAssemble_Sycl(sycl::queue &sycl_queue, const CeedOperator_Sycl *impl, … in CeedOperatorLinearAssemble_Sycl() argument
1223 if (!sycl_queue.is_in_order()) e = {sycl_queue.ext_oneapi_submit_barrier()}; in CeedOperatorLinearAssemble_Sycl()
1224 sycl_queue.parallel_for<CeedOperatorSyclLinearAssemble>(kernel_range, e, [=](sycl::id<3> idx) { in CeedOperatorLinearAssemble_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()