Global enum and defines

Classes
struct	dim3
struct	hipLaunchParams_t
struct	hipExternalMemoryHandleDesc_st
struct	hipExternalMemoryBufferDesc_st

Macros
#define	hipStreamDefault    0x00
	Flags that can be used with hipStreamCreateWithFlags. More...
#define	hipStreamNonBlocking   0x01
	Stream does not implicitly synchronize with null stream.
#define	hipEventDefault   0x0
	Flags that can be used with hipEventCreateWithFlags: More...
#define	hipEventBlockingSync    0x1
	Waiting will yield CPU. Power-friendly and usage-friendly but may increase latency.
#define	hipEventDisableTiming    0x2
	Disable event's capability to record timing information. May improve performance.
#define	hipEventInterprocess   0x4
	Event can support IPC. More...
#define	hipEventReleaseToDevice    0x40000000
#define	hipEventReleaseToSystem    0x80000000
#define	hipHostMallocDefault   0x0
	Flags that can be used with hipHostMalloc. More...
#define	hipHostMallocPortable   0x1
	Memory is considered allocated by all contexts.
#define	hipHostMallocMapped    0x2
	can be obtained with hipHostGetDevicePointer. More...
#define	hipHostMallocWriteCombined   0x4
#define	hipHostMallocNumaUser    0x20000000
	Host memory allocation will follow numa policy set by user.
#define	hipHostMallocCoherent    0x40000000
	allocation. More...
#define	hipHostMallocNonCoherent    0x80000000
	allocation. More...
#define	hipMemAttachGlobal   0x01
	Memory can be accessed by any stream on any device.
#define	hipMemAttachHost   0x02
	Memory cannot be accessed by any stream on any device.
#define	hipMemAttachSingle   0x04
	the associated device More...
#define	hipDeviceMallocDefault   0x0
#define	hipDeviceMallocFinegrained   0x1
	Memory is allocated in fine grained region of device.
#define	hipMallocSignalMemory   0x2
	Memory represents a HSA signal.
#define	hipHostRegisterDefault   0x0
	Flags that can be used with hipHostRegister. More...
#define	hipHostRegisterPortable   0x1
	Memory is considered registered by all contexts.
#define	hipHostRegisterMapped    0x2
	can be obtained with hipHostGetDevicePointer. More...
#define	hipHostRegisterIoMemory   0x4
	Not supported.
#define	hipExtHostRegisterCoarseGrained   0x8
	Coarse Grained host memory lock.
#define	hipDeviceScheduleAuto   0x0
	Automatically select between Spin and Yield.
#define	hipDeviceScheduleSpin    0x1
	may consume more power. More...
#define	hipDeviceScheduleYield    0x2
	power and is friendlier to other threads in the system. More...
#define	hipDeviceScheduleBlockingSync   0x4
#define	hipDeviceScheduleMask   0x7
#define	hipDeviceMapHost   0x8
#define	hipDeviceLmemResizeToMax   0x16
#define	hipArrayDefault   0x00
	Default HIP array allocation flag.
#define	hipArrayLayered   0x01
#define	hipArraySurfaceLoadStore   0x02
#define	hipArrayCubemap   0x04
#define	hipArrayTextureGather   0x08
#define	hipOccupancyDefault   0x00
#define	hipCooperativeLaunchMultiDeviceNoPreSync   0x01
#define	hipCooperativeLaunchMultiDeviceNoPostSync   0x02
#define	hipCpuDeviceId   ((int)-1)
#define	hipInvalidDeviceId   ((int)-2)
#define	hipExtAnyOrderLaunch   0x01
	AnyOrderLaunch of kernels.
#define	hipStreamWaitValueGte   0x0
#define	hipStreamWaitValueEq   0x1
#define	hipStreamWaitValueAnd   0x2
#define	hipStreamWaitValueNor   0x3
#define	__HIP_NODISCARD

