Lines Matching refs:sycl
71 static inline int CeedJitCompileSource_Sycl(Ceed ceed, const sycl::device &sycl_device, const std::… in CeedJitCompileSource_Sycl()
73 …sycl::ext::libceed::online_compiler<sycl::ext::libceed::source_language::opencl_c> compiler(sycl_d…
77 } catch (sycl::ext::libceed::online_compile_error &e) {
86 static int CeedLoadModule_Sycl(Ceed ceed, const sycl::context &sycl_context, const sycl::device &sy… in CeedLoadModule_Sycl()
88 auto lz_context = sycl::get_native<sycl::backend::ext_oneapi_level_zero>(sycl_context); in CeedLoadModule_Sycl()
89 auto lz_device = sycl::get_native<sycl::backend::ext_oneapi_level_zero>(sycl_device); in CeedLoadModule_Sycl()
116 …*sycl_module = new SyclModule_t(sycl::make_kernel_bundle<sycl::backend::ext_oneapi_level_zero, syc… in CeedLoadModule_Sycl()
117 {lz_module, sycl::ext::oneapi::level_zero::ownership::transfer}, sycl_context)); in CeedLoadModule_Sycl()
143 …ed ceed, const SyclModule_t *sycl_module, const std::string &kernel_name, sycl::kernel **sycl_kern… in CeedGetKernel_Sycl()
150 …ze_module_handle_t lz_module = sycl::get_native<sycl::backend::ext_oneapi_level_zero>(*sycl_module… in CeedGetKernel_Sycl()
160 …*sycl_kernel = new sycl::kernel(sycl::make_kernel<sycl::backend::ext_oneapi_level_zero>({*sycl_mod… in CeedGetKernel_Sycl()
161 … sycl::ext::oneapi::level_zero::ownership::transfer}, in CeedGetKernel_Sycl()
169 int CeedRunKernelDimSharedSycl(Ceed ceed, sycl::kernel *kernel, const int grid_size, const int bloc… in CeedRunKernelDimSharedSycl()
171 sycl::range<3> local_range(block_size_z, block_size_y, block_size_x); in CeedRunKernelDimSharedSycl()
172 sycl::range<3> global_range(grid_size * block_size_z, block_size_y, block_size_x); in CeedRunKernelDimSharedSycl()
173 sycl::nd_range<3> kernel_range(global_range, local_range); in CeedRunKernelDimSharedSycl()
180 sycl::event e = ceed_Sycl->sycl_queue.ext_oneapi_submit_barrier(); in CeedRunKernelDimSharedSycl()
182 ceed_Sycl->sycl_queue.submit([&](sycl::handler &cgh) { in CeedRunKernelDimSharedSycl()