Crate cubecl_hip_sys Copy item path Source pub use hipconfig ::*;hipconfig HIP_ARRAY3D_DESCRIPTOR HIP 3D array descriptor HIP_ARRAY_DESCRIPTOR HIP array descriptor HIP_LAUNCH_CONFIG_st HIP driver extensible launch configuration HIP_MEMCPY3D HIP 3D memory copy HIP_RESOURCE_DESC_st HIP resource view descriptor struct HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_1 HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_2 HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_3 HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_4 HIP_RESOURCE_DESC_st__bindgen_ty_1__bindgen_ty_5 HIP_RESOURCE_VIEW_DESC_st Resource view descriptor HIP_TEXTURE_DESC_st HIP texture descriptor __BindgenBitfieldUnit __atomic_wide_counter__bindgen_ty_1 __fsid_t __hip_surface An opaque value that represents a hip surface object __hip_texture An opaque value that represents a hip texture object __once_flag __pthread_cond_s __pthread_internal_list __pthread_internal_slist __pthread_mutex_s __pthread_rwlock_arch_t __sigset_t _hipGraphicsResource _hiprtcProgram char1 char2 char3 char4 dim3 Struct for data in 3D div_t double1 double2 double3 double4 drand48_data fd_set float1 float2 float3 float4 hipAccessPolicyWindow hipArray hipArrayMapInfo Map info for arrays hipArrayMapInfo__bindgen_ty_2__bindgen_ty_1 hipArrayMapInfo__bindgen_ty_2__bindgen_ty_2 hipBatchMemOpNodeParams @brief Structure representing node parameters for batch memory operations in HIP graphs. hipChannelFormatDesc HIP channel format descriptor hipChildGraphNodeParams Child graph node params hipDeviceArch_t @defgroup GlobalDefs Global enum and defines
@{ hipDeviceProp_tR0600 hipDeviceProp hipEventRecordNodeParams Event record node params hipEventWaitNodeParams Event record node params hipExtent HIP extent hipExternalMemoryBufferDesc_st hipExternalMemoryHandleDesc_st hipExternalMemoryHandleDesc_st__bindgen_ty_1__bindgen_ty_1 hipExternalMemoryMipmappedArrayDesc_st hipExternalSemaphoreHandleDesc_st hipExternalSemaphoreHandleDesc_st__bindgen_ty_1__bindgen_ty_1 hipExternalSemaphoreSignalNodeParams External semaphore signal node parameters hipExternalSemaphoreSignalParams_st hipExternalSemaphoreSignalParams_st__bindgen_ty_1 hipExternalSemaphoreSignalParams_st__bindgen_ty_1__bindgen_ty_1 hipExternalSemaphoreSignalParams_st__bindgen_ty_1__bindgen_ty_3 hipExternalSemaphoreWaitNodeParams External semaphore wait node parameters hipExternalSemaphoreWaitParams_st External semaphore wait parameters, compatible with driver type hipExternalSemaphoreWaitParams_st__bindgen_ty_1 hipExternalSemaphoreWaitParams_st__bindgen_ty_1__bindgen_ty_1 hipExternalSemaphoreWaitParams_st__bindgen_ty_1__bindgen_ty_3 hipFuncAttributes hipFunctionLaunchParams_t struct hipFunctionLaunchParams_t hipGraphEdgeData hipGraphExec hipGraphInstantiateParams Graph Instantiation parameters hipGraphNode hipGraphNodeParams Params for different graph nodes hipHostNodeParams hipIpcEventHandle_st hipIpcMemHandle_st hipKernelNodeParams hipLaunchAttribute_st Used to specify custom attributes for launching kernels hipLaunchConfig_st HIP extensible launch configuration hipLaunchParams_t struct hipLaunchParams_t hipMemAccessDesc Memory access descriptor structure is used to specify memory access
permissions for a virtual memory region in Virtual Memory Management API.
This structure changes read, and write permissions for
specific memory regions. hipMemAllocNodeParams hipMemAllocationProp Memory allocation properties hipMemAllocationProp__bindgen_ty_2 hipMemFreeNodeParams Memory free node params hipMemLocation Specifies a memory location. hipMemPoolProps Specifies the properties of allocations made from the pool. hipMemPoolPtrExportData Opaque data structure for exporting a pool allocation hipMemcpy3DParms HIP 3D memory copy parameters hipMemcpyNodeParams Memcpy node params hipMemsetParams hipMipmappedArray HIP mipmapped array hipPitchedPtr HIP pithed pointer hipPointerAttribute_t Pointer attributes hipPos HIP position hipResourceDesc HIP resource descriptor hipResourceDesc__bindgen_ty_1__bindgen_ty_1 hipResourceDesc__bindgen_ty_1__bindgen_ty_2 hipResourceDesc__bindgen_ty_1__bindgen_ty_3 hipResourceDesc__bindgen_ty_1__bindgen_ty_4 hipResourceViewDesc HIP resource view descriptor hipStreamBatchMemOpParams_union_hipStreamMemOpFlushRemoteWritesParams_t hipStreamBatchMemOpParams_union_hipStreamMemOpMemoryBarrierParams_t hipStreamBatchMemOpParams_union_hipStreamMemOpWaitValueParams_t hipStreamBatchMemOpParams_union_hipStreamMemOpWriteValueParams_t hipTextureDesc hip texture descriptor hipUUID_t hipUserObject hip_Memcpy2D HIP 2D memory copy parameters ihipCtx_t ihipEvent_t ihipGraph ihipLinkState_t ihipMemGenericAllocationHandle ihipMemPoolHandle_t ihipModuleSymbol_t ihipModule_t ihipStream_t ihiprtcLinkState int1 int2 int3 int4 ldiv_t lldiv_t long1 long2 long3 long4 longlong1 longlong2 longlong3 longlong4 random_data short1 short2 short3 short4 surfaceReference hip surface reference textureReference hip texture reference timespec timeval uchar1 uchar2 uchar3 uchar4 uint1 uint2 uint3 uint4 ulong1 ulong2 ulong3 ulong4 ulonglong1 ulonglong2 ulonglong3 ulonglong4 ushort1 ushort2 ushort3 ushort4 AIO_PRIO_DELTA_MAX ARG_MAX BC_BASE_MAX BC_DIM_MAX BC_SCALE_MAX BC_STRING_MAX BIG_ENDIAN BYTE_ORDER CHARCLASS_NAME_MAX COLL_WEIGHTS_MAX DELAYTIMER_MAX EXIT_FAILURE EXIT_SUCCESS EXPR_NEST_MAX FD_SETSIZE GENERIC_GRID_LAUNCH HIP_DEPRECATED_MSG HIP_ERROR_INVALID_VALUE HIP_ERROR_LAUNCH_OUT_OF_RESOURCES HIP_ERROR_NOT_INITIALIZED HIP_IMAGE_OBJECT_SIZE_DWORD HIP_IPC_HANDLE_SIZE HIP_SAMPLER_OBJECT_OFFSET_DWORD HIP_SAMPLER_OBJECT_SIZE_DWORD HIP_SUCCESS HIP_TEXTURE_OBJECT_SIZE_DWORD HIP_TRSA_OVERRIDE_FORMAT HIP_TRSF_NORMALIZED_COORDINATES HIP_TRSF_READ_AS_INTEGER HIP_TRSF_SRGB HIP_VERSION HIP_VERSION_BUILD_ID HIP_VERSION_BUILD_NAME HIP_VERSION_GITHASH HIP_VERSION_MAJOR HIP_VERSION_MINOR HIP_VERSION_PATCH HIPaddress_mode_enum_HIP_TR_ADDRESS_MODE_BORDER < Border address mode HIPaddress_mode_enum_HIP_TR_ADDRESS_MODE_CLAMP < Clamp address mode HIPaddress_mode_enum_HIP_TR_ADDRESS_MODE_MIRROR < Mirror address mode HIPaddress_mode_enum_HIP_TR_ADDRESS_MODE_WRAP < Wrap address mode HIPfilter_mode_enum_HIP_TR_FILTER_MODE_LINEAR < Filter mode linear HIPfilter_mode_enum_HIP_TR_FILTER_MODE_POINT < Filter mode point HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_1X16 < 1 channel, 16-bit floating point HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_1X32 < 1 channel, 32-bit floating point HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_2X16 < 2 channels, 16-bit floating point HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_2X32 < 2 channels, 32-bit floating point HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_4X16 < 4 channels, 16-bit floating point HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_FLOAT_4X32 < 4 channels, 32-bit floating point HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_NONE < No resource view format (use underlying resource format) HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SIGNED_BC4 < Block-compressed 4 signed HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SIGNED_BC5 < Block-compressed 5 signed HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SIGNED_BC6H < Block-compressed 6 signed half-float HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_1X8 < 1 channel, signed 8-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_1X16 < 1 channel, signed 16-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_1X32 < 1 channel, signed 32-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_2X8 < 2 channels, signed 8-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_2X16 < 2 channels, signed 16-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_2X32 < 2 channels, signed 32-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_4X8 < 4 channels, signed 8-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_4X16 < 4 channels, signed 16-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_SINT_4X32 < 4 channels, signed 32-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_1X8 < 1 channel, unsigned 8-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_1X16 < 1 channel, unsigned 16-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_1X32 < 1 channel, unsigned 32-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_2X8 < 2 channels, unsigned 8-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_2X16 < 2 channels, unsigned 16-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_2X32 < 2 channels, unsigned 32-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_4X8 < 4 channels, unsigned 8-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_4X16 < 4 channels, unsigned 16-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UINT_4X32 < 4 channels, unsigned 32-bit integers HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC1 < Block-compressed 1 HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC2 < Block-compressed 2 HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC3 < Block-compressed 3 HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC4 < Block-compressed 4 unsigned HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC5 < Block-compressed 5 unsigned HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC7 < Block-compressed 7 HIPresourceViewFormat_enum_HIP_RES_VIEW_FORMAT_UNSIGNED_BC6H < Block-compressed 6 unsigned half-float HIPresourcetype_enum_HIP_RESOURCE_TYPE_ARRAY < Array resource HIPresourcetype_enum_HIP_RESOURCE_TYPE_LINEAR < Linear resource HIPresourcetype_enum_HIP_RESOURCE_TYPE_MIPMAPPED_ARRAY < Mipmapped array resource HIPresourcetype_enum_HIP_RESOURCE_TYPE_PITCH2D < Pitch 2D resource HOST_NAME_MAX INT8_MAX INT8_MIN INT16_MAX INT16_MIN INT32_MAX INT32_MIN INTPTR_MAX INTPTR_MIN INT_FAST8_MAX INT_FAST8_MIN INT_FAST16_MAX INT_FAST16_MIN INT_FAST32_MAX INT_FAST32_MIN INT_LEAST8_MAX INT_LEAST8_MIN INT_LEAST16_MAX INT_LEAST16_MIN INT_LEAST32_MAX INT_LEAST32_MIN LINE_MAX LINK_MAX LITTLE_ENDIAN LOGIN_NAME_MAX MAX_CANON MAX_INPUT MB_LEN_MAX MQ_PRIO_MAX NAME_MAX NGROUPS_MAX NR_OPEN PATH_MAX PDP_ENDIAN PIPE_BUF PTHREAD_DESTRUCTOR_ITERATIONS PTHREAD_KEYS_MAX PTHREAD_STACK_MIN PTRDIFF_MAX PTRDIFF_MIN RAND_MAX RE_DUP_MAX RTSIG_MAX SEM_VALUE_MAX SIG_ATOMIC_MAX SIG_ATOMIC_MIN SIZE_MAX TTY_NAME_MAX UINT8_MAX UINT16_MAX UINT32_MAX UINTPTR_MAX UINT_FAST8_MAX UINT_FAST16_MAX UINT_FAST32_MAX UINT_LEAST8_MAX UINT_LEAST16_MAX UINT_LEAST32_MAX WCONTINUED WEXITED WINT_MAX WINT_MIN WNOHANG WNOWAIT WSTOPPED WUNTRACED XATTR_LIST_MAX XATTR_NAME_MAX XATTR_SIZE_MAX _ALLOCA_H _ATFILE_SOURCE _BITS_BYTESWAP_H _BITS_ENDIANNESS_H _BITS_ENDIAN_H _BITS_POSIX1_LIM_H _BITS_POSIX2_LIM_H _BITS_PTHREADTYPES_ARCH_H _BITS_PTHREADTYPES_COMMON_H _BITS_STDINT_INTN_H _BITS_STDINT_LEAST_H _BITS_STDINT_UINTN_H _BITS_TIME64_H _BITS_TYPESIZES_H _BITS_TYPES_H _BITS_UINTN_IDENTITY_H _BITS_WCHAR_H _DEFAULT_SOURCE _ENDIAN_H _FEATURES_H _LIBC_LIMITS_H_ _POSIX2_BC_BASE_MAX _POSIX2_BC_DIM_MAX _POSIX2_BC_SCALE_MAX _POSIX2_BC_STRING_MAX _POSIX2_CHARCLASS_NAME_MAX _POSIX2_COLL_WEIGHTS_MAX _POSIX2_EXPR_NEST_MAX _POSIX2_LINE_MAX _POSIX2_RE_DUP_MAX _POSIX_AIO_LISTIO_MAX _POSIX_AIO_MAX _POSIX_ARG_MAX _POSIX_CHILD_MAX _POSIX_CLOCKRES_MIN _POSIX_C_SOURCE _POSIX_DELAYTIMER_MAX _POSIX_HOST_NAME_MAX _POSIX_LINK_MAX _POSIX_LOGIN_NAME_MAX _POSIX_MAX_CANON _POSIX_MAX_INPUT _POSIX_MQ_OPEN_MAX _POSIX_MQ_PRIO_MAX _POSIX_NAME_MAX _POSIX_NGROUPS_MAX _POSIX_OPEN_MAX _POSIX_PATH_MAX _POSIX_PIPE_BUF _POSIX_RE_DUP_MAX _POSIX_RTSIG_MAX _POSIX_SEM_NSEMS_MAX _POSIX_SEM_VALUE_MAX _POSIX_SIGQUEUE_MAX _POSIX_SOURCE _POSIX_SSIZE_MAX _POSIX_STREAM_MAX _POSIX_SYMLINK_MAX _POSIX_SYMLOOP_MAX _POSIX_THREAD_DESTRUCTOR_ITERATIONS _POSIX_THREAD_KEYS_MAX _POSIX_THREAD_THREADS_MAX _POSIX_TIMER_MAX _POSIX_TTY_NAME_MAX _POSIX_TZNAME_MAX _STDC_PREDEF_H _STDINT_H _STDLIB_H _STRUCT_TIMESPEC _SYS_CDEFS_H _SYS_SELECT_H _SYS_TYPES_H _THREAD_MUTEX_INTERNAL_H _THREAD_SHARED_TYPES_H __BIG_ENDIAN __BIT_TYPES_DEFINED__ __BYTE_ORDER __FD_SETSIZE __FLOAT_WORD_ORDER __GLIBC_MINOR__ __GLIBC_USE_C2X_STRTOL __GLIBC_USE_DEPRECATED_GETS __GLIBC_USE_DEPRECATED_SCANF __GLIBC_USE_IEC_60559_BFP_EXT __GLIBC_USE_IEC_60559_BFP_EXT_C2X __GLIBC_USE_IEC_60559_EXT __GLIBC_USE_IEC_60559_FUNCS_EXT __GLIBC_USE_IEC_60559_FUNCS_EXT_C2X __GLIBC_USE_IEC_60559_TYPES_EXT __GLIBC_USE_ISOC2X __GLIBC_USE_LIB_EXT2 __GLIBC__ __GNU_LIBRARY__ __HAVE_DISTINCT_FLOAT16 __HAVE_DISTINCT_FLOAT32 __HAVE_DISTINCT_FLOAT64 __HAVE_DISTINCT_FLOAT32X __HAVE_DISTINCT_FLOAT64X __HAVE_DISTINCT_FLOAT128 __HAVE_DISTINCT_FLOAT128X __HAVE_FLOAT16 __HAVE_FLOAT32 __HAVE_FLOAT64 __HAVE_FLOAT32X __HAVE_FLOAT64X __HAVE_FLOAT64X_LONG_DOUBLE __HAVE_FLOAT128 __HAVE_FLOAT128X __HAVE_FLOATN_NOT_TYPEDEF __HAVE_GENERIC_SELECTION __HIP_ARCH_HAS_3DGRID__ __HIP_ARCH_HAS_DOUBLES__ __HIP_ARCH_HAS_DYNAMIC_PARALLEL__ __HIP_ARCH_HAS_FLOAT_ATOMIC_ADD__ __HIP_ARCH_HAS_GLOBAL_FLOAT_ATOMIC_EXCH__ __HIP_ARCH_HAS_GLOBAL_INT32_ATOMICS__ __HIP_ARCH_HAS_GLOBAL_INT64_ATOMICS__ __HIP_ARCH_HAS_SHARED_FLOAT_ATOMIC_EXCH__ __HIP_ARCH_HAS_SHARED_INT32_ATOMICS__ __HIP_ARCH_HAS_SHARED_INT64_ATOMICS__ __HIP_ARCH_HAS_SURFACE_FUNCS__ __HIP_ARCH_HAS_SYNC_THREAD_EXT__ __HIP_ARCH_HAS_THREAD_FENCE_SYSTEM__ __HIP_ARCH_HAS_WARP_BALLOT__ __HIP_ARCH_HAS_WARP_FUNNEL_SHIFT__ __HIP_ARCH_HAS_WARP_SHUFFLE__ __HIP_ARCH_HAS_WARP_VOTE__ __HIP_HAS_GET_PCH __HIP_USE_NATIVE_VECTOR__ __INO_T_MATCHES_INO64_T __KERNEL_OLD_TIMEVAL_MATCHES_TIMEVAL64 __LDOUBLE_REDIRECTS_TO_FLOAT128_ABI __LITTLE_ENDIAN __OFF_T_MATCHES_OFF64_T __PDP_ENDIAN __PTHREAD_MUTEX_HAVE_PREV __RLIM_T_MATCHES_RLIM64_T __SIZEOF_PTHREAD_ATTR_T __SIZEOF_PTHREAD_BARRIERATTR_T __SIZEOF_PTHREAD_BARRIER_T __SIZEOF_PTHREAD_CONDATTR_T __SIZEOF_PTHREAD_COND_T __SIZEOF_PTHREAD_MUTEXATTR_T __SIZEOF_PTHREAD_MUTEX_T __SIZEOF_PTHREAD_RWLOCKATTR_T __SIZEOF_PTHREAD_RWLOCK_T __STATFS_MATCHES_STATFS64 __STDC_IEC_559_COMPLEX__ __STDC_IEC_559__ __STDC_IEC_60559_BFP__ __STDC_IEC_60559_COMPLEX__ __STDC_ISO_10646__ __SYSCALL_WORDSIZE __TIMESIZE __USE_ATFILE __USE_FORTIFY_LEVEL __USE_ISOC11 __USE_ISOC95 __USE_ISOC99 __USE_MISC __USE_POSIX __USE_POSIX2 __USE_POSIX199309 __USE_POSIX199506 __USE_POSIX_IMPLICITLY __USE_XOPEN2K __USE_XOPEN2K8 __WALL __WCLONE __WCOREFLAG __WNOTHREAD __WORDSIZE __WORDSIZE_TIME64_COMPAT32 __W_CONTINUED __clock_t_defined __clockid_t_defined __glibc_c99_flexarr_available __have_pthread_attr_t __ldiv_t_defined __lldiv_t_defined __sigset_t_defined __time_t_defined __timer_t_defined __timeval_defined hipAccessProperty_hipAccessPropertyNormal hipAccessProperty_hipAccessPropertyPersisting hipAccessProperty_hipAccessPropertyStreaming hipArrayCubemap hipArrayDefault hipArrayLayered hipArraySparseSubresourceType_hipArraySparseSubresourceTypeMiptail < Miptail hipArraySparseSubresourceType_hipArraySparseSubresourceTypeSparseLevel < Sparse level hipArraySurfaceLoadStore hipArrayTextureGather hipArray_Format_HIP_AD_FORMAT_FLOAT < Float array format hipArray_Format_HIP_AD_FORMAT_HALF < Half array format hipArray_Format_HIP_AD_FORMAT_SIGNED_INT8 < Signed 8-bit array format hipArray_Format_HIP_AD_FORMAT_SIGNED_INT16 < Signed 16-bit array format hipArray_Format_HIP_AD_FORMAT_SIGNED_INT32 < Signed 32-bit array format hipArray_Format_HIP_AD_FORMAT_UNSIGNED_INT8 < Unsigned 8-bit array format hipArray_Format_HIP_AD_FORMAT_UNSIGNED_INT16 < Unsigned 16-bit array format hipArray_Format_HIP_AD_FORMAT_UNSIGNED_INT32 < Unsigned 32-bit array format hipChannelFormatKind_hipChannelFormatKindFloat < Float channel format hipChannelFormatKind_hipChannelFormatKindNone < No channel format hipChannelFormatKind_hipChannelFormatKindSigned < Signed channel format hipChannelFormatKind_hipChannelFormatKindUnsigned < Unsigned channel format hipComputeMode_hipComputeModeDefault hipComputeMode_hipComputeModeExclusive hipComputeMode_hipComputeModeExclusiveProcess hipComputeMode_hipComputeModeProhibited hipCooperativeLaunchMultiDeviceNoPostSync hipCooperativeLaunchMultiDeviceNoPreSync hipDeviceAttribute_t_hipDeviceAttributeAccessPolicyMaxWindowSize < Cuda only. The maximum size of the window policy in bytes. hipDeviceAttribute_t_hipDeviceAttributeAmdSpecificBegin hipDeviceAttribute_t_hipDeviceAttributeAmdSpecificEnd hipDeviceAttribute_t_hipDeviceAttributeAsicRevision < Revision of the GPU in this device hipDeviceAttribute_t_hipDeviceAttributeAsyncEngineCount < Asynchronous engines number. hipDeviceAttribute_t_hipDeviceAttributeCanMapHostMemory < Whether host memory can be mapped into device address space hipDeviceAttribute_t_hipDeviceAttributeCanUseHostPointerForRegisteredMem < Device can access host registered memory
< at the same virtual address as the CPU hipDeviceAttribute_t_hipDeviceAttributeCanUseStreamWaitValue < ‘1’ if Device supports hipStreamWaitValue32() and
< hipStreamWaitValue64(), ‘0’ otherwise. hipDeviceAttribute_t_hipDeviceAttributeClockInstructionRate < Frequency in khz of the timer used by the device-side “clock*” hipDeviceAttribute_t_hipDeviceAttributeClockRate < Peak clock frequency in kilohertz. hipDeviceAttribute_t_hipDeviceAttributeComputeCapabilityMajor < Major compute capability version number. hipDeviceAttribute_t_hipDeviceAttributeComputeCapabilityMinor < Minor compute capability version number. hipDeviceAttribute_t_hipDeviceAttributeComputeMode < Compute mode that device is currently in. hipDeviceAttribute_t_hipDeviceAttributeComputePreemptionSupported < Device supports Compute Preemption. hipDeviceAttribute_t_hipDeviceAttributeConcurrentKernels < Device can possibly execute multiple kernels concurrently. hipDeviceAttribute_t_hipDeviceAttributeConcurrentManagedAccess < Device can coherently access managed memory concurrently with the CPU hipDeviceAttribute_t_hipDeviceAttributeCooperativeLaunch < Support cooperative launch hipDeviceAttribute_t_hipDeviceAttributeCooperativeMultiDeviceLaunch < Support cooperative launch on multiple devices hipDeviceAttribute_t_hipDeviceAttributeCooperativeMultiDeviceUnmatchedBlockDim < Supports cooperative launch on multiple
< devices with unmatched block dimensions hipDeviceAttribute_t_hipDeviceAttributeCooperativeMultiDeviceUnmatchedFunc < Supports cooperative launch on multiple
< devices with unmatched functions hipDeviceAttribute_t_hipDeviceAttributeCooperativeMultiDeviceUnmatchedGridDim < Supports cooperative launch on multiple
< devices with unmatched grid dimensions hipDeviceAttribute_t_hipDeviceAttributeCooperativeMultiDeviceUnmatchedSharedMem < Supports cooperative launch on multiple
< devices with unmatched shared memories hipDeviceAttribute_t_hipDeviceAttributeCudaCompatibleBegin hipDeviceAttribute_t_hipDeviceAttributeCudaCompatibleEnd hipDeviceAttribute_t_hipDeviceAttributeDeviceOverlap < Device can concurrently copy memory and execute a kernel.
< Deprecated. Use instead asyncEngineCount. hipDeviceAttribute_t_hipDeviceAttributeDirectManagedMemAccessFromHost < Host can directly access managed memory on
< the device without migration hipDeviceAttribute_t_hipDeviceAttributeEccEnabled < Whether ECC support is enabled. hipDeviceAttribute_t_hipDeviceAttributeFineGrainSupport < ‘1’ if Device supports fine grain, ‘0’ otherwise hipDeviceAttribute_t_hipDeviceAttributeGlobalL1CacheSupported < Device supports caching globals in L1 hipDeviceAttribute_t_hipDeviceAttributeHdpMemFlushCntl < Address of the HDP_MEM_COHERENCY_FLUSH_CNTL register hipDeviceAttribute_t_hipDeviceAttributeHdpRegFlushCntl < Address of the HDP_REG_COHERENCY_FLUSH_CNTL register hipDeviceAttribute_t_hipDeviceAttributeHostNativeAtomicSupported < Link between the device and the host supports native atomic operations hipDeviceAttribute_t_hipDeviceAttributeHostRegisterSupported < Can device support host memory registration via hipHostRegister hipDeviceAttribute_t_hipDeviceAttributeImageSupport < ‘1’ if Device supports image, ‘0’ otherwise. hipDeviceAttribute_t_hipDeviceAttributeIntegrated < Device is integrated GPU hipDeviceAttribute_t_hipDeviceAttributeIsLargeBar < Whether it is LargeBar hipDeviceAttribute_t_hipDeviceAttributeIsMultiGpuBoard < Multiple GPU devices. hipDeviceAttribute_t_hipDeviceAttributeKernelExecTimeout < Run time limit for kernels executed on the device hipDeviceAttribute_t_hipDeviceAttributeL2CacheSize < Size of L2 cache in bytes. 0 if the device doesn’t have L2 cache. hipDeviceAttribute_t_hipDeviceAttributeLocalL1CacheSupported < caching locals in L1 is supported hipDeviceAttribute_t_hipDeviceAttributeLuid < 8-byte locally unique identifier in 8 bytes. Undefined on TCC and non-Windows platforms hipDeviceAttribute_t_hipDeviceAttributeLuidDeviceNodeMask < Luid device node mask. Undefined on TCC and non-Windows platforms hipDeviceAttribute_t_hipDeviceAttributeManagedMemory < Device supports allocating managed memory on this system hipDeviceAttribute_t_hipDeviceAttributeMaxBlockDimX < Max block size in width. hipDeviceAttribute_t_hipDeviceAttributeMaxBlockDimY < Max block size in height. hipDeviceAttribute_t_hipDeviceAttributeMaxBlockDimZ < Max block size in depth. hipDeviceAttribute_t_hipDeviceAttributeMaxBlocksPerMultiProcessor < Max block size per multiprocessor hipDeviceAttribute_t_hipDeviceAttributeMaxGridDimX < Max grid size in width. hipDeviceAttribute_t_hipDeviceAttributeMaxGridDimY < Max grid size in height. hipDeviceAttribute_t_hipDeviceAttributeMaxGridDimZ < Max grid size in depth. hipDeviceAttribute_t_hipDeviceAttributeMaxPitch < Maximum pitch in bytes allowed by memory copies hipDeviceAttribute_t_hipDeviceAttributeMaxRegistersPerBlock < 32-bit registers available to a thread block. This number is shared
< by all thread blocks simultaneously resident on a multiprocessor. hipDeviceAttribute_t_hipDeviceAttributeMaxRegistersPerMultiprocessor < 32-bit registers available per block. hipDeviceAttribute_t_hipDeviceAttributeMaxSharedMemoryPerBlock < Maximum shared memory available per block in bytes. hipDeviceAttribute_t_hipDeviceAttributeMaxSharedMemoryPerMultiprocessor < Maximum Shared Memory PerMultiprocessor. hipDeviceAttribute_t_hipDeviceAttributeMaxSurface1D < Maximum size of 1D surface. hipDeviceAttribute_t_hipDeviceAttributeMaxSurface1DLayered < Cuda only. Maximum dimensions of 1D layered surface. hipDeviceAttribute_t_hipDeviceAttributeMaxSurface2D < Maximum dimension (width, height) of 2D surface. hipDeviceAttribute_t_hipDeviceAttributeMaxSurface2DLayered < Cuda only. Maximum dimensions of 2D layered surface. hipDeviceAttribute_t_hipDeviceAttributeMaxSurface3D < Maximum dimension (width, height, depth) of 3D surface. hipDeviceAttribute_t_hipDeviceAttributeMaxSurfaceCubemap < Cuda only. Maximum dimensions of Cubemap surface. hipDeviceAttribute_t_hipDeviceAttributeMaxSurfaceCubemapLayered < Cuda only. Maximum dimension of Cubemap layered surface. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture1DLayered < Maximum dimensions of 1D layered texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture1DLinear < Maximum number of elements allocatable in a 1D linear texture.
< Use cudaDeviceGetTexture1DLinearMaxWidth() instead on Cuda. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture1DMipmap < Maximum size of 1D mipmapped texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture1DWidth < Maximum size of 1D texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DGather < Maximum dimensions of 2D texture if gather operations performed. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DHeight < Maximum dimension hight of 2D texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DLayered < Maximum dimensions of 2D layered texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DLinear < Maximum dimensions (width, height, pitch) of 2D textures bound to pitched memory. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DMipmap < Maximum dimensions of 2D mipmapped texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture2DWidth < Maximum dimension width of 2D texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture3DAlt < Maximum dimensions of alternate 3D texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture3DDepth < Maximum dimension depth of 3D texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture3DHeight < Maximum dimension height of 3D texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTexture3DWidth < Maximum dimension width of 3D texture. hipDeviceAttribute_t_hipDeviceAttributeMaxTextureCubemap < Maximum dimensions of Cubemap texture hipDeviceAttribute_t_hipDeviceAttributeMaxTextureCubemapLayered < Maximum dimensions of Cubemap layered texture. hipDeviceAttribute_t_hipDeviceAttributeMaxThreadsDim < Maximum dimension of a block hipDeviceAttribute_t_hipDeviceAttributeMaxThreadsPerBlock < Maximum number of threads per block. hipDeviceAttribute_t_hipDeviceAttributeMaxThreadsPerMultiProcessor < Maximum resident threads per multiprocessor. hipDeviceAttribute_t_hipDeviceAttributeMemoryBusWidth < Global memory bus width in bits. hipDeviceAttribute_t_hipDeviceAttributeMemoryClockRate < Peak memory clock frequency in kilohertz. hipDeviceAttribute_t_hipDeviceAttributeMemoryPoolSupportedHandleTypes < Supported handle mask for HIP Stream Ordered Memory Allocator hipDeviceAttribute_t_hipDeviceAttributeMemoryPoolsSupported < Device supports HIP Stream Ordered Memory Allocator hipDeviceAttribute_t_hipDeviceAttributeMultiGpuBoardGroupID < Unique ID of device group on the same multi-GPU board hipDeviceAttribute_t_hipDeviceAttributeMultiprocessorCount < Number of multiprocessors on the device. hipDeviceAttribute_t_hipDeviceAttributeNumberOfXccs < The number of XCC(s) on the device hipDeviceAttribute_t_hipDeviceAttributePageableMemoryAccess < Device supports coherently accessing pageable memory
< without calling hipHostRegister on it hipDeviceAttribute_t_hipDeviceAttributePageableMemoryAccessUsesHostPageTables < Device accesses pageable memory via the host’s page tables hipDeviceAttribute_t_hipDeviceAttributePciBusId < PCI Bus ID. hipDeviceAttribute_t_hipDeviceAttributePciChipId < PCI Chip ID. Returns gpu manufacturer device id hipDeviceAttribute_t_hipDeviceAttributePciDeviceId < PCI Device ID. hipDeviceAttribute_t_hipDeviceAttributePciDomainID < PCI Domain ID, for backward compatibility. hipDeviceAttribute_t_hipDeviceAttributePciDomainId < PCI Domain Id. hipDeviceAttribute_t_hipDeviceAttributePersistingL2CacheMaxSize < Maximum l2 persisting lines capacity in bytes hipDeviceAttribute_t_hipDeviceAttributePhysicalMultiProcessorCount < All available physical compute
< units for the device hipDeviceAttribute_t_hipDeviceAttributeReservedSharedMemPerBlock < Shared memory reserved by CUDA driver per block. hipDeviceAttribute_t_hipDeviceAttributeSharedMemPerBlockOptin < Maximum shared memory per block usable by special opt in. hipDeviceAttribute_t_hipDeviceAttributeSharedMemPerMultiprocessor < Shared memory available per multiprocessor. hipDeviceAttribute_t_hipDeviceAttributeSingleToDoublePrecisionPerfRatio < Cuda only. Performance ratio of single precision to double precision. hipDeviceAttribute_t_hipDeviceAttributeStreamPrioritiesSupported < Whether to support stream priorities. hipDeviceAttribute_t_hipDeviceAttributeSurfaceAlignment < Alignment requirement for surfaces hipDeviceAttribute_t_hipDeviceAttributeTccDriver < Cuda only. Whether device is a Tesla device using TCC driver hipDeviceAttribute_t_hipDeviceAttributeTextureAlignment < Alignment requirement for textures hipDeviceAttribute_t_hipDeviceAttributeTexturePitchAlignment < Pitch alignment requirement for 2D texture references bound to pitched memory; hipDeviceAttribute_t_hipDeviceAttributeTotalConstantMemory < Constant memory size in bytes. hipDeviceAttribute_t_hipDeviceAttributeTotalGlobalMem < Global memory available on devicice. hipDeviceAttribute_t_hipDeviceAttributeUnifiedAddressing < Cuda only. An unified address space shared with the host. hipDeviceAttribute_t_hipDeviceAttributeUnused1 < Previously hipDeviceAttributeName hipDeviceAttribute_t_hipDeviceAttributeUnused2 < Previously hipDeviceAttributeUuid hipDeviceAttribute_t_hipDeviceAttributeUnused3 < Previously hipDeviceAttributeArch hipDeviceAttribute_t_hipDeviceAttributeUnused4 < Previously hipDeviceAttributeGcnArch hipDeviceAttribute_t_hipDeviceAttributeUnused5 < Previously hipDeviceAttributeGcnArchName hipDeviceAttribute_t_hipDeviceAttributeVendorSpecificBegin hipDeviceAttribute_t_hipDeviceAttributeVirtualMemoryManagementSupported < Device supports HIP virtual memory management hipDeviceAttribute_t_hipDeviceAttributeWallClockRate < Constant frequency of wall clock in kilohertz. hipDeviceAttribute_t_hipDeviceAttributeWarpSize < Warp size in threads. hipDeviceLmemResizeToMax hipDeviceMallocContiguous hipDeviceMallocDefault hipDeviceMallocFinegrained hipDeviceMallocUncached hipDeviceMapHost hipDeviceP2PAttr_hipDevP2PAttrAccessSupported hipDeviceP2PAttr_hipDevP2PAttrHipArrayAccessSupported hipDeviceP2PAttr_hipDevP2PAttrNativeAtomicSupported hipDeviceP2PAttr_hipDevP2PAttrPerformanceRank hipDeviceScheduleAuto hipDeviceScheduleBlockingSync hipDeviceScheduleMask hipDeviceScheduleSpin hipDeviceScheduleYield hipDriverProcAddressQueryResult_HIP_GET_PROC_ADDRESS_SUCCESS hipDriverProcAddressQueryResult_HIP_GET_PROC_ADDRESS_SYMBOL_NOT_FOUND hipDriverProcAddressQueryResult_HIP_GET_PROC_ADDRESS_VERSION_NOT_SUFFICIENT hipError_t_hipErrorAlreadyAcquired hipError_t_hipErrorAlreadyMapped hipError_t_hipErrorArrayIsMapped hipError_t_hipErrorAssert < Produced when the kernel calls assert. hipError_t_hipErrorCapturedEvent < The operation is not permitted on an event which was last
< recorded in a capturing stream. hipError_t_hipErrorContextAlreadyCurrent hipError_t_hipErrorContextAlreadyInUse < The context is already in use hipError_t_hipErrorContextIsDestroyed < The context is already destroyed hipError_t_hipErrorCooperativeLaunchTooLarge < This error indicates that the number of blocks
< launched per grid for a kernel that was launched
< via cooperative launch APIs exceeds the maximum
< number of allowed blocks for the current device. hipError_t_hipErrorDeinitialized < Deinitialized hipError_t_hipErrorECCNotCorrectable hipError_t_hipErrorFileNotFound < the file is not found. hipError_t_hipErrorGraphExecUpdateFailure < This error indicates that the graph update
< not performed because it included changes which
< violated constraintsspecific to instantiated graph
< update. hipError_t_hipErrorHostMemoryAlreadyRegistered < Produced when trying to lock a page-locked
< memory. hipError_t_hipErrorHostMemoryNotRegistered < Produced when trying to unlock a non-page-locked
< memory. hipError_t_hipErrorIllegalAddress hipError_t_hipErrorIllegalState < Resource required is not in a valid state to perform operation. hipError_t_hipErrorInitializationError hipError_t_hipErrorInsufficientDriver hipError_t_hipErrorInvalidChannelDescriptor < Invalid channel descriptor. hipError_t_hipErrorInvalidConfiguration < Invalide configuration hipError_t_hipErrorInvalidContext < Produced when input context is invalid. hipError_t_hipErrorInvalidDevice < DeviceID must be in range from 0 to compute-devices. hipError_t_hipErrorInvalidDeviceFunction < Invalid device function hipError_t_hipErrorInvalidDevicePointer < Invalid Device Pointer hipError_t_hipErrorInvalidGraphicsContext hipError_t_hipErrorInvalidHandle < Invalide handle hipError_t_hipErrorInvalidImage < Invalid image hipError_t_hipErrorInvalidKernelFile < In CUDA DRV, it is CUDA_ERROR_INVALID_PTX hipError_t_hipErrorInvalidMemcpyDirection < Invalid memory copy direction hipError_t_hipErrorInvalidPitchValue < Invalid pitch value hipError_t_hipErrorInvalidResourceHandle < Resource handle (hipEvent_t or hipStream_t) invalid. hipError_t_hipErrorInvalidSource < Invalid source. hipError_t_hipErrorInvalidSymbol < Invalid symbol hipError_t_hipErrorInvalidTexture < Invalid texture. hipError_t_hipErrorInvalidValue < One or more of the parameters passed to the API call is NULL
< or not in an acceptable range. hipError_t_hipErrorLaunchFailure < An exception occurred on the device while executing a kernel. hipError_t_hipErrorLaunchOutOfResources < Out of resources error. hipError_t_hipErrorLaunchTimeOut < Timeout for the launch. hipError_t_hipErrorMapBufferObjectFailed < Produced when the IPC memory attach failed from ROCr. hipError_t_hipErrorMapFailed hipError_t_hipErrorMemoryAllocation < Memory allocation error. hipError_t_hipErrorMissingConfiguration hipError_t_hipErrorNoBinaryForGpu hipError_t_hipErrorNoDevice < Call to hipGetDeviceCount returned 0 devices hipError_t_hipErrorNotFound < Not found hipError_t_hipErrorNotInitialized < Invalid not initialized hipError_t_hipErrorNotMapped hipError_t_hipErrorNotMappedAsArray hipError_t_hipErrorNotMappedAsPointer hipError_t_hipErrorNotReady < Indicates that asynchronous operations enqueued earlier are not
< ready. This is not actually an error, but is used to distinguish
< from hipSuccess (which indicates completion). APIs that return
< this error include hipEventQuery and hipStreamQuery. hipError_t_hipErrorNotSupported < Produced when the hip API is not supported/implemented hipError_t_hipErrorOperatingSystem < Not the correct operating system hipError_t_hipErrorOutOfMemory < out of memory range. hipError_t_hipErrorPeerAccessAlreadyEnabled < Peer access was already enabled from the current
< device. hipError_t_hipErrorPeerAccessNotEnabled < Peer access was never enabled from the current device. hipError_t_hipErrorPeerAccessUnsupported hipError_t_hipErrorPriorLaunchFailure hipError_t_hipErrorProfilerAlreadyStarted hipError_t_hipErrorProfilerAlreadyStopped hipError_t_hipErrorProfilerDisabled hipError_t_hipErrorProfilerNotInitialized hipError_t_hipErrorRuntimeMemory < HSA runtime memory call returned error. Typically not seen
< in production systems. hipError_t_hipErrorRuntimeOther < HSA runtime call other than memory returned error. Typically
< not seen in production systems. hipError_t_hipErrorSetOnActiveProcess < The process is active. hipError_t_hipErrorSharedObjectInitFailed < Failed to initialize shared object. hipError_t_hipErrorSharedObjectSymbolNotFound hipError_t_hipErrorStreamCaptureImplicit < The operation would have resulted in a disallowed
< implicit dependency on a current capture sequence
< from hipStreamLegacy. hipError_t_hipErrorStreamCaptureInvalidated < The current capture sequence on the stream
< has been invalidated due to a previous error. hipError_t_hipErrorStreamCaptureIsolation < A dependency would have been created which crosses
< the capture sequence boundary. Only implicit
< in-stream ordering dependencies are allowed
< to cross the boundary hipError_t_hipErrorStreamCaptureMerge < The operation would have resulted in a merge of
< two independent capture sequences. hipError_t_hipErrorStreamCaptureUnjoined < The capture sequence contains a fork that was not
< joined to the primary stream. hipError_t_hipErrorStreamCaptureUnmatched < The capture was not initiated in this stream. hipError_t_hipErrorStreamCaptureUnsupported < The operation is not permitted when the stream
< is capturing. hipError_t_hipErrorStreamCaptureWrongThread < A stream capture sequence not initiated with
< the hipStreamCaptureModeRelaxed argument to
< hipStreamBeginCapture was passed to
< hipStreamEndCapture in a different thread. hipError_t_hipErrorTbd < Marker that more error codes are needed. hipError_t_hipErrorUnknown < Unknown error. hipError_t_hipErrorUnmapFailed hipError_t_hipErrorUnsupportedLimit < Unsupported limit hipError_t_hipSuccess < Successful completion. hipEventBlockingSync hipEventDefault hipEventDisableSystemFence hipEventDisableTiming hipEventInterprocess hipEventRecordDefault hipEventRecordExternal hipEventReleaseToDevice hipEventReleaseToSystem hipEventWaitDefault hipEventWaitExternal hipExtAnyOrderLaunch hipExtHostRegisterCoarseGrained hipExtHostRegisterUncached hipExternalMemoryDedicated hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeD3D11Resource hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeD3D11ResourceKmt hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeD3D12Heap hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeD3D12Resource hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeNvSciBuf hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeOpaqueFd hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeOpaqueWin32 hipExternalMemoryHandleType_enum_hipExternalMemoryHandleTypeOpaqueWin32Kmt hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeD3D11Fence hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeD3D12Fence hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeKeyedMutex hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeKeyedMutexKmt hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeNvSciSync hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeOpaqueFd hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeOpaqueWin32 hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeOpaqueWin32Kmt hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeTimelineSemaphoreFd hipExternalSemaphoreHandleType_enum_hipExternalSemaphoreHandleTypeTimelineSemaphoreWin32 hipFlushGPUDirectRDMAWritesOptions_hipFlushGPUDirectRDMAWritesOptionHost hipFlushGPUDirectRDMAWritesOptions_hipFlushGPUDirectRDMAWritesOptionMemOps hipFuncAttribute_hipFuncAttributeMax hipFuncAttribute_hipFuncAttributeMaxDynamicSharedMemorySize < The maximum number of bytes requested for dynamically allocated shared memory hipFuncAttribute_hipFuncAttributePreferredSharedMemoryCarveout < Sets the percentage of total shared memory allocated as the shared memory carveout hipFuncCache_t_hipFuncCachePreferEqual < prefer equal size L1 cache and shared memory hipFuncCache_t_hipFuncCachePreferL1 < prefer larger L1 cache and smaller shared memory hipFuncCache_t_hipFuncCachePreferNone < no preference for shared memory or L1 (default) hipFuncCache_t_hipFuncCachePreferShared < prefer larger shared memory and smaller L1 cache hipFunction_attribute_HIP_FUNC_ATTRIBUTE_BINARY_VERSION < Binary version hipFunction_attribute_HIP_FUNC_ATTRIBUTE_CACHE_MODE_CA < Cache mode hipFunction_attribute_HIP_FUNC_ATTRIBUTE_CONST_SIZE_BYTES < The user-allocated constant memory by the function in bytes. hipFunction_attribute_HIP_FUNC_ATTRIBUTE_LOCAL_SIZE_BYTES < The local memory usage of each thread by this function in bytes. hipFunction_attribute_HIP_FUNC_ATTRIBUTE_MAX hipFunction_attribute_HIP_FUNC_ATTRIBUTE_MAX_DYNAMIC_SHARED_SIZE_BYTES < The maximum dynamic shared memory per block for this function in bytes. hipFunction_attribute_HIP_FUNC_ATTRIBUTE_MAX_THREADS_PER_BLOCK < The maximum number of threads per block. Depends on function and device. hipFunction_attribute_HIP_FUNC_ATTRIBUTE_NUM_REGS < The number of registers used by each thread of this function. hipFunction_attribute_HIP_FUNC_ATTRIBUTE_PREFERRED_SHARED_MEMORY_CARVEOUT < The shared memory carveout preference in percent of the maximum shared memory. hipFunction_attribute_HIP_FUNC_ATTRIBUTE_PTX_VERSION < PTX version hipFunction_attribute_HIP_FUNC_ATTRIBUTE_SHARED_SIZE_BYTES < The statically allocated shared memory size in bytes per block required by the function. hipGPUDirectRDMAWritesOrdering_hipGPUDirectRDMAWritesOrderingAllDevices hipGPUDirectRDMAWritesOrdering_hipGPUDirectRDMAWritesOrderingNone hipGPUDirectRDMAWritesOrdering_hipGPUDirectRDMAWritesOrderingOwner hipGraphDebugDotFlags_hipGraphDebugDotFlagsEventNodeParams hipGraphDebugDotFlags_hipGraphDebugDotFlagsExtSemasSignalNodeParams hipGraphDebugDotFlags_hipGraphDebugDotFlagsExtSemasWaitNodeParams hipGraphDebugDotFlags_hipGraphDebugDotFlagsHandles hipGraphDebugDotFlags_hipGraphDebugDotFlagsHostNodeParams < Adds hipHostNodeParams to output hipGraphDebugDotFlags_hipGraphDebugDotFlagsKernelNodeAttributes hipGraphDebugDotFlags_hipGraphDebugDotFlagsKernelNodeParams < Adds hipKernelNodeParams to output hipGraphDebugDotFlags_hipGraphDebugDotFlagsMemcpyNodeParams < Adds hipMemcpy3DParms to output hipGraphDebugDotFlags_hipGraphDebugDotFlagsMemsetNodeParams < Adds hipMemsetParams to output hipGraphDebugDotFlags_hipGraphDebugDotFlagsVerbose hipGraphDependencyType_hipGraphDependencyTypeDefault hipGraphDependencyType_hipGraphDependencyTypeProgrammatic hipGraphExecUpdateResult_hipGraphExecUpdateError < The update failed for an unexpected reason which is described
< in the return value of the function hipGraphExecUpdateResult_hipGraphExecUpdateErrorFunctionChanged hipGraphExecUpdateResult_hipGraphExecUpdateErrorNodeTypeChanged < The update failed because a node type changed hipGraphExecUpdateResult_hipGraphExecUpdateErrorNotSupported hipGraphExecUpdateResult_hipGraphExecUpdateErrorParametersChanged hipGraphExecUpdateResult_hipGraphExecUpdateErrorTopologyChanged < The update failed because the topology changed hipGraphExecUpdateResult_hipGraphExecUpdateErrorUnsupportedFunctionChange hipGraphExecUpdateResult_hipGraphExecUpdateSuccess < The update succeeded hipGraphInstantiateFlags_hipGraphInstantiateFlagAutoFreeOnLaunch hipGraphInstantiateFlags_hipGraphInstantiateFlagDeviceLaunch hipGraphInstantiateFlags_hipGraphInstantiateFlagUpload hipGraphInstantiateFlags_hipGraphInstantiateFlagUseNodePriority hipGraphInstantiateResult_hipGraphInstantiateError < Instantiation failed for an
unexpected reason which is described in the return value of the function hipGraphInstantiateResult_hipGraphInstantiateInvalidStructure < Instantiation failed due
to invalid structure, such as cycles hipGraphInstantiateResult_hipGraphInstantiateMultipleDevicesNotSupported < Instantiation for device launch failed
due to the nodes belonging to different contexts hipGraphInstantiateResult_hipGraphInstantiateNodeOperationNotSupported < Instantiation for device launch failed
because the graph contained an unsupported operation hipGraphInstantiateResult_hipGraphInstantiateSuccess < Instantiation Success hipGraphKernelNodePortDefault hipGraphKernelNodePortLaunchCompletion hipGraphKernelNodePortProgrammatic hipGraphMemAttributeType_hipGraphMemAttrReservedMemCurrent < Amount of memory, in bytes, currently allocated for graphs. hipGraphMemAttributeType_hipGraphMemAttrReservedMemHigh < High watermark of memory, in bytes, currently allocated for graphs hipGraphMemAttributeType_hipGraphMemAttrUsedMemCurrent < Amount of memory, in bytes, currently associated with graphs hipGraphMemAttributeType_hipGraphMemAttrUsedMemHigh < High watermark of memory, in bytes, associated with graphs since the last time. hipGraphNodeType_hipGraphNodeTypeBatchMemOp < BatchMemOp node hipGraphNodeType_hipGraphNodeTypeCount hipGraphNodeType_hipGraphNodeTypeEmpty < Empty (no-op) node hipGraphNodeType_hipGraphNodeTypeEventRecord < External event record node hipGraphNodeType_hipGraphNodeTypeExtSemaphoreSignal < External Semaphore signal node hipGraphNodeType_hipGraphNodeTypeExtSemaphoreWait < External Semaphore wait node hipGraphNodeType_hipGraphNodeTypeGraph < Node which executes an embedded graph hipGraphNodeType_hipGraphNodeTypeHost < Host (executable) node hipGraphNodeType_hipGraphNodeTypeKernel < GPU kernel node hipGraphNodeType_hipGraphNodeTypeMemAlloc < Memory alloc node hipGraphNodeType_hipGraphNodeTypeMemFree < Memory free node hipGraphNodeType_hipGraphNodeTypeMemcpy < Memcpy node hipGraphNodeType_hipGraphNodeTypeMemcpyFromSymbol < MemcpyFromSymbol node hipGraphNodeType_hipGraphNodeTypeMemcpyToSymbol < MemcpyToSymbol node hipGraphNodeType_hipGraphNodeTypeMemset < Memset node hipGraphNodeType_hipGraphNodeTypeWaitEvent < External event wait node hipGraphicsRegisterFlags_hipGraphicsRegisterFlagsNone hipGraphicsRegisterFlags_hipGraphicsRegisterFlagsReadOnly < HIP will not write to this registered resource hipGraphicsRegisterFlags_hipGraphicsRegisterFlagsSurfaceLoadStore < HIP will bind this resource to a surface hipGraphicsRegisterFlags_hipGraphicsRegisterFlagsTextureGather hipGraphicsRegisterFlags_hipGraphicsRegisterFlagsWriteDiscard hipHostAllocDefault hipHostAllocMapped hipHostAllocPortable hipHostAllocUncached hipHostAllocWriteCombined hipHostMallocCoherent hipHostMallocDefault hipHostMallocMapped hipHostMallocNonCoherent hipHostMallocNumaUser hipHostMallocPortable hipHostMallocUncached hipHostMallocWriteCombined hipHostRegisterDefault hipHostRegisterIoMemory hipHostRegisterMapped hipHostRegisterPortable hipHostRegisterReadOnly hipIpcMemLazyEnablePeerAccess hipJitCacheMode_hipJitCacheOptionCA hipJitCacheMode_hipJitCacheOptionCG hipJitCacheMode_hipJitCacheOptionNone hipJitFallback_hipJitPreferBinary hipJitFallback_hipJitPreferPTX hipJitInputType_hipJitInputCubin < Cuda only Input cubin hipJitInputType_hipJitInputFatBinary < Cuda Only Input FAT Binary hipJitInputType_hipJitInputLLVMArchivesOfBundledBitcode < HIP Only LLVM Archive of Bundled Bitcode hipJitInputType_hipJitInputLLVMBitcode < HIP Only LLVM Bitcode or IR assembly hipJitInputType_hipJitInputLLVMBundledBitcode < HIP Only LLVM Clang Bundled Code hipJitInputType_hipJitInputLibrary < Cuda Only Archive of Host Objects with embedded
< device code hipJitInputType_hipJitInputNvvm < @deprecated Cuda only High Level intermediate
< code for LTO hipJitInputType_hipJitInputObject < Cuda Only Host Object with embedded device code hipJitInputType_hipJitInputPtx < Cuda only Input PTX hipJitInputType_hipJitInputSpirv < HIP Only SPIRV Code Object hipJitInputType_hipJitNumInputTypes < Count of Input Types hipJitInputType_hipJitNumLegacyInputTypes < Count of Legacy Input Types hipJitOption_hipJitOptionCacheMode < CUDA Only Set cache mode hipJitOption_hipJitOptionErrorLogBuffer < CUDA Only Pointer to the buffer with logged error(s) hipJitOption_hipJitOptionErrorLogBufferSizeBytes < CUDA Only Size of the buffer in bytes for logged error(s) hipJitOption_hipJitOptionFallbackStrategy < CUDA Only Fallback strategy hipJitOption_hipJitOptionFastCompile < CUDA Only Set fast compile hipJitOption_hipJitOptionFma < @deprecated CUDA Only Enable floating-point multiplies and
< adds/subtracts operations hipJitOption_hipJitOptionFtz < @deprecated CUDA Only Set single-precision denormals. hipJitOption_hipJitOptionGenerateDebugInfo < CUDA Only Generate debug information hipJitOption_hipJitOptionGenerateLineInfo < CUDA Only Generate line number information hipJitOption_hipJitOptionGlobalSymbolAddresses < CUDA Only Array of host addresses to be relocated to the device hipJitOption_hipJitOptionGlobalSymbolCount < CUDA Only Number of symbol count. hipJitOption_hipJitOptionGlobalSymbolNames < CUDA Only Array of device symbol names to be relocated to the host hipJitOption_hipJitOptionIRtoISAOptCountExt < Hip Only Count of linker options to be passed on to compiler hipJitOption_hipJitOptionIRtoISAOptExt < Hip Only Linker options to be passed on to compiler hipJitOption_hipJitOptionInfoLogBuffer < CUDA Only Pointer to the buffer with logged information hipJitOption_hipJitOptionInfoLogBufferSizeBytes < CUDA Only Size of the buffer in bytes for logged info hipJitOption_hipJitOptionLogVerbose < CUDA Only Generate log verbose hipJitOption_hipJitOptionLto < @deprecated CUDA Only Enable link-time optimization for device code hipJitOption_hipJitOptionMaxRegisters < CUDA Only Maximum registers may be used in a thread,
< passed to compiler hipJitOption_hipJitOptionMaxThreadsPerBlock < CUDA only Maximum number of threads in a thread block hipJitOption_hipJitOptionMinCTAPerSM < CUDA Only Hints to JIT compiler the minimum number of CTAs frin kernel’s
< grid to be mapped to SM hipJitOption_hipJitOptionNumOptions < Number of options hipJitOption_hipJitOptionOptimizationLevel < Value of optimization level for generated codes, acceptable options
< -O0, -O1, -O2, -O3 hipJitOption_hipJitOptionOverrideDirectiveValues < Cuda only Override Directive values hipJitOption_hipJitOptionPositionIndependentCode < CUDA Only Generates Position Independent code hipJitOption_hipJitOptionPrecDiv < @deprecated CUDA Only Set single-precision floating-point division
< and reciprocals hipJitOption_hipJitOptionPrecSqrt < @deprecated CUDA Only Set single-precision floating-point square root hipJitOption_hipJitOptionSm3xOpt < @deprecated CUDA Only New SM3X option. hipJitOption_hipJitOptionTarget < CUDA Only JIT target hipJitOption_hipJitOptionTargetFromContext < CUDA Only The target context, which is the default hipJitOption_hipJitOptionThreadsPerBlock < CUDA Only Number of thread per block hipJitOption_hipJitOptionWallTime < CUDA Only Value for total wall clock time hipLaunchAttributeID_hipLaunchAttributeAccessPolicyWindow < Valid for Streams, graph nodes, launches hipLaunchAttributeID_hipLaunchAttributeCooperative < Valid for graph nodes, launches hipLaunchAttributeID_hipLaunchAttributeMax hipLaunchAttributeID_hipLaunchAttributePriority < Valid for graph node, streams, launches hipLimit_t_hipExtLimitScratchCurrent < Current scratch limit threshold in bytes on this
< device. Must be between hipExtLimitScratchMin and
< hipExtLimitScratchMaxValid values. Valid only on Rocm
< device. This can be modified. hipLimit_t_hipExtLimitScratchMax < Maximum allowed value in bytes for scratch limit on this
< device. Valid only on Rocm device. This is read only. hipLimit_t_hipExtLimitScratchMin < Minimum allowed value in bytes for scratch limit on this
< device. Valid only on Rocm device. This is read only. hipLimit_t_hipLimitMallocHeapSize < Limit of heap size in bytes on the current device, should
< be less than the global memory size on the device hipLimit_t_hipLimitPrintfFifoSize < Size limit in bytes of fifo used by printf call on the
< device. Currently not supported hipLimit_t_hipLimitRange < Supported limit range hipLimit_t_hipLimitStackSize < Limit of stack size in bytes on the current device, per
< thread. The size is in units of 256 dwords, up to the
< limit of (128K - 16) hipMallocSignalMemory hipMemAccessFlags_hipMemAccessFlagsProtNone < Default, make the address range not accessible hipMemAccessFlags_hipMemAccessFlagsProtRead < Set the address range read accessible hipMemAccessFlags_hipMemAccessFlagsProtReadWrite < Set the address range read-write accessible hipMemAllocationGranularity_flags_hipMemAllocationGranularityMinimum < Minimum granularity hipMemAllocationGranularity_flags_hipMemAllocationGranularityRecommended < Recommended granularity for performance hipMemAllocationHandleType_hipMemHandleTypeNone < Does not allow any export mechanism hipMemAllocationHandleType_hipMemHandleTypePosixFileDescriptor < Allows a file descriptor for exporting. Permitted only on POSIX systems hipMemAllocationHandleType_hipMemHandleTypeWin32 < Allows a Win32 NT handle for exporting. (HANDLE) hipMemAllocationHandleType_hipMemHandleTypeWin32Kmt < Allows a Win32 KMT handle for exporting. (D3DKMT_HANDLE) hipMemAllocationType_hipMemAllocationTypeInvalid hipMemAllocationType_hipMemAllocationTypeMax This allocation type is ‘pinned’, i.e. cannot migrate from its current
location while the application is actively using it hipMemAllocationType_hipMemAllocationTypePinned This allocation type is ‘pinned’, i.e. cannot migrate from its current
location while the application is actively using it hipMemAttachGlobal hipMemAttachHost hipMemAttachSingle hipMemHandleType_hipMemHandleTypeGeneric < Generic handle type hipMemLocationType_hipMemLocationTypeDevice < Device location, thus it’s HIP device ID hipMemLocationType_hipMemLocationTypeInvalid hipMemOperationType_hipMemOperationTypeMap < Map operation hipMemOperationType_hipMemOperationTypeUnmap < Unmap operation hipMemPoolAttr_hipMemPoolAttrReleaseThreshold (value type = uint64_t)
Amount of reserved memory in bytes to hold onto before trying
to release memory back to the OS. When more than the release
threshold bytes of memory are held by the memory pool, the
allocator will try to release memory back to the OS on the
next call to stream, event or context synchronize. (default 0) hipMemPoolAttr_hipMemPoolAttrReservedMemCurrent (value type = uint64_t)
Amount of backing memory currently allocated for the mempool. hipMemPoolAttr_hipMemPoolAttrReservedMemHigh (value type = uint64_t)
High watermark of backing memory allocated for the mempool since the
last time it was reset. High watermark can only be reset to zero. hipMemPoolAttr_hipMemPoolAttrUsedMemCurrent (value type = uint64_t)
Amount of memory from the pool that is currently in use by the application. hipMemPoolAttr_hipMemPoolAttrUsedMemHigh (value type = uint64_t)
High watermark of the amount of memory from the pool that was in use by the application since
the last time it was reset. High watermark can only be reset to zero. hipMemPoolAttr_hipMemPoolReuseAllowInternalDependencies (value type = int)
Allow @p hipMemAllocAsync to insert new stream dependencies
in order to establish the stream ordering required to reuse
a piece of memory released by cuFreeAsync (default enabled). hipMemPoolAttr_hipMemPoolReuseAllowOpportunistic (value type = int)
Allow reuse of already completed frees when there is no dependency
between the free and allocation. (default enabled) hipMemPoolAttr_hipMemPoolReuseFollowEventDependencies (value type = int)
Allow @p hipMemAllocAsync to use memory asynchronously freed
in another streams as long as a stream ordering dependency
of the allocating stream on the free action exists.
hip events and null stream interactions can create the required
stream ordered dependencies. (default enabled) hipMemRangeAttribute_hipMemRangeAttributeAccessedBy < Memory range has hipMemAdviseSetAccessedBy
< set for the specified device hipMemRangeAttribute_hipMemRangeAttributeCoherencyMode < Returns coherency mode
< @ref hipMemRangeCoherencyMode for the range hipMemRangeAttribute_hipMemRangeAttributeLastPrefetchLocation < The last location to where the range was
< prefetched hipMemRangeAttribute_hipMemRangeAttributePreferredLocation < The preferred location of the range hipMemRangeAttribute_hipMemRangeAttributeReadMostly < Whether the range will mostly be read and
< only occassionally be written to hipMemRangeCoherencyMode_hipMemRangeCoherencyModeCoarseGrain < Writes to memory with this attribute can be
< performed by a single device at a time hipMemRangeCoherencyMode_hipMemRangeCoherencyModeFineGrain < Updates to memory with this attribute can be
< done coherently from all devices hipMemRangeCoherencyMode_hipMemRangeCoherencyModeIndeterminate < Memory region queried contains subregions with
< both hipMemRangeCoherencyModeFineGrain and
< hipMemRangeCoherencyModeCoarseGrain attributes hipMemRangeFlags_hipMemRangeFlagDmaBufMappingTypePcie hipMemRangeFlags_hipMemRangeFlagsMax hipMemRangeHandleType_hipMemRangeHandleTypeDmaBufFd hipMemRangeHandleType_hipMemRangeHandleTypeMax hipMemcpyKind_hipMemcpyDefault < Runtime will automatically determine
<copy-kind based on virtual addresses. hipMemcpyKind_hipMemcpyDeviceToDevice < Device-to-Device Copy hipMemcpyKind_hipMemcpyDeviceToDeviceNoCU < Device-to-Device Copy without using compute units hipMemcpyKind_hipMemcpyDeviceToHost < Device-to-Host Copy hipMemcpyKind_hipMemcpyHostToDevice < Host-to-Device Copy hipMemcpyKind_hipMemcpyHostToHost < Host-to-Host Copy hipMemoryAdvise_hipMemAdviseSetAccessedBy < Data will be accessed by the specified device
< so prevent page faults as much as possible hipMemoryAdvise_hipMemAdviseSetCoarseGrain < The default memory model is fine-grain. That allows
< coherent operations between host and device, while
< executing kernels. The coarse-grain can be used
< for data that only needs to be coherent at dispatch
< boundaries for better performance hipMemoryAdvise_hipMemAdviseSetPreferredLocation < Set the preferred location for the data as
< the specified device hipMemoryAdvise_hipMemAdviseSetReadMostly < Data will mostly be read and only occassionally
< be written to hipMemoryAdvise_hipMemAdviseUnsetAccessedBy < Let HIP to decide on the page faulting policy
< for the specified device hipMemoryAdvise_hipMemAdviseUnsetCoarseGrain < Restores cache coherency policy back to fine-grain hipMemoryAdvise_hipMemAdviseUnsetPreferredLocation < Clear the preferred location for the data hipMemoryAdvise_hipMemAdviseUnsetReadMostly < Undo the effect of hipMemAdviseSetReadMostly hipMemoryType_hipMemoryTypeArray < Array memory, physically located on device. (see deviceId for
< specific device) hipMemoryType_hipMemoryTypeDevice < Memory is physically located on device. (see deviceId for
< specific device) hipMemoryType_hipMemoryTypeHost < Memory is physically located on host hipMemoryType_hipMemoryTypeManaged < Managed memory, automaticallly managed by the unified
< memory system
< place holder for new values. hipMemoryType_hipMemoryTypeUnified < unified address space hipMemoryType_hipMemoryTypeUnregistered < Unregistered memory hipOccupancyDefault hipOccupancyDisableCachingOverride hipPointer_attribute_HIP_POINTER_ATTRIBUTE_ACCESS_FLAGS < Returns the access flags the device associated with
< for the corresponding memory referenced by the ptr hipPointer_attribute_HIP_POINTER_ATTRIBUTE_ALLOWED_HANDLE_TYPES < Bitmask of allowed hipmemAllocationHandleType
< for this allocation @warning This attribute is not supported in HIP hipPointer_attribute_HIP_POINTER_ATTRIBUTE_BUFFER_ID < Unique ID for an allocated memory region hipPointer_attribute_HIP_POINTER_ATTRIBUTE_CONTEXT < The context on which a pointer was allocated
< @warning This attribute is not supported in HIP hipPointer_attribute_HIP_POINTER_ATTRIBUTE_DEVICE_ORDINAL < device ordinal of a device on which a pointer
< was allocated or registered hipPointer_attribute_HIP_POINTER_ATTRIBUTE_DEVICE_POINTER < address at which the pointer is allocated on the device hipPointer_attribute_HIP_POINTER_ATTRIBUTE_HOST_POINTER < address at which the pointer is allocated on the host hipPointer_attribute_HIP_POINTER_ATTRIBUTE_IS_GPU_DIRECT_RDMA_CAPABLE < returns if the memory referenced by
< this pointer can be used with the GPUDirect RDMA API
< @warning This attribute is not supported in HIP hipPointer_attribute_HIP_POINTER_ATTRIBUTE_IS_LEGACY_HIP_IPC_CAPABLE < if this pointer maps to an allocation
< that is suitable for hipIpcGetMemHandle
< @warning This attribute is not supported in HIP hipPointer_attribute_HIP_POINTER_ATTRIBUTE_IS_MANAGED < Indicates if the pointer points to managed memory hipPointer_attribute_HIP_POINTER_ATTRIBUTE_MAPPED < tells if this pointer is in a valid address range
< that is mapped to a backing allocation hipPointer_attribute_HIP_POINTER_ATTRIBUTE_MEMORY_TYPE < memory type describing the location of a pointer hipPointer_attribute_HIP_POINTER_ATTRIBUTE_MEMPOOL_HANDLE < Returns the mempool handle for the allocation if
< it was allocated from a mempool
< @warning This attribute is not supported in HIP hipPointer_attribute_HIP_POINTER_ATTRIBUTE_P2P_TOKENS < A pair of tokens for use with Linux kernel interface
< @warning This attribute is not supported in HIP hipPointer_attribute_HIP_POINTER_ATTRIBUTE_RANGE_SIZE < Size of the address range for this requested pointer hipPointer_attribute_HIP_POINTER_ATTRIBUTE_RANGE_START_ADDR < Starting address for this requested pointer hipPointer_attribute_HIP_POINTER_ATTRIBUTE_SYNC_MEMOPS < Synchronize every synchronous memory operation
< initiated on this region hipResourceType_hipResourceTypeArray < Array resource hipResourceType_hipResourceTypeLinear < Linear resource hipResourceType_hipResourceTypeMipmappedArray < Mipmapped array resource hipResourceType_hipResourceTypePitch2D < Pitch 2D resource hipResourceViewFormat_hipResViewFormatFloat1 < 1 channel, 32-bit floating point hipResourceViewFormat_hipResViewFormatFloat2 < 2 channels, 32-bit floating point hipResourceViewFormat_hipResViewFormatFloat4 < 4 channels, 32-bit floating point hipResourceViewFormat_hipResViewFormatHalf1 < 1 channel, 16-bit floating point hipResourceViewFormat_hipResViewFormatHalf2 < 2 channels, 16-bit floating point hipResourceViewFormat_hipResViewFormatHalf4 < 4 channels, 16-bit floating point hipResourceViewFormat_hipResViewFormatNone < No resource view format (use underlying resource format) hipResourceViewFormat_hipResViewFormatSignedBlockCompressed4 < Block-compressed 4 signed hipResourceViewFormat_hipResViewFormatSignedBlockCompressed5 < Block-compressed 5 signed hipResourceViewFormat_hipResViewFormatSignedBlockCompressed6H < Block-compressed 6 signed half-float hipResourceViewFormat_hipResViewFormatSignedChar1 < 1 channel, signed 8-bit integers hipResourceViewFormat_hipResViewFormatSignedChar2 < 2 channels, signed 8-bit integers hipResourceViewFormat_hipResViewFormatSignedChar4 < 4 channels, signed 8-bit integers hipResourceViewFormat_hipResViewFormatSignedInt1 < 1 channel, signed 32-bit integers hipResourceViewFormat_hipResViewFormatSignedInt2 < 2 channels, signed 32-bit integers hipResourceViewFormat_hipResViewFormatSignedInt4 < 4 channels, signed 32-bit integers hipResourceViewFormat_hipResViewFormatSignedShort1 < 1 channel, signed 16-bit integers hipResourceViewFormat_hipResViewFormatSignedShort2 < 2 channels, signed 16-bit integers hipResourceViewFormat_hipResViewFormatSignedShort4 < 4 channels, signed 16-bit integers hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed1 < Block-compressed 1 hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed2 < Block-compressed 2 hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed3 < Block-compressed 3 hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed4 < Block-compressed 4 unsigned hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed5 < Block-compressed 5 unsigned hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed7 < Block-compressed 7 hipResourceViewFormat_hipResViewFormatUnsignedBlockCompressed6H < Block-compressed 6 unsigned half-float hipResourceViewFormat_hipResViewFormatUnsignedChar1 < 1 channel, unsigned 8-bit integers hipResourceViewFormat_hipResViewFormatUnsignedChar2 < 2 channels, unsigned 8-bit integers hipResourceViewFormat_hipResViewFormatUnsignedChar4 < 4 channels, unsigned 8-bit integers hipResourceViewFormat_hipResViewFormatUnsignedInt1 < 1 channel, unsigned 32-bit integers hipResourceViewFormat_hipResViewFormatUnsignedInt2 < 2 channels, unsigned 32-bit integers hipResourceViewFormat_hipResViewFormatUnsignedInt4 < 4 channels, unsigned 32-bit integers hipResourceViewFormat_hipResViewFormatUnsignedShort1 < 1 channel, unsigned 16-bit integers hipResourceViewFormat_hipResViewFormatUnsignedShort2 < 2 channels, unsigned 16-bit integers hipResourceViewFormat_hipResViewFormatUnsignedShort4 < 4 channels, unsigned 16-bit integers hipSharedMemConfig_hipSharedMemBankSizeDefault < The compiler selects a device-specific value for the banking. hipSharedMemConfig_hipSharedMemBankSizeEightByte < Shared mem is banked at 8-byte intervals and performs best
< when adjacent threads access data 4 bytes apart. hipSharedMemConfig_hipSharedMemBankSizeFourByte < Shared mem is banked at 4-bytes intervals and performs best
< when adjacent threads access data 4 bytes apart. hipStreamBatchMemOpType_hipStreamMemOpBarrier < Currently not supported hipStreamBatchMemOpType_hipStreamMemOpFlushRemoteWrites < Currently not supported hipStreamBatchMemOpType_hipStreamMemOpWaitValue32 hipStreamBatchMemOpType_hipStreamMemOpWaitValue64 hipStreamBatchMemOpType_hipStreamMemOpWriteValue32 hipStreamBatchMemOpType_hipStreamMemOpWriteValue64 hipStreamCaptureMode_hipStreamCaptureModeGlobal hipStreamCaptureMode_hipStreamCaptureModeRelaxed hipStreamCaptureMode_hipStreamCaptureModeThreadLocal hipStreamCaptureStatus_hipStreamCaptureStatusActive < Stream is actively capturing hipStreamCaptureStatus_hipStreamCaptureStatusInvalidated < Stream is part of a capture sequence that has been
< invalidated, but not terminated hipStreamCaptureStatus_hipStreamCaptureStatusNone < Stream is not capturing hipStreamDefault hipStreamNonBlocking hipStreamUpdateCaptureDependenciesFlags_hipStreamAddCaptureDependencies < Add new nodes to the dependency set hipStreamUpdateCaptureDependenciesFlags_hipStreamSetCaptureDependencies < Replace the dependency set with the new nodes hipStreamWaitValueAnd hipStreamWaitValueEq hipStreamWaitValueGte hipStreamWaitValueNor hipSurfaceBoundaryMode_hipBoundaryModeClamp hipSurfaceBoundaryMode_hipBoundaryModeTrap hipSurfaceBoundaryMode_hipBoundaryModeZero hipTextureAddressMode_hipAddressModeBorder hipTextureAddressMode_hipAddressModeClamp hipTextureAddressMode_hipAddressModeMirror hipTextureAddressMode_hipAddressModeWrap hipTextureFilterMode_hipFilterModeLinear hipTextureFilterMode_hipFilterModePoint hipTextureReadMode_hipReadModeElementType hipTextureReadMode_hipReadModeNormalizedFloat hipTextureType1D hipTextureType1DLayered hipTextureType2D hipTextureType2DLayered hipTextureType3D hipTextureTypeCubemap hipTextureTypeCubemapLayered hipUserObjectFlags_hipUserObjectNoDestructorSync < Destructor execution is not synchronized. hipUserObjectRetainFlags_hipGraphUserObjectMove < Add new reference or retain. hiprtcResult_HIPRTC_ERROR_BUILTIN_OPERATION_FAILURE < Failed in builtin operation hiprtcResult_HIPRTC_ERROR_COMPILATION < Compilation error hiprtcResult_HIPRTC_ERROR_INTERNAL_ERROR < Internal error hiprtcResult_HIPRTC_ERROR_INVALID_INPUT < Invalid input hiprtcResult_HIPRTC_ERROR_INVALID_OPTION < Invalid option hiprtcResult_HIPRTC_ERROR_INVALID_PROGRAM < Invalid program hiprtcResult_HIPRTC_ERROR_LINKING < Error in linking hiprtcResult_HIPRTC_ERROR_NAME_EXPRESSION_NOT_VALID < Invalid name expression hiprtcResult_HIPRTC_ERROR_NO_LOWERED_NAMES_BEFORE_COMPILATION < No lowered names before compilation hiprtcResult_HIPRTC_ERROR_NO_NAME_EXPRESSIONS_AFTER_COMPILATION < No name expression after compilation hiprtcResult_HIPRTC_ERROR_OUT_OF_MEMORY < Out of memory hiprtcResult_HIPRTC_ERROR_PROGRAM_CREATION_FAILURE < Failed to create program hiprtcResult_HIPRTC_SUCCESS < Success _Exit ⚠ __ctype_get_mb_cur_max ⚠ __hipGetPCH ⚠ Internal use only. This API may change in the future
Pre-Compiled header for online compilation __hipPopCallConfiguration ⚠ @brief Pop configuration of a kernel launch. __hipPushCallConfiguration ⚠ @brief Push configuration of a kernel launch. a64l ⚠ abort ⚠ abs ⚠ aligned_alloc ⚠ alloca ⚠ arc4random ⚠ arc4random_buf ⚠ arc4random_uniform ⚠ at_quick_exit ⚠ atexit ⚠ atof ⚠ atoi ⚠ atol ⚠ atoll ⚠ bsearch ⚠ calloc ⚠ clearenv ⚠ div ⚠ drand48 ⚠ drand48_r ⚠ ecvt ⚠ ecvt_r ⚠ erand48 ⚠ erand48_r ⚠ exit ⚠ fcvt ⚠ fcvt_r ⚠ free ⚠ gcvt ⚠ getenv ⚠ getloadavg ⚠ getsubopt ⚠ hipApiName ⚠ @defgroup Callback Callback Activity APIs
@{
This section describes the callback/Activity of HIP runtime API.
/
/**
@brief Returns HIP API name by ID. hipArray3DCreate ⚠ @brief Create a 3D array memory pointer on the device. hipArray3DGetDescriptor ⚠ @brief Gets a 3D array descriptor hipArrayCreate ⚠ @brief Create an array memory pointer on the device. hipArrayDestroy ⚠ @brief Destroy an array memory pointer on the device. hipArrayGetDescriptor ⚠ @brief Gets a 1D or 2D array descriptor hipArrayGetInfo ⚠ @brief Gets info about the specified array hipBindTexture ⚠ @brief Binds a memory area to a texture [Deprecated] hipBindTexture2D ⚠ @brief Binds a 2D memory area to a texture [Deprecated] hipBindTextureToArray ⚠ @brief Binds a memory area to a texture [Deprecated] hipBindTextureToMipmappedArray ⚠ @brief Binds a mipmapped array to a texture [Deprecated] hipChooseDeviceR0600 ⚠ @brief Device which matches hipDeviceProp_t is returned hipConfigureCall ⚠ @}
/
/** hipCreateChannelDesc ⚠ hipCreateSurfaceObject ⚠ @brief Create a surface object. hipCreateTextureObject ⚠ @brief Creates a texture object. hipCtxCreate ⚠ @brief Create a context and set it as current/default context hipCtxDestroy ⚠ @brief Destroy a HIP context [Deprecated] hipCtxDisablePeerAccess ⚠ @brief Disable direct access from current context’s virtual address space to memory allocations
physically located on a peer context.Disables direct access to memory allocations in a peer
context and unregisters any registered allocations [Deprecated] hipCtxEnablePeerAccess ⚠ @brief Enables direct access to memory allocations in a peer context [Deprecated] hipCtxGetApiVersion ⚠ @brief Returns the approximate HIP api version. hipCtxGetCacheConfig ⚠ @brief Get Cache configuration for a specific function [Deprecated] hipCtxGetCurrent ⚠ @brief Get the handle of the current/ default context [Deprecated] hipCtxGetDevice ⚠ @brief Get the handle of the device associated with current/default context [Deprecated] hipCtxGetFlags ⚠ @brief Return flags used for creating default context [Deprecated] hipCtxGetSharedMemConfig ⚠ @brief Get Shared memory bank configuration [Deprecated] hipCtxPopCurrent ⚠ @brief Pop the current/default context and return the popped context [Deprecated] hipCtxPushCurrent ⚠ @brief Push the context to be set as current/ default context [Deprecated] hipCtxSetCacheConfig ⚠ @brief Set L1/Shared cache partition [Deprecated] hipCtxSetCurrent ⚠ @brief Set the passed context as current/default [Deprecated] hipCtxSetSharedMemConfig ⚠ @brief Set Shared memory bank configuration [Deprecated] hipCtxSynchronize ⚠ @brief Blocks until the default context has completed all preceding requested tasks [Deprecated] hipDestroyExternalMemory ⚠ @brief Destroys an external memory object. hipDestroyExternalSemaphore ⚠ @brief Destroys an external semaphore object and releases any references to the underlying resource. Any outstanding signals or waits must have completed before the semaphore is destroyed. hipDestroySurfaceObject ⚠ @brief Destroy a surface object. hipDestroyTextureObject ⚠ @brief Destroys a texture object. hipDeviceCanAccessPeer ⚠ @}
/
/** hipDeviceComputeCapability ⚠ @brief Returns the compute capability of the device
@param [out] major Major compute capability version number
@param [out] minor Minor compute capability version number
@param [in] device Device ordinal hipDeviceDisablePeerAccess ⚠ @brief Disables direct access to memory allocations on a peer device. hipDeviceEnablePeerAccess ⚠ @brief Enables direct access to memory allocations on a peer device. hipDeviceGet ⚠ @brief Returns a handle to a compute device
@param [out] device Handle of device
@param [in] ordinal Device ordinal hipDeviceGetAttribute ⚠ @brief Query for a specific device attribute. hipDeviceGetByPCIBusId ⚠ @brief Returns a handle to a compute device.
@param [out] device The handle of the device
@param [in] pciBusId The string of PCI Bus Id for the device hipDeviceGetCacheConfig ⚠ @brief Get Cache configuration for a specific Device hipDeviceGetDefaultMemPool ⚠ @brief Returns the default memory pool of the specified device hipDeviceGetGraphMemAttribute ⚠ @brief Get the mem attribute for graphs. hipDeviceGetLimit ⚠ @brief Gets resource limits of current device hipDeviceGetMemPool ⚠ @brief Gets the current memory pool for the specified device hipDeviceGetName ⚠ @brief Returns an identifer string for the device.
@param [out] name String of the device name
@param [in] len Maximum length of string to store in device name
@param [in] device Device ordinal hipDeviceGetP2PAttribute ⚠ @brief Returns a value for attribute of link between two devices
@param [out] value Pointer of the value for the attrubute
@param [in] attr enum of hipDeviceP2PAttr to query
@param [in] srcDevice The source device of the link
@param [in] dstDevice The destination device of the link hipDeviceGetPCIBusId ⚠ @brief Returns a PCI Bus Id string for the device, overloaded to take int device ID.
@param [out] pciBusId The string of PCI Bus Id format for the device
@param [in] len Maximum length of string
@param [in] device The device ordinal hipDeviceGetSharedMemConfig ⚠ @brief Returns bank width of shared memory for current device hipDeviceGetStreamPriorityRange ⚠ @brief Returns numerical values that correspond to the least and greatest stream priority. hipDeviceGetTexture1DLinearMaxWidth ⚠ @brief Gets the maximum width for 1D linear textures on the specified device hipDeviceGetUuid ⚠ @brief Returns an UUID for the device.[BETA]
@param [out] uuid UUID for the device
@param [in] device device ordinal hipDeviceGraphMemTrim ⚠ @brief Free unused memory reserved for graphs on a specific device and return it back to the OS. hipDevicePrimaryCtxGetState ⚠ @brief Get the state of the primary context [Deprecated] hipDevicePrimaryCtxRelease ⚠ @brief Release the primary context on the GPU. hipDevicePrimaryCtxReset ⚠ @brief Resets the primary context on the GPU [Deprecated] hipDevicePrimaryCtxRetain ⚠ @brief Retain the primary context on the GPU [Deprecated] hipDevicePrimaryCtxSetFlags ⚠ @brief Set flags for the primary context [Deprecated] hipDeviceReset ⚠ @brief The state of current device is discarded and updated to a fresh state. hipDeviceSetCacheConfig ⚠ @brief Set L1/Shared cache partition. hipDeviceSetGraphMemAttribute ⚠ @brief Set the mem attribute for graphs. hipDeviceSetLimit ⚠ @brief Sets resource limits of current device. hipDeviceSetMemPool ⚠ @brief Sets the current memory pool of a device hipDeviceSetSharedMemConfig ⚠ @brief The bank width of shared memory on current device is set hipDeviceSynchronize ⚠ @}
/
/**
@defgroup Device Device Management
@{
This section describes the device management functions of HIP runtime API.
/
/**
@brief Waits on all active streams on current device hipDeviceTotalMem ⚠ @brief Returns the total amount of memory on the device.
@param [out] bytes The size of memory in bytes, on the device
@param [in] device The ordinal of the device hipDriverGetVersion ⚠ @brief Returns the approximate HIP driver version. hipDrvGetErrorName ⚠ @brief Return hip error as text string form. hipDrvGetErrorString ⚠ @brief Return handy text string message to explain the error which occurred hipDrvGraphAddMemFreeNode ⚠ @brief Creates a memory free node and adds it to a graph hipDrvGraphAddMemcpyNode ⚠ @brief Creates a memcpy node and adds it to a graph. hipDrvGraphAddMemsetNode ⚠ @brief Creates a memset node and adds it to a graph. hipDrvGraphExecMemcpyNodeSetParams ⚠ @brief Sets the parameters for a memcpy node in the given graphExec. hipDrvGraphExecMemsetNodeSetParams ⚠ @brief Sets the parameters for a memset node in the given graphExec. hipDrvGraphMemcpyNodeGetParams ⚠ @brief Gets a memcpy node’s parameters. hipDrvGraphMemcpyNodeSetParams ⚠ @brief Sets a memcpy node’s parameters. hipDrvLaunchKernelEx ⚠ @brief Launches a HIP kernel using the driver API with the specified configuration.
@ingroup Execution hipDrvMemcpy2DUnaligned ⚠ Copies memory for 2D arrays. hipDrvMemcpy3D ⚠ @brief Copies data between host and device. hipDrvMemcpy3DAsync ⚠ @brief Copies data between host and device asynchronously. hipDrvPointerGetAttributes ⚠ @brief Returns information about the specified pointer.[BETA] hipEventCreate ⚠ Create an event hipEventCreateWithFlags ⚠ @}
/
/** hipEventDestroy ⚠ @brief Destroy the specified event. hipEventElapsedTime ⚠ @brief Return the elapsed time between two events. hipEventQuery ⚠ @brief Query event status hipEventRecord ⚠ hipEventRecordWithFlags ⚠ @brief Record an event in the specified stream. hipEventRecord_spt ⚠ hipEventSynchronize ⚠ @brief Wait for an event to complete. hipExtGetLastError ⚠ @brief Return last error returned by any HIP runtime API call and resets the stored error code to
#hipSuccess hipExtGetLinkTypeAndHopCount ⚠ @brief Returns the link type and hop count between two devices hipExtLaunchKernel ⚠ @brief Launches kernel from the pointer address, with arguments and shared memory on stream. hipExtLaunchMultiKernelMultiDevice ⚠ @brief Launches kernels on multiple devices and guarantees all specified kernels are dispatched
on respective streams before enqueuing any other work on the specified streams from any other threads
@ingroup Execution
@param [in] launchParamsList List of launch parameters, one per device.
@param [in] numDevices Size of the launchParamsList array.
@param [in] flags Flags to control launch behavior. hipExtMallocWithFlags ⚠ @brief Allocate memory on the default accelerator hipExtStreamCreateWithCUMask ⚠ @brief Creates an asynchronous stream with the specified CU mask. hipExtStreamGetCUMask ⚠ @brief Gets CU mask associated with an asynchronous stream hipExternalMemoryGetMappedBuffer ⚠ @brief Maps a buffer onto an imported memory object. hipExternalMemoryGetMappedMipmappedArray ⚠ @brief Maps a mipmapped array onto an external memory object. hipFree ⚠ @brief Free memory allocated by the HIP-Clang hip memory allocation API.
This API performs an implicit hipDeviceSynchronize() call.
If pointer is NULL, the hip runtime is initialized and hipSuccess is returned. hipFreeArray ⚠ @brief Frees an array on the device. hipFreeAsync ⚠ @brief Frees memory with stream ordered semantics hipFreeHost ⚠ @brief Frees page-locked memory
This API performs an implicit hipDeviceSynchronize() call.
If pointer is NULL, the hip runtime is initialized and hipSuccess is returned. hipFreeMipmappedArray ⚠ @brief Frees a mipmapped array on the device. hipFuncGetAttribute ⚠ @brief Find out a specific attribute for a given function.
@ingroup Execution
@param [out] value Pointer to the value
@param [in] attrib Attributes of the given funtion
@param [in] hfunc Function to get attributes from hipFuncGetAttributes ⚠ @brief Find out attributes for a given function.
@ingroup Execution
@param [out] attr Attributes of funtion
@param [in] func Pointer to the function handle hipFuncSetAttribute ⚠ @}
/
/** hipFuncSetCacheConfig ⚠ @brief Set Cache configuration for a specific function hipFuncSetSharedMemConfig ⚠ @brief Set shared memory configuation for a specific function hipGetChannelDesc ⚠ @brief Gets the channel descriptor in an array. hipGetDevice ⚠ @brief Return the default device id for the calling host thread. hipGetDeviceCount ⚠ @brief Return number of compute-capable devices. hipGetDeviceFlags ⚠ @brief Gets the flags set for current device hipGetDevicePropertiesR0600 ⚠ @brief Returns device properties. hipGetErrorName ⚠ @brief Return hip error as text string form. hipGetErrorString ⚠ @brief Return handy text string message to explain the error which occurred hipGetFuncBySymbol ⚠ @brief Gets pointer to device entry function that matches entry function symbolPtr. hipGetLastError ⚠ @}
/
/** hipGetMipmappedArrayLevel ⚠ @brief Gets a mipmap level of a HIP mipmapped array. hipGetProcAddress ⚠ @brief Gets the pointer of requested HIP driver function. hipGetStreamDeviceId ⚠ @brief Returns device ID on the stream. hipGetSymbolAddress ⚠ @brief Gets device pointer associated with symbol on the device. hipGetSymbolSize ⚠ @brief Gets the size of the given symbol on the device. hipGetTextureAlignmentOffset ⚠ @brief Get the offset of the alignment in a texture [Deprecated] hipGetTextureObjectResourceDesc ⚠ @brief Gets resource descriptor for the texture object. hipGetTextureObjectResourceViewDesc ⚠ @brief Gets resource view descriptor for the texture object. hipGetTextureObjectTextureDesc ⚠ @brief Gets texture descriptor for the texture object. hipGetTextureReference ⚠ @brief Gets the texture reference related with the symbol [Deprecated] hipGraphAddBatchMemOpNode ⚠ @brief Creates a batch memory operation node and adds it to a graph.[BETA] hipGraphAddChildGraphNode ⚠ @brief Creates a child graph node and adds it to a graph. hipGraphAddDependencies ⚠ @brief Adds dependency edges to a graph. hipGraphAddEmptyNode ⚠ @brief Creates an empty node and adds it to a graph. hipGraphAddEventRecordNode ⚠ @brief Creates an event record node and adds it to a graph. hipGraphAddEventWaitNode ⚠ @brief Creates an event wait node and adds it to a graph. hipGraphAddExternalSemaphoresSignalNode ⚠ @brief Creates a external semaphor signal node and adds it to a graph. hipGraphAddExternalSemaphoresWaitNode ⚠ @brief Creates a external semaphor wait node and adds it to a graph. hipGraphAddHostNode ⚠ @brief Creates a host execution node and adds it to a graph. hipGraphAddKernelNode ⚠ @brief Creates a kernel execution node and adds it to a graph. hipGraphAddMemAllocNode ⚠ @brief Creates a memory allocation node and adds it to a graph hipGraphAddMemFreeNode ⚠ @brief Creates a memory free node and adds it to a graph hipGraphAddMemcpyNode ⚠ @brief Creates a memcpy node and adds it to a graph. hipGraphAddMemcpyNode1D ⚠ @brief Creates a 1D memcpy node and adds it to a graph. hipGraphAddMemcpyNodeFromSymbol ⚠ @brief Creates a memcpy node to copy from a symbol on the device and adds it to a graph. hipGraphAddMemcpyNodeToSymbol ⚠ @brief Creates a memcpy node to copy to a symbol on the device and adds it to a graph. hipGraphAddMemsetNode ⚠ @brief Creates a memset node and adds it to a graph. hipGraphAddNode ⚠ @brief Creates a kernel execution node and adds it to a graph. hipGraphBatchMemOpNodeGetParams ⚠ @brief Returns a batch mem op node’s parameters.[BETA] hipGraphBatchMemOpNodeSetParams ⚠ @brief Sets the batch mem op node’s parameters.[BETA] hipGraphChildGraphNodeGetGraph ⚠ @brief Gets a handle to the embedded graph of a child graph node. hipGraphClone ⚠ @brief Clones a graph. hipGraphCreate ⚠ @brief Creates a graph hipGraphDebugDotPrint ⚠ @brief Write a DOT file describing graph structure. hipGraphDestroy ⚠ @brief Destroys a graph hipGraphDestroyNode ⚠ @brief Remove a node from the graph. hipGraphEventRecordNodeGetEvent ⚠ @brief Returns the event associated with an event record node. hipGraphEventRecordNodeSetEvent ⚠ @brief Sets an event record node’s event. hipGraphEventWaitNodeGetEvent ⚠ @brief Returns the event associated with an event wait node. hipGraphEventWaitNodeSetEvent ⚠ @brief Sets an event wait node’s event. hipGraphExecBatchMemOpNodeSetParams ⚠ @brief Sets the parameters for a batch mem op node in the given graphExec.[BETA] hipGraphExecChildGraphNodeSetParams ⚠ @brief Updates node parameters in the child graph node in the given graphExec. hipGraphExecDestroy ⚠ @brief Destroys an executable graph hipGraphExecEventRecordNodeSetEvent ⚠ @brief Sets the event for an event record node in the given graphExec. hipGraphExecEventWaitNodeSetEvent ⚠ @brief Sets the event for an event record node in the given graphExec. hipGraphExecExternalSemaphoresSignalNodeSetParams ⚠ @brief Updates node parameters in the external semaphore signal node in the given graphExec. hipGraphExecExternalSemaphoresWaitNodeSetParams ⚠ @brief Updates node parameters in the external semaphore wait node in the given graphExec. hipGraphExecGetFlags ⚠ @brief Return the flags of an executable graph. hipGraphExecHostNodeSetParams ⚠ @brief Sets the parameters for a host node in the given graphExec. hipGraphExecKernelNodeSetParams ⚠ @brief Sets the parameters for a kernel node in the given graphExec. hipGraphExecMemcpyNodeSetParams ⚠ @brief Sets the parameters of a memcpy node in the given graphExec. hipGraphExecMemcpyNodeSetParams1D ⚠ @brief Sets the parameters for a memcpy node in the given graphExec to perform a 1-dimensional
copy. hipGraphExecMemcpyNodeSetParamsFromSymbol ⚠ @brief Sets the parameters for a memcpy node in the given graphExec to copy from a symbol on the hipGraphExecMemcpyNodeSetParamsToSymbol ⚠ @brief Sets the parameters for a memcpy node in the given graphExec to copy to a symbol on the
device.
@param [in] hGraphExec - Instance of the executable graph with the node.
@param [in] node - Instance of the node to set parameters of.
@param [in] symbol - Device symbol address.
@param [in] src - Pointer to memory address of the src.
@param [in] count - Size of the memory to copy.
@param [in] offset - Offset from start of symbol in bytes.
@param [in] kind - Type of memory copy.
@returns #hipSuccess, #hipErrorInvalidValue hipGraphExecMemsetNodeSetParams ⚠ @brief Sets the parameters for a memset node in the given graphExec. hipGraphExecNodeSetParams ⚠ @brief Updates parameters of an executable graph’s node. hipGraphExecUpdate ⚠ @brief Check whether an executable graph can be updated with a graph and perform the update if *
possible. hipGraphExternalSemaphoresSignalNodeGetParams ⚠ @brief Returns external semaphore signal node params. hipGraphExternalSemaphoresSignalNodeSetParams ⚠ @brief Updates node parameters in the external semaphore signal node. hipGraphExternalSemaphoresWaitNodeGetParams ⚠ @brief Returns external semaphore wait node params. hipGraphExternalSemaphoresWaitNodeSetParams ⚠ @brief Updates node parameters in the external semaphore wait node. hipGraphGetEdges ⚠ @brief Returns a graph’s dependency edges. hipGraphGetNodes ⚠ @brief Returns a graph’s nodes. hipGraphGetRootNodes ⚠ @brief Returns a graph’s root nodes. hipGraphHostNodeGetParams ⚠ @brief Returns a host node’s parameters. hipGraphHostNodeSetParams ⚠ @brief Sets a host node’s parameters. hipGraphInstantiate ⚠ @brief Creates an executable graph from a graph hipGraphInstantiateWithFlags ⚠ @brief Creates an executable graph from a graph. hipGraphInstantiateWithParams ⚠ @brief Creates an executable graph from a graph. hipGraphKernelNodeCopyAttributes ⚠ @brief Copies attributes from source node to destination node. hipGraphKernelNodeGetAttribute ⚠ @brief Gets a node’s attribute. hipGraphKernelNodeGetParams ⚠ @brief Gets kernel node’s parameters. hipGraphKernelNodeSetAttribute ⚠ @brief Sets a node’s attribute. hipGraphKernelNodeSetParams ⚠ @brief Sets a kernel node’s parameters. hipGraphLaunch ⚠ @brief Launches an executable graph in the specified stream. hipGraphLaunch_spt ⚠ hipGraphMemAllocNodeGetParams ⚠ @brief Returns parameters for memory allocation node hipGraphMemFreeNodeGetParams ⚠ @brief Returns parameters for memory free node hipGraphMemcpyNodeGetParams ⚠ @brief Gets a memcpy node’s parameters. hipGraphMemcpyNodeSetParams ⚠ @brief Sets a memcpy node’s parameters. hipGraphMemcpyNodeSetParams1D ⚠ @brief Sets a memcpy node’s parameters to perform a 1-dimensional copy. hipGraphMemcpyNodeSetParamsFromSymbol ⚠ @brief Sets a memcpy node’s parameters to copy from a symbol on the device. hipGraphMemcpyNodeSetParamsToSymbol ⚠ @brief Sets a memcpy node’s parameters to copy to a symbol on the device. hipGraphMemsetNodeGetParams ⚠ @brief Gets a memset node’s parameters. hipGraphMemsetNodeSetParams ⚠ @brief Sets a memset node’s parameters. hipGraphNodeFindInClone ⚠ @brief Finds a cloned version of a node. hipGraphNodeGetDependencies ⚠ @brief Returns a node’s dependencies. hipGraphNodeGetDependentNodes ⚠ @brief Returns a node’s dependent nodes. hipGraphNodeGetEnabled ⚠ @brief Query whether a node in the given graphExec is enabled hipGraphNodeGetType ⚠ @brief Returns a node’s type. hipGraphNodeSetEnabled ⚠ @brief Enables or disables the specified node in the given graphExec hipGraphNodeSetParams ⚠ @brief Updates parameters of a graph’s node. hipGraphReleaseUserObject ⚠ @brief Release user object from graphs. hipGraphRemoveDependencies ⚠ @brief Removes dependency edges from a graph. hipGraphRetainUserObject ⚠ @brief Retain user object for graphs. hipGraphUpload ⚠ @brief Uploads an executable graph to a stream hipGraphicsMapResources ⚠ @brief Maps a graphics resource for access. hipGraphicsResourceGetMappedPointer ⚠ @brief Gets device accessible address of a graphics resource. hipGraphicsSubResourceGetMappedArray ⚠ @brief Get an array through which to access a subresource of a mapped graphics resource. hipGraphicsUnmapResources ⚠ @brief Unmaps graphics resources. hipGraphicsUnregisterResource ⚠ @brief Unregisters a graphics resource. hipHostAlloc ⚠ @brief Allocate device accessible page locked host memory hipHostFree ⚠ @brief Free memory allocated by the HIP-Clang hip host memory allocation API
This API performs an implicit hipDeviceSynchronize() call.
If pointer is NULL, the hip runtime is initialized and hipSuccess is returned. hipHostGetDevicePointer ⚠ @brief Get Device pointer from Host Pointer allocated through hipHostMalloc hipHostGetFlags ⚠ @brief Return flags associated with host pointer hipHostMalloc ⚠ @}
/
/**
@brief Allocates device accessible page locked (pinned) host memory hipHostRegister ⚠ @brief Register host memory so it can be accessed from the current device. hipHostUnregister ⚠ @brief Un-register host pointer hipImportExternalMemory ⚠ @brief Imports an external memory object. hipImportExternalSemaphore ⚠ hipInit ⚠ @}
/
/**
@defgroup API HIP API
@{ hipIpcCloseMemHandle ⚠ @brief Close memory mapped with hipIpcOpenMemHandle hipIpcGetEventHandle ⚠ @brief Gets an opaque interprocess handle for an event. hipIpcGetMemHandle ⚠ @brief Gets an interprocess memory handle for an existing device memory
allocation hipIpcOpenEventHandle ⚠ @brief Opens an interprocess event handles. hipIpcOpenMemHandle ⚠ @brief Opens an interprocess memory handle exported from another process
and returns a device pointer usable in the local process. hipKernelNameRef ⚠ @brief Returns kernel name reference by function name. hipKernelNameRefByPtr ⚠ @brief Retrives kernel for a given host pointer, unless stated otherwise. hipLaunchByPtr ⚠ @brief Launch a kernel. hipLaunchCooperativeKernel ⚠ @brief Launches kernel f with launch parameters and shared memory on stream with arguments passed
to kernelparams or extra, where thread blocks can cooperate and synchronize as they execute. hipLaunchCooperativeKernelMultiDevice ⚠ @brief Launches kernels on multiple devices where thread blocks can cooperate and
synchronize as they execute. hipLaunchCooperativeKernel_spt ⚠ hipLaunchHostFunc ⚠ @brief Enqueues a host function call in a stream. hipLaunchHostFunc_spt ⚠ hipLaunchKernel ⚠ @brief C compliant kernel launch API hipLaunchKernelExC ⚠ @brief Launches a HIP kernel using a generic function pointer and the specified configuration.
@ingroup Execution hipLaunchKernel_spt ⚠ hipLinkAddData ⚠ @brief Adds bitcode data to be linked with options.
@param [in] state hip link state
@param [in] type Type of the input data or bitcode
@param [in] data Input data which is null terminated
@param [in] size Size of the input data
@param [in] name Optional name for this input
@param [in] numOptions Size of the options
@param [in] options Array of options applied to this input
@param [in] optionValues Array of option values cast to void* hipLinkAddFile ⚠ @brief Adds a file with bitcode to be linked with options.
@param [in] state hip link state
@param [in] type Type of the input data or bitcode
@param [in] path Path to the input file where bitcode is present
@param [in] numOptions Size of the options
@param [in] options Array of options applied to this input
@param [in] optionValues Array of option values cast to void* hipLinkComplete ⚠ @brief Completes the linking of the given program.
@param [in] state hip link state
@param [out] hipBinOut Upon success, points to the output binary
@param [out] sizeOut Size of the binary is stored (optional) hipLinkCreate ⚠ @brief Creates a linker instance with options.
@param [in] numOptions Number of options
@param [in] option Array of options
@param [in] optionValues Array of option values cast to void*
@param [out] stateOut hip link state created upon success hipLinkDestroy ⚠ @brief Deletes the linker instance.
@param [in] state link state instance hipMalloc ⚠ @}
/
/**
@brief Allocate memory on the default accelerator hipMalloc3D ⚠ @brief Create a 3D memory pointer on the device. hipMalloc3DArray ⚠ @brief Allocate an array on the device. hipMallocArray ⚠ @brief Allocate an array on the device. hipMallocAsync ⚠ @brief Allocates memory with stream ordered semantics hipMallocFromPoolAsync ⚠ @brief Allocates memory from a specified pool with stream ordered semantics. hipMallocHost ⚠ @brief Allocate pinned host memory [Deprecated] hipMallocManaged ⚠ hipMallocMipmappedArray ⚠ @brief Allocate a mipmapped array on the device. hipMallocPitch ⚠ Allocates at least width (in bytes) * height bytes of linear memory
Padding may occur to ensure alighnment requirements are met for the given row
The change in width size due to padding will be returned in *pitch.
Currently the alignment is set to 128 bytes hipMemAddressFree ⚠ @brief Frees an address range reservation made via hipMemAddressReserve hipMemAddressReserve ⚠ @brief Reserves an address range hipMemAdvise ⚠ @brief Advise about the usage of a given memory range to HIP. hipMemAllocHost ⚠ @brief Allocate pinned host memory [Deprecated] hipMemAllocPitch ⚠ Allocates at least width (in bytes) * height bytes of linear memory
Padding may occur to ensure alighnment requirements are met for the given row
The change in width size due to padding will be returned in *pitch.
Currently the alignment is set to 128 bytes hipMemCreate ⚠ @brief Creates a memory allocation described by the properties and size hipMemExportToShareableHandle ⚠ @brief Exports an allocation to a requested shareable handle type. hipMemGetAccess ⚠ @brief Get the access flags set for the given location and ptr. hipMemGetAddressRange ⚠ @brief Get information on memory allocations. hipMemGetAllocationGranularity ⚠ @brief Calculates either the minimal or recommended granularity. hipMemGetAllocationPropertiesFromHandle ⚠ @brief Retrieve the property structure of the given handle. hipMemGetHandleForAddressRange ⚠ @brief Returns a handle for the address range requested. hipMemGetInfo ⚠ @brief Query memory info. hipMemImportFromShareableHandle ⚠ @brief Imports an allocation from a requested shareable handle type. hipMemMap ⚠ @brief Maps an allocation handle to a reserved virtual address range. hipMemMapArrayAsync ⚠ @brief Maps or unmaps subregions of sparse HIP arrays and sparse HIP mipmapped arrays. hipMemPoolCreate ⚠ @brief Creates a memory pool hipMemPoolDestroy ⚠ @brief Destroys the specified memory pool hipMemPoolExportPointer ⚠ @brief Export data to share a memory pool allocation between processes. hipMemPoolExportToShareableHandle ⚠ @brief Exports a memory pool to the requested handle type. hipMemPoolGetAccess ⚠ @brief Returns the accessibility of a pool from a device hipMemPoolGetAttribute ⚠ @brief Gets attributes of a memory pool hipMemPoolImportFromShareableHandle ⚠ @brief Imports a memory pool from a shared handle. hipMemPoolImportPointer ⚠ @brief Import a memory pool allocation from another process. hipMemPoolSetAccess ⚠ @brief Controls visibility of the specified pool between devices hipMemPoolSetAttribute ⚠ @brief Sets attributes of a memory pool hipMemPoolTrimTo ⚠ @brief Releases freed memory back to the OS hipMemPrefetchAsync ⚠ @brief Prefetches memory to the specified destination device using HIP. hipMemPtrGetInfo ⚠ @brief Get allocated memory size via memory pointer. hipMemRangeGetAttribute ⚠ @brief Query an attribute of a given memory range in HIP. hipMemRangeGetAttributes ⚠ @brief Query attributes of a given memory range in HIP. hipMemRelease ⚠ @brief Release a memory handle representing a memory allocation which was previously allocated through hipMemCreate. hipMemRetainAllocationHandle ⚠ @brief Returns the allocation handle of the backing memory allocation given the address. hipMemSetAccess ⚠ @brief Set the access flags for each location specified in desc for the given virtual address range. hipMemUnmap ⚠ @brief Unmap memory allocation of a given address range. hipMemcpy ⚠ @brief Copy data from src to dst. hipMemcpy2D ⚠ @brief Copies data between host and device. hipMemcpy2DArrayToArray ⚠ @brief Copies data between host and device. hipMemcpy2DAsync ⚠ @brief Copies data between host and device asynchronously. hipMemcpy2DAsync_spt ⚠ hipMemcpy2DFromArray ⚠ @brief Copies data between host and device. hipMemcpy2DFromArrayAsync ⚠ @brief Copies data between host and device asynchronously. hipMemcpy2DFromArrayAsync_spt ⚠ hipMemcpy2DFromArray_spt ⚠ hipMemcpy2DToArray ⚠ @brief Copies data between host and device. hipMemcpy2DToArrayAsync ⚠ @brief Copies data between host and device. hipMemcpy2DToArrayAsync_spt ⚠ hipMemcpy2DToArray_spt ⚠ hipMemcpy2D_spt ⚠ hipMemcpy3D ⚠ @brief Copies data between host and device. hipMemcpy3DAsync ⚠ @brief Copies data between host and device asynchronously. hipMemcpy3DAsync_spt ⚠ hipMemcpy3D_spt ⚠ hipMemcpyAsync ⚠ @brief Copies data from src to dst asynchronously. hipMemcpyAsync_spt ⚠ hipMemcpyAtoA ⚠ @brief Copies from one 1D array to another. hipMemcpyAtoD ⚠ @brief Copies from one 1D array to device memory. hipMemcpyAtoH ⚠ @brief Copies data between host and device. hipMemcpyAtoHAsync ⚠ @brief Copies from one 1D array to host memory. hipMemcpyDtoA ⚠ @brief Copies from device memory to a 1D array. hipMemcpyDtoD ⚠ @brief Copy data from Device to Device hipMemcpyDtoDAsync ⚠ @brief Copy data from Device to Device asynchronously hipMemcpyDtoH ⚠ @brief Copy data from Device to Host hipMemcpyDtoHAsync ⚠ @brief Copy data from Device to Host asynchronously hipMemcpyFromArray ⚠ @brief Copies data between host and device [Deprecated] hipMemcpyFromArray_spt ⚠ hipMemcpyFromSymbol ⚠ @brief Copies data from the given symbol on the device. hipMemcpyFromSymbolAsync ⚠ @brief Copies data from the given symbol on the device asynchronously. hipMemcpyFromSymbolAsync_spt ⚠ hipMemcpyFromSymbol_spt ⚠ hipMemcpyHtoA ⚠ @brief Copies data between host and device. hipMemcpyHtoAAsync ⚠ @brief Copies from host memory to a 1D array. hipMemcpyHtoD ⚠ @brief Copy data from Host to Device hipMemcpyHtoDAsync ⚠ @brief Copy data from Host to Device asynchronously hipMemcpyParam2D ⚠ @brief Copies memory for 2D arrays.
@param[in] pCopy Parameters for the memory copy
@returns #hipSuccess, #hipErrorInvalidValue, #hipErrorInvalidPitchValue,
#hipErrorInvalidDevicePointer, #hipErrorInvalidMemcpyDirection hipMemcpyParam2DAsync ⚠ @brief Copies memory for 2D arrays.
@param[in] pCopy Parameters for the memory copy
@param[in] stream Stream to use
@returns #hipSuccess, #hipErrorInvalidValue, #hipErrorInvalidPitchValue,
#hipErrorInvalidDevicePointer, #hipErrorInvalidMemcpyDirection hipMemcpyPeer ⚠ @brief Copies memory between two peer accessible devices. hipMemcpyPeerAsync ⚠ @brief Copies memory between two peer accessible devices asynchronously. hipMemcpyToArray ⚠ @brief Copies data between host and device [Deprecated] hipMemcpyToSymbol ⚠ @brief Copies data to the given symbol on the device.
Symbol HIP APIs allow a kernel to define a device-side data symbol which can be accessed on
the host side. The symbol can be in __constant or device space.
Note that the symbol name needs to be encased in the HIP_SYMBOL macro.
This also applies to hipMemcpyFromSymbol, hipGetSymbolAddress, and hipGetSymbolSize.
For detailed usage, see the
memcpyToSymbol example
in the HIP Porting Guide. hipMemcpyToSymbolAsync ⚠ @brief Copies data to the given symbol on the device asynchronously. hipMemcpyToSymbolAsync_spt ⚠ hipMemcpyToSymbol_spt ⚠ hipMemcpyWithStream ⚠ @brief Memory copy on the stream.
It allows single or multiple devices to do memory copy on single or multiple streams. hipMemcpy_spt ⚠ hipMemset ⚠ @brief Fills the first sizeBytes bytes of the memory area pointed to by dest with the constant
byte value value. hipMemset2D ⚠ @brief Fills the memory area pointed to by dst with the constant value. hipMemset2DAsync ⚠ @brief Fills asynchronously the memory area pointed to by dst with the constant value. hipMemset2DAsync_spt ⚠ hipMemset2D_spt ⚠ hipMemset3D ⚠ @brief Fills synchronously the memory area pointed to by pitchedDevPtr with the constant value. hipMemset3DAsync ⚠ @brief Fills asynchronously the memory area pointed to by pitchedDevPtr with the constant value. hipMemset3DAsync_spt ⚠ hipMemset3D_spt ⚠ hipMemsetAsync ⚠ @brief Fills the first sizeBytes bytes of the memory area pointed to by dev with the constant
byte value value. hipMemsetAsync_spt ⚠ hipMemsetD8 ⚠ @brief Fills the first sizeBytes bytes of the memory area pointed to by dest with the constant
byte value value. hipMemsetD8Async ⚠ @brief Fills the first sizeBytes bytes of the memory area pointed to by dest with the constant
byte value value. hipMemsetD16 ⚠ @brief Fills the first sizeBytes bytes of the memory area pointed to by dest with the constant
short value value. hipMemsetD32 ⚠ @brief Fills the memory area pointed to by dest with the constant integer
value for specified number of times. hipMemsetD16Async ⚠ @brief Fills the first sizeBytes bytes of the memory area pointed to by dest with the constant
short value value. hipMemsetD32Async ⚠ @brief Fills the memory area pointed to by dev with the constant integer
value for specified number of times. hipMemset_spt ⚠ hipMipmappedArrayCreate ⚠ @brief Create a mipmapped array. hipMipmappedArrayDestroy ⚠ @brief Destroy a mipmapped array. hipMipmappedArrayGetLevel ⚠ @brief Get a mipmapped array on a mipmapped level. hipModuleGetFunction ⚠ @brief Function with kname will be extracted if present in module hipModuleGetGlobal ⚠ @brief Returns a global pointer from a module.
@ingroup Module hipModuleGetTexRef ⚠ @brief returns the handle of the texture reference with the name from the module. hipModuleLaunchCooperativeKernel ⚠ \addtogroup ModuleCooperativeG Cooperative groups kernel launch of Module management.
\ingroup Module
@{ /
/ *
@brief launches kernel f with launch parameters and shared memory on stream with arguments passed
to kernelParams, where thread blocks can cooperate and synchronize as they execute hipModuleLaunchCooperativeKernelMultiDevice ⚠ @brief Launches kernels on multiple devices where thread blocks can cooperate and
synchronize as they execute. hipModuleLaunchKernel ⚠ @brief launches kernel f with launch parameters and shared memory on stream with arguments passed
to kernelparams or extra
@ingroup Execution
@param [in] f Kernel to launch.
@param [in] gridDimX X grid dimension specified as multiple of blockDimX.
@param [in] gridDimY Y grid dimension specified as multiple of blockDimY.
@param [in] gridDimZ Z grid dimension specified as multiple of blockDimZ.
@param [in] blockDimX X block dimensions specified in work-items
@param [in] blockDimY Y grid dimension specified in work-items
@param [in] blockDimZ Z grid dimension specified in work-items
@param [in] sharedMemBytes Amount of dynamic shared memory to allocate for this kernel. The
HIP-Clang compiler provides support for extern shared declarations.
@param [in] stream Stream where the kernel should be dispatched. May be 0, in which case th
default stream is used with associated synchronization rules.
@param [in] kernelParams Kernel parameters to launch
@param [in] extra Pointer to kernel arguments. These are passed directly to the kernel and
must be in the memory layout and alignment expected by the kernel.
All passed arguments must be naturally aligned according to their type. The memory address of each
argument should be a multiple of its size in bytes. Please refer to hip_porting_driver_api.md
for sample usage. hipModuleLoad ⚠ @}
/
/** hipModuleLoadData ⚠ @brief builds module from code object which resides in host memory. Image is pointer to that
location. hipModuleLoadDataEx ⚠ @brief builds module from code object which resides in host memory. Image is pointer to that
location. Options are not used. hipModuleLoadData is called. hipModuleOccupancyMaxActiveBlocksPerMultiprocessor ⚠ @brief Returns occupancy for a device function. hipModuleOccupancyMaxActiveBlocksPerMultiprocessorWithFlags ⚠ @brief Returns occupancy for a device function. hipModuleOccupancyMaxPotentialBlockSize ⚠ hipModuleOccupancyMaxPotentialBlockSizeWithFlags ⚠ @brief determine the grid and block sizes to achieves maximum occupancy for a kernel hipModuleUnload ⚠ @brief Frees the module hipOccupancyMaxActiveBlocksPerMultiprocessor ⚠ @brief Returns occupancy for a device function. hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags ⚠ @brief Returns occupancy for a device function. hipOccupancyMaxPotentialBlockSize ⚠ @brief determine the grid and block sizes to achieves maximum occupancy for a kernel hipPeekAtLastError ⚠ @brief Return last error returned by any HIP runtime API call. hipPointerGetAttribute ⚠ @brief Returns information about the specified pointer.[BETA] hipPointerGetAttributes ⚠ @brief Returns attributes for the specified pointer hipPointerSetAttribute ⚠ @brief Sets information on the specified pointer.[BETA] hipProfilerStart ⚠ @brief Start recording of profiling information [Deprecated]
When using this API, start the profiler with profiling disabled. (–startdisabled)
@returns #hipErrorNotSupported
@warning hipProfilerStart API is deprecated, use roctracer/rocTX instead. hipProfilerStop ⚠ @brief Stop recording of profiling information [Deprecated]
When using this API, start the profiler with profiling disabled. (–startdisabled)
@returns #hipErrorNotSupported
@warning hipProfilerStart API is deprecated, use roctracer/rocTX instead. hipRuntimeGetVersion ⚠ @brief Returns the approximate HIP Runtime version. hipSetDevice ⚠ @brief Set default device to be used for subsequent hip API calls from this thread. hipSetDeviceFlags ⚠ @brief The current device behavior is changed according to the flags passed. hipSetValidDevices ⚠ @brief Set a list of devices that can be used. hipSetupArgument ⚠ @brief Set a kernel argument. hipSignalExternalSemaphoresAsync ⚠ @brief Signals a set of external semaphore objects. hipStreamAddCallback ⚠ @brief Adds a callback to be called on the host after all currently enqueued items in the stream
have completed. For each hipStreamAddCallback call, a callback will be executed exactly once.
The callback will block later work in the stream until it is finished. hipStreamAddCallback_spt ⚠ hipStreamAttachMemAsync ⚠ @brief Attach memory to a stream asynchronously in HIP. hipStreamBatchMemOp ⚠ @brief Enqueues an array of stream memory operations in the stream.[BETA] hipStreamBeginCapture ⚠ @brief Begins graph capture on a stream. hipStreamBeginCaptureToGraph ⚠ @brief Begins graph capture on a stream to an existing graph. hipStreamBeginCapture_spt ⚠ hipStreamCreate ⚠ @brief Creates an asynchronous stream. hipStreamCreateWithFlags ⚠ @brief Creates an asynchronous stream with flag. hipStreamCreateWithPriority ⚠ @brief Creates an asynchronous stream with the specified priority. hipStreamDestroy ⚠ @brief Destroys the specified stream. hipStreamEndCapture ⚠ @brief Ends capture on a stream, returning the captured graph. hipStreamEndCapture_spt ⚠ hipStreamGetCaptureInfo ⚠ @brief Get capture status of a stream. hipStreamGetCaptureInfo_spt ⚠ hipStreamGetCaptureInfo_v2 ⚠ @brief Get stream’s capture state hipStreamGetCaptureInfo_v2_spt ⚠ hipStreamGetDevice ⚠ @brief Gets the device associated with the stream. hipStreamGetFlags ⚠ @brief Returns flags associated with this stream. hipStreamGetFlags_spt ⚠ hipStreamGetPriority ⚠ @brief Queries the priority of a stream. hipStreamGetPriority_spt ⚠ hipStreamIsCapturing ⚠ @brief Get stream’s capture state hipStreamIsCapturing_spt ⚠ hipStreamQuery ⚠ @brief Returns #hipSuccess if all of the operations in the specified @p stream have completed, or
#hipErrorNotReady if not. hipStreamQuery_spt ⚠ hipStreamSynchronize ⚠ @brief Waits for all commands in the stream to complete. hipStreamSynchronize_spt ⚠ hipStreamUpdateCaptureDependencies ⚠ @brief Update the set of dependencies in a capturing stream hipStreamWaitEvent ⚠ @brief Makes the specified compute stream wait for the specified event hipStreamWaitEvent_spt ⚠ hipStreamWaitValue32 ⚠ @brief Enqueues a wait command to the stream.[BETA] hipStreamWaitValue64 ⚠ @brief Enqueues a wait command to the stream.[BETA] hipStreamWriteValue32 ⚠ @brief Enqueues a write command to the stream.[BETA] hipStreamWriteValue64 ⚠ @brief Enqueues a write command to the stream.[BETA] hipTexObjectCreate ⚠ @brief Creates a texture object. hipTexObjectDestroy ⚠ @brief Destroys a texture object. hipTexObjectGetResourceDesc ⚠ @brief Gets resource descriptor of a texture object. hipTexObjectGetResourceViewDesc ⚠ @brief Gets resource view descriptor of a texture object. hipTexObjectGetTextureDesc ⚠ @brief Gets texture descriptor of a texture object. hipTexRefGetAddress ⚠ @brief Gets the address for a texture reference [Deprecated] hipTexRefGetAddressMode ⚠ @brief Gets the address mode for a texture reference [Deprecated] hipTexRefGetArray ⚠ @brief Gets the array bound to a texture reference [Deprecated] hipTexRefGetBorderColor ⚠ @brief Gets the border color used by a texture reference [Deprecated] hipTexRefGetFilterMode ⚠ @brief Gets filter mode for a texture reference [Deprecated] hipTexRefGetFlags ⚠ @brief Gets flags for a texture reference [Deprecated] hipTexRefGetFormat ⚠ @brief Gets texture format for a texture reference [Deprecated] hipTexRefGetMaxAnisotropy ⚠ @brief Gets the maximum anisotropy for a texture reference [Deprecated] hipTexRefGetMipMappedArray ⚠ @brief Gets the mipmapped array bound to a texture reference [Deprecated] hipTexRefGetMipmapFilterMode ⚠ @brief Gets the mipmap filter mode for a texture reference [Deprecated] hipTexRefGetMipmapLevelBias ⚠ @brief Gets the mipmap level bias for a texture reference [Deprecated] hipTexRefGetMipmapLevelClamp ⚠ @brief Gets the minimum and maximum mipmap level clamps for a texture reference [Deprecated] hipTexRefSetAddress ⚠ @brief Sets an bound address for a texture reference [Deprecated] hipTexRefSetAddress2D ⚠ @brief Set a bind an address as a 2D texture reference [Deprecated] hipTexRefSetAddressMode ⚠ @brief Sets address mode for a texture reference [Deprecated] hipTexRefSetArray ⚠ @brief Binds an array as a texture reference [Deprecated] hipTexRefSetBorderColor ⚠ @brief Sets border color for a texture reference [Deprecated] hipTexRefSetFilterMode ⚠ @brief Set filter mode for a texture reference [Deprecated] hipTexRefSetFlags ⚠ @brief Set flags for a texture reference [Deprecated] hipTexRefSetFormat ⚠ @brief Set format for a texture reference [Deprecated] hipTexRefSetMaxAnisotropy ⚠ @brief Sets the maximum anisotropy for a texture reference [Deprecated] hipTexRefSetMipmapFilterMode ⚠ @brief Sets mipmap filter mode for a texture reference [Deprecated] hipTexRefSetMipmapLevelBias ⚠ @brief Sets mipmap level bias for a texture reference [Deprecated] hipTexRefSetMipmapLevelClamp ⚠ @brief Sets mipmap level clamp for a texture reference [Deprecated] hipTexRefSetMipmappedArray ⚠ @brief Binds mipmapped array to a texture reference [Deprecated] hipThreadExchangeStreamCaptureMode ⚠ @brief Swaps the stream capture mode of a thread. hipUnbindTexture ⚠ @brief Unbinds a texture [Deprecated] hipUserObjectCreate ⚠ @brief Create an instance of userObject to manage lifetime of a resource. hipUserObjectRelease ⚠ @brief Release number of references to resource. hipUserObjectRetain ⚠ @brief Retain number of references to resource. hipWaitExternalSemaphoresAsync ⚠ @brief Waits on a set of external semaphore objects hiprtcAddNameExpression ⚠ @ingroup Runtime
@brief Adds the given name exprssion to the runtime compilation program. hiprtcCompileProgram ⚠ @ingroup Runtime
@brief Compiles the given runtime compilation program. hiprtcCreateProgram ⚠ @ingroup Runtime
@brief Creates an instance of hiprtcProgram with the given input parameters,
and sets the output hiprtcProgram prog with it. hiprtcDestroyProgram ⚠ @brief Destroys an instance of given hiprtcProgram.
@ingroup Runtime
@param [in] prog runtime compilation program instance.
@returns #HIPRTC_SUCCESS hiprtcGetBitcode ⚠ @brief Gets the pointer of compiled bitcode by the runtime compilation program instance. hiprtcGetBitcodeSize ⚠ @brief Gets the size of compiled bitcode by the runtime compilation program instance.
@ingroup Runtime hiprtcGetCode ⚠ @brief Gets the pointer of compilation binary by the runtime compilation program instance.
@ingroup Runtime
@param [in] prog runtime compilation program instance.
@param [out] code char pointer to binary.
@returns #HIPRTC_SUCCESS hiprtcGetCodeSize ⚠ @brief Gets the size of compilation binary by the runtime compilation program instance.
@ingroup Runtime
@param [in] prog runtime compilation program instance.
@param [out] codeSizeRet the size of binary.
@returns #HIPRTC_SUCCESS hiprtcGetErrorString ⚠ @ingroup Runtime hiprtcGetLoweredName ⚠ @brief Gets the lowered (mangled) name from an instance of hiprtcProgram with the given input parameters,
and sets the output lowered_name with it.
@ingroup Runtime
@param [in] prog runtime compilation program instance.
@param [in] name_expression const char pointer to the name expression.
@param [in, out] lowered_name const char array to the lowered (mangled) name.
@returns #HIPRTC_SUCCESS hiprtcGetProgramLog ⚠ @brief Gets the log generated by the runtime compilation program instance.
@ingroup Runtime
@param [in] prog runtime compilation program instance.
@param [out] log memory pointer to the generated log.
@returns #HIPRTC_SUCCESS hiprtcGetProgramLogSize ⚠ @brief Gets the size of log generated by the runtime compilation program instance. hiprtcLinkAddData ⚠ @brief Completes the linking of the given program.
@ingroup Runtime
@param [in] hip_link_state hiprtc link state
@param [in] input_type Type of the input data or bitcode
@param [in] image Input data which is null terminated
@param [in] image_size Size of the input data
@param [in] name Optional name for this input
@param [in] num_options Size of the options
@param [in] options_ptr Array of options applied to this input
@param [in] option_values Array of option values cast to void* hiprtcLinkAddFile ⚠ @brief Adds a file with bit code to be linked with options
@ingroup Runtime
@param [in] hip_link_state hiprtc link state
@param [in] input_type Type of the input data or bitcode
@param [in] file_path Path to the input file where bitcode is present
@param [in] num_options Size of the options
@param [in] options_ptr Array of options applied to this input
@param [in] option_values Array of option values cast to void* hiprtcLinkComplete ⚠ @brief Completes the linking of the given program.
@ingroup Runtime
@param [in] hip_link_state hiprtc link state
@param [out] bin_out Upon success, points to the output binary
@param [out] size_out Size of the binary is stored (optional) hiprtcLinkCreate ⚠ @brief Creates the link instance via hiprtc APIs.
@ingroup Runtime
@param [in] num_options Number of options
@param [in] option_ptr Array of options
@param [in] option_vals_pptr Array of option values cast to void*
@param [out] hip_link_state_ptr hiprtc link state created upon success hiprtcLinkDestroy ⚠ @brief Deletes the link instance via hiprtc APIs.
@ingroup Runtime
@param [in] hip_link_state link state instance hiprtcVersion ⚠ @ingroup Runtime
@brief Sets the parameters as major and minor version. initstate ⚠ initstate_r ⚠ jrand48 ⚠ jrand48_r ⚠ l64a ⚠ labs ⚠ lcong48 ⚠ lcong48_r ⚠ ldiv ⚠ llabs ⚠ lldiv ⚠ lrand48 ⚠ lrand48_r ⚠ malloc ⚠ mblen ⚠ mbstowcs ⚠ mbtowc ⚠ mkdtemp ⚠ mkstemp ⚠ mkstemps ⚠ mktemp ⚠ mrand48 ⚠ mrand48_r ⚠ nrand48 ⚠ nrand48_r ⚠ on_exit ⚠ posix_memalign ⚠ pselect ⚠ putenv ⚠ qecvt ⚠ qecvt_r ⚠ qfcvt ⚠ qfcvt_r ⚠ qgcvt ⚠ qsort ⚠ quick_exit ⚠ rand ⚠ rand_r ⚠ random ⚠ random_r ⚠ realloc ⚠ reallocarray ⚠ realpath ⚠ rpmatch ⚠ seed48 ⚠ seed48_r ⚠ select ⚠ setenv ⚠ setstate ⚠ setstate_r ⚠ srand ⚠ srand48 ⚠ srand48_r ⚠ srandom ⚠ srandom_r ⚠ strtod ⚠ strtof ⚠ strtol ⚠ strtold ⚠ strtoll ⚠ strtoq ⚠ strtoul ⚠ strtoull ⚠ strtouq ⚠ system ⚠ unsetenv ⚠ valloc ⚠ wcstombs ⚠ wctomb ⚠ HIP_LAUNCH_CONFIG HIP driver extensible launch configuration HIP_RESOURCE_DESC HIP resource view descriptor struct HIP_RESOURCE_VIEW_DESC Resource view descriptor HIP_TEXTURE_DESC HIP texture descriptor HIPaddress_mode HIP texture address modes
HIP texture address modes HIPaddress_mode_enum HIP texture address modes HIPfilter_mode HIP filter modes
HIP filter modes HIPfilter_mode_enum HIP filter modes HIPresourceViewFormat HIP texture resource view formats
HIP texture resource view formats HIPresourceViewFormat_enum HIP texture resource view formats HIPresourcetype HIPresourcetype_enum _Float32 _Float64 _Float32x _Float64x __blkcnt64_t __blkcnt_t __blksize_t __caddr_t __clock_t __clockid_t __compar_fn_t __daddr_t __dev_t __fd_mask __fsblkcnt64_t __fsblkcnt_t __fsfilcnt64_t __fsfilcnt_t __fsword_t __gid_t __id_t __ino64_t __ino_t __int8_t __int16_t __int32_t __int64_t __int_least8_t __int_least16_t __int_least32_t __int_least64_t __intmax_t __intptr_t __key_t __loff_t __mode_t __nlink_t __off64_t __off_t __pid_t __pthread_list_t __pthread_slist_t __quad_t __rlim64_t __rlim_t __sig_atomic_t __socklen_t __ssize_t __suseconds64_t __suseconds_t __syscall_slong_t __syscall_ulong_t __thrd_t __time_t __timer_t __tss_t __u_char __u_int __u_long __u_quad_t __u_short __uid_t __uint8_t __uint16_t __uint32_t __uint64_t __uint_least8_t __uint_least16_t __uint_least32_t __uint_least64_t __uintmax_t __useconds_t _bindgen_ty_1 blkcnt_t blksize_t caddr_t clock_t clockid_t daddr_t dev_t fd_mask fsblkcnt_t fsfilcnt_t fsid_t gid_t hipAccessProperty hipArraySparseSubresourceType Subresource types for sparse arrays hipArray_Format HIP array format hipArray_const_t hipArray_t hipChannelFormatKind HIP channel format kinds hipComputeMode hipCtx_t hipDeviceAttribute_t hipDeviceAttribute_t
hipDeviceAttributeUnused number: 5 hipDeviceP2PAttr hipDevice_t hipDeviceptr_t @defgroup DriverTypes Driver Types
@{
This section describes the driver data types. hipDriverProcAddressQueryResult hipError_t HIP error type hipEvent_t hipExternalMemoryBufferDesc hipExternalMemoryHandleDesc hipExternalMemoryHandleType hipExternalMemoryHandleType_enum hipExternalMemoryMipmappedArrayDesc hipExternalMemory_t hipExternalSemaphoreHandleDesc hipExternalSemaphoreHandleType hipExternalSemaphoreHandleType_enum hipExternalSemaphoreSignalParams hipExternalSemaphoreWaitParams External semaphore wait parameters, compatible with driver type hipExternalSemaphore_t hipFlushGPUDirectRDMAWritesOptions hipFuncAttribute @warning On AMD devices and some Nvidia devices, these hints and controls are ignored. hipFuncCache_t @warning On AMD devices and some Nvidia devices, these hints and controls are ignored. hipFunctionLaunchParams struct hipFunctionLaunchParams_t hipFunction_attribute hipFunction_t hipGPUDirectRDMAWritesOrdering hipGraphDebugDotFlags hipGraphDependencyType hipGraphExecUpdateResult Graph execution update result hipGraphExec_t An opaque value that represents a hip graph Exec hipGraphInstantiateFlags hipGraphInstantiateResult hipGraphInstantiateWithParams results hipGraphMemAttributeType hipGraphNodeType hipGraphNodeType hipGraphNode_t An opaque value that represents a hip graph node hipGraph_t An opaque value that represents a hip graph hipGraphicsRegisterFlags HIP Access falgs for Interop resources. hipGraphicsResource hipGraphicsResource_t hipHostFn_t hipIpcEventHandle_t hipIpcMemHandle_t hipJitCacheMode hipJitCacheMode hipJitFallback hipJitFallback hipJitInputType hipJitInputType hipJitOption hipJitOption hipLaunchAttribute Used to specify custom attributes for launching kernels hipLaunchAttributeID Launch Attribute ID hipLaunchConfig_t HIP extensible launch configuration hipLaunchParams struct hipLaunchParams_t hipLimit_t hipLimit hipLinkState_t hipMemAccessFlags Specifies the memory protection flags for mapping hipMemAllocationGranularity_flags Flags for granularity hipMemAllocationHandleType Flags for specifying handle types for memory pool allocations hipMemAllocationType Defines the allocation types hipMemGenericAllocationHandle_t Generic handle for memory allocation hipMemHandleType Memory handle type hipMemLocationType Specifies the type of location hipMemOperationType Memory operation types hipMemPoolAttr HIP memory pool attributes hipMemPool_t HIP memory pool hipMemRangeAttribute HIP range attributes hipMemRangeCoherencyMode HIP Coherency Mode hipMemRangeFlags Mem Range Flags used in hipMemGetHandleForAddressRange. hipMemRangeHandleType Requested handle type for address range. hipMemcpyKind hipMemoryAdvise HIP Memory Advise values hipMemoryType hipMemoryType (for pointer attributes) hipMipmappedArray_const_t hipMipmappedArray_t HIP mipmapped array pointer hipModule_t hipPointer_attribute hipResourceType HIP resource types hipResourceViewFormat HIP texture resource view formats hipResourcetype hipSharedMemConfig @warning On AMD devices and some Nvidia devices, these hints and controls are ignored. hipStreamBatchMemOpParams @brief Union representing batch memory operation parameters for HIP streams. hipStreamBatchMemOpType Operations for hipStreamBatchMemOp hipStreamCallback_t Stream CallBack struct hipStreamCaptureMode hipStreamCaptureStatus hipStreamUpdateCaptureDependenciesFlags hipStream_t hipSurfaceBoundaryMode hip surface boundary modes hipSurfaceObject_t hipTextureAddressMode hip texture address modes hipTextureFilterMode hip texture filter modes hipTextureObject_t hipTextureReadMode hip texture read modes hipUUID hipUserObjectFlags hipUserObjectRetainFlags hipUserObject_t An opaque value that represents a user obj hipmipmappedArray hiprtcLinkState hiprtc link state hiprtcProgram hiprtc program hiprtcResult @addtogroup GlobalDefs
@{ id_t ino_t int_fast8_t int_fast16_t int_fast32_t int_fast64_t int_least8_t int_least16_t int_least32_t int_least64_t intmax_t key_t loff_t mode_t nlink_t off_t pid_t pthread_key_t pthread_once_t pthread_spinlock_t pthread_t quad_t register_t sigset_t suseconds_t time_t timer_t u_char u_int u_int8_t u_int16_t u_int32_t u_int64_t u_long u_quad_t u_short uid_t uint uint_fast8_t uint_fast16_t uint_fast32_t uint_fast64_t uint_least8_t uint_least16_t uint_least32_t uint_least64_t uintmax_t ulong ushort wchar_t HIP_RESOURCE_DESC_st__bindgen_ty_1 __atomic_wide_counter hipArrayMapInfo__bindgen_ty_1 hipArrayMapInfo__bindgen_ty_2 hipArrayMapInfo__bindgen_ty_3 hipExternalMemoryHandleDesc_st__bindgen_ty_1 hipExternalSemaphoreHandleDesc_st__bindgen_ty_1 hipExternalSemaphoreSignalParams_st__bindgen_ty_1__bindgen_ty_2 hipExternalSemaphoreWaitParams_st__bindgen_ty_1__bindgen_ty_2 hipGraphNodeParams__bindgen_ty_1 hipLaunchAttributeValue Launch Attribute Value hipLaunchAttribute_st__bindgen_ty_1 hipMemAllocationProp__bindgen_ty_1 hipResourceDesc__bindgen_ty_1 hipStreamBatchMemOpParams_union @brief Union representing batch memory operation parameters for HIP streams. hipStreamBatchMemOpParams_union_hipStreamMemOpWaitValueParams_t__bindgen_ty_1 hipStreamBatchMemOpParams_union_hipStreamMemOpWriteValueParams_t__bindgen_ty_1 pthread_attr_t pthread_barrier_t pthread_barrierattr_t pthread_cond_t pthread_condattr_t pthread_mutex_t pthread_mutexattr_t pthread_rwlock_t pthread_rwlockattr_t