Typedefs
typedef enum hipMemoryAdvise	hipMemoryAdvise
typedef enum hipMemRangeAttribute	hipMemRangeAttribute
typedef enum hipJitOption	hipJitOption
typedef enum hipFuncAttribute	hipFuncAttribute
typedef enum hipFuncCache_t	hipFuncCache_t
typedef enum hipSharedMemConfig	hipSharedMemConfig
typedef struct dim3	dim3
typedef struct hipLaunchParams_t	hipLaunchParams
typedef enum hipExternalMemoryHandleType_enum	hipExternalMemoryHandleType
typedef struct hipExternalMemoryHandleDesc_st	hipExternalMemoryHandleDesc
typedef struct hipExternalMemoryBufferDesc_st	hipExternalMemoryBufferDesc
typedef void *	hipExternalMemory_t
typedef enum __HIP_NODISCARD hipError_t	hipError_t
typedef enum hipDeviceAttribute_t	hipDeviceAttribute_t

Enumerations
enum	hipMemoryAdvise {   hipMemAdviseSetReadMostly = 1 , hipMemAdviseUnsetReadMostly = 2 , hipMemAdviseSetPreferredLocation = 3 , hipMemAdviseUnsetPreferredLocation = 4 ,   hipMemAdviseSetAccessedBy = 5 , hipMemAdviseUnsetAccessedBy = 6 , hipMemAdviseSetReadMostly , hipMemAdviseUnsetReadMostly ,   hipMemAdviseSetPreferredLocation , hipMemAdviseUnsetPreferredLocation , hipMemAdviseSetAccessedBy , hipMemAdviseUnsetAccessedBy }
enum	hipMemRangeAttribute { hipMemRangeAttributeReadMostly = 1 , hipMemRangeAttributePreferredLocation = 2 , hipMemRangeAttributeAccessedBy = 3 , hipMemRangeAttributeLastPrefetchLocation = 4 }
enum	hipJitOption {   hipJitOptionMaxRegisters = 0 , hipJitOptionThreadsPerBlock , hipJitOptionWallTime , hipJitOptionInfoLogBuffer ,   hipJitOptionInfoLogBufferSizeBytes , hipJitOptionErrorLogBuffer , hipJitOptionErrorLogBufferSizeBytes , hipJitOptionOptimizationLevel ,   hipJitOptionTargetFromContext , hipJitOptionTarget , hipJitOptionFallbackStrategy , hipJitOptionGenerateDebugInfo ,   hipJitOptionLogVerbose , hipJitOptionGenerateLineInfo , hipJitOptionCacheMode , hipJitOptionSm3xOpt ,   hipJitOptionFastCompile , hipJitOptionNumOptions }
enum	hipFuncAttribute { hipFuncAttributeMaxDynamicSharedMemorySize = 8 , hipFuncAttributePreferredSharedMemoryCarveout = 9 , hipFuncAttributeMax }
enum	hipFuncCache_t { hipFuncCachePreferNone , hipFuncCachePreferShared , hipFuncCachePreferL1 , hipFuncCachePreferEqual }
enum	hipSharedMemConfig { hipSharedMemBankSizeDefault , hipSharedMemBankSizeFourByte , hipSharedMemBankSizeEightByte }
enum	hipExternalMemoryHandleType_enum {   hipExternalMemoryHandleTypeOpaqueFd = 1 , hipExternalMemoryHandleTypeOpaqueWin32 = 2 , hipExternalMemoryHandleTypeOpaqueWin32Kmt = 3 , hipExternalMemoryHandleTypeD3D12Heap = 4 ,   hipExternalMemoryHandleTypeD3D12Resource = 5 , hipExternalMemoryHandleTypeD3D11Resource = 6 , hipExternalMemoryHandleTypeD3D11ResourceKmt = 7 }
enum	hipDeviceAttribute_t {   hipDeviceAttributeMaxThreadsPerBlock , hipDeviceAttributeMaxBlockDimX , hipDeviceAttributeMaxBlockDimY , hipDeviceAttributeMaxBlockDimZ ,   hipDeviceAttributeMaxGridDimX , hipDeviceAttributeMaxGridDimY , hipDeviceAttributeMaxGridDimZ , hipDeviceAttributeMaxSharedMemoryPerBlock ,   hipDeviceAttributeTotalConstantMemory , hipDeviceAttributeWarpSize , hipDeviceAttributeMaxRegistersPerBlock , hipDeviceAttributeClockRate ,   hipDeviceAttributeMemoryClockRate , hipDeviceAttributeMemoryBusWidth , hipDeviceAttributeMultiprocessorCount , hipDeviceAttributeComputeMode ,   hipDeviceAttributeL2CacheSize , hipDeviceAttributeMaxThreadsPerMultiProcessor , hipDeviceAttributeComputeCapabilityMajor , hipDeviceAttributeComputeCapabilityMinor ,   hipDeviceAttributeConcurrentKernels , hipDeviceAttributePciBusId , hipDeviceAttributePciDeviceId , hipDeviceAttributeMaxSharedMemoryPerMultiprocessor ,   hipDeviceAttributeIsMultiGpuBoard , hipDeviceAttributeIntegrated , hipDeviceAttributeCooperativeLaunch , hipDeviceAttributeCooperativeMultiDeviceLaunch ,   hipDeviceAttributeMaxTexture1DWidth , hipDeviceAttributeMaxTexture2DWidth , hipDeviceAttributeMaxTexture2DHeight , hipDeviceAttributeMaxTexture3DWidth ,   hipDeviceAttributeMaxTexture3DHeight , hipDeviceAttributeMaxTexture3DDepth , hipDeviceAttributeHdpMemFlushCntl , hipDeviceAttributeHdpRegFlushCntl ,   hipDeviceAttributeMaxPitch , hipDeviceAttributeTextureAlignment , hipDeviceAttributeTexturePitchAlignment , hipDeviceAttributeKernelExecTimeout ,   hipDeviceAttributeCanMapHostMemory , hipDeviceAttributeEccEnabled , hipDeviceAttributeCooperativeMultiDeviceUnmatchedFunc , hipDeviceAttributeCooperativeMultiDeviceUnmatchedGridDim ,   hipDeviceAttributeCooperativeMultiDeviceUnmatchedBlockDim , hipDeviceAttributeCooperativeMultiDeviceUnmatchedSharedMem , hipDeviceAttributeAsicRevision , hipDeviceAttributeManagedMemory ,   hipDeviceAttributeDirectManagedMemAccessFromHost , hipDeviceAttributeConcurrentManagedAccess , hipDeviceAttributePageableMemoryAccess , hipDeviceAttributePageableMemoryAccessUsesHostPageTables ,   hipDeviceAttributeCanUseStreamWaitValue }
enum	hipComputeMode { hipComputeModeDefault = 0 , hipComputeModeExclusive = 1 , hipComputeModeProhibited = 2 , hipComputeModeExclusiveProcess = 3 }

