45 #ifndef KOKKOS_SYCL_HPP 46 #define KOKKOS_SYCL_HPP 48 #include <Kokkos_Macros.hpp> 50 #ifdef KOKKOS_ENABLE_SYCL 51 #include <CL/sycl.hpp> 52 #include <Kokkos_SYCL_Space.hpp> 54 #include <Kokkos_ScratchSpace.hpp> 55 #include <impl/Kokkos_ExecSpaceInitializer.hpp> 56 #include <impl/Kokkos_Profiling_Interface.hpp> 57 #include <impl/Kokkos_HostSharedPtr.hpp> 74 using execution_space = SYCL;
75 using memory_space = SYCLDeviceUSMSpace;
76 using device_type = Kokkos::Device<execution_space, memory_space>;
78 using array_layout = LayoutLeft;
79 using size_type = memory_space::size_type;
81 using scratch_memory_space = ScratchMemorySpace<SYCL>;
84 explicit SYCL(
const sycl::queue&);
86 uint32_t impl_instance_id() const noexcept {
return 0; }
88 sycl::context sycl_context() const noexcept {
89 return m_space_instance->m_queue->get_context();
97 KOKKOS_INLINE_FUNCTION
static int in_parallel() {
98 #if defined(__SYCL_DEVICE_ONLY__) 112 static void impl_static_fence();
116 void print_configuration(std::ostream&,
const bool detail =
false);
119 static void impl_finalize();
126 SYCLDevice() : SYCLDevice(sycl::default_selector()) {}
127 explicit SYCLDevice(sycl::device d);
128 explicit SYCLDevice(
const sycl::device_selector& selector);
129 explicit SYCLDevice(
size_t id);
131 sycl::device get_device()
const;
133 friend std::ostream& operator<<(std::ostream& os,
const SYCLDevice& that) {
134 return SYCL::impl_sycl_info(os, that.m_device);
138 sycl::device m_device;
141 static void impl_initialize(SYCLDevice = SYCLDevice());
143 int sycl_device()
const;
145 static bool impl_is_initialized();
147 static int concurrency();
148 static const char* name();
150 inline Impl::SYCLInternal* impl_internal_space_instance()
const {
151 return m_space_instance.get();
155 static std::ostream& impl_sycl_info(std::ostream& os,
156 const sycl::device& device);
158 Kokkos::Impl::HostSharedPtr<Impl::SYCLInternal> m_space_instance;
163 class SYCLSpaceInitializer :
public Kokkos::Impl::ExecSpaceInitializerBase {
165 void initialize(
const InitArguments& args)
final;
166 void finalize(
const bool)
final;
168 void print_configuration(std::ostream& msg, const
bool detail) final;
177 struct DeviceTypeTraits<
Kokkos::Experimental::SYCL> {
179 static constexpr DeviceType
id = DeviceType::SYCL;
Declaration of various MemoryLayout options.