.. _global: .. index:: pair: namespace; global Global Namespace ================ .. toctree:: :hidden: namespace_dpctl.rst enum_DPCTLGlobalMemCacheType.rst enum_DPCTLKernelArgType.rst enum_DPCTLPartitionAffinityDomainType.rst enum_DPCTLQueuePropertyType.rst enum_DPCTLSyclAspectType.rst enum_DPCTLSyclBackendType.rst enum_DPCTLSyclDeviceType.rst enum_DPCTLSyclEventStatusType.rst enum_DPCTLSyclUSMType.rst struct_MDLocalAccessorTy.rst struct_RawWorkGroupMemoryTy.rst Overview ~~~~~~~~ .. ref-code-block:: cpp :class: doxyrest-overview-code-block // namespaces namespace :ref:`dpctl`; namespace :ref:`dpctl::syclinterface`; // typedefs typedef void :ref:`error_handler_callback`(int err_code); typedef struct DPCTLOpaqueSyclWorkGroupMemory* :target:`DPCTLSyclWorkGroupMemoryRef`; typedef :ref:`DPCTL_C_EXTERN_C_BEGIN` struct :ref:`RawWorkGroupMemoryTy` :target:`RawWorkGroupMemory`; typedef struct :ref:`MDLocalAccessorTy` :ref:`MDLocalAccessor`; typedef struct DPCTLOpaqueSyclContext* :ref:`DPCTLSyclContextRef`; typedef struct DPCTLOpaqueSyclDevice* :ref:`DPCTLSyclDeviceRef`; typedef struct DPCTLOpaqueSyclDeviceSelector* :ref:`DPCTLSyclDeviceSelectorRef`; typedef struct DPCTLOpaqueSyclEvent* :ref:`DPCTLSyclEventRef`; typedef struct DPCTLOpaqueSyclKernelBundle* :ref:`DPCTLSyclKernelBundleRef`; typedef struct DPCTLOpaqueSyclKernel* :ref:`DPCTLSyclKernelRef`; typedef struct DPCTLOpaqueSyclPlatform* :ref:`DPCTLSyclPlatformRef`; typedef struct DPCTLOpaqueSyclQueue* :ref:`DPCTLSyclQueueRef`; typedef struct DPCTLOpaqueSyclUSM* :ref:`DPCTLSyclUSMRef`; // enums enum :ref:`DPCTLGlobalMemCacheType`; enum :ref:`DPCTLKernelArgType`; enum :ref:`DPCTLPartitionAffinityDomainType`; enum :ref:`DPCTLQueuePropertyType`; enum :ref:`DPCTLSyclAspectType`; enum :ref:`DPCTLSyclBackendType`; enum :ref:`DPCTLSyclDeviceType`; enum :ref:`DPCTLSyclEventStatusType`; enum :ref:`DPCTLSyclUSMType`; // structs struct :ref:`MDLocalAccessorTy`; struct :ref:`RawWorkGroupMemoryTy`; // global functions :ref:`DPCTL_API` uint32_t :ref:`DPCTLDevice_GetGlobalMemCacheLineSize`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` uint64_t :ref:`DPCTLDevice_GetGlobalMemCacheSize`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` :ref:`DPCTLGlobalMemCacheType` :ref:`DPCTLDevice_GetGlobalMemCacheType`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` size_t :ref:`DPCTLDevice_GetImage2dMaxHeight`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` size_t :ref:`DPCTLDevice_GetImage2dMaxWidth`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` size_t :ref:`DPCTLDevice_GetImage3dMaxDepth`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` size_t :ref:`DPCTLDevice_GetImage3dMaxHeight`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` size_t :ref:`DPCTLDevice_GetImage3dMaxWidth`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` uint32_t :ref:`DPCTLDevice_GetMaxClockFrequency`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` uint64_t :ref:`DPCTLDevice_GetMaxMemAllocSize`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` uint32_t :ref:`DPCTLDevice_GetMaxReadImageArgs`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` uint32_t :ref:`DPCTLDevice_GetMaxWriteImageArgs`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` :ref:`__dpctl_give` :ref:`DPCTLSyclDeviceRef` :ref:`DPCTLDevice_GetParentDevice`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` uint32_t :ref:`DPCTLDevice_GetPartitionMaxSubDevices`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` size_t :ref:`DPCTLDevice_GetProfilingTimerResolution`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` size_t :ref:`DPCTLDevice_Hash`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef); :ref:`DPCTL_API` bool :target:`DPCTLWorkGroupMemory_Available`(); :ref:`DPCTL_API` :ref:`__dpctl_give` :ref:`DPCTLSyclWorkGroupMemoryRef` :target:`DPCTLWorkGroupMemory_Create`(size_t nbytes); :ref:`DPCTL_API` void :target:`DPCTLWorkGroupMemory_Delete`(:ref:`__dpctl_take` :ref:`DPCTLSyclWorkGroupMemoryRef` Ref); :ref:`DPCTL_API` :ref:`__dpctl_give` :ref:`DPCTLSyclEventRef` :ref:`DPCTLQueue_SubmitBarrier`(:ref:`__dpctl_keep` const :ref:`DPCTLSyclQueueRef` QRef); :ref:`DPCTL_API` :ref:`__dpctl_give` :ref:`DPCTLSyclEventRef` :ref:`DPCTLQueue_SubmitBarrierForEvents`( :ref:`__dpctl_keep` const :ref:`DPCTLSyclQueueRef` QRef, :ref:`__dpctl_keep` const :ref:`DPCTLSyclEventRef`* DepEvents, size_t NDepEvents ); :ref:`DPCTL_C_EXTERN_C_BEGIN` :ref:`DPCTL_API` void :ref:`DPCTLCString_Delete`(:ref:`__dpctl_take` const char* str); :ref:`DPCTL_API` void :ref:`DPCTLSize_t_Array_Delete`(:ref:`__dpctl_take` size_t* arr); // macros #define :target:`DPCTL_C_EXTERN_C_BEGIN` #define :target:`DPCTL_C_EXTERN_C_END` #define :target:`DPCTL_DECLARE_VECTOR`(EL) #define :target:`DPCTL_DECLARE_VECTOR_FN`(EL) #define :ref:`DPCTL_DECLARE_VECTOR_TYPE`(EL) #define :target:`DPCTL_DPCPP_VERSION` #define :target:`DPCTL_ENABLE_L0_PROGRAM_CREATION` #define :target:`DPCTL_LIBCL_LOADER_FILENAME` #define :target:`DPCTL_LIBZE_LOADER_FILENAME` #define :ref:`HUGE_VALF` #define :ref:`INT64_MAX` #define :ref:`INT64_MIN` #define :ref:`UINT64_MAX` #define :target:`__SYCL_COMPILER_VERSION_REQUIRED` .. _details-global: Detailed Documentation ~~~~~~~~~~~~~~~~~~~~~~ Typedefs -------- .. index:: pair: typedef; error_handler_callback .. _doxid-de/d75/dpctl__error__handler__type_8h_1aeb0f262687ced57ead8f8b7d0b7dcefe: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef void error_handler_callback(int err_code) Type of function to be used in SYCL async error handler provide by DPCTL. .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - err_code - Error code extracted from an SYCL asynchronous error. .. index:: pair: typedef; MDLocalAccessor .. _doxid-da/db8/dpctl__sycl__queue__interface_8h_1a7779ae83e3fd4db1174768e1ba62f30b: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef struct :ref:`MDLocalAccessorTy` MDLocalAccessor Structure to be used to specify dimensionality and type of local_accessor kernel type argument. .. index:: pair: typedef; DPCTLSyclContextRef .. _doxid-df/d57/dpctl__sycl__types_8h_1accf78808322af80b73da617cb2f15f08: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef struct DPCTLOpaqueSyclContext* DPCTLSyclContextRef Opaque pointer to a ``sycl::context`` .. index:: pair: typedef; DPCTLSyclDeviceRef .. _doxid-df/d57/dpctl__sycl__types_8h_1a8dae76b436012ecbdebbd568e77f440d: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef struct DPCTLOpaqueSyclDevice* DPCTLSyclDeviceRef Opaque pointer to a ``sycl::device`` .. index:: pair: typedef; DPCTLSyclDeviceSelectorRef .. _doxid-df/d57/dpctl__sycl__types_8h_1a50a1c6c98f4ca4a27a88e53a7f3eeb83: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef struct DPCTLOpaqueSyclDeviceSelector* DPCTLSyclDeviceSelectorRef Opaque pointer to a ``sycl::device_selector`` .. index:: pair: typedef; DPCTLSyclEventRef .. _doxid-df/d57/dpctl__sycl__types_8h_1a42590892ae4324c54f6ddef34009ca03: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef struct DPCTLOpaqueSyclEvent* DPCTLSyclEventRef Opaque pointer to a ``sycl::event`` .. index:: pair: typedef; DPCTLSyclKernelBundleRef .. _doxid-df/d57/dpctl__sycl__types_8h_1a6d9c52ea7d2e9394ddf7ba7e7f01bebd: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef struct DPCTLOpaqueSyclKernelBundle* DPCTLSyclKernelBundleRef Opaque pointer to a ``sycl::kernel_bundle`` .. index:: pair: typedef; DPCTLSyclKernelRef .. _doxid-df/d57/dpctl__sycl__types_8h_1a3f6be07fdf695c015719ce0b0c237844: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef struct DPCTLOpaqueSyclKernel* DPCTLSyclKernelRef Opaque pointer to a ``sycl::kernel`` .. index:: pair: typedef; DPCTLSyclPlatformRef .. _doxid-df/d57/dpctl__sycl__types_8h_1aae750289dcff2c3739f4870086ac7ed0: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef struct DPCTLOpaqueSyclPlatform* DPCTLSyclPlatformRef Opaque pointer to a ``sycl::platform`` .. index:: pair: typedef; DPCTLSyclQueueRef .. _doxid-df/d57/dpctl__sycl__types_8h_1af23137a8bf20ff63b10db9f7f987799a: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef struct DPCTLOpaqueSyclQueue* DPCTLSyclQueueRef Opaque pointer to a ``sycl::queue`` .. index:: pair: typedef; DPCTLSyclUSMRef .. _doxid-df/d57/dpctl__sycl__types_8h_1a8c78ad1413045f90e15f5b6a2727d2e6: .. ref-code-block:: cpp :class: doxyrest-title-code-block typedef struct DPCTLOpaqueSyclUSM* DPCTLSyclUSMRef Used to pass a ``sycl::usm`` memory opaquely through DPCTL interfaces. Global Functions ---------------- .. index:: pair: function; DPCTLDevice_GetGlobalMemCacheLineSize .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1ac47e84e08c40272eb54358b6ab76c0f0: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` uint32_t DPCTLDevice_GetGlobalMemCacheLineSize(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the size of global memory cache line in bytes as uint32_t. .. index:: pair: function; DPCTLDevice_GetGlobalMemCacheSize .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1ae4641fb22da8c78a1c5b3c9a0c0fd913: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` uint64_t DPCTLDevice_GetGlobalMemCacheSize(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the size of global memory cache in bytes as uint64_t. .. index:: pair: function; DPCTLDevice_GetGlobalMemCacheType .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1a34aef85cc31edf294aece8d68f5bccba: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` :ref:`DPCTLGlobalMemCacheType` DPCTLDevice_GetGlobalMemCacheType(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the type of global memory cache supported. .. index:: pair: function; DPCTLDevice_GetImage2dMaxHeight .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1a4ef25a38cbf63e618016302e8ebf480d: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` size_t DPCTLDevice_GetImage2dMaxHeight(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info(). .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the maximum height of a 2D image or 1D image in pixels. The minimum value is 8192 if the SYCL device has aspect::image. .. index:: pair: function; DPCTLDevice_GetImage2dMaxWidth .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1ad1f6957fdc5fb51ed873fa444af17c13: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` size_t DPCTLDevice_GetImage2dMaxWidth(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info(). .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the maximum width of a 2D image or 1D image in pixels. The minimum value is 8192 if the SYCL device has aspect::image. .. index:: pair: function; DPCTLDevice_GetImage3dMaxDepth .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1ac64423a160a010d1841b36ae2ab48658: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` size_t DPCTLDevice_GetImage3dMaxDepth(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info(). .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the maximum depth of a 3D image The minimum value is 2048 if the SYCL device has aspect::image. .. index:: pair: function; DPCTLDevice_GetImage3dMaxHeight .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1ac041263954e4e4c2a5bf58eeb08c0b7e: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` size_t DPCTLDevice_GetImage3dMaxHeight(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info(). .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the maximum height of a 3D image The minimum value is 2048 if the SYCL device has aspect::image. .. index:: pair: function; DPCTLDevice_GetImage3dMaxWidth .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1a775e74dcd25c38e1d1575df3262b6f60: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` size_t DPCTLDevice_GetImage3dMaxWidth(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info(). .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the maximum width of a 3D image in pixels. The minimum value is 2048 if the SYCL device has aspect::image. .. index:: pair: function; DPCTLDevice_GetMaxClockFrequency .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1a8a86e895dc25e747f8f4349100d85809: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` uint32_t DPCTLDevice_GetMaxClockFrequency(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the maximum clock frequency in MHz as uint32_t. .. index:: pair: function; DPCTLDevice_GetMaxMemAllocSize .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1ad546933b32f0c9917982f39ddf0be5c6: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` uint64_t DPCTLDevice_GetMaxMemAllocSize(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the maximum size of memory object in bytes as uint64_t. .. index:: pair: function; DPCTLDevice_GetMaxReadImageArgs .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1a9810a239416c53427e3742bfb72ea0a6: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` uint32_t DPCTLDevice_GetMaxReadImageArgs(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info(). .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the maximum number of simultaneous image objects that can be read from by a kernel. The minimum value is 128 if the SYCL device has aspect::image. .. index:: pair: function; DPCTLDevice_GetMaxWriteImageArgs .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1a34dbd5b5dbde22ba5f1d5205de298d81: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` uint32_t DPCTLDevice_GetMaxWriteImageArgs(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info(). .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the maximum number of simultaneous image objects that can be written to by a kernel. The minimum value is 8 if the SYCL device has aspect::image. .. index:: pair: function; DPCTLDevice_GetParentDevice .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1acccdc3f034e6c5fd2a249907355169bc: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` :ref:`__dpctl_give` :ref:`DPCTLSyclDeviceRef` DPCTLDevice_GetParentDevice(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns an opaque pointer to the parent device for a sub-device, or nullptr otherwise. .. index:: pair: function; DPCTLDevice_GetPartitionMaxSubDevices .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1ab48d25118cd217ccd917993afba98570: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` uint32_t DPCTLDevice_GetPartitionMaxSubDevices(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the maximum number of sub-devices that can be created when this device is partitioned. .. index:: pair: function; DPCTLDevice_GetProfilingTimerResolution .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1a5fe67bf4915e62ce08d80d810f0e8632: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` size_t DPCTLDevice_GetProfilingTimerResolution(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over device.get_info .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns the resolution of device timer in nanoseconds. .. index:: pair: function; DPCTLDevice_Hash .. _doxid-d4/d5a/dpctl__sycl__device__interface_8h_1a28538fa8029a6d4c7ff4d972ec690b97: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` size_t DPCTLDevice_Hash(:ref:`__dpctl_keep` const :ref:`DPCTLSyclDeviceRef` DRef) Wrapper over std::hash's operator() .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - DRef - Opaque pointer to a sycl::device .. rubric:: Returns: Returns hash value. .. index:: pair: function; DPCTLQueue_SubmitBarrier .. _doxid-da/db8/dpctl__sycl__queue__interface_8h_1a2453786e50a7d7e51a0d240b2ce52f53: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` :ref:`__dpctl_give` :ref:`DPCTLSyclEventRef` DPCTLQueue_SubmitBarrier(:ref:`__dpctl_keep` const :ref:`DPCTLSyclQueueRef` QRef) C-API wrapper for ``sycl::queue::submit_barrier()``. .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - QRef - An opaque pointer to the ``sycl::queue``. .. rubric:: Returns: An opaque pointer to the ``sycl::event`` returned by the ``sycl::queue::submit_barrier()`` function. .. index:: pair: function; DPCTLQueue_SubmitBarrierForEvents .. _doxid-da/db8/dpctl__sycl__queue__interface_8h_1a1666c1e2da52e7736cfc662a7c0ad6fb: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` :ref:`__dpctl_give` :ref:`DPCTLSyclEventRef` DPCTLQueue_SubmitBarrierForEvents( :ref:`__dpctl_keep` const :ref:`DPCTLSyclQueueRef` QRef, :ref:`__dpctl_keep` const :ref:`DPCTLSyclEventRef`* DepEvents, size_t NDepEvents ) C-API wrapper for ``sycl::queue::submit_barrier(event_vector)``. .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - QRef - An opaque pointer to the ``sycl::queue``. * - DepEvents - List of dependent DPCTLSyclEventRef objects (events) for the barrier. We call ``sycl::handler.depends_on`` for each of the provided events. * - NDepEvents - Size of the DepEvents list. .. rubric:: Returns: An opaque pointer to the ``sycl::event`` returned by the ``sycl::queue::submit_barrier()`` function. .. index:: pair: function; DPCTLCString_Delete .. _doxid-da/d48/dpctl__utils_8h_1a33267597953b5a15fc3a052e0d09ef06: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_C_EXTERN_C_BEGIN` :ref:`DPCTL_API` void DPCTLCString_Delete(:ref:`__dpctl_take` const char* str) Deletes the C String argument. .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - str - C string to be deleted .. index:: pair: function; DPCTLSize_t_Array_Delete .. _doxid-da/d48/dpctl__utils_8h_1a8666dbbe5583326eb3b57293be168ffc: .. ref-code-block:: cpp :class: doxyrest-title-code-block :ref:`DPCTL_API` void DPCTLSize_t_Array_Delete(:ref:`__dpctl_take` size_t* arr) Deletes an array of size_t elements. .. rubric:: Parameters: .. list-table:: :widths: 20 80 * - arr - Array to be deleted. Macros ------ .. index:: pair: define; DPCTL_DECLARE_VECTOR_TYPE .. _doxid-d4/d64/dpctl__vector_8h_1a83a0669601a2adec6b227cc2276a1538: .. ref-code-block:: cpp :class: doxyrest-title-code-block #define DPCTL_DECLARE_VECTOR_TYPE(EL) Declare an opaque pointer type for a std::vector of opaque pointers wrapping SYCL data types. .. index:: pair: define; HUGE_VALF .. _doxid-dd/d1c/dpctl__data__types_8h_1acd69981d54c27fe0ff514645dbfc6359: .. ref-code-block:: cpp :class: doxyrest-title-code-block #define HUGE_VALF Represents a positive expression of type float. .. index:: pair: define; INT64_MAX .. _doxid-dd/d1c/dpctl__data__types_8h_1ad0d744f05898e32d01f73f8af3cd2071: .. ref-code-block:: cpp :class: doxyrest-title-code-block #define INT64_MAX Represents the largest possible value of a 64 bit signed integer. .. index:: pair: define; INT64_MIN .. _doxid-dd/d1c/dpctl__data__types_8h_1ab21f12f372f67b8ff0aa3432336ede67: .. ref-code-block:: cpp :class: doxyrest-title-code-block #define INT64_MIN Represents the smallest possible value of a 64 bit signed integer. .. index:: pair: define; UINT64_MAX .. _doxid-dd/d1c/dpctl__data__types_8h_1a30654b4b67d97c42ca3f9b6052dda916: .. ref-code-block:: cpp :class: doxyrest-title-code-block #define UINT64_MAX Represents the largest possible value of a 64bit unsigned integer.