Detailed Description

Macro Definition Documentation

hipDeviceScheduleSpin

#define hipDeviceScheduleSpin    0x1

may consume more power.

Dedicate a CPU core to spin-wait. Provides lowest latency, but burns a CPU core and

hipDeviceScheduleYield

#define hipDeviceScheduleYield    0x2

power and is friendlier to other threads in the system.

Yield the CPU to the operating system when waiting. May increase latency, but lowers

hipEventDefault

#define hipEventDefault   0x0

Flags that can be used with hipEventCreateWithFlags:

Default flags

hipEventInterprocess

#define hipEventInterprocess   0x4

Event can support IPC.

Warning

- not supported in HIP.

hipEventReleaseToSystem

#define hipEventReleaseToSystem    0x80000000

< Use a device-scope release when recording this event. This flag is useful to obtain more precise timings of commands between events. The flag is a no-op on CUDA platforms.

hipHostMallocCoherent

#define hipHostMallocCoherent    0x40000000

allocation.

Allocate coherent memory. Overrides HIP_COHERENT_HOST_ALLOC for specific

hipHostMallocDefault

#define hipHostMallocDefault   0x0

Flags that can be used with hipHostMalloc.

< Use a system-scope release when recording this event. This flag is useful to make non-coherent host memory visible to the host. The flag is a no-op on CUDA platforms.

hipHostMallocMapped

#define hipHostMallocMapped    0x2

can be obtained with hipHostGetDevicePointer.

Map the allocation into the address space for the current device. The device pointer

hipHostMallocNonCoherent

#define hipHostMallocNonCoherent    0x80000000

allocation.

Allocate non-coherent memory. Overrides HIP_COHERENT_HOST_ALLOC for specific

hipHostRegisterDefault

#define hipHostRegisterDefault   0x0

Flags that can be used with hipHostRegister.

Memory is Mapped and Portable

hipHostRegisterMapped

#define hipHostRegisterMapped    0x2

can be obtained with hipHostGetDevicePointer.

Map the allocation into the address space for the current device. The device pointer

