Provides an abstraction of a SYCL kernel. More...

#include <sycl/kernel.hpp>

Inheritance diagram for sycl::_V1::kernel:

Collaboration diagram for sycl::_V1::kernel:

Public Member Functions
	kernel (const kernel &RHS)=default
	Constructs a SYCL kernel instance from an OpenCL cl_kernel. More...

	kernel (kernel &&RHS)=default

kernel &	operator= (const kernel &RHS)=default

kernel &	operator= (kernel &&RHS)=default

bool	operator== (const kernel &RHS) const

bool	operator!= (const kernel &RHS) const

	__SYCL2020_DEPRECATED ("is_host() is deprecated as the host device is no longer supported.") bool is_host() const
	Get a valid OpenCL kernel handle. More...

context	get_context () const
	Get the context that this kernel is defined for. More...

backend	get_backend () const noexcept
	Returns the backend associated with this kernel. More...

kernel_bundle< bundle_state::executable >	get_kernel_bundle () const
	Get the kernel_bundle associated with this kernel. More...

template<typename Param >
detail::is_kernel_info_desc< Param >::return_type	get_info () const
	Query information from the kernel object using the info::kernel_info descriptor. More...

template<typename Param >
detail::is_kernel_device_specific_info_desc< Param >::return_type	get_info (const device &Device) const
	Query device-specific information from the kernel object using the info::kernel_device_specific descriptor. More...

template<typename Param >
detail::is_kernel_device_specific_info_desc< Param >::return_type	get_info (const device &Device, const range< 3 > &WGSize) const
	Query device-specific information from a kernel using the info::kernel_device_specific descriptor for a specific device and value. More...

template<typename Param >
Param::return_type	ext_oneapi_get_info (const queue &q) const

Public Member Functions inherited from sycl::_V1::detail::OwnerLessBase< kernel >
bool	ext_oneapi_owner_before (const ext::oneapi::detail::weak_object_base< kernel > &Other) const noexcept
	Compares the object against a weak object using an owner-based implementation-defined ordering. More...

bool	ext_oneapi_owner_before (const kernel &Other) const noexcept
	Compares the object against another object using an owner-based implementation-defined ordering. More...

Friends
template<class T >
T	detail::createSyclObjFromImpl (decltype(T::impl) ImplObj)

template<backend BackendName, class SyclObjectT >
auto	get_native (const SyclObjectT &Obj) -> backend_return_t< BackendName, SyclObjectT >

Detailed Description

Provides an abstraction of a SYCL kernel.

See also: sycl_api_exec; program; queue

Definition at line 74 of file kernel.hpp.

Constructor & Destructor Documentation

◆ kernel() [1/2]

sycl::_V1::kernel::kernel ( const kernel & RHS )

default

Constructs a SYCL kernel instance from an OpenCL cl_kernel.

The requirements for this constructor are described in section 4.3.1 of the SYCL specification.

Parameters

ClKernel	is a valid OpenCL cl_kernel instance
SyclContext	is a valid SYCL context

◆ kernel() [2/2]

sycl::_V1::kernel::kernel ( kernel && RHS )

default

Member Function Documentation

◆ __SYCL2020_DEPRECATED()

sycl::_V1::kernel::__SYCL2020_DEPRECATED ( "is_host() is deprecated as the host device is no longer supported." ) const

Get a valid OpenCL kernel handle.

If this kernel encapsulates an instance of OpenCL kernel, a valid cl_kernel will be returned. If this kernel is a host kernel, an invalid_object_error exception will be thrown.

Returns: a valid cl_kernel instance Check if the associated SYCL context is a SYCL host context.; true if this SYCL kernel is a host kernel.

◆ ext_oneapi_get_info()

template<typename Param >

Param::return_type sycl::_V1::kernel::ext_oneapi_get_info ( const queue & q ) const

◆ get_backend()

backend sycl::_V1::kernel::get_backend ( ) const

noexcept

Returns the backend associated with this kernel.

Returns: the backend associated with this kernel.

Definition at line 43 of file kernel.cpp.

◆ get_context()

context sycl::_V1::kernel::get_context ( ) const

Get the context that this kernel is defined for.

The value returned must be equal to that returned by get_info<info::kernel::context>().

Returns: a valid SYCL context

Definition at line 39 of file kernel.cpp.

◆ get_info() [1/3]

template<typename Param >

detail::is_kernel_info_desc< Param >::return_type sycl::_V1::kernel::get_info

Query information from the kernel object using the info::kernel_info descriptor.

Returns: depends on information being queried.

Definition at line 53 of file kernel.cpp.

◆ get_info() [2/3]

template<typename Param >

detail::is_kernel_device_specific_info_desc< Param >::return_type sycl::_V1::kernel::get_info ( const device & Device ) const

Query device-specific information from the kernel object using the info::kernel_device_specific descriptor.

Parameters

Device is a valid SYCL device to query info for.

Returns: depends on information being queried.

Definition at line 66 of file kernel.cpp.

◆ get_info() [3/3]

template<typename Param >

detail::is_kernel_device_specific_info_desc< Param >::return_type sycl::_V1::kernel::get_info	(	const device &	Device,
		const range< 3 > &	WGSize
	)		const

Query device-specific information from a kernel using the info::kernel_device_specific descriptor for a specific device and value.

max_sub_group_size is the only valid descriptor for this function.

Parameters

Device	is a valid SYCL device.
WGSize	is the work-group size the sub-group size is requested for.

Returns: depends on information being queried.

Definition at line 74 of file kernel.cpp.

◆ get_kernel_bundle()

kernel_bundle< sycl::bundle_state::executable > sycl::_V1::kernel::get_kernel_bundle ( ) const

Get the kernel_bundle associated with this kernel.

Returns: a valid kernel_bundle<bundle_state::executable>

Definition at line 46 of file kernel.cpp.

◆ operator!=()

bool sycl::_V1::kernel::operator!= ( const kernel & RHS ) const

inline

Definition at line 97 of file kernel.hpp.

◆ operator=() [1/2]

kernel& sycl::_V1::kernel::operator= ( const kernel & RHS )

default

◆ operator=() [2/2]

kernel& sycl::_V1::kernel::operator= ( kernel && RHS )

default

◆ operator==()

bool sycl::_V1::kernel::operator== ( const kernel & RHS ) const

inline

Definition at line 95 of file kernel.hpp.

Friends And Related Function Documentation

◆ detail::createSyclObjFromImpl

template<class T >

T detail::createSyclObjFromImpl ( decltype(T::impl) ImplObj )

friend

◆ get_native

template<backend BackendName, class SyclObjectT >

auto get_native ( const SyclObjectT & Obj ) -> backend_return_t< BackendName, SyclObjectT >

friend

Definition at line 136 of file backend.hpp.

The documentation for this class was generated from the following files:

include/sycl/kernel.hpp
plugins/unified_runtime/ur/adapters/native_cpu/kernel.cpp

Public Member Functions

Friends

Detailed Description

Constructor & Destructor Documentation

◆ kernel() [1/2]

◆ kernel() [2/2]

Member Function Documentation

◆ __SYCL2020_DEPRECATED()

◆ ext_oneapi_get_info()

◆ get_backend()

◆ get_context()

◆ get_info() [1/3]

◆ get_info() [2/3]

◆ get_info() [3/3]

◆ get_kernel_bundle()

◆ operator!=()

◆ operator=() [1/2]

◆ operator=() [2/2]

◆ operator==()

Friends And Related Function Documentation

◆ detail::createSyclObjFromImpl

◆ get_native