|
DPC++ Runtime
Runtime libraries for oneAPI DPC++
|
|
|
DPC++ Runtime
Runtime libraries for oneAPI DPC++
|
|
Encapsulates a single SYCL queue which schedules kernels on a SYCL device. More...
#include <sycl/queue.hpp>
Public Member Functions | |
| queue (const property_list &PropList={}) | |
| Constructs a SYCL queue instance using the device returned by an instance of default_selector. More... | |
| queue (const async_handler &AsyncHandler, const property_list &PropList={}) | |
| Constructs a SYCL queue instance with an async_handler using the device returned by an instance of default_selector. More... | |
| template<typename DeviceSelector , typename = detail::EnableIfSYCL2020DeviceSelectorInvocable<DeviceSelector>> | |
| queue (const DeviceSelector &deviceSelector, const async_handler &AsyncHandler, const property_list &PropList={}) | |
| Constructs a SYCL queue instance using the device identified by the device selector provided. More... | |
| template<typename DeviceSelector , typename = detail::EnableIfSYCL2020DeviceSelectorInvocable<DeviceSelector>> | |
| queue (const DeviceSelector &deviceSelector, const property_list &PropList={}) | |
| Constructs a SYCL queue instance using the device identified by the device selector provided. More... | |
| template<typename DeviceSelector , typename = detail::EnableIfSYCL2020DeviceSelectorInvocable<DeviceSelector>> | |
| queue (const context &syclContext, const DeviceSelector &deviceSelector, const property_list &propList={}) | |
| Constructs a SYCL queue instance using the device identified by the device selector provided. More... | |
| template<typename DeviceSelector , typename = detail::EnableIfSYCL2020DeviceSelectorInvocable<DeviceSelector>> | |
| queue (const context &syclContext, const DeviceSelector &deviceSelector, const async_handler &AsyncHandler, const property_list &propList={}) | |
| Constructs a SYCL queue instance using the device identified by the device selector provided. More... | |
| __SYCL2020_DEPRECATED ("SYCL 1.2.1 device selectors are deprecated. Please " "use SYCL 2020 device selectors instead.") queue(const device_selector &DeviceSelector | |
| Constructs a SYCL queue instance using the device returned by the DeviceSelector provided. More... | |
| __SYCL2020_DEPRECATED ("SYCL 1.2.1 device selectors are deprecated. Please " "use SYCL 2020 device selectors instead.") queue(const context &SyclContext | |
| Constructs a SYCL queue instance that is associated with the context provided, using the device returned by the device selector. More... | |
| __SYCL2020_DEPRECATED ("SYCL 1.2.1 device selectors are deprecated. Please " "use SYCL 2020 device selectors instead.") queue(const context &SyclContext | |
| Constructs a SYCL queue instance with an async_handler that is associated with the context provided, using the device returned by the device selector. More... | |
| queue (const context &SyclContext, const device &SyclDevice, const property_list &PropList={}) | |
| Constructs a SYCL queue associated with the given context, device and optional properties list. More... | |
| queue (const context &SyclContext, const device &SyclDevice, const async_handler &AsyncHandler, const property_list &PropList={}) | |
| Constructs a SYCL queue associated with the given context, device, asynchronous exception handler and optional properties list. More... | |
| queue (const queue &RHS)=default | |
| Constructs a SYCL queue with an optional async_handler from an OpenCL cl_command_queue. More... | |
| queue (queue &&RHS)=default | |
| queue & | operator= (const queue &RHS)=default |
| queue & | operator= (queue &&RHS)=default |
| bool | operator== (const queue &RHS) const |
| bool | operator!= (const queue &RHS) const |
| context | get_context () const |
| device | get_device () const |
| ext::oneapi::experimental::queue_state | ext_oneapi_get_state () const |
| __SYCL2020_DEPRECATED ("is_host() is deprecated as the host device is no longer supported.") bool is_host() const | |
| template<typename Param > | |
| detail::is_queue_info_desc< Param >::return_type | get_info () const |
| Queries SYCL queue for information. More... | |
| template<typename T > | |
| std::enable_if_t< std::is_invocable_r_v< void, T, handler & >, event > | submit (T CGF, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Submits a command group function object to the queue, in order to be scheduled for execution on the device. More... | |
| template<typename T > | |
| std::enable_if_t< std::is_invocable_r_v< void, T, handler & >, event > | submit (T CGF, queue &SecondaryQueue, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Submits a command group function object to the queue, in order to be scheduled for execution on the device. More... | |
| event | ext_oneapi_submit_barrier (const detail::code_location &CodeLoc=detail::code_location::current()) |
| Prevents any commands submitted afterward to this queue from executing until all commands previously submitted to this queue have entered the complete state. More... | |
| event | ext_oneapi_submit_barrier (const std::vector< event > &WaitList, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Prevents any commands submitted afterward to this queue from executing until all events in WaitList have entered the complete state. More... | |
| void | wait (const detail::code_location &CodeLoc=detail::code_location::current()) |
| Performs a blocking wait for the completion of all enqueued tasks in the queue. More... | |
| void | wait_and_throw (const detail::code_location &CodeLoc=detail::code_location::current()) |
| Performs a blocking wait for the completion of all enqueued tasks in the queue. More... | |
| void | wait_proxy (const detail::code_location &CodeLoc) |
| Proxy method for wait to forward the code location information to the implementation. More... | |
| void | wait_and_throw_proxy (const detail::code_location &CodeLoc) |
| Proxy method for wait_and_throw to forward the code location information to the implementation. More... | |
| void | throw_asynchronous () |
| Checks if any asynchronous errors have been produced by the queue and if so reports them to the async_handler passed on the queue construction. More... | |
| template<typename PropertyT > | |
| bool | has_property () const noexcept |
| template<typename PropertyT > | |
| PropertyT | get_property () const |
| template<typename T > | |
| event | fill (void *Ptr, const T &Pattern, size_t Count, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the specified memory with the specified pattern. More... | |
| template<typename T > | |
| event | fill (void *Ptr, const T &Pattern, size_t Count, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the specified memory with the specified pattern. More... | |
| template<typename T > | |
| event | fill (void *Ptr, const T &Pattern, size_t Count, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the specified memory with the specified pattern. More... | |
| event | memset (void *Ptr, int Value, size_t Count, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the memory pointed by a USM pointer with the value specified. More... | |
| event | memset (void *Ptr, int Value, size_t Count, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the memory pointed by a USM pointer with the value specified. More... | |
| event | memset (void *Ptr, int Value, size_t Count, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the memory pointed by a USM pointer with the value specified. More... | |
| event | memcpy (void *Dest, const void *Src, size_t Count, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue. More... | |
| event | memcpy (void *Dest, const void *Src, size_t Count, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue. More... | |
| event | memcpy (void *Dest, const void *Src, size_t Count, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue. More... | |
| template<typename T > | |
| event | copy (const T *Src, T *Dest, size_t Count, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue. More... | |
| template<typename T > | |
| event | copy (const T *Src, T *Dest, size_t Count, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue. More... | |
| template<typename T > | |
| event | copy (const T *Src, T *Dest, size_t Count, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue. More... | |
| event | mem_advise (const void *Ptr, size_t Length, pi_mem_advice Advice, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Provides additional information to the underlying runtime about how different allocations are used. More... | |
| event | mem_advise (const void *Ptr, size_t Length, int Advice, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Provides additional information to the underlying runtime about how different allocations are used. More... | |
| event | mem_advise (const void *Ptr, size_t Length, int Advice, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Provides additional information to the underlying runtime about how different allocations are used. More... | |
| event | mem_advise (const void *Ptr, size_t Length, int Advice, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Provides additional information to the underlying runtime about how different allocations are used. More... | |
| event | prefetch (const void *Ptr, size_t Count, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Provides hints to the runtime library that data should be made available on a device earlier than Unified Shared Memory would normally require it to be available. More... | |
| event | prefetch (const void *Ptr, size_t Count, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Provides hints to the runtime library that data should be made available on a device earlier than Unified Shared Memory would normally require it to be available. More... | |
| event | prefetch (const void *Ptr, size_t Count, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Provides hints to the runtime library that data should be made available on a device earlier than Unified Shared Memory would normally require it to be available. More... | |
| template<typename T = unsigned char, typename = std::enable_if_t<std::is_same_v<T, unsigned char>>> | |
| event | ext_oneapi_memcpy2d (void *Dest, size_t DestPitch, const void *Src, size_t SrcPitch, size_t Width, size_t Height, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one 2D memory region to another, both pointed by USM pointers. More... | |
| template<typename T = unsigned char, typename = std::enable_if_t<std::is_same_v<T, unsigned char>>> | |
| event | ext_oneapi_memcpy2d (void *Dest, size_t DestPitch, const void *Src, size_t SrcPitch, size_t Width, size_t Height, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one 2D memory region to another, both pointed by USM pointers. More... | |
| template<typename T = unsigned char, typename = std::enable_if_t<std::is_same_v<T, unsigned char>>> | |
| event | ext_oneapi_memcpy2d (void *Dest, size_t DestPitch, const void *Src, size_t SrcPitch, size_t Width, size_t Height, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one 2D memory region to another, both pointed by USM pointers. More... | |
| template<typename T > | |
| event | ext_oneapi_copy2d (const T *Src, size_t SrcPitch, T *Dest, size_t DestPitch, size_t Width, size_t Height, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one 2D memory region to another, both pointed by USM pointers. More... | |
| template<typename T > | |
| event | ext_oneapi_copy2d (const T *Src, size_t SrcPitch, T *Dest, size_t DestPitch, size_t Width, size_t Height, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one 2D memory region to another, both pointed by USM pointers. More... | |
| template<typename T > | |
| event | ext_oneapi_copy2d (const T *Src, size_t SrcPitch, T *Dest, size_t DestPitch, size_t Width, size_t Height, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one 2D memory region to another, both pointed by USM pointers. More... | |
| template<typename T = unsigned char, typename = std::enable_if_t<std::is_same_v<T, unsigned char>>> | |
| event | ext_oneapi_memset2d (void *Dest, size_t DestPitch, int Value, size_t Width, size_t Height, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the memory pointed by a USM pointer with the value specified. More... | |
| template<typename T = unsigned char, typename = std::enable_if_t<std::is_same_v<T, unsigned char>>> | |
| event | ext_oneapi_memset2d (void *Dest, size_t DestPitch, int Value, size_t Width, size_t Height, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the memory pointed by a USM pointer with the value specified. More... | |
| template<typename T = unsigned char, typename = std::enable_if_t<std::is_same_v<T, unsigned char>>> | |
| event | ext_oneapi_memset2d (void *Dest, size_t DestPitch, int Value, size_t Width, size_t Height, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the memory pointed by a USM pointer with the value specified. More... | |
| template<typename T > | |
| event | ext_oneapi_fill2d (void *Dest, size_t DestPitch, const T &Pattern, size_t Width, size_t Height, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the memory pointed by a USM pointer with the value specified. More... | |
| template<typename T > | |
| event | ext_oneapi_fill2d (void *Dest, size_t DestPitch, const T &Pattern, size_t Width, size_t Height, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the memory pointed by a USM pointer with the value specified. More... | |
| template<typename T > | |
| event | ext_oneapi_fill2d (void *Dest, size_t DestPitch, const T &Pattern, size_t Width, size_t Height, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the memory pointed by a USM pointer with the value specified. More... | |
| template<typename T , typename PropertyListT > | |
| event | memcpy (ext::oneapi::experimental::device_global< T, PropertyListT > &Dest, const void *Src, size_t NumBytes, size_t Offset, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from a USM memory region to a device_global. More... | |
| template<typename T , typename PropertyListT > | |
| event | memcpy (ext::oneapi::experimental::device_global< T, PropertyListT > &Dest, const void *Src, size_t NumBytes, size_t Offset, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from a USM memory region to a device_global. More... | |
| template<typename T , typename PropertyListT > | |
| event | memcpy (ext::oneapi::experimental::device_global< T, PropertyListT > &Dest, const void *Src, size_t NumBytes=sizeof(T), size_t Offset=0, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from a USM memory region to a device_global. More... | |
| template<typename T , typename PropertyListT > | |
| event | memcpy (void *Dest, const ext::oneapi::experimental::device_global< T, PropertyListT > &Src, size_t NumBytes, size_t Offset, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from a device_global to USM memory. More... | |
| template<typename T , typename PropertyListT > | |
| event | memcpy (void *Dest, const ext::oneapi::experimental::device_global< T, PropertyListT > &Src, size_t NumBytes, size_t Offset, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from a device_global to USM memory. More... | |
| template<typename T , typename PropertyListT > | |
| event | memcpy (void *Dest, const ext::oneapi::experimental::device_global< T, PropertyListT > &Src, size_t NumBytes=sizeof(T), size_t Offset=0, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from a device_global to USM memory. More... | |
| template<typename T , typename PropertyListT > | |
| event | copy (const std::remove_all_extents_t< T > *Src, ext::oneapi::experimental::device_global< T, PropertyListT > &Dest, size_t Count, size_t StartIndex, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies elements of type std::remove_all_extents_t<T> from a USM memory region to a device_global. More... | |
| template<typename T , typename PropertyListT > | |
| event | copy (const std::remove_all_extents_t< T > *Src, ext::oneapi::experimental::device_global< T, PropertyListT > &Dest, size_t Count, size_t StartIndex, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies elements of type std::remove_all_extents_t<T> from a USM memory region to a device_global. More... | |
| template<typename T , typename PropertyListT > | |
| event | copy (const std::remove_all_extents_t< T > *Src, ext::oneapi::experimental::device_global< T, PropertyListT > &Dest, size_t Count=sizeof(T)/sizeof(std::remove_all_extents_t< T >), size_t StartIndex=0, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies elements of type std::remove_all_extents_t<T> from a USM memory region to a device_global. More... | |
| template<typename T , typename PropertyListT > | |
| event | copy (const ext::oneapi::experimental::device_global< T, PropertyListT > &Src, std::remove_all_extents_t< T > *Dest, size_t Count, size_t StartIndex, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies elements of type std::remove_all_extents_t<T> from a device_global to a USM memory region. More... | |
| template<typename T , typename PropertyListT > | |
| event | copy (const ext::oneapi::experimental::device_global< T, PropertyListT > &Src, std::remove_all_extents_t< T > *Dest, size_t Count, size_t StartIndex, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies elements of type std::remove_all_extents_t<T> from a device_global to a USM memory region. More... | |
| template<typename T , typename PropertyListT > | |
| event | copy (const ext::oneapi::experimental::device_global< T, PropertyListT > &Src, std::remove_all_extents_t< T > *Dest, size_t Count=sizeof(T)/sizeof(std::remove_all_extents_t< T >), size_t StartIndex=0, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies elements of type std::remove_all_extents_t<T> from a device_global to a USM memory region. More... | |
| event | ext_oneapi_copy (void *Src, ext::oneapi::experimental::image_mem_handle Dest, const ext::oneapi::experimental::image_descriptor &DestImgDesc, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle wrapper. More... | |
| event | ext_oneapi_copy (void *Src, sycl::range< 3 > SrcOffset, sycl::range< 3 > SrcExtent, ext::oneapi::experimental::image_mem_handle Dest, sycl::range< 3 > DestOffset, const ext::oneapi::experimental::image_descriptor &DestImgDesc, sycl::range< 3 > CopyExtent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle. More... | |
| event | ext_oneapi_copy (void *Src, ext::oneapi::experimental::image_mem_handle Dest, const ext::oneapi::experimental::image_descriptor &DestImgDesc, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle wrapper. More... | |
| event | ext_oneapi_copy (void *Src, sycl::range< 3 > SrcOffset, sycl::range< 3 > SrcExtent, ext::oneapi::experimental::image_mem_handle Dest, sycl::range< 3 > DestOffset, const ext::oneapi::experimental::image_descriptor &DestImgDesc, sycl::range< 3 > CopyExtent, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle. More... | |
| event | ext_oneapi_copy (void *Src, ext::oneapi::experimental::image_mem_handle Dest, const ext::oneapi::experimental::image_descriptor &DestImgDesc, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle wrapper. More... | |
| event | ext_oneapi_copy (void *Src, sycl::range< 3 > SrcOffset, sycl::range< 3 > SrcExtent, ext::oneapi::experimental::image_mem_handle Dest, sycl::range< 3 > DestOffset, const ext::oneapi::experimental::image_descriptor &DestImgDesc, sycl::range< 3 > CopyExtent, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle. More... | |
| event | ext_oneapi_copy (ext::oneapi::experimental::image_mem_handle Src, void *Dest, const ext::oneapi::experimental::image_descriptor &SrcImgDesc, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer. More... | |
| event | ext_oneapi_copy (ext::oneapi::experimental::image_mem_handle Src, sycl::range< 3 > SrcOffset, const ext::oneapi::experimental::image_descriptor &SrcImgDesc, void *Dest, sycl::range< 3 > DestOffset, sycl::range< 3 > DestExtent, sycl::range< 3 > CopyExtent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer. More... | |
| event | ext_oneapi_copy (ext::oneapi::experimental::image_mem_handle Src, void *Dest, const ext::oneapi::experimental::image_descriptor &SrcImgDesc, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer. More... | |
| event | ext_oneapi_copy (ext::oneapi::experimental::image_mem_handle Src, sycl::range< 3 > SrcOffset, const ext::oneapi::experimental::image_descriptor &SrcImgDesc, void *Dest, sycl::range< 3 > DestOffset, sycl::range< 3 > DestExtent, sycl::range< 3 > CopyExtent, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer. More... | |
| event | ext_oneapi_copy (ext::oneapi::experimental::image_mem_handle Src, void *Dest, const ext::oneapi::experimental::image_descriptor &SrcImgDesc, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer. More... | |
| event | ext_oneapi_copy (ext::oneapi::experimental::image_mem_handle Src, sycl::range< 3 > SrcOffset, const ext::oneapi::experimental::image_descriptor &SrcImgDesc, void *Dest, sycl::range< 3 > DestOffset, sycl::range< 3 > DestExtent, sycl::range< 3 > CopyExtent, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer. More... | |
| event | ext_oneapi_copy (void *Src, void *Dest, const ext::oneapi::experimental::image_descriptor &DeviceImgDesc, size_t DeviceRowPitch, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src and Dest are USM pointers. More... | |
| event | ext_oneapi_copy (void *Src, sycl::range< 3 > SrcOffset, void *Dest, sycl::range< 3 > DestOffset, const ext::oneapi::experimental::image_descriptor &DeviceImgDesc, size_t DeviceRowPitch, sycl::range< 3 > HostExtent, sycl::range< 3 > CopyExtent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src and Dest are USM pointers. More... | |
| event | ext_oneapi_copy (void *Src, void *Dest, const ext::oneapi::experimental::image_descriptor &DeviceImgDesc, size_t DeviceRowPitch, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src and Dest are USM pointers. More... | |
| event | ext_oneapi_copy (void *Src, sycl::range< 3 > SrcOffset, void *Dest, sycl::range< 3 > DestOffset, const ext::oneapi::experimental::image_descriptor &DeviceImgDesc, size_t DeviceRowPitch, sycl::range< 3 > HostExtent, sycl::range< 3 > CopyExtent, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src and Dest are USM pointers. More... | |
| event | ext_oneapi_copy (void *Src, void *Dest, const ext::oneapi::experimental::image_descriptor &DeviceImgDesc, size_t DeviceRowPitch, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src and Dest are USM pointers. More... | |
| event | ext_oneapi_copy (void *Src, sycl::range< 3 > SrcOffset, void *Dest, sycl::range< 3 > DestOffset, const ext::oneapi::experimental::image_descriptor &DeviceImgDesc, size_t DeviceRowPitch, sycl::range< 3 > HostExtent, sycl::range< 3 > CopyExtent, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
Copies data from one memory region to another, where Src and Dest are USM pointers. More... | |
| event | ext_oneapi_wait_external_semaphore (sycl::ext::oneapi::experimental::interop_semaphore_handle SemaphoreHandle, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Instruct the queue with a non-blocking wait on an external semaphore. More... | |
| event | ext_oneapi_wait_external_semaphore (sycl::ext::oneapi::experimental::interop_semaphore_handle SemaphoreHandle, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Instruct the queue with a non-blocking wait on an external semaphore. More... | |
| event | ext_oneapi_wait_external_semaphore (sycl::ext::oneapi::experimental::interop_semaphore_handle SemaphoreHandle, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Instruct the queue with a non-blocking wait on an external semaphore. More... | |
| event | ext_oneapi_signal_external_semaphore (sycl::ext::oneapi::experimental::interop_semaphore_handle SemaphoreHandle, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Instruct the queue to signal the external semaphore once all previous commands have completed execution. More... | |
| event | ext_oneapi_signal_external_semaphore (sycl::ext::oneapi::experimental::interop_semaphore_handle SemaphoreHandle, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Instruct the queue to signal the external semaphore once all previous commands have completed execution. More... | |
| event | ext_oneapi_signal_external_semaphore (sycl::ext::oneapi::experimental::interop_semaphore_handle SemaphoreHandle, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Instruct the queue to signal the external semaphore once all previous commands have completed execution. More... | |
| template<typename KernelName = detail::auto_name, typename KernelType , typename PropertiesT > | |
| std::enable_if_t< ext::oneapi::experimental::is_property_list< PropertiesT >::value, event > | single_task (PropertiesT Properties, _KERNELFUNCPARAM(KernelFunc), const detail::code_location &CodeLoc=detail::code_location::current()) |
| single_task version with a kernel represented as a lambda. More... | |
| template<typename KernelName = detail::auto_name, typename KernelType > | |
| event | single_task (_KERNELFUNCPARAM(KernelFunc), const detail::code_location &CodeLoc=detail::code_location::current()) |
| single_task version with a kernel represented as a lambda. More... | |
| template<typename KernelName = detail::auto_name, typename KernelType , typename PropertiesT > | |
| std::enable_if_t< ext::oneapi::experimental::is_property_list< PropertiesT >::value, event > | single_task (event DepEvent, PropertiesT Properties, _KERNELFUNCPARAM(KernelFunc), const detail::code_location &CodeLoc=detail::code_location::current()) |
| single_task version with a kernel represented as a lambda. More... | |
| template<typename KernelName = detail::auto_name, typename KernelType > | |
| event | single_task (event DepEvent, _KERNELFUNCPARAM(KernelFunc), const detail::code_location &CodeLoc=detail::code_location::current()) |
| single_task version with a kernel represented as a lambda. More... | |
| template<typename KernelName = detail::auto_name, typename KernelType , typename PropertiesT > | |
| std::enable_if_t< ext::oneapi::experimental::is_property_list< PropertiesT >::value, event > | single_task (const std::vector< event > &DepEvents, PropertiesT Properties, _KERNELFUNCPARAM(KernelFunc), const detail::code_location &CodeLoc=detail::code_location::current()) |
| single_task version with a kernel represented as a lambda. More... | |
| template<typename KernelName = detail::auto_name, typename KernelType > | |
| event | single_task (const std::vector< event > &DepEvents, _KERNELFUNCPARAM(KernelFunc), const detail::code_location &CodeLoc=detail::code_location::current()) |
| single_task version with a kernel represented as a lambda. More... | |
| template<typename KernelName = detail::auto_name, typename... RestT> | |
| event | parallel_for (range< 1 > Range, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + range that specifies global size only. More... | |
| template<typename KernelName = detail::auto_name, typename... RestT> | |
| event | parallel_for (range< 2 > Range, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + range that specifies global size only. More... | |
| template<typename KernelName = detail::auto_name, typename... RestT> | |
| event | parallel_for (range< 3 > Range, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + range that specifies global size only. More... | |
| template<typename KernelName = detail::auto_name, typename... RestT> | |
| event | parallel_for (range< 1 > Range, event DepEvent, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + range that specifies global size only. More... | |
| template<typename KernelName = detail::auto_name, typename... RestT> | |
| event | parallel_for (range< 2 > Range, event DepEvent, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + range that specifies global size only. More... | |
| template<typename KernelName = detail::auto_name, typename... RestT> | |
| event | parallel_for (range< 3 > Range, event DepEvent, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + range that specifies global size only. More... | |
| template<typename KernelName = detail::auto_name, typename... RestT> | |
| event | parallel_for (range< 1 > Range, const std::vector< event > &DepEvents, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + range that specifies global size only. More... | |
| template<typename KernelName = detail::auto_name, typename... RestT> | |
| event | parallel_for (range< 2 > Range, const std::vector< event > &DepEvents, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + range that specifies global size only. More... | |
| template<typename KernelName = detail::auto_name, typename... RestT> | |
| event | parallel_for (range< 3 > Range, const std::vector< event > &DepEvents, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + range that specifies global size only. More... | |
| template<typename KernelName = detail::auto_name, typename KernelType , int Dim> | |
| event | parallel_for (range< Dim > Range, id< Dim > WorkItemOffset, const std::vector< event > &DepEvents, _KERNELFUNCPARAM(KernelFunc)) |
| parallel_for version with a kernel represented as a lambda + range and offset that specify global size and global offset correspondingly. More... | |
| template<typename KernelName = detail::auto_name, typename KernelType , int Dims> | |
| event | parallel_for_impl (range< Dims > Range, id< Dims > WorkItemOffset, _KERNELFUNCPARAM(KernelFunc)) |
| parallel_for version with a kernel represented as a lambda + range and offset that specify global size and global offset correspondingly. More... | |
| template<typename KernelName = detail::auto_name, typename KernelType , int Dims> | |
| event | parallel_for_impl (range< Dims > Range, id< Dims > WorkItemOffset, event DepEvent, _KERNELFUNCPARAM(KernelFunc)) |
| parallel_for version with a kernel represented as a lambda + range and offset that specify global size and global offset correspondingly. More... | |
| template<typename KernelName = detail::auto_name, typename KernelType , int Dims> | |
| event | parallel_for_impl (range< Dims > Range, id< Dims > WorkItemOffset, const std::vector< event > &DepEvents, _KERNELFUNCPARAM(KernelFunc)) |
| parallel_for version with a kernel represented as a lambda + range and offset that specify global size and global offset correspondingly. More... | |
| template<typename KernelName = detail::auto_name, int Dims, typename PropertiesT , typename... RestT> | |
| std::enable_if_t< detail::AreAllButLastReductions< RestT... >::value &&ext::oneapi::experimental::is_property_list< PropertiesT >::value, event > | parallel_for (nd_range< Dims > Range, PropertiesT Properties, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + nd_range that specifies global, local sizes and offset. More... | |
| template<typename KernelName = detail::auto_name, int Dims, typename... RestT> | |
| std::enable_if_t< detail::AreAllButLastReductions< RestT... >::value, event > | parallel_for (nd_range< Dims > Range, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + nd_range that specifies global, local sizes and offset. More... | |
| template<typename KernelName = detail::auto_name, int Dims, typename... RestT> | |
| event | parallel_for (nd_range< Dims > Range, event DepEvent, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + nd_range that specifies global, local sizes and offset. More... | |
| template<typename KernelName = detail::auto_name, int Dims, typename... RestT> | |
| event | parallel_for (nd_range< Dims > Range, const std::vector< event > &DepEvents, RestT &&...Rest) |
| parallel_for version with a kernel represented as a lambda + nd_range that specifies global, local sizes and offset. More... | |
| template<typename SrcT , int SrcDims, access_mode SrcMode, target SrcTgt, access::placeholder IsPlaceholder, typename DestT > | |
| event | copy (accessor< SrcT, SrcDims, SrcMode, SrcTgt, IsPlaceholder > Src, std::shared_ptr< DestT > Dest, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from a memory region pointed to by a placeholder accessor to another memory region pointed to by a shared_ptr. More... | |
| template<typename SrcT , typename DestT , int DestDims, access_mode DestMode, target DestTgt, access::placeholder IsPlaceholder> | |
| event | copy (std::shared_ptr< SrcT > Src, accessor< DestT, DestDims, DestMode, DestTgt, IsPlaceholder > Dest, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from a memory region pointed to by a shared_ptr to another memory region pointed to by a placeholder accessor. More... | |
| template<typename SrcT , int SrcDims, access_mode SrcMode, target SrcTgt, access::placeholder IsPlaceholder, typename DestT > | |
| event | copy (accessor< SrcT, SrcDims, SrcMode, SrcTgt, IsPlaceholder > Src, DestT *Dest, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from a memory region pointed to by a placeholder accessor to another memory region pointed to by a raw pointer. More... | |
| template<typename SrcT , typename DestT , int DestDims, access_mode DestMode, target DestTgt, access::placeholder IsPlaceholder> | |
| event | copy (const SrcT *Src, accessor< DestT, DestDims, DestMode, DestTgt, IsPlaceholder > Dest, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from a memory region pointed to by a raw pointer to another memory region pointed to by a placeholder accessor. More... | |
| template<typename SrcT , int SrcDims, access_mode SrcMode, target SrcTgt, access::placeholder IsSrcPlaceholder, typename DestT , int DestDims, access_mode DestMode, target DestTgt, access::placeholder IsDestPlaceholder> | |
| event | copy (accessor< SrcT, SrcDims, SrcMode, SrcTgt, IsSrcPlaceholder > Src, accessor< DestT, DestDims, DestMode, DestTgt, IsDestPlaceholder > Dest, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Copies data from one memory region to another, both pointed by placeholder accessors. More... | |
| template<typename T , int Dims, access_mode Mode, target Tgt, access::placeholder IsPlaceholder> | |
| event | update_host (accessor< T, Dims, Mode, Tgt, IsPlaceholder > Acc, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Provides guarantees that the memory object accessed via Acc is updated on the host after operation is complete. More... | |
| template<typename T , int Dims, access_mode Mode, target Tgt, access::placeholder IsPlaceholder> | |
| event | fill (accessor< T, Dims, Mode, Tgt, IsPlaceholder > Dest, const T &Src, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Fills the specified memory with the specified data. More... | |
| bool | ext_codeplay_supports_fusion () const |
| Returns true if the queue was created with the ext::codeplay::experimental::property::queue::enable_fusion property. More... | |
| event | ext_oneapi_graph (ext::oneapi::experimental::command_graph< ext::oneapi::experimental::graph_state::executable > Graph, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Shortcut for executing a graph of commands. More... | |
| event | ext_oneapi_graph (ext::oneapi::experimental::command_graph< ext::oneapi::experimental::graph_state::executable > Graph, event DepEvent, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Shortcut for executing a graph of commands with a single dependency. More... | |
| event | ext_oneapi_graph (ext::oneapi::experimental::command_graph< ext::oneapi::experimental::graph_state::executable > Graph, const std::vector< event > &DepEvents, const detail::code_location &CodeLoc=detail::code_location::current()) |
| Shortcut for executing a graph of commands with multiple dependencies. More... | |
| bool | is_in_order () const |
| Returns whether the queue is in order or OoO. More... | |
| backend | get_backend () const noexcept |
| Returns the backend associated with this queue. More... | |
| bool | ext_oneapi_empty () const |
| Allows to check status of the queue (completed vs noncompleted). More... | |
| pi_native_handle | getNative (int32_t &NativeHandleDesc) const |
 Public Member Functions inherited from sycl::_V1::detail::OwnerLessBase< queue > | |
| bool | ext_oneapi_owner_before (const ext::oneapi::detail::weak_object_base< queue > &Other) const noexcept |
| Compares the object against a weak object using an owner-based implementation-defined ordering. More... | |
| bool | ext_oneapi_owner_before (const queue &Other) const noexcept |
| Compares the object against another object using an owner-based implementation-defined ordering. More... | |
Public Attributes | |
| const property_list & | PropList |
| const device_selector & | DeviceSelector |
| const device_selector const property_list & | PropList = {}) |
| const device_selector const async_handler & | AsyncHandler |
| const device_selector const async_handler const property_list & | PropList = {}) |
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 > |
Encapsulates a single SYCL queue which schedules kernels on a SYCL device.
A SYCL queue can be used to submit command groups to be executed by the SYCL runtime.
|
inlineexplicit |
|
inline |
|
inlineexplicit |
Constructs a SYCL queue instance using the device identified by the device selector provided.
| DeviceSelector | is SYCL 2020 Device Selector, a simple callable that takes a device and returns an int |
| AsyncHandler | is a SYCL asynchronous exception handler. |
| PropList | is a list of properties for queue construction. |
|
inlineexplicit |
Constructs a SYCL queue instance using the device identified by the device selector provided.
| DeviceSelector | is SYCL 2020 Device Selector, a simple callable that takes a device and returns an int |
| PropList | is a list of properties for queue construction. |
|
inlineexplicit |
Constructs a SYCL queue instance using the device identified by the device selector provided.
| SyclContext | is an instance of SYCL context. |
| DeviceSelector | is SYCL 2020 Device Selector, a simple callable that takes a device and returns an int |
| PropList | is a list of properties for queue construction. |
|
inlineexplicit |
Constructs a SYCL queue instance using the device identified by the device selector provided.
| SyclContext | is an instance of SYCL context. |
| DeviceSelector | is SYCL 2020 Device Selector, a simple callable that takes a device and returns an int |
| AsyncHandler | is a SYCL asynchronous exception handler. |
| PropList | is a list of properties for queue construction. |
| sycl::_V1::queue::queue | ( | const context & | SyclContext, |
| const device & | SyclDevice, | ||
| const property_list & | PropList = {} |
||
| ) |
| sycl::_V1::queue::queue | ( | const context & | SyclContext, |
| const device & | SyclDevice, | ||
| const async_handler & | AsyncHandler, | ||
| const property_list & | PropList = {} |
||
| ) |
Constructs a SYCL queue associated with the given context, device, asynchronous exception handler and optional properties list.
| SyclContext | is an instance of SYCL context. |
| SyclDevice | is an instance of SYCL device. |
| AsyncHandler | is a SYCL asynchronous exception handler. |
| PropList | is a list of properties for queue construction. |
Definition at line 40 of file queue.cpp.
References AsyncHandler, sycl::_V1::detail::getSyclObjImpl(), and PropList.
|
default |
Constructs a SYCL queue with an optional async_handler from an OpenCL cl_command_queue.
The instance of cl_command_queue is retained on construction.
| ClQueue | is a valid instance of OpenCL queue. |
| SyclContext | is a valid SYCL context. |
| AsyncHandler | is a SYCL asynchronous exception handler. |
|
default |
| sycl::_V1::queue::__SYCL2020_DEPRECATED | ( | "is_host() is deprecated as the host device is no longer supported." | ) | const |
| sycl::_V1::queue::__SYCL2020_DEPRECATED | ( | "SYCL 1.2.1 device selectors are deprecated. Please " "use SYCL 2020 device selectors instead." | ) | const & |
Constructs a SYCL queue instance that is associated with the context provided, using the device returned by the device selector.
| SyclContext | is an instance of SYCL context. |
| DeviceSelector | is an instance of SYCL device selector. |
| PropList | is a list of properties for queue construction. |
| sycl::_V1::queue::__SYCL2020_DEPRECATED | ( | "SYCL 1.2.1 device selectors are deprecated. Please " "use SYCL 2020 device selectors instead." | ) | const & |
Constructs a SYCL queue instance with an async_handler that is associated with the context provided, using the device returned by the device selector.
| SyclContext | is an instance of SYCL context. |
| DeviceSelector | is an instance of SYCL device selector. |
| AsyncHandler | is a SYCL asynchronous exception handler. |
| PropList | is a list of properties for queue construction. |
| sycl::_V1::queue::__SYCL2020_DEPRECATED | ( | "SYCL 1.2.1 device selectors are deprecated. Please " "use SYCL 2020 device selectors instead." | ) | const & |
Constructs a SYCL queue instance using the device returned by the DeviceSelector provided.
| DeviceSelector | is an instance of a SYCL 1.2.1 device_selector. |
| PropList | is a list of properties for queue construction. |
|
inline |
Copies data from a memory region pointed to by a placeholder accessor to another memory region pointed to by a raw pointer.
| Src | is a placeholder accessor to the source memory. |
| Dest | is a raw pointer to the destination memory. |
Definition at line 2619 of file queue.hpp.
References sycl::_V1::handler::copy(), and sycl::_V1::handler::require().
|
inline |
Copies data from a memory region pointed to by a placeholder accessor to another memory region pointed to by a shared_ptr.
| Src | is a placeholder accessor to the source memory. |
| Dest | is a shared_ptr to the destination memory. |
Definition at line 2579 of file queue.hpp.
References sycl::_V1::handler::copy(), and sycl::_V1::handler::require().
|
inline |
Copies data from one memory region to another, both pointed by placeholder accessors.
| Src | is a placeholder accessor to the source memory. |
| Dest | is a placeholder accessor to the destination memory. |
Definition at line 2660 of file queue.hpp.
References sycl::_V1::handler::copy(), and sycl::_V1::handler::require().
|
inline |
Copies elements of type std::remove_all_extents_t<T> from a device_global to a USM memory region.
Throws an exception if the copy operation intends to write outside the memory range
| Src,as | specified through |
| Count | and |
| StartIndex. | |
| Src | is the source device_global. |
| Dest | is a USM pointer to copy to. |
| Count | is a number of elements to copy. |
| StartIndex | is the index of the first element in Src to copy from. |
| DepEvents | is a vector of events that specifies the operation dependencies. |
Definition at line 1410 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies elements of type std::remove_all_extents_t<T> from a device_global to a USM memory region.
Throws an exception if the copy operation intends to write outside the memory range
| Src,as | specified through |
| Count | and |
| StartIndex. | |
| Src | is the source device_global. |
| Dest | is a USM pointer to copy to. |
| Count | is a number of elements to copy. |
| StartIndex | is the index of the first element in Src to copy from. |
| DepEvent | is a vector of event that specifies the operation dependency. |
Definition at line 1435 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies elements of type std::remove_all_extents_t<T> from a device_global to a USM memory region.
Throws an exception if the copy operation intends to write outside the memory range
| Src,as | specified through |
| Count | and |
| StartIndex. | |
| Src | is the source device_global. |
| Dest | is a USM pointer to copy to. |
| Count | is a number of elements to copy. |
| StartIndex | is the index of the first element in Src to copy from. |
Definition at line 1458 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies data from a memory region pointed to by a raw pointer to another memory region pointed to by a placeholder accessor.
| Src | is a raw pointer to the source memory. |
| Dest | is a placeholder accessor to the destination memory. |
Definition at line 2638 of file queue.hpp.
References sycl::_V1::handler::copy(), and sycl::_V1::handler::require().
|
inline |
Copies elements of type std::remove_all_extents_t<T> from a USM memory region to a device_global.
Throws an exception if the copy operation intends to write outside the memory range
| Dest,as | specified through |
| Count | and |
| StartIndex. | |
| Src | is a USM pointer to the source memory. |
| Dest | is the destination device_glboal. |
| Count | is a number of elements to copy. |
| StartIndex | is the index of the first element in Dest to copy to. |
| DepEvents | is a vector of events that specifies the operation dependencies. |
Definition at line 1337 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies elements of type std::remove_all_extents_t<T> from a USM memory region to a device_global.
Throws an exception if the copy operation intends to write outside the memory range
| Dest,as | specified through |
| Count | and |
| StartIndex. | |
| Src | is a USM pointer to the source memory. |
| Dest | is the destination device_glboal. |
| Count | is a number of elements to copy. |
| StartIndex | is the index of the first element in Dest to copy to. |
| DepEvent | is a vector of event that specifies the operation dependency. |
Definition at line 1362 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies elements of type std::remove_all_extents_t<T> from a USM memory region to a device_global.
Throws an exception if the copy operation intends to write outside the memory range
| Dest,as | specified through |
| Count | and |
| StartIndex. | |
| Src | is a USM pointer to the source memory. |
| Dest | is the destination device_glboal. |
| Count | is a number of elements to copy. |
| StartIndex | is the index of the first element in Dest to copy to. |
Definition at line 1385 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue.
No operations is done if
| Count | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr. The behavior is undefined if any of the pointer parameters is invalid. |
| Src | is a USM pointer to the source memory. |
| Dest | is a USM pointer to the destination memory. |
| Count | is a number of elements of type T to copy. |
| CodeLoc | contains the code location of user code |
Definition at line 647 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue.
No operations is done if
| Count | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr. The behavior is undefined if any of the pointer parameters is invalid. |
| Src | is a USM pointer to the source memory. |
| Dest | is a USM pointer to the destination memory. |
| Count | is a number of elements of type T to copy. |
| DepEvents | is a vector of events that specifies the kernel |
| CodeLoc | contains the code location of user code |
Definition at line 689 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue.
No operations is done if
| Count | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr. The behavior is undefined if any of the pointer parameters is invalid. |
| Src | is a USM pointer to the source memory. |
| Dest | is a USM pointer to the destination memory. |
| Count | is a number of elements of type T to copy. |
| DepEvent | is an event that specifies the kernel dependencies. |
| CodeLoc | contains the code location of user code |
Definition at line 668 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies data from a memory region pointed to by a shared_ptr to another memory region pointed to by a placeholder accessor.
| Src | is a shared_ptr to the source memory. |
| Dest | is a placeholder accessor to the destination memory. |
Definition at line 2599 of file queue.hpp.
References sycl::_V1::handler::copy(), and sycl::_V1::handler::require().
| bool sycl::_V1::queue::ext_codeplay_supports_fusion | ( | ) | const |
Returns true if the queue was created with the ext::codeplay::experimental::property::queue::enable_fusion property.
Equivalent to has_property<ext::codeplay::experimental::property::queue::enable_fusion>().
Definition at line 266 of file queue.cpp.
Referenced by sycl::_V1::ext::codeplay::experimental::fusion_wrapper::fusion_wrapper().
|
inline |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer.
Allows for a sub-region copy, where SrcOffset , DestOffset , and CopyExtent are used to determine the sub-region. Pixel size is determined by SrcImgDesc An exception is thrown if either Src is nullptr or Dest is incomplete.
| Src | is an opaque image memory handle to the source memory. |
| SrcOffset | is an offset from the origin of source measured in pixels (pixel size determined by SrcImgDesc ) |
| SrcImgDesc | is the source image descriptor |
| Dest | is a USM pointer to the destination memory. |
| DestOffset | is an offset from the destination origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| DestExtent | is the extent of the dest memory to copy, measured in pixels (pixel size determined by DestImgDesc ) |
| CopyExtent | is the width, height, and depth of the region to copy measured in pixels (pixel size determined by SrcImgDesc ) |
Definition at line 1694 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer.
Allows for a sub-region copy, where SrcOffset , DestOffset , and CopyExtent are used to determine the sub-region. Pixel size is determined by SrcImgDesc An exception is thrown if either Src is nullptr or Dest is incomplete.
| Src | is an opaque image memory handle to the source memory. |
| SrcOffset | is an offset from the origin of source measured in pixels (pixel size determined by SrcImgDesc ) |
| SrcImgDesc | is the source image descriptor |
| Dest | is a USM pointer to the destination memory. |
| DestOffset | is an offset from the destination origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| DestExtent | is the extent of the dest memory to copy, measured in pixels (pixel size determined by DestImgDesc ) |
| CopyExtent | is the width, height, and depth of the region to copy measured in pixels (pixel size determined by SrcImgDesc ) |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 1821 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer.
Allows for a sub-region copy, where SrcOffset , DestOffset , and CopyExtent are used to determine the sub-region. Pixel size is determined by SrcImgDesc An exception is thrown if either Src is nullptr or Dest is incomplete.
| Src | is an opaque image memory handle to the source memory. |
| SrcOffset | is an offset from the origin of source measured in pixels (pixel size determined by SrcImgDesc ) |
| SrcImgDesc | is the source image descriptor |
| Dest | is a USM pointer to the destination memory. |
| DestOffset | is an offset from the destination origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| DestExtent | is the extent of the dest memory to copy, measured in pixels (pixel size determined by DestImgDesc ) |
| CopyExtent | is the width, height, and depth of the region to copy measured in pixels (pixel size determined by SrcImgDesc ) |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 1756 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer.
An exception is thrown if either Src is incomplete or Dest is nullptr. The behavior is undefined if SrcImgDesc is inconsistent with the allocated memory region.
| Src | is an opaque image memory handle to the source memory. |
| Dest | is a USM pointer to the destination memory. |
| SrcImgDesc | is the source image descriptor. |
Definition at line 1663 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer.
An exception is thrown if either Src is incomplete or Dest is nullptr. The behavior is undefined if SrcImgDesc is inconsistent with the allocated memory region.
| Src | is an opaque image memory handle to the source memory. |
| Dest | is a USM pointer to the destination memory. |
| SrcImgDesc | is the image descriptor (format, order, dimensions). |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 1784 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is an opaque image memory handle and Dest is a USM pointer.
An exception is thrown if either Src is incomplete or Dest is nullptr. The behavior is undefined if SrcImgDesc is inconsistent with the allocated memory region.
| Src | is an opaque image memory handle to the source memory. |
| Dest | is a USM pointer to the destination memory. |
| SrcImgDesc | is the image descriptor (format, order, dimensions). |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 1720 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle wrapper.
An exception is thrown if either Src is nullptr or Dest is incomplete. The behavior is undefined if DestImgDesc is inconsistent with the allocated memory region.
| Src | is a USM pointer to the source memory. |
| Dest | is a wrapper for an opaque image memory handle to the destination memory. |
| DestImgDesc | is the image descriptor (format, order, dimensions). |
Definition at line 1480 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle wrapper.
An exception is thrown if either Src is nullptr or Dest is incomplete. The behavior is undefined if DestImgDesc is inconsistent with the allocated memory region.
| Src | is a USM pointer to the source memory. |
| Dest | is a wrapper for an opaque image memory handle to the destination memory. |
| DestImgDesc | is the destination image descriptor |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 1601 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle wrapper.
An exception is thrown if either Src is nullptr or Dest is incomplete. The behavior is undefined if DestImgDesc is inconsistent with the allocated memory region.
| Src | is a USM pointer to the source memory. |
| Dest | is a wrapper for an opaque image memory handle to the destination memory. |
| DestImgDesc | is the destination image descriptor |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 1537 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle.
Allows for a sub-region copy, where SrcOffset , DestOffset , and CopyExtent are used to determine the sub-region. An exception is thrown if either Src is nullptr or CopyExtent is incomplete.
| Src | is a USM pointer to the source memory. |
| SrcOffset | is an offset from the origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| SrcExtent | is the extent of the source memory to copy, measured in pixels (pixel size determined by DestImgDesc ) |
| Dest | is an opaque image memory handle to the destination memory. |
| DestOffset | is an offset from the destination origin measured in pixels (pixel size determined by DestImgDesc ) |
| DestImgDesc | is the destination image descriptor |
| CopyExtent | is the width, height, and depth of the region to copy measured in pixels as determined by DestImgDesc |
Definition at line 1509 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle.
Allows for a sub-region copy, where SrcOffset , DestOffset , and CopyExtent are used to determine the sub-region. An exception is thrown if either Src is nullptr or Dest is incomplete.
| Src | is a USM pointer to the source memory. |
| SrcOffset | is an offset from the origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| SrcExtent | is the extent of the source memory to copy, measured in pixels (pixel size determined by DestImgDesc ) |
| Dest | is an opaque image memory handle to the destination memory. |
| DestOffset | is an offset from the destination origin measured in pixels (pixel size determined by DestImgDesc ) |
| DestImgDesc | is the destination image descriptor |
| CopyExtent | is the width, height, and depth of the region to copy measured in pixels as determined by DestImgDesc |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 1636 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src is a USM pointer and Dest is an opaque image memory handle.
Allows for a sub-region copy, where SrcOffset , DestOffset , and CopyExtent are used to determine the sub-region. An exception is thrown if either Src is nullptr or Dest is incomplete.
| Src | is a USM pointer to the source memory. |
| SrcOffset | is an offset from the origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| SrcExtent | is the extent of the source memory to copy, measured in pixels (pixel size determined by DestImgDesc ) |
| Dest | is an opaque image memory handle to the destination memory. |
| DestOffset | is an offset from the destination origin measured in pixels (pixel size determined by DestImgDesc ) |
| DestImgDesc | is the destination image descriptor |
| CopyExtent | is the width, height, and depth of the region to copy measured in pixels as determined by DestImgDesc |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 1571 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src and Dest are USM pointers.
Allows for a sub-region copy, where SrcOffset , DestOffset , and Extent are used to determine the sub-region. An exception is thrown if either Src is nullptr or Dest is incomplete.
| Src | is a USM pointer to the source memory. |
| SrcOffset | is an destination offset from the origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| Dest | is a USM pointer to the destination memory. |
| DestOffset | is an destination offset from the origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| DeviceImgDesc | is the device image descriptor |
| DeviceRowPitch | is the row pitch on the device |
| HostExtent | is the extent of the host memory to copy, measured in pixels (pixel size determined by DeviceImgDesc ) |
| CopyExtent | is the width, height, and depth of the region to copy measured in pixels (pixel size determined by DeviceImgDesc ) |
Definition at line 1883 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src and Dest are USM pointers.
Allows for a sub-region copy, where SrcOffset , DestOffset , and Extent are used to determine the sub-region. An exception is thrown if either Src is nullptr or Dest is incomplete.
| Src | is a USM pointer to the source memory. |
| SrcOffset | is an destination offset from the origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| Dest | is a USM pointer to the destination memory. |
| DestOffset | is an destination offset from the origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| DeviceImgDesc | is the destination image descriptor |
| DeviceRowPitch | is the row pitch on the device |
| HostExtent | is the extent of the host memory to copy, measured in pixels (pixel size determined by DeviceImgDesc ) |
| CopyExtent | is the width, height, and depth of the region to copy measured in pixels (pixel size determined by DeviceImgDesc ) |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 2016 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src and Dest are USM pointers.
Allows for a sub-region copy, where SrcOffset , DestOffset , and Extent are used to determine the sub-region. An exception is thrown if either Src is nullptr or Dest is incomplete.
| Src | is a USM pointer to the source memory. |
| SrcOffset | is an destination offset from the origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| Dest | is a USM pointer to the destination memory. |
| DestOffset | is an destination offset from the origin where the x, y, and z components are measured in bytes, rows, and slices respectively |
| DeviceImgDesc | is the destination image descriptor |
| DeviceRowPitch | is the row pitch on the device |
| HostExtent | is the extent of the host memory to copy, measured in pixels (pixel size determined by DeviceImgDesc ) |
| CopyExtent | is the width, height, and depth of the region to copy measured in pixels (pixel size determined by DeviceImgDesc ) |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 1948 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src and Dest are USM pointers.
An exception is thrown if either Src is nullptr, Dest is nullptr, or Pitch is inconsistent with hardware requirements. The behavior is undefined if DeviceImgDesc is inconsistent with the allocated memory region.
| Src | is a USM pointer to the source memory. |
| Dest | is a USM pointer to the destination memory. |
| DeviceImgDesc | is the image descriptor |
| DeviceRowPitch | is the DeviceRowPitch of the rows on the device. |
Definition at line 1848 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src and Dest are USM pointers.
An exception is thrown if either Src is nullptr, Dest is nullptr, or Pitch is inconsistent with hardware requirements. The behavior is undefined if DeviceImgDesc is inconsistent with the allocated memory region.
| Src | is a USM pointer to the source memory. |
| Dest | is a USM pointer to the destination memory. |
| DeviceImgDesc | is the image descriptor |
| DeviceRowPitch | is the pitch of the rows on the device. |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 1978 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one memory region to another, where Src and Dest are USM pointers.
An exception is thrown if either Src is nullptr, Dest is nullptr, or Pitch is inconsistent with hardware requirements. The behavior is undefined if DeviceImgDesc is inconsistent with the allocated memory region.
| Src | is a USM pointer to the source memory. |
| Dest | is a USM pointer to the destination memory. |
| DeviceImgDesc | is the image descriptor |
| DeviceRowPitch | is the pitch of the rows on the device. |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 1911 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy().
|
inline |
Copies data from one 2D memory region to another, both pointed by USM pointers.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than either |
| DestPitch | or |
| SrcPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
| Src | is a USM pointer to the source memory. |
| SrcPitch | is the pitch of the rows in |
| Src. | |
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Width | is the width in number of elements of the 2D region to copy. |
| Height | is the height in number of rows of the 2D region to copy. |
Definition at line 917 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_copy2d().
|
inline |
Copies data from one 2D memory region to another, both pointed by USM pointers.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than either |
| DestPitch | or |
| SrcPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
| Src | is a USM pointer to the source memory. |
| SrcPitch | is the pitch of the rows in |
| Src. | |
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Width | is the width in number of elements of the 2D region to copy. |
| Height | is the height in number of rows of the 2D region to copy. |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 977 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy2d().
|
inline |
Copies data from one 2D memory region to another, both pointed by USM pointers.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than either |
| DestPitch | or |
| SrcPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
| Src | is a USM pointer to the source memory. |
| SrcPitch | is the pitch of the rows in |
| Src. | |
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Width | is the width in number of elements of the 2D region to copy. |
| Height | is the height in number of rows of the 2D region to copy. |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 946 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_copy2d().
| bool sycl::_V1::queue::ext_oneapi_empty | ( | ) | const |
|
inline |
Fills the memory pointed by a USM pointer with the value specified.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than |
| DestPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Pattern | is the pattern to fill into the memory. T should be trivially copyable. |
| Width | is the width in number of elements of the 2D region to fill. |
| Height | is the height in number of rows of the 2D region to fill. |
Definition at line 1095 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_fill2d().
|
inline |
Fills the memory pointed by a USM pointer with the value specified.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than |
| DestPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Pattern | is the pattern to fill into the memory. T should be trivially copyable. |
| Width | is the width in number of elements of the 2D region to fill. |
| Height | is the height in number of rows of the 2D region to fill. |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 1149 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_fill2d().
|
inline |
Fills the memory pointed by a USM pointer with the value specified.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than |
| DestPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Pattern | is the pattern to fill into the memory. T should be trivially copyable. |
| Width | is the width in number of elements of the 2D region to fill. |
| Height | is the height in number of rows of the 2D region to fill. |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 1121 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_fill2d().
| ext::oneapi::experimental::queue_state sycl::_V1::queue::ext_oneapi_get_state | ( | ) | const |
Definition at line 79 of file queue.cpp.
References sycl::_V1::ext::oneapi::experimental::executing, and sycl::_V1::ext::oneapi::experimental::recording.
|
inline |
Shortcut for executing a graph of commands.
| Graph | the graph of commands to execute |
Definition at line 2725 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_graph().
|
inline |
Shortcut for executing a graph of commands with multiple dependencies.
| Graph | the graph of commands to execute |
| DepEvents | is a vector of events that specifies the graph execution dependencies. |
Definition at line 2759 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_graph().
|
inline |
Shortcut for executing a graph of commands with a single dependency.
| Graph | the graph of commands to execute |
| DepEvent | is an event that specifies the graph execution dependencies. |
Definition at line 2739 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_graph().
|
inline |
Copies data from one 2D memory region to another, both pointed by USM pointers.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than either |
| DestPitch | or |
| SrcPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
NOTE: Function is dependent to prevent the fallback kernels from materializing without the use of the function.
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Src | is a USM pointer to the source memory. |
| SrcPitch | is the pitch of the rows in |
| Src. | |
| Width | is the width in bytes of the 2D region to copy. |
| Height | is the height in number of rows of the 2D region to copy. |
Definition at line 820 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_memcpy2d().
|
inline |
Copies data from one 2D memory region to another, both pointed by USM pointers.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than either |
| DestPitch | or |
| SrcPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
NOTE: Function is dependent to prevent the fallback kernels from materializing without the use of the function.
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Src | is a USM pointer to the source memory. |
| SrcPitch | is the pitch of the rows in |
| Src. | |
| Width | is the width in bytes of the 2D region to copy. |
| Height | is the height in number of rows of the 2D region to copy. |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 888 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_memcpy2d().
|
inline |
Copies data from one 2D memory region to another, both pointed by USM pointers.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than either |
| DestPitch | or |
| SrcPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
NOTE: Function is dependent to prevent the fallback kernels from materializing without the use of the function.
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Src | is a USM pointer to the source memory. |
| SrcPitch | is the pitch of the rows in |
| Src. | |
| Width | is the width in bytes of the 2D region to copy. |
| Height | is the height in number of rows of the 2D region to copy. |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 853 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_memcpy2d().
|
inline |
Fills the memory pointed by a USM pointer with the value specified.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than |
| DestPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
NOTE: Function is dependent to prevent the fallback kernels from materializing without the use of the function.
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Value | is the value to fill into the region in |
| Dest. | Value is cast as an unsigned char. |
| Width | is the width in number of elements of the 2D region to fill. |
| Height | is the height in number of rows of the 2D region to fill. |
Definition at line 1008 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_memset2d().
|
inline |
Fills the memory pointed by a USM pointer with the value specified.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than |
| DestPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
NOTE: Function is dependent to prevent the fallback kernels from materializing without the use of the function.
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Value | is the value to fill into the region in |
| Dest. | Value is cast as an unsigned char. |
| Width | is the width in number of elements of the 2D region to fill. |
| Height | is the height in number of rows of the 2D region to fill. |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 1069 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_memset2d().
|
inline |
Fills the memory pointed by a USM pointer with the value specified.
No operations is done if
| Width | or |
| Height | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr or if |
| Width | is strictly greater than |
| DestPitch. | The behavior is undefined if any of the pointer parameters is invalid. |
NOTE: Function is dependent to prevent the fallback kernels from materializing without the use of the function.
| Dest | is a USM pointer to the destination memory. |
| DestPitch | is the pitch of the rows in |
| Dest. | |
| Value | is the value to fill into the region in |
| Dest. | Value is cast as an unsigned char. |
| Width | is the width in number of elements of the 2D region to fill. |
| Height | is the height in number of rows of the 2D region to fill. |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 1037 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_memset2d().
|
inline |
Instruct the queue to signal the external semaphore once all previous commands have completed execution.
An exception is thrown if SemaphoreHandle is incomplete.
| SemaphoreHandle | is an opaque external interop semaphore handle |
Definition at line 2094 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_signal_external_semaphore().
|
inline |
Instruct the queue to signal the external semaphore once all previous commands have completed execution.
An exception is thrown if SemaphoreHandle is incomplete.
| SemaphoreHandle | is an opaque external interop semaphore handle |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 2133 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_signal_external_semaphore().
|
inline |
Instruct the queue to signal the external semaphore once all previous commands have completed execution.
An exception is thrown if SemaphoreHandle is incomplete.
| SemaphoreHandle | is an opaque external interop semaphore handle |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 2112 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_signal_external_semaphore().
|
inline |
Prevents any commands submitted afterward to this queue from executing until all commands previously submitted to this queue have entered the complete state.
| CodeLoc | is the code location of the submit call (default argument) |
Definition at line 414 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_barrier().
|
inline |
Prevents any commands submitted afterward to this queue from executing until all events in WaitList have entered the complete state.
If WaitList is empty, then ext_oneapi_submit_barrier has no effect.
| WaitList | is a vector of valid SYCL events that need to complete before barrier command can be executed. |
| CodeLoc | is the code location of the submit call (default argument) |
Definition at line 428 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_barrier().
|
inline |
Instruct the queue with a non-blocking wait on an external semaphore.
An exception is thrown if SemaphoreHandle is incomplete.
| SemaphoreHandle | is an opaque external interop semaphore handle |
Definition at line 2038 of file queue.hpp.
References sycl::_V1::handler::ext_oneapi_wait_external_semaphore().
|
inline |
Instruct the queue with a non-blocking wait on an external semaphore.
An exception is thrown if SemaphoreHandle is incomplete.
| SemaphoreHandle | is an opaque external interop semaphore handle |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 2075 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_wait_external_semaphore().
|
inline |
Instruct the queue with a non-blocking wait on an external semaphore.
An exception is thrown if SemaphoreHandle is incomplete.
| SemaphoreHandle | is an opaque external interop semaphore handle |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 2055 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::ext_oneapi_wait_external_semaphore().
|
inline |
Fills the specified memory with the specified data.
| Dest | is the placeholder accessor to the memory to fill. |
| Src | is the data to fill the memory with. T should be trivially copyable. |
Definition at line 2699 of file queue.hpp.
References sycl::_V1::handler::fill(), and sycl::_V1::handler::require().
|
inline |
Fills the specified memory with the specified pattern.
| Ptr | is the pointer to the memory to fill. |
| Pattern | is the pattern to fill into the memory. T should be trivially copyable. |
| Count | is the number of times to fill Pattern into Ptr. |
Definition at line 491 of file queue.hpp.
References sycl::_V1::handler::fill().
Referenced by syclcompat::detail::get_pitch().
|
inline |
Fills the specified memory with the specified pattern.
| Ptr | is the pointer to the memory to fill. |
| Pattern | is the pattern to fill into the memory. T should be trivially copyable. |
| Count | is the number of times to fill Pattern into Ptr. |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 530 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::fill().
|
inline |
Fills the specified memory with the specified pattern.
| Ptr | is the pointer to the memory to fill. |
| Pattern | is the pattern to fill into the memory. T should be trivially copyable. |
| Count | is the number of times to fill Pattern into Ptr. |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 508 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::fill().
|
noexcept |
Returns the backend associated with this queue.
Definition at line 231 of file queue.cpp.
References sycl::_V1::detail::getImplBackend().
| context sycl::_V1::queue::get_context | ( | ) | const |
Definition at line 75 of file queue.cpp.
Referenced by sycl::_V1::aligned_alloc(), sycl::_V1::aligned_alloc_device(), sycl::_V1::aligned_alloc_host(), sycl::_V1::aligned_alloc_shared(), sycl::_V1::ext::oneapi::experimental::alloc_image_mem(), sycl::_V1::ext::oneapi::experimental::create_image(), sycl::_V1::ext::oneapi::experimental::destroy_external_semaphore(), sycl::_V1::ext::oneapi::experimental::destroy_image_handle(), sycl::_V1::free(), sycl::_V1::ext::oneapi::experimental::free_image_mem(), sycl::_V1::ext::oneapi::experimental::get_image_channel_type(), sycl::_V1::ext::oneapi::experimental::get_image_num_channels(), sycl::_V1::ext::oneapi::experimental::get_image_range(), sycl::_V1::ext::oneapi::experimental::get_mip_level_mem_handle(), sycl::_V1::ext::oneapi::experimental::import_external_memory< external_mem_fd >(), sycl::_V1::ext::oneapi::experimental::import_external_semaphore(), sycl::_V1::malloc(), syclcompat::malloc(), sycl::_V1::ext::oneapi::experimental::malloc_annotated(), sycl::_V1::malloc_device(), sycl::_V1::malloc_host(), sycl::_V1::malloc_shared(), sycl::_V1::ext::oneapi::experimental::map_external_image_memory(), syclcompat::device_memory< T, Memory, 1 >::operator[](), sycl::_V1::ext::oneapi::experimental::pitched_alloc_device(), sycl::_V1::ext::oneapi::experimental::prepare_for_device_copy(), sycl::_V1::ext::oneapi::experimental::release_external_memory(), and sycl::_V1::ext::oneapi::experimental::release_from_device_copy().
| device sycl::_V1::queue::get_device | ( | ) | const |
Definition at line 77 of file queue.cpp.
Referenced by sycl::_V1::aligned_alloc(), sycl::_V1::aligned_alloc_device(), sycl::_V1::aligned_alloc_shared(), sycl::_V1::ext::oneapi::experimental::alloc_image_mem(), sycl::_V1::ext::oneapi::experimental::create_image(), sycl::_V1::ext::oneapi::experimental::destroy_external_semaphore(), sycl::_V1::ext::oneapi::experimental::destroy_image_handle(), sycl::_V1::ext::oneapi::experimental::free_image_mem(), sycl::_V1::ext::oneapi::experimental::get_image_channel_type(), sycl::_V1::ext::oneapi::experimental::get_image_num_channels(), sycl::_V1::ext::oneapi::experimental::get_image_range(), sycl::_V1::ext::oneapi::experimental::get_mip_level_mem_handle(), sycl::_V1::detail::reduction_impl_algo< T, BinaryOperation, Dims, Extent, ExplicitIdentity, RedOutVar >::getGroupsCounterAccDiscrete(), sycl::_V1::ext::oneapi::experimental::import_external_memory< external_mem_fd >(), sycl::_V1::ext::oneapi::experimental::import_external_semaphore(), sycl::_V1::malloc(), sycl::_V1::ext::oneapi::experimental::malloc_annotated(), sycl::_V1::malloc_device(), sycl::_V1::malloc_shared(), sycl::_V1::ext::oneapi::experimental::map_external_image_memory(), syclcompat::device_memory< T, Memory, 1 >::operator[](), sycl::_V1::ext::oneapi::experimental::pitched_alloc_device(), sycl::_V1::ext::intel::experimental::pipe< _name, _dataT, _min_capacity, _propertiesT, class >::read(), sycl::_V1::ext::oneapi::experimental::release_external_memory(), and sycl::_V1::ext::intel::experimental::pipe< _name, _dataT, _min_capacity, _propertiesT, class >::write().
| detail::is_queue_info_desc< Param >::return_type sycl::_V1::queue::get_info |
| PropertyT sycl::_V1::queue::get_property |
| pi_native_handle sycl::_V1::queue::getNative | ( | int32_t & | NativeHandleDesc | ) | const |
|
noexcept |
| bool sycl::_V1::queue::is_in_order | ( | ) | const |
Returns whether the queue is in order or OoO.
Equivalent to has_property<property::queue::in_order>()
| event sycl::_V1::queue::mem_advise | ( | const void * | Ptr, |
| size_t | Length, | ||
| int | Advice, | ||
| const detail::code_location & | CodeLoc = detail::code_location::current() |
||
| ) |
Provides additional information to the underlying runtime about how different allocations are used.
| Ptr | is a USM pointer to the allocation. |
| Length | is a number of bytes in the allocation. |
| Advice | is a device-defined advice for the specified allocation. |
| event sycl::_V1::queue::mem_advise | ( | const void * | Ptr, |
| size_t | Length, | ||
| int | Advice, | ||
| const std::vector< event > & | DepEvents, | ||
| const detail::code_location & | CodeLoc = detail::code_location::current() |
||
| ) |
Provides additional information to the underlying runtime about how different allocations are used.
| Ptr | is a USM pointer to the allocation. |
| Length | is a number of bytes in the allocation. |
| Advice | is a device-defined advice for the specified allocation. |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
| event sycl::_V1::queue::mem_advise | ( | const void * | Ptr, |
| size_t | Length, | ||
| int | Advice, | ||
| event | DepEvent, | ||
| const detail::code_location & | CodeLoc = detail::code_location::current() |
||
| ) |
Provides additional information to the underlying runtime about how different allocations are used.
| Ptr | is a USM pointer to the allocation. |
| Length | is a number of bytes in the allocation. |
| Advice | is a device-defined advice for the specified allocation. |
| DepEvent | is an event that specifies the kernel dependencies. |
| event sycl::_V1::queue::mem_advise | ( | const void * | Ptr, |
| size_t | Length, | ||
| pi_mem_advice | Advice, | ||
| const detail::code_location & | CodeLoc = detail::code_location::current() |
||
| ) |
Provides additional information to the underlying runtime about how different allocations are used.
| Ptr | is a USM pointer to the allocation. |
| Length | is a number of bytes in the allocation. |
| Advice | is a device-defined advice for the specified allocation. |
|
inline |
Copies data from a USM memory region to a device_global.
Throws an exception if the copy operation intends to write outside the memory range
| Dest,as | specified through |
| NumBytes | and |
| Offset. | |
| Dest | is the destination device_glboal. |
| Src | is a USM pointer to the source memory. |
| NumBytes | is a number of bytes to copy. |
| Offset | is the offset into |
| Dest | to copy to. |
| DepEvents | is a vector of events that specifies the operation dependencies. |
Definition at line 1174 of file queue.hpp.
References sycl::_V1::handler::depends_on(), sycl::_V1::ext::oneapi::experimental::has_property(), sycl::_V1::invalid, sycl::_V1::detail::isDeviceGlobalUsedInKernel(), sycl::_V1::make_error_code(), and sycl::_V1::handler::memcpy().
|
inline |
Copies data from a USM memory region to a device_global.
Throws an exception if the copy operation intends to write outside the memory range
| Dest,as | specified through |
| NumBytes | and |
| Offset. | |
| Dest | is the destination device_glboal. |
| Src | is a USM pointer to the source memory. |
| NumBytes | is a number of bytes to copy. |
| Offset | is the offset into |
| Dest | to copy to. |
| DepEvent | is a vector of event that specifies the operation dependency. |
Definition at line 1214 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies data from a USM memory region to a device_global.
Throws an exception if the copy operation intends to write outside the memory range
| Dest,as | specified through |
| NumBytes | and |
| Offset. | |
| Dest | is the destination device_glboal. |
| Src | is a USM pointer to the source memory. |
| NumBytes | is a number of bytes to copy. |
| Offset | is the offset into |
| Dest | to copy to. |
Definition at line 1234 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies data from a device_global to USM memory.
Throws an exception if the copy operation intends to read outside the memory range
| Src,as | specified through |
| NumBytes | and |
| Offset. | |
| Dest | is a USM pointer to copy to. |
| Src | is the source device_global. |
| NumBytes | is a number of bytes to copy. |
| Offset | is the offset into |
| Src | to copy from. |
| DepEvents | is a vector of events that specifies the operation dependencies. |
Definition at line 1255 of file queue.hpp.
References sycl::_V1::handler::depends_on(), sycl::_V1::ext::oneapi::experimental::has_property(), sycl::_V1::invalid, sycl::_V1::detail::isDeviceGlobalUsedInKernel(), sycl::_V1::make_error_code(), and sycl::_V1::handler::memcpy().
|
inline |
Copies data from a device_global to USM memory.
Throws an exception if the copy operation intends to read outside the memory range
| Src,as | specified through |
| NumBytes | and |
| Offset. | |
| Dest | is a USM pointer to copy to. |
| Src | is the source device_global. |
| NumBytes | is a number of bytes to copy. |
| Offset | is the offset into |
| Src | to copy from. |
| DepEvent | is a vector of event that specifies the operation dependency. |
Definition at line 1293 of file queue.hpp.
References sycl::_V1::detail::memcpy().
|
inline |
Copies data from a device_global to USM memory.
Throws an exception if the copy operation intends to read outside the memory range
| Src,as | specified through |
| NumBytes | and |
| Offset. | |
| Dest | is a USM pointer to copy to. |
| Src | is the source device_global. |
| NumBytes | is a number of bytes to copy. |
| Offset | is the offset into |
| Src | to copy from. |
Definition at line 1314 of file queue.hpp.
References sycl::_V1::detail::memcpy().
| event sycl::_V1::queue::memcpy | ( | void * | Dest, |
| const void * | Src, | ||
| size_t | Count, | ||
| const detail::code_location & | CodeLoc = detail::code_location::current() |
||
| ) |
Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue.
No operations is done if
| Count | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr. The behavior is undefined if any of the pointer parameters is invalid. |
| Dest | is a USM pointer to the destination memory. |
| Src | is a USM pointer to the source memory. |
| Count | is a number of bytes to copy. |
| event sycl::_V1::queue::memcpy | ( | void * | Dest, |
| const void * | Src, | ||
| size_t | Count, | ||
| const std::vector< event > & | DepEvents, | ||
| const detail::code_location & | CodeLoc = detail::code_location::current() |
||
| ) |
Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue.
No operations is done if
| Count | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr. The behavior is undefined if any of the pointer parameters is invalid. |
| Dest | is a USM pointer to the destination memory. |
| Src | is a USM pointer to the source memory. |
| Count | is a number of bytes to copy. |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
| event sycl::_V1::queue::memcpy | ( | void * | Dest, |
| const void * | Src, | ||
| size_t | Count, | ||
| event | DepEvent, | ||
| const detail::code_location & | CodeLoc = detail::code_location::current() |
||
| ) |
Copies data from one memory region to another, each is either a host pointer or a pointer within USM allocation accessible on the device associated with this queue.
No operations is done if
| Count | is zero. An exception is thrown if either |
| Dest | or |
| Src | is nullptr. The behavior is undefined if any of the pointer parameters is invalid. |
| Dest | is a USM pointer to the destination memory. |
| Src | is a USM pointer to the source memory. |
| Count | is a number of bytes to copy. |
| DepEvent | is an event that specifies the kernel dependencies. |
| event sycl::_V1::queue::memset | ( | void * | Ptr, |
| int | Value, | ||
| size_t | Count, | ||
| const detail::code_location & | CodeLoc = detail::code_location::current() |
||
| ) |
Fills the memory pointed by a USM pointer with the value specified.
No operations is done if
| Count | is zero. An exception is thrown if |
| Ptr | is nullptr. The behavior is undefined if |
| Ptr | is invalid. |
| Ptr | is a USM pointer to the memory to fill. |
| Value | is a value to be set. Value is cast as an unsigned char. |
| Count | is a number of bytes to fill. |
Definition at line 93 of file queue.cpp.
Referenced by sycl::_V1::detail::reduction_impl_algo< T, BinaryOperation, Dims, Extent, ExplicitIdentity, RedOutVar >::getGroupsCounterAccDiscrete(), and syclcompat::detail::malloc().
| event sycl::_V1::queue::memset | ( | void * | Ptr, |
| int | Value, | ||
| size_t | Count, | ||
| const std::vector< event > & | DepEvents, | ||
| const detail::code_location & | CodeLoc = detail::code_location::current() |
||
| ) |
Fills the memory pointed by a USM pointer with the value specified.
No operations is done if
| Count | is zero. An exception is thrown if |
| Ptr | is nullptr. The behavior is undefined if |
| Ptr | is invalid. |
| Ptr | is a USM pointer to the memory to fill. |
| Value | is a value to be set. Value is cast as an unsigned char. |
| Count | is a number of bytes to fill. |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
| event sycl::_V1::queue::memset | ( | void * | Ptr, |
| int | Value, | ||
| size_t | Count, | ||
| event | DepEvent, | ||
| const detail::code_location & | CodeLoc = detail::code_location::current() |
||
| ) |
Fills the memory pointed by a USM pointer with the value specified.
No operations is done if
| Count | is zero. An exception is thrown if |
| Ptr | is nullptr. The behavior is undefined if |
| Ptr | is invalid. |
| Ptr | is a USM pointer to the memory to fill. |
| Value | is a value to be set. Value is cast as an unsigned char. |
| Count | is a number of bytes to fill. |
| DepEvent | is an event that specifies the kernel dependencies. |
|
inline |
parallel_for version with a kernel represented as a lambda + nd_range that specifies global, local sizes and offset.
| Range | specifies the global and local work spaces of the kernel |
| DepEvents | is a vector of events that specifies the kernel dependencies |
| Rest | acts as-if: "ReductionTypes&&... Reductions, const KernelType &KernelFunc". |
Definition at line 2556 of file queue.hpp.
References sycl::_V1::handler::depends_on().
|
inline |
parallel_for version with a kernel represented as a lambda + nd_range that specifies global, local sizes and offset.
| Range | specifies the global and local work spaces of the kernel |
| DepEvent | is an event that specifies the kernel dependencies |
| Rest | acts as-if: "ReductionTypes&&... Reductions, const KernelType &KernelFunc". |
Definition at line 2532 of file queue.hpp.
References sycl::_V1::handler::depends_on().
|
inline |
parallel_for version with a kernel represented as a lambda + nd_range that specifies global, local sizes and offset.
| Range | specifies the global and local work spaces of the kernel |
| Properties | is the kernel properties. |
| Rest | acts as-if: "ReductionTypes&&... Reductions, const KernelType &KernelFunc". |
|
inline |
parallel_for version with a kernel represented as a lambda + nd_range that specifies global, local sizes and offset.
| Range | specifies the global and local work spaces of the kernel |
| Rest | acts as-if: "ReductionTypes&&... Reductions, const KernelType &KernelFunc". |
|
inline |
parallel_for version with a kernel represented as a lambda + range that specifies global size only.
| Range | specifies the global work space of the kernel |
| DepEvents | is a vector of events that specifies the kernel dependencies |
| Rest | acts as-if: "ReductionTypes&&... Reductions, const KernelType &KernelFunc". |
|
inline |
parallel_for version with a kernel represented as a lambda + range that specifies global size only.
| Range | specifies the global work space of the kernel |
| DepEvent | is an event that specifies the kernel dependencies |
| Rest | acts as-if: "ReductionTypes&&... Reductions, const KernelType &KernelFunc". |
|
inline |
parallel_for version with a kernel represented as a lambda + range that specifies global size only.
| Range | specifies the global work space of the kernel |
| DepEvents | is a vector of events that specifies the kernel dependencies |
| Rest | acts as-if: "ReductionTypes&&... Reductions, const KernelType &KernelFunc". |
|
inline |
parallel_for version with a kernel represented as a lambda + range that specifies global size only.
| Range | specifies the global work space of the kernel |
| DepEvent | is an event that specifies the kernel dependencies |
| Rest | acts as-if: "ReductionTypes&&... Reductions, const KernelType &KernelFunc". |
|
inline |
parallel_for version with a kernel represented as a lambda + range that specifies global size only.
| Range | specifies the global work space of the kernel |
| DepEvents | is a vector of events that specifies the kernel dependencies |
| Rest | acts as-if: "ReductionTypes&&... Reductions, const KernelType &KernelFunc". |
|
inline |
parallel_for version with a kernel represented as a lambda + range that specifies global size only.
| Range | specifies the global work space of the kernel |
| DepEvent | is an event that specifies the kernel dependencies |
| Rest | acts as-if: "ReductionTypes&&... Reductions, const KernelType &KernelFunc". |
|
inline |
parallel_for version with a kernel represented as a lambda + range and offset that specify global size and global offset correspondingly.
| Range | specifies the global work space of the kernel |
| WorkItemOffset | specifies the offset for each work item id |
| KernelFunc | is the Kernel functor or lambda |
| CodeLoc | contains the code location of user code |
|
inline |
parallel_for version with a kernel represented as a lambda + range and offset that specify global size and global offset correspondingly.
| Range | specifies the global work space of the kernel |
| WorkItemOffset | specifies the offset for each work item id |
| KernelFunc | is the Kernel functor or lambda |
| CodeLoc | contains the code location of user code |
|
inline |
parallel_for version with a kernel represented as a lambda + range and offset that specify global size and global offset correspondingly.
| Range | specifies the global work space of the kernel |
| WorkItemOffset | specifies the offset for each work item id |
| DepEvents | is a vector of events that specifies the kernel dependencies |
| KernelFunc | is the Kernel functor or lambda |
| CodeLoc | contains the code location of user code |
Definition at line 2469 of file queue.hpp.
References sycl::_V1::handler::depends_on().
|
inline |
parallel_for version with a kernel represented as a lambda + range and offset that specify global size and global offset correspondingly.
| Range | specifies the global work space of the kernel |
| WorkItemOffset | specifies the offset for each work item id |
| DepEvent | is an event that specifies the kernel dependencies |
| KernelFunc | is the Kernel functor or lambda |
| CodeLoc | contains the code location of user code |
Definition at line 2444 of file queue.hpp.
References sycl::_V1::handler::depends_on().
|
inline |
Provides hints to the runtime library that data should be made available on a device earlier than Unified Shared Memory would normally require it to be available.
| Ptr | is a USM pointer to the memory to be prefetched to the device. |
| Count | is a number of bytes to be prefetched. |
Definition at line 752 of file queue.hpp.
References sycl::_V1::handler::prefetch().
|
inline |
Provides hints to the runtime library that data should be made available on a device earlier than Unified Shared Memory would normally require it to be available.
| Ptr | is a USM pointer to the memory to be prefetched to the device. |
| Count | is a number of bytes to be prefetched. |
| DepEvents | is a vector of events that specifies the kernel dependencies. |
Definition at line 788 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::prefetch().
|
inline |
Provides hints to the runtime library that data should be made available on a device earlier than Unified Shared Memory would normally require it to be available.
| Ptr | is a USM pointer to the memory to be prefetched to the device. |
| Count | is a number of bytes to be prefetched. |
| DepEvent | is an event that specifies the kernel dependencies. |
Definition at line 767 of file queue.hpp.
References sycl::_V1::handler::depends_on(), and sycl::_V1::handler::prefetch().
|
inline |
|
inline |
|
inline |
single_task version with a kernel represented as a lambda.
| DepEvents | is a vector of events that specifies the kernel dependencies |
| Properties | is the kernel properties. |
| KernelFunc | is the Kernel functor or lambda |
| CodeLoc | contains the code location of user code |
Definition at line 2243 of file queue.hpp.
References sycl::_V1::handler::depends_on().
|
inline |
|
inline |
single_task version with a kernel represented as a lambda.
| DepEvent | is an event that specifies the kernel dependencies |
| Properties | is the kernel properties. |
| KernelFunc | is the Kernel functor or lambda |
| CodeLoc | contains the code location of user code |
Definition at line 2197 of file queue.hpp.
References sycl::_V1::handler::depends_on().
|
inline |
|
inline |
Submits a command group function object to the queue, in order to be scheduled for execution on the device.
| CGF | is a function object containing command group. |
| CodeLoc | is the code location of the submit call (default argument) |
Definition at line 342 of file queue.hpp.
References sycl::_V1::ext::oneapi::experimental::device_has.
Referenced by syclcompat::detail::memcpy(), sycl::_V1::ext::intel::experimental::pipe< _name, _dataT, _min_capacity, _propertiesT, class >::read(), and sycl::_V1::ext::intel::experimental::pipe< _name, _dataT, _min_capacity, _propertiesT, class >::write().
|
inline |
Submits a command group function object to the queue, in order to be scheduled for execution on the device.
On a kernel error, this command group function object is then scheduled for execution on a secondary queue.
| CGF | is a function object containing command group. |
| SecondaryQueue | is a fallback SYCL queue. |
| CodeLoc | is the code location of the submit call (default argument) |
Definition at line 379 of file queue.hpp.
References sycl::_V1::ext::oneapi::experimental::device_has.
| void sycl::_V1::queue::throw_asynchronous | ( | ) |
|
inline |
Provides guarantees that the memory object accessed via Acc is updated on the host after operation is complete.
| Acc | is a SYCL accessor that needs to be updated on host. |
Definition at line 2680 of file queue.hpp.
References sycl::_V1::handler::require(), and sycl::_V1::handler::update_host().
|
inline |
|
inline |
Performs a blocking wait for the completion of all enqueued tasks in the queue.
Synchronous errors will be reported through SYCL exceptions. Asynchronous errors will be passed to the async_handler passed to the queue on construction. If no async_handler was provided then asynchronous exceptions will be lost.
| CodeLoc | is the code location of the submit call (default argument) |
| void sycl::_V1::queue::wait_and_throw_proxy | ( | const detail::code_location & | CodeLoc | ) |
| void sycl::_V1::queue::wait_proxy | ( | const detail::code_location & | CodeLoc | ) |
|
friend |
|
friend |
Definition at line 136 of file backend.hpp.
| const device_selector const async_handler& sycl::_V1::queue::AsyncHandler |
| const device_selector & sycl::_V1::queue::DeviceSelector |
| const property_list& sycl::_V1::queue::PropList |
| const device_selector const property_list& sycl::_V1::queue::PropList = {}) |
| const device_selector const async_handler const property_list& sycl::_V1::queue::PropList = {}) |
1.8.17