Lines Matching refs:sycl

60       sycl::range<3>    local_range(lrange[2], lrange[1], lrange[0]);  in CeedBasisApplyTensor_Sycl_shared()
61 sycl::range<3> global_range(group_count * lrange[2], lrange[1], lrange[0]); in CeedBasisApplyTensor_Sycl_shared()
62 sycl::nd_range<3> kernel_range(global_range, local_range); in CeedBasisApplyTensor_Sycl_shared()
64sycl::kernel *interp_kernel = (t_mode == CEED_TRANSPOSE) ? impl->interp_transpose_kernel : impl->i… in CeedBasisApplyTensor_Sycl_shared()
66 std::vector<sycl::event> e; in CeedBasisApplyTensor_Sycl_shared()
69 ceed_Sycl->sycl_queue.submit([&](sycl::handler &cgh) { in CeedBasisApplyTensor_Sycl_shared()
81 sycl::range<3> local_range(lrange[2], lrange[1], lrange[0]); in CeedBasisApplyTensor_Sycl_shared()
82 sycl::range<3> global_range(group_count * lrange[2], lrange[1], lrange[0]); in CeedBasisApplyTensor_Sycl_shared()
83 sycl::nd_range<3> kernel_range(global_range, local_range); in CeedBasisApplyTensor_Sycl_shared()
85sycl::kernel *grad_kernel = (t_mode == CEED_TRANSPOSE) ? impl->grad_transpose_kernel : impl->g… in CeedBasisApplyTensor_Sycl_shared()
88 std::vector<sycl::event> e; in CeedBasisApplyTensor_Sycl_shared()
92 ceed_Sycl->sycl_queue.submit([&](sycl::handler &cgh) { in CeedBasisApplyTensor_Sycl_shared()
103 sycl::range<3> local_range(lrange[2], lrange[1], lrange[0]); in CeedBasisApplyTensor_Sycl_shared()
104 sycl::range<3> global_range(group_count * lrange[2], lrange[1], lrange[0]); in CeedBasisApplyTensor_Sycl_shared()
105 sycl::nd_range<3> kernel_range(global_range, local_range); in CeedBasisApplyTensor_Sycl_shared()
107 std::vector<sycl::event> e; in CeedBasisApplyTensor_Sycl_shared()
112 ceed_Sycl->sycl_queue.submit([&](sycl::handler &cgh) { in CeedBasisApplyTensor_Sycl_shared()
147 if (impl->d_q_weight_1d) CeedCallSycl(ceed, sycl::free(impl->d_q_weight_1d, data->sycl_context)); in CeedBasisDestroy_Sycl_shared()
148 CeedCallSycl(ceed, sycl::free(impl->d_interp_1d, data->sycl_context)); in CeedBasisDestroy_Sycl_shared()
149 CeedCallSycl(ceed, sycl::free(impl->d_grad_1d, data->sycl_context)); in CeedBasisDestroy_Sycl_shared()
150 CeedCallSycl(ceed, sycl::free(impl->d_collo_grad_1d, data->sycl_context)); in CeedBasisDestroy_Sycl_shared()
198 std::vector<sycl::event> e; in CeedBasisCreateTensorH1_Sycl_shared()
203 std::vector<sycl::event> copy_events; in CeedBasisCreateTensorH1_Sycl_shared()
205 …CeedCallSycl(ceed, impl->d_q_weight_1d = sycl::malloc_device<CeedScalar>(Q_1d, data->sycl_device, … in CeedBasisCreateTensorH1_Sycl_shared()
206sycl::event copy_weight = data->sycl_queue.copy<CeedScalar>(q_weight_1d, impl->d_q_weight_1d, Q_1d… in CeedBasisCreateTensorH1_Sycl_shared()
211 …CeedCallSycl(ceed, impl->d_interp_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_d… in CeedBasisCreateTensorH1_Sycl_shared()
212sycl::event copy_interp = data->sycl_queue.copy<CeedScalar>(interp_1d, impl->d_interp_1d, interp_l… in CeedBasisCreateTensorH1_Sycl_shared()
215 …CeedCallSycl(ceed, impl->d_grad_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_dev… in CeedBasisCreateTensorH1_Sycl_shared()
216sycl::event copy_grad = data->sycl_queue.copy<CeedScalar>(grad_1d, impl->d_grad_1d, interp_length,… in CeedBasisCreateTensorH1_Sycl_shared()
219 CeedCallSycl(ceed, sycl::event::wait_and_throw(copy_events)); in CeedBasisCreateTensorH1_Sycl_shared()
231 …CeedCallSycl(ceed, impl->d_collo_grad_1d = sycl::malloc_device<CeedScalar>(cgrad_length, data->syc… in CeedBasisCreateTensorH1_Sycl_shared()