hipMemAttachSingle

#define hipMemAttachSingle   0x04

the associated device

Memory can only be accessed by a single stream on

hipStreamDefault

#define hipStreamDefault    0x00

Flags that can be used with hipStreamCreateWithFlags.

Default stream creation flags. These are used with hipStreamCreate().

Typedef Documentation

dim3

typedef struct dim3 dim3

Struct for data in 3D

hipFuncAttribute

typedef enum hipFuncAttribute hipFuncAttribute

Warning

On AMD devices and some Nvidia devices, these hints and controls are ignored.

hipFuncCache_t

typedef enum hipFuncCache_t hipFuncCache_t

Warning

On AMD devices and some Nvidia devices, these hints and controls are ignored.

hipSharedMemConfig

typedef enum hipSharedMemConfig hipSharedMemConfig

Warning

On AMD devices and some Nvidia devices, these hints and controls are ignored.

Enumeration Type Documentation

hipDeviceAttribute_t

enum hipDeviceAttribute_t

Enumerator
hipDeviceAttributeMaxThreadsPerBlock	Maximum number of threads per block.
hipDeviceAttributeMaxBlockDimX	Maximum x-dimension of a block.
hipDeviceAttributeMaxBlockDimY	Maximum y-dimension of a block.
hipDeviceAttributeMaxBlockDimZ	Maximum z-dimension of a block.
hipDeviceAttributeMaxGridDimX	Maximum x-dimension of a grid.
hipDeviceAttributeMaxGridDimY	Maximum y-dimension of a grid.
hipDeviceAttributeMaxGridDimZ	Maximum z-dimension of a grid.
hipDeviceAttributeMaxSharedMemoryPerBlock	Maximum shared memory available per block in bytes.
hipDeviceAttributeTotalConstantMemory	Constant memory size in bytes.
hipDeviceAttributeWarpSize	Warp size in threads.
hipDeviceAttributeMaxRegistersPerBlock	Maximum number of 32-bit registers available to a thread block. This number is shared by all thread blocks simultaneously resident on a multiprocessor.
hipDeviceAttributeClockRate	Peak clock frequency in kilohertz.
hipDeviceAttributeMemoryClockRate	Peak memory clock frequency in kilohertz.
hipDeviceAttributeMemoryBusWidth	Global memory bus width in bits.
hipDeviceAttributeMultiprocessorCount	Number of multiprocessors on the device.
hipDeviceAttributeComputeMode	Compute mode that device is currently in.
hipDeviceAttributeL2CacheSize	Size of L2 cache in bytes. 0 if the device doesn't have L2 cache.
hipDeviceAttributeMaxThreadsPerMultiProcessor	Maximum resident threads per multiprocessor.
hipDeviceAttributeComputeCapabilityMajor	Major compute capability version number.
hipDeviceAttributeComputeCapabilityMinor	Minor compute capability version number.
hipDeviceAttributeConcurrentKernels	Device can possibly execute multiple kernels concurrently.
hipDeviceAttributePciBusId	PCI Bus ID.
hipDeviceAttributePciDeviceId	PCI Device ID.
hipDeviceAttributeMaxSharedMemoryPerMultiprocessor	Maximum Shared Memory Per Multiprocessor.
hipDeviceAttributeIsMultiGpuBoard	Multiple GPU devices.
hipDeviceAttributeIntegrated	iGPU
hipDeviceAttributeCooperativeLaunch	Support cooperative launch.
hipDeviceAttributeCooperativeMultiDeviceLaunch	Support cooperative launch on multiple devices.
hipDeviceAttributeMaxTexture1DWidth	Maximum number of elements in 1D images.
hipDeviceAttributeMaxTexture2DWidth	Maximum dimension width of 2D images in image elements.
hipDeviceAttributeMaxTexture2DHeight	Maximum dimension height of 2D images in image elements.
hipDeviceAttributeMaxTexture3DWidth	Maximum dimension width of 3D images in image elements.
hipDeviceAttributeMaxTexture3DHeight	Maximum dimensions height of 3D images in image elements.
hipDeviceAttributeMaxTexture3DDepth	Maximum dimensions depth of 3D images in image elements.
hipDeviceAttributeHdpMemFlushCntl	Address of the HDP_MEM_COHERENCY_FLUSH_CNTL register.
hipDeviceAttributeHdpRegFlushCntl	Address of the HDP_REG_COHERENCY_FLUSH_CNTL register.
hipDeviceAttributeMaxPitch	Maximum pitch in bytes allowed by memory copies.
hipDeviceAttributeTextureAlignment	Alignment requirement for textures.
hipDeviceAttributeTexturePitchAlignment	Pitch alignment requirement for 2D texture references bound to pitched memory;.
hipDeviceAttributeKernelExecTimeout	Run time limit for kernels executed on the device.
hipDeviceAttributeCanMapHostMemory	Device can map host memory into device address space.
hipDeviceAttributeEccEnabled	Device has ECC support enabled.
hipDeviceAttributeCooperativeMultiDeviceUnmatchedFunc	Supports cooperative launch on multiple devices with unmatched functions
hipDeviceAttributeCooperativeMultiDeviceUnmatchedGridDim	Supports cooperative launch on multiple devices with unmatched grid dimensions
hipDeviceAttributeCooperativeMultiDeviceUnmatchedBlockDim	Supports cooperative launch on multiple devices with unmatched block dimensions
hipDeviceAttributeCooperativeMultiDeviceUnmatchedSharedMem	Supports cooperative launch on multiple devices with unmatched shared memories
hipDeviceAttributeAsicRevision	Revision of the GPU in this device.
hipDeviceAttributeManagedMemory	Device supports allocating managed memory on this system.
hipDeviceAttributeDirectManagedMemAccessFromHost	Host can directly access managed memory on the device without migration
hipDeviceAttributeConcurrentManagedAccess	Device can coherently access managed memory concurrently with the CPU
hipDeviceAttributePageableMemoryAccess	Device supports coherently accessing pageable memory without calling hipHostRegister on it
hipDeviceAttributePageableMemoryAccessUsesHostPageTables	Device accesses pageable memory via the host's page tables
hipDeviceAttributeCanUseStreamWaitValue	'1' if Device supports hipStreamWaitValue32() and hipStreamWaitValue64() , '0' otherwise.

