Lines Matching refs: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()
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()
769 std::vector<sycl::event> e; in CeedOperatorAssembleDiagonalSetup_Sycl()
773 std::vector<sycl::event> copy_events; in CeedOperatorAssembleDiagonalSetup_Sycl()
778 …CeedCallSycl(ceed, diag->d_identity = sycl::malloc_device<CeedScalar>(i_len, sycl_data->sycl_devic… in CeedOperatorAssembleDiagonalSetup_Sycl()
779sycl::event identity_copy = sycl_data->sycl_queue.copy<CeedScalar>(identity, diag->d_identity, i_l… in CeedOperatorAssembleDiagonalSetup_Sycl()
785 …CeedCallSycl(ceed, diag->d_interp_in = sycl::malloc_device<CeedScalar>(i_len, sycl_data->sycl_devi… in CeedOperatorAssembleDiagonalSetup_Sycl()
786sycl::event interp_in_copy = sycl_data->sycl_queue.copy<CeedScalar>(interp_in, diag->d_interp_in, … in CeedOperatorAssembleDiagonalSetup_Sycl()
790 …CeedCallSycl(ceed, diag->d_interp_out = sycl::malloc_device<CeedScalar>(i_len, sycl_data->sycl_dev… in CeedOperatorAssembleDiagonalSetup_Sycl()
791sycl::event interp_out_copy = sycl_data->sycl_queue.copy<CeedScalar>(interp_out, diag->d_interp_ou… in CeedOperatorAssembleDiagonalSetup_Sycl()
796 …CeedCallSycl(ceed, diag->d_grad_in = sycl::malloc_device<CeedScalar>(g_len, sycl_data->sycl_device… in CeedOperatorAssembleDiagonalSetup_Sycl()
797sycl::event grad_in_copy = sycl_data->sycl_queue.copy<CeedScalar>(grad_in, diag->d_grad_in, g_len,… in CeedOperatorAssembleDiagonalSetup_Sycl()
801 …CeedCallSycl(ceed, diag->d_grad_out = sycl::malloc_device<CeedScalar>(g_len, sycl_data->sycl_devic… in CeedOperatorAssembleDiagonalSetup_Sycl()
802sycl::event grad_out_copy = sycl_data->sycl_queue.copy<CeedScalar>(grad_out, diag->d_grad_out, g_l… in CeedOperatorAssembleDiagonalSetup_Sycl()
806 …CeedCallSycl(ceed, diag->d_eval_mode_in = sycl::malloc_device<CeedEvalMode>(num_eval_mode_in, sycl… in CeedOperatorAssembleDiagonalSetup_Sycl()
807sycl::event eval_mode_in_copy = sycl_data->sycl_queue.copy<CeedEvalMode>(eval_mode_in, diag->d_eva… in CeedOperatorAssembleDiagonalSetup_Sycl()
810 …CeedCallSycl(ceed, diag->d_eval_mode_out = sycl::malloc_device<CeedEvalMode>(num_eval_mode_out, sy… in CeedOperatorAssembleDiagonalSetup_Sycl()
811sycl::event eval_mode_out_copy = sycl_data->sycl_queue.copy<CeedEvalMode>(eval_mode_out, diag->d_e… in CeedOperatorAssembleDiagonalSetup_Sycl()
819 CeedCallSycl(ceed, sycl::event::wait_and_throw(copy_events)); in CeedOperatorAssembleDiagonalSetup_Sycl()
832 static int CeedOperatorLinearDiagonal_Sycl(sycl::queue &sycl_queue, const bool is_point_block, cons… in CeedOperatorLinearDiagonal_Sycl()
847 sycl::range<1> kernel_range(num_elem * num_nodes); in CeedOperatorLinearDiagonal_Sycl()
849 std::vector<sycl::event> e; in CeedOperatorLinearDiagonal_Sycl()
853 sycl_queue.parallel_for<CeedOperatorSyclLinearDiagonal>(kernel_range, e, [=](sycl::id<1> idx) { in CeedOperatorLinearDiagonal_Sycl()
1127 …CeedCallSycl(ceed, asmb->d_B_in = sycl::malloc_device<CeedScalar>(size_B_in, sycl_data->sycl_devic… in CeedOperatorAssembleSingleSetup_Sycl()
1132 std::vector<sycl::event> e; in CeedOperatorAssembleSingleSetup_Sycl()
1138 std::vector<sycl::event> e; in CeedOperatorAssembleSingleSetup_Sycl()
1159 …CeedCallSycl(ceed, asmb->d_B_out = sycl::malloc_device<CeedScalar>(size_B_out, sycl_data->sycl_dev… in CeedOperatorAssembleSingleSetup_Sycl()
1164 std::vector<sycl::event> e; in CeedOperatorAssembleSingleSetup_Sycl()
1170 std::vector<sycl::event> e; in CeedOperatorAssembleSingleSetup_Sycl()
1189 static int CeedOperatorLinearAssemble_Sycl(sycl::queue &sycl_queue, const CeedOperator_Sycl *impl, … in CeedOperatorLinearAssemble_Sycl()
1219 sycl::range<3> kernel_range(num_elem, block_size_y, block_size_x); in CeedOperatorLinearAssemble_Sycl()
1221 std::vector<sycl::event> e; in CeedOperatorLinearAssemble_Sycl()
1224 sycl_queue.parallel_for<CeedOperatorSyclLinearAssemble>(kernel_range, e, [=](sycl::id<3> idx) { in CeedOperatorLinearAssemble_Sycl()