Home
last modified time | relevance | path

Searched refs:sycl_device (Results 1 – 11 of 11) sorted by relevance

/libCEED/backends/sycl/
H A Dceed-sycl-common.sycl.cpp44 sycl::device sycl_device{sycl_devices[device_id]}; in CeedInit_Sycl() local
46 if (!sycl_device.has(sycl::aspect::usm_device_allocations)) { in CeedInit_Sycl()
67 sycl::context sycl_context{sycl_device.get_platform().get_devices()}; in CeedInit_Sycl()
68 …sycl::queue sycl_queue{sycl_context, sycl_device, sycl_async_handler, sycl::property::queue::in_… in CeedInit_Sycl()
72 data->sycl_device = sycl_device; in CeedInit_Sycl()
102 …CeedCheck(data->sycl_device == q->get_device(), ceed, CEED_ERROR_BACKEND, "Device mismatch between… in CeedSetStream_Sycl()
103 data->sycl_device = q->get_device(); in CeedSetStream_Sycl()
H A Dceed-sycl-compile.sycl.cpp71 static inline int CeedJitCompileSource_Sycl(Ceed ceed, const sycl::device &sycl_device, const std::… in CeedJitCompileSource_Sycl() argument
73 …ext::libceed::online_compiler<sycl::ext::libceed::source_language::opencl_c> compiler(sycl_device);
86 …Sycl(Ceed ceed, const sycl::context &sycl_context, const sycl::device &sycl_device, const ByteVect… in CeedLoadModule_Sycl() argument
89 auto lz_device = sycl::get_native<sycl::backend::ext_oneapi_level_zero>(sycl_device); in CeedLoadModule_Sycl()
133 CeedCallBackend(CeedJitCompileSource_Sycl(ceed, data->sycl_device, jit_source, il_binary, flags)); in CeedBuildModule_Sycl()
134 …CeedCallBackend(CeedLoadModule_Sycl(ceed, data->sycl_context, data->sycl_device, il_binary, sycl_m… in CeedBuildModule_Sycl()
H A Dceed-sycl-common.hpp36 sycl::device sycl_device; member
/libCEED/backends/sycl-gen/
H A Dceed-sycl-gen-operator.sycl.cpp220 …impl->indices = sycl::malloc_device<FieldsInt_Sycl>(1, sycl_data->sycl_device, sycl_data->sycl_con… in CeedOperatorCreate_Sycl_gen()
222 …impl->B = sycl::malloc_device<Fields_Sycl>(1, sycl_data->sycl_device, sycl_data->sycl_contex… in CeedOperatorCreate_Sycl_gen()
223 …impl->G = sycl::malloc_device<Fields_Sycl>(1, sycl_data->sycl_device, sycl_data->sycl_contex… in CeedOperatorCreate_Sycl_gen()
224 …impl->W = sycl::malloc_device<CeedScalar>(1, sycl_data->sycl_device, sycl_data->sycl_context… in CeedOperatorCreate_Sycl_gen()
H A Dceed-sycl-gen-operator-build.sycl.cpp227 …std::vector allowed_sg_sizes = sycl_data->sycl_device.get_info<sycl::info::device::sub_group_size… in CeedOperatorBuildKernel_Sycl_gen()
/libCEED/backends/sycl-shared/
H A Dceed-sycl-shared-basis.sycl.cpp205 …eed, impl->d_q_weight_1d = sycl::malloc_device<CeedScalar>(Q_1d, data->sycl_device, data->sycl_con… in CeedBasisCreateTensorH1_Sycl_shared()
211 …pl->d_interp_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_device, data->sycl_con… in CeedBasisCreateTensorH1_Sycl_shared()
215 …impl->d_grad_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_device, data->sycl_con… in CeedBasisCreateTensorH1_Sycl_shared()
231 …>d_collo_grad_1d = sycl::malloc_device<CeedScalar>(cgrad_length, data->sycl_device, data->sycl_con… in CeedBasisCreateTensorH1_Sycl_shared()
/libCEED/backends/sycl-ref/
H A Dceed-sycl-ref-basis.sycl.cpp45 const sycl::device &sycl_device = sycl_queue.get_device(); in CeedBasisApplyInterp_Sycl() local
149 const sycl::device &sycl_device = sycl_queue.get_device(); in CeedBasisApplyGrad_Sycl() local
592 …eed, impl->d_q_weight_1d = sycl::malloc_device<CeedScalar>(Q_1d, data->sycl_device, data->sycl_con… in CeedBasisCreateTensorH1_Sycl()
598 …pl->d_interp_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_device, data->sycl_con… in CeedBasisCreateTensorH1_Sycl()
602 …impl->d_grad_1d = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_device, data->sycl_con… in CeedBasisCreateTensorH1_Sycl()
655 …ed, impl->d_q_weight = sycl::malloc_device<CeedScalar>(num_qpts, data->sycl_device, data->sycl_con… in CeedBasisCreateH1_Sycl()
661 … impl->d_interp = sycl::malloc_device<CeedScalar>(interp_length, data->sycl_device, data->sycl_con… in CeedBasisCreateH1_Sycl()
666 …CeedCallSycl(ceed, impl->d_grad = sycl::malloc_device<CeedScalar>(grad_length, data->sycl_device, … in CeedBasisCreateH1_Sycl()
H A Dceed-sycl-restriction.sycl.cpp314 … impl->d_l_vec_indices = sycl::malloc_device<CeedInt>(num_nodes, data->sycl_device, data->sycl_con… in CeedElemRestrictionOffset_Sycl()
317 …, impl->d_t_offsets = sycl::malloc_device<CeedInt>(size_offsets, data->sycl_device, data->sycl_con… in CeedElemRestrictionOffset_Sycl()
320 …, impl->d_t_indices = sycl::malloc_device<CeedInt>(size_indices, data->sycl_device, data->sycl_con… in CeedElemRestrictionOffset_Sycl()
421 …ceed, impl->d_offsets_owned = sycl::malloc_device<CeedInt>(size, data->sycl_device, data->sycl_con… in CeedElemRestrictionCreate_Sycl()
436 …ceed, impl->d_offsets_owned = sycl::malloc_device<CeedInt>(size, data->sycl_device, data->sycl_con… in CeedElemRestrictionCreate_Sycl()
H A Dceed-sycl-ref-operator.sycl.cpp778 …, diag->d_identity = sycl::malloc_device<CeedScalar>(i_len, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
785 … diag->d_interp_in = sycl::malloc_device<CeedScalar>(i_len, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
790 …diag->d_interp_out = sycl::malloc_device<CeedScalar>(i_len, sycl_data->sycl_device, sycl_data->syc… 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()
801 …, diag->d_grad_out = sycl::malloc_device<CeedScalar>(g_len, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
806 …de_in = sycl::malloc_device<CeedEvalMode>(num_eval_mode_in, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
810 …_out = sycl::malloc_device<CeedEvalMode>(num_eval_mode_out, sycl_data->sycl_device, sycl_data->syc… in CeedOperatorAssembleDiagonalSetup_Sycl()
1127 …, asmb->d_B_in = sycl::malloc_device<CeedScalar>(size_B_in, sycl_data->sycl_device, sycl_data->syc… 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()
H A Dceed-sycl-ref-qfunctioncontext.sycl.cpp37 …CeedCallSycl(ceed, impl->d_data_owned = sycl::malloc_device(ctx_size, sycl_data->sycl_device, sycl… in CeedQFunctionContextSyncH2D_Sycl()
217 …CeedCallSycl(ceed, impl->d_data_owned = sycl::malloc_device(ctx_size, sycl_data->sycl_device, sycl… in CeedQFunctionContextSetDataDevice_Sycl()
H A Dceed-sycl-vector.sycl.cpp58 …d, impl->d_array_owned = sycl::malloc_device<CeedScalar>(length, data->sycl_device, data->sycl_con… in CeedVectorSyncH2D_Sycl()
220 …d, impl->d_array_owned = sycl::malloc_device<CeedScalar>(length, data->sycl_device, data->sycl_con… in CeedVectorSetArrayDevice_Sycl()