hipFuncAttribute

enum hipFuncAttribute

Warning

On AMD devices and some Nvidia devices, these hints and controls are ignored.

hipFuncCache_t

enum hipFuncCache_t

Warning

On AMD devices and some Nvidia devices, these hints and controls are ignored.

Enumerator
hipFuncCachePreferNone	no preference for shared memory or L1 (default)
hipFuncCachePreferShared	prefer larger shared memory and smaller L1 cache
hipFuncCachePreferL1	prefer larger L1 cache and smaller shared memory
hipFuncCachePreferEqual	prefer equal size L1 cache and shared memory

hipMemoryAdvise

enum hipMemoryAdvise

Enumerator
hipMemAdviseSetReadMostly	Data will mostly be read and only occassionally be written to
hipMemAdviseUnsetReadMostly	Undo the effect of hipMemAdviseSetReadMostly.
hipMemAdviseSetPreferredLocation	Set the preferred location for the data as the specified device
hipMemAdviseUnsetPreferredLocation	Clear the preferred location for the data.
hipMemAdviseSetAccessedBy	Data will be accessed by the specified device, so prevent page faults as much as possible
hipMemAdviseUnsetAccessedBy	Let the Unified Memory subsystem decide on the page faulting policy for the specified device

hipMemRangeAttribute

enum hipMemRangeAttribute

Enumerator
hipMemRangeAttributeReadMostly	Whether the range will mostly be read and only occassionally be written to
hipMemRangeAttributePreferredLocation	The preferred location of the range.
hipMemRangeAttributeAccessedBy	Memory range has cudaMemAdviseSetAccessedBy set for specified device
hipMemRangeAttributeLastPrefetchLocation	The last location to which the range was prefetched.

hipSharedMemConfig

enum hipSharedMemConfig

Warning

On AMD devices and some Nvidia devices, these hints and controls are ignored.

Enumerator
hipSharedMemBankSizeDefault	The compiler selects a device-specific value for the banking.
hipSharedMemBankSizeFourByte	Shared mem is banked at 4-bytes intervals and performs best when adjacent threads access data 4 bytes apart.
hipSharedMemBankSizeEightByte	Shared mem is banked at 8-byte intervals and performs best when adjacent threads access data 4 bytes apart.