include/hip/hip_runtime_api.h Source File

include/hip/hip_runtime_api.h Source File#

HIP Runtime API Reference: include/hip/hip_runtime_api.h Source File
hip_runtime_api.h
Go to the documentation of this file.
1/*
2 * Copyright (c) Advanced Micro Devices, Inc., or its affiliates.
3 *
4 * SPDX-License-Identifier: MIT
5 */
6
15#ifndef HIP_INCLUDE_HIP_HIP_RUNTIME_API_H
16#define HIP_INCLUDE_HIP_HIP_RUNTIME_API_H
17
18#if __cplusplus
19#include <climits>
20#include <cstdint>
21#include <cstdlib>
22#include <utility>
23#else
24#include <limits.h>
25#include <stdint.h>
26#include <stdlib.h>
27#endif
28
29#include <hip/hip_version.h>
30#include <hip/hip_common.h>
31#include <hip/linker_types.h>
32
33#if HIP_FORCE_API_VERSION > HIP_API_VERSION
34# error "HIP_FORCE_API_VERSION is newer than the installed HIP headers"
35#endif
36
37enum {
42};
43// hack to get these to show up in Doxygen:
53typedef struct {
54 // 32-bit Atomics
55 unsigned hasGlobalInt32Atomics : 1;
57 unsigned hasSharedInt32Atomics : 1;
59 unsigned hasFloatAtomicAdd : 1;
60
61 // 64-bit Atomics
62 unsigned hasGlobalInt64Atomics : 1;
63 unsigned hasSharedInt64Atomics : 1;
64
65 // Doubles
66 unsigned hasDoubles : 1;
67
68 // Warp cross-lane operations
69 unsigned hasWarpVote : 1;
70 unsigned hasWarpBallot : 1;
71 unsigned hasWarpShuffle : 1;
72 unsigned hasFunnelShift : 1;
73
74 // Sync
75 unsigned hasThreadFenceSystem : 1;
76 unsigned hasSyncThreadsExt : 1;
77
78 // Misc
79 unsigned hasSurfaceFuncs : 1;
80 unsigned has3dGrid : 1;
81 unsigned hasDynamicParallelism : 1;
83
84typedef struct hipUUID_t {
85 char bytes[16];
86} hipUUID;
87
88//---
89// Common headers for both NVCC and HIP-Clang paths:
90
91// Ignoring error-code return values from hip APIs is discouraged. On C++17,
92// we can make that yield a warning
93#if __cplusplus >= 201703L
94#define __HIP_NODISCARD [[nodiscard]]
95#else
96#define __HIP_NODISCARD
97#endif
98
99#if defined(_MSC_VER) && (_MSC_VER >= 1800)
100#define UINT32_BASE :uint32_t
101#else
102#define UINT32_BASE
103#endif
104
109// Developer note - when updating these, update the hipErrorName and hipErrorString functions in
110// NVCC and HIP-Clang paths Also update the hipCUDAErrorTohipError function in NVCC path.
111
117 // Deprecated
120 // Deprecated
142 // Deprecated
164 // Deprecated
224 // HSA Runtime Error Codes start here.
232 hipErrorTbd
234
235#undef __HIP_NODISCARD
236#undef UINT32_BASE
237
238/*
239 Versioning struct. Because each public API must use the versioned struct to
240 ensure ABI compatibility, we must typedef the actual struct name here.
241*/
242
243#if HIP_FORCE_API_VERSION < 600
244
245#include <hip/hip_deprecated.h>
246// Legacy version, HIP_ABI_IMPL is on the latest version, so it must not see this.
248// Dummy struct for hip_prof_str.h
250
251#endif
252
253#if HIP_FORCE_API_VERSION >= 600
254// Latest version.
255
260typedef struct hipDeviceProp_t {
261 char name[256];
263 char luid[8];
264 unsigned int luidDeviceNodeMask;
269 size_t memPitch;
273 int maxGridSize[3];
277 int major;
281 int minor;
370 unsigned int
377 int reserved[63];
378
379 int hipReserved[32];
380
381 /* HIP Only struct members */
382 char gcnArchName[256];
387 unsigned int* hdpMemFlushCntl;
388 unsigned int* hdpRegFlushCntl;
404
405// Latest version, HIP_ABI_IMPL should see this.
407#endif
408
429
433typedef struct hipPointerAttribute_t {
439 unsigned allocationFlags; /* flags specified when memory was allocated*/
440 /* peers? */
442
449
597
600
646
649 // Extended attributes for vendors
651
652// Flags that can be used with hipGetProcAddress.
656#define HIP_GET_PROC_ADDRESS_DEFAULT 0x0
657
659#define HIP_GET_PROC_ADDRESS_LEGACY_STREAM 0x1
660
663#define HIP_GET_PROC_ADDRESS_PER_THREAD_DEFAULT_STREAM 0x2
664
670
677
682
688
695
707
708#if defined(__HIP_PLATFORM_AMD__) && !defined(__HIP_PLATFORM_NVIDIA__)
709
710#ifndef GENERIC_GRID_LAUNCH
711#define GENERIC_GRID_LAUNCH 1
712#endif
713#include <hip/amd_detail/host_defines.h>
714#include <hip/driver_types.h>
715#include <hip/texture_types.h>
716#include <hip/surface_types.h>
717
718#if defined(HIP_ABI_IMPL)
719// Nothing is deprecated if we are implementing the HIP ABI.
720#define HIP_DEPRECATED(x)
721#elif defined(_MSC_VER)
722#define HIP_DEPRECATED(msg) __declspec(deprecated(msg))
723#else // !defined(_MSC_VER)
724#define HIP_DEPRECATED(msg) __attribute__((deprecated(msg)))
725#endif // !defined(_MSC_VER)
726
727#define HIP_DEPRECATED_MSG \
728 "This API is marked as deprecated and might not be supported in future releases. For more " \
729 "details please refer " \
730 "https://github.com/ROCm/HIP/blob/develop/docs/reference/deprecated_api_list.md"
731#define HIP_LAUNCH_PARAM_BUFFER_POINTER ((void*)0x01)
732#define HIP_LAUNCH_PARAM_BUFFER_SIZE ((void*)0x02)
733#define HIP_LAUNCH_PARAM_END ((void*)0x03)
734#ifdef __cplusplus
735#define __dparm(x) = x
736#else
737#define __dparm(x)
738#endif
739#ifdef __GNUC__
740#pragma GCC visibility push(default)
741#endif
742#ifdef __cplusplus
743namespace hip_impl {
745} // namespace hip_impl
746#endif
747// Structure definitions:
748#ifdef __cplusplus
749extern "C" {
750#endif
751//---
752// API-visible structures
753typedef struct ihipCtx_t* hipCtx_t;
754typedef struct ihipExecutionCtx_t* hipExecutionCtx_t;
755typedef struct ihipDevResourceDesc_t* hipDevResourceDesc_t;
774
775#define HIP_RESOURCE_ABI_BYTES 40
776
777typedef struct hipDevSmResource {
778 unsigned int smCount;
779 unsigned int minSmPartitionSize;
781 unsigned int flags;
783
789
793
794typedef struct hipDevResource_st {
796 unsigned char _internal_padding[92];
797 union {
801 unsigned char _oversize[HIP_RESOURCE_ABI_BYTES];
802 };
803 struct hipDevResource_st* nextResource;
805
806typedef struct hipDevSmResourceGroupParams_st {
807 unsigned int smCount;
808 unsigned int coscheduledSmCount;
810 unsigned int flags;
811 unsigned int reserved[12];
813
814// Note many APIs also use integer deviceIds as an alternative to the device pointer:
815typedef int hipDevice_t;
827typedef struct ihipStream_t* hipStream_t;
828#define hipIpcMemLazyEnablePeerAccess 0x01
829#define HIP_IPC_HANDLE_SIZE 64
830typedef struct hipIpcMemHandle_st {
831 char reserved[HIP_IPC_HANDLE_SIZE];
833typedef struct hipIpcEventHandle_st {
834 char reserved[HIP_IPC_HANDLE_SIZE];
836typedef struct hipMemFabricHandle_st {
837 unsigned char data[HIP_IPC_HANDLE_SIZE];
839typedef struct ihipModule_t* hipModule_t;
840typedef struct ihipModuleSymbol_t* hipFunction_t;
841typedef struct ihipLinkState_t* hipLinkState_t;
842typedef struct ihipLibrary_t* hipLibrary_t;
843typedef struct ihipKernel_t* hipKernel_t;
847typedef struct ihipMemPoolHandle_t* hipMemPool_t;
848
861typedef struct ihipEvent_t* hipEvent_t;
862
887
891// Flags that can be used with hipStreamCreateWithFlags.
893#define hipStreamDefault 0x00
894
896#define hipStreamNonBlocking 0x01
897
898// Flags that can be used with hipEventCreateWithFlags.
900#define hipEventDefault 0x0
901
903#define hipEventBlockingSync 0x1
904
906#define hipEventDisableTiming 0x2
907
909#define hipEventInterprocess 0x4
910
911// Flags that can be used with hipEventRecordWithFlags.
913#define hipEventRecordDefault 0x00
914
916#define hipEventRecordExternal 0x01
917
918//Flags that can be used with hipStreamWaitEvent.
920#define hipEventWaitDefault 0x00
921
923#define hipEventWaitExternal 0x01
924
933#define hipEventDisableSystemFence 0x20000000
934
937#define hipEventReleaseToDevice 0x40000000
938
941#define hipEventReleaseToSystem 0x80000000
942
943// Flags that can be used with hipGetDriverEntryPoint.
947#define hipEnableDefault 0x0
948
950#define hipEnableLegacyStream 0x1
951
954#define hipEnablePerThreadDefaultStream 0x2
955
956// Flags that can be used with hipHostMalloc/hipHostAlloc.
958#define hipHostAllocDefault 0x0
959
962#define hipHostMallocDefault 0x0
963
965#define hipHostAllocPortable 0x1
966
969#define hipHostMallocPortable 0x1
970
973#define hipHostAllocMapped 0x2
974
978#define hipHostMallocMapped 0x2
979
985#define hipHostAllocWriteCombined 0x4
986
993#define hipHostMallocWriteCombined 0x4
994
1000#define hipHostMallocUncached 0x10000000
1001#define hipHostAllocUncached hipHostMallocUncached
1002
1007#define hipHostMallocNumaUser 0x20000000
1008
1010#define hipHostMallocCoherent 0x40000000
1011
1013#define hipHostMallocNonCoherent 0x80000000
1014
1016#define hipMemAttachGlobal 0x01
1017
1019#define hipMemAttachHost 0x02
1020
1022#define hipMemAttachSingle 0x04
1023
1024#define hipDeviceMallocDefault 0x0
1025
1027#define hipDeviceMallocFinegrained 0x1
1028
1030#define hipMallocSignalMemory 0x2
1031
1033#define hipDeviceMallocUncached 0x3
1034
1036#define hipDeviceMallocContiguous 0x4
1037
1038// Flags that can be used with hipHostRegister.
1040#define hipHostRegisterDefault 0x0
1041
1043#define hipHostRegisterPortable 0x1
1044
1047#define hipHostRegisterMapped 0x2
1048
1053#define hipHostRegisterIoMemory 0x4
1054
1056#define hipHostRegisterReadOnly 0x08
1057
1059#define hipExtHostRegisterCoarseGrained 0x8
1060
1064#define hipExtHostRegisterUncached 0x80000000
1065
1067#define hipDeviceScheduleAuto 0x0
1068
1071#define hipDeviceScheduleSpin 0x1
1072
1075#define hipDeviceScheduleYield 0x2
1076#define hipDeviceScheduleBlockingSync 0x4
1077#define hipDeviceScheduleMask 0x7
1078#define hipDeviceMapHost 0x8
1079#define hipDeviceLmemResizeToMax 0x10
1081#define hipInitDeviceFlagsAreValid 0x1
1083#define hipArrayDefault 0x00
1084#define hipArrayLayered 0x01
1085#define hipArraySurfaceLoadStore 0x02
1086#define hipArrayCubemap 0x04
1087#define hipArrayTextureGather 0x08
1088#define hipOccupancyDefault 0x00
1089#define hipOccupancyDisableCachingOverride 0x01
1090#define hipCooperativeLaunchMultiDeviceNoPreSync 0x01
1091#define hipCooperativeLaunchMultiDeviceNoPostSync 0x02
1092#define hipCpuDeviceId ((int)-1)
1093#define hipInvalidDeviceId ((int)-2)
1094// Flags that can be used with hipExtLaunch Set of APIs.
1096#define hipExtAnyOrderLaunch 0x01
1097// Flags to be used with hipStreamWaitValue32 and hipStreamWaitValue64.
1098#define hipStreamWaitValueGte 0x0
1099#define hipStreamWaitValueEq 0x1
1100#define hipStreamWaitValueAnd 0x2
1101#define hipStreamWaitValueNor 0x3
1102// Flags to be used with hipStreamWriteValue32 and hipStreamWriteValue64.
1103#define hipStreamWriteValueDefault 0x0
1104#define hipExtStreamWriteValueIncrement 0x1000
1105#define hipExtStreamWriteValueDecrement 0x1001
1106
1116
1153typedef union hipStreamBatchMemOpParams_union {
1158 union {
1159 uint32_t value;
1160 uint64_t value64;
1161 };
1162 unsigned int flags;
1164 } waitValue;
1168 union {
1169 uint32_t value;
1170 uint64_t value64;
1171 };
1172 unsigned int flags;
1174 } writeValue;
1183 uint64_t pad[6];
1185
1219
1220// Stream per thread
1222#define hipStreamPerThread ((hipStream_t)2)
1223
1224#define hipStreamLegacy ((hipStream_t)1)
1225
1226// Indicates that the external memory object is a dedicated resource
1227#define hipExternalMemoryDedicated 0x1
1277
1336
1401 unsigned char reserved[64];
1403
1440typedef struct dim3 {
1441 uint32_t x;
1442 uint32_t y;
1443 uint32_t z;
1444#ifdef __cplusplus
1445 constexpr __host__ __device__ dim3(uint32_t _x = 1, uint32_t _y = 1, uint32_t _z = 1)
1446 : x(_x), y(_y), z(_z) {};
1447#endif
1448} dim3;
1452typedef struct hipLaunchParams_t {
1453 void* func;
1456 void** args;
1457 size_t sharedMem;
1463typedef struct hipFunctionLaunchParams_t {
1465 unsigned int gridDimX;
1466 unsigned int gridDimY;
1467 unsigned int gridDimZ;
1468 unsigned int blockDimX;
1469 unsigned int blockDimY;
1470 unsigned int blockDimZ;
1471 unsigned int sharedMemBytes;
1485typedef struct hipExternalMemoryHandleDesc_st {
1487 union {
1488 int fd;
1489 struct {
1490 void* handle;
1491 const void* name;
1492 } win32;
1493 const void* nvSciBufObject;
1494 } handle;
1495 unsigned long long size;
1496 unsigned int flags;
1497 unsigned int reserved[16];
1499typedef struct hipExternalMemoryBufferDesc_st {
1500 unsigned long long offset;
1501 unsigned long long size;
1502 unsigned int flags;
1503 unsigned int reserved[16];
1505typedef struct hipExternalMemoryMipmappedArrayDesc_st {
1506 unsigned long long offset;
1509 unsigned int flags;
1510 unsigned int numLevels;
1525typedef struct hipExternalSemaphoreHandleDesc_st {
1527 union {
1528 int fd;
1529 struct {
1530 void* handle;
1531 const void* name;
1532 } win32;
1533 const void* NvSciSyncObj;
1534 } handle;
1535 unsigned int flags;
1536 unsigned int reserved[16];
1539typedef struct hipExternalSemaphoreSignalParams_st {
1540 struct {
1541 struct {
1542 unsigned long long value;
1543 } fence;
1544 union {
1545 void* fence;
1546 unsigned long long reserved;
1547 } nvSciSync;
1548 struct {
1549 unsigned long long key;
1550 } keyedMutex;
1551 unsigned int reserved[12];
1552 } params;
1553 unsigned int flags;
1554 unsigned int reserved[16];
1559typedef struct hipExternalSemaphoreWaitParams_st {
1560 struct {
1561 struct {
1562 unsigned long long value;
1563 } fence;
1564 union {
1565 void* fence;
1566 unsigned long long reserved;
1567 } nvSciSync;
1568 struct {
1569 unsigned long long key;
1570 unsigned int timeoutMs;
1571 } keyedMutex;
1572 unsigned int reserved[10];
1573 } params;
1574 unsigned int flags;
1575 unsigned int reserved[16];
1577
1582void __hipGetPCH(const char** pch, unsigned int* size);
1583
1596
1597typedef struct _hipGraphicsResource hipGraphicsResource;
1598
1600
1604typedef struct ihipGraph* hipGraph_t;
1608typedef struct hipGraphNode* hipGraphNode_t;
1612typedef struct hipGraphExec* hipGraphExec_t;
1613
1617typedef struct hipUserObject* hipUserObject_t;
1618
1619
1641
1642typedef void (*hipHostFn_t)(void* userData);
1655typedef struct hipMemsetParams {
1656 void* dst;
1657 unsigned int elementSize;
1658 size_t height;
1659 size_t pitch;
1660 unsigned int value;
1661 size_t width;
1663
1673
1682
1683/***
1684 * Specifies access policy for a window, a contiguous extent of memory
1685 * beginning at base_ptr and ending at base_ptr + num_bytes.
1686 */
1694
1699 unsigned char default_;
1700 unsigned char remote;
1702
1710
1721/* Cluster scheduling policies passed to hipFuncSetAttribute
1722*/
1729
1737
1752
1758#define HIP_EXT_DYN_DATA_PREFETCH_MAX_REGIONS 2
1759
1775
1792
1793
1834
1838#define hipStreamAttrID hipLaunchAttributeID
1839#define hipStreamAttributeAccessPolicyWindow hipLaunchAttributeAccessPolicyWindow
1840#define hipStreamAttributeSynchronizationPolicy hipLaunchAttributeSynchronizationPolicy
1841#define hipStreamAttributeMemSyncDomainMap hipLaunchAttributeMemSyncDomainMap
1842#define hipStreamAttributeMemSyncDomain hipLaunchAttributeMemSyncDomain
1843#define hipStreamAttributePriority hipLaunchAttributePriority
1844
1845#define hipStreamAttrValue hipLaunchAttributeValue
1846
1850#define hipKernelNodeAttrID hipLaunchAttributeID
1851#define hipKernelNodeAttributeAccessPolicyWindow hipLaunchAttributeAccessPolicyWindow
1852#define hipKernelNodeAttributeCooperative hipLaunchAttributeCooperative
1853#define hipKernelNodeAttributePriority hipLaunchAttributePriority
1854
1858#define hipKernelNodeAttrValue hipLaunchAttributeValue
1859
1863#define hipDrvLaunchAttributeCooperative hipLaunchAttributeCooperative
1864
1865#define hipDrvLaunchAttributeID hipLaunchAttributeID
1866#define hipDrvLaunchAttributeValue hipLaunchAttributeValue
1867#define hipDrvLaunchAttribute hipLaunchAttribute
1868
1886
1898
1903
1917
1921
1932
1951
1966
1977
1978
1982typedef struct hipMemAllocationProp {
1984 union {
1985 hipMemAllocationHandleType requestedHandleType;
1986 hipMemAllocationHandleType requestedHandleTypes;
1987 };
1990 struct {
1991 unsigned char compressionType;
1992 unsigned char gpuDirectRDMACapable;
1993 unsigned short usage;
1996
2008
2020
2024typedef struct ihipMemGenericAllocationHandle* hipMemGenericAllocationHandle_t;
2025
2033
2040
2048
2056
2060typedef struct hipArrayMapInfo {
2062 union {
2063 hipMipmappedArray mipmap;
2067 union {
2068 struct {
2069 unsigned int
2070 level;
2071 unsigned int
2072 layer;
2073 unsigned int offsetX;
2074 unsigned int offsetY;
2075 unsigned int offsetZ;
2076 unsigned int extentWidth;
2077 unsigned int extentHeight;
2078 unsigned int extentDepth;
2079 } sparseLevel;
2080 struct {
2081 unsigned int
2082 layer;
2083 unsigned long long offset;
2084 unsigned long long size;
2085 } miptail;
2092 unsigned long long offset;
2093 unsigned int deviceBitMask;
2094 unsigned int flags;
2095 unsigned int reserved[2];
2097
2106
2114
2121
2128
2135
2139typedef struct hipGraphNodeParams {
2142 union {
2143 long long reserved1[29];
2144 hipKernelNodeParams kernel;
2145 hipMemcpyNodeParams memcpy;
2146 hipMemsetParams memset;
2147 hipHostNodeParams host;
2149 hipEventWaitNodeParams eventWait;
2150 hipEventRecordNodeParams eventRecord;
2155 };
2156
2157 long long reserved2;
2159
2163#define hipGraphKernelNodePortDefault 0
2164
2168#define hipGraphKernelNodePortLaunchCompletion 2
2169
2175#define hipGraphKernelNodePortProgrammatic 1
2176
2181
2182typedef struct hipGraphEdgeData {
2183 unsigned char
2191 unsigned char reserved[5];
2192 unsigned char
2194 unsigned char type;
2196
2197
2201typedef struct hipLaunchAttribute_st {
2203 char pad[8 - sizeof(hipLaunchAttributeID)];
2204 union {
2207 };
2209
2221
2225typedef struct HIP_LAUNCH_CONFIG_st {
2226 unsigned int gridDimX;
2227 unsigned int gridDimY;
2228 unsigned int gridDimZ;
2229 unsigned int blockDimX;
2230 unsigned int blockDimY;
2231 unsigned int blockDimZ;
2232 unsigned int sharedMemBytes;
2235 unsigned int numAttrs;
2237
2245
2253
2261
2262
2263// Doxygen end group GlobalDefs
2295// TODO-ctx - more description on error codes.
2296hipError_t hipInit(unsigned int flags);
2297
2339
2348hipError_t hipDeviceComputeCapability(int* major, int* minor, hipDevice_t device);
2357hipError_t hipDeviceGetName(char* name, int len, hipDevice_t device);
2383hipError_t hipDeviceGetLuid(char* luid, unsigned int* deviceNodeMask, hipDevice_t device);
2394 int dstDevice);
2403hipError_t hipDeviceGetPCIBusId(char* pciBusId, int len, int device);
2411hipError_t hipDeviceGetByPCIBusId(int* device, const char* pciBusId);
2420// doxygen end initialization
2496hipError_t hipSetValidDevices(int* device_arr, int len);
2614
2615// hipDeviceProp_t and hipGetDeviceProperties/hipChooseDevice are versioned.
2616// See HIP_FORCE_API_VERSION in hip_common.h.
2617
2618#if HIP_FORCE_API_VERSION >= 600
2619
2621
2635static inline hipError_t hipGetDeviceProperties(hipDeviceProp_t* prop, int deviceId) {
2636 return hipGetDevicePropertiesR0600(prop, deviceId);
2637}
2638
2639#endif
2640
2641
2659 int device);
2696hipError_t hipDeviceGetLimit(size_t* pValue, enum hipLimit_t limit);
2716hipError_t hipDeviceSetLimit(enum hipLimit_t limit, size_t value);
2736hipError_t hipGetDeviceFlags(unsigned int* flags);
2781
2782#if HIP_FORCE_API_VERSION >= 600
2784
2793static inline hipError_t hipChooseDevice(int* device, const hipDeviceProp_t* prop) {
2794 return hipChooseDeviceR0600(device, prop);
2795}
2796
2797#endif
2798
2823hipError_t hipInitDevice(int device, unsigned int deviceFlags, unsigned int flags);
2824
2838hipError_t hipExtGetLinkTypeAndHopCount(int device1, int device2, uint32_t* linktype,
2839 uint32_t* hopcount);
2840// TODO: implement IPC apis
2900hipError_t hipIpcOpenMemHandle(void** devPtr, hipIpcMemHandle_t handle, unsigned int flags);
2919
2937
2957
2958// end doxygen Device
2982hipError_t hipFuncSetAttribute(const void* func, hipFuncAttribute attr, int value);
2983
3000
3028 int device);
3029
3039
3066// doxygen end execution
3089
3102
3122const char* hipGetErrorName(hipError_t hip_error);
3131const char* hipGetErrorString(hipError_t hipError);
3141hipError_t hipDrvGetErrorName(hipError_t hipError, const char** errorString);
3151hipError_t hipDrvGetErrorString(hipError_t hipError, const char** errorString);
3152// end doxygen Error
3228hipError_t hipStreamCreateWithPriority(hipStream_t* stream, unsigned int flags, int priority);
3247hipError_t hipDeviceGetStreamPriorityRange(int* leastPriority, int* greatestPriority);
3331hipError_t hipStreamWaitEvent(hipStream_t stream, hipEvent_t event, unsigned int flags __dparm(0));
3341hipError_t hipStreamGetFlags(hipStream_t stream, unsigned int* flags);
3351hipError_t hipStreamGetId(hipStream_t stream, unsigned long long* streamId);
3394 const uint32_t* cuMask);
3407hipError_t hipExtStreamGetCUMask(hipStream_t stream, uint32_t cuMaskSize, uint32_t* cuMask);
3411typedef void (*hipStreamCallback_t)(hipStream_t stream, hipError_t status, void* userData);
3428 unsigned int flags);
3429
3438 const hipStreamAttrValue* value);
3439
3448 hipStreamAttrValue* value_out);
3449
3457
3458// end doxygen Stream
3506hipError_t hipStreamWaitValue32(hipStream_t stream, void* ptr, uint32_t value, unsigned int flags,
3507 uint32_t mask __dparm(0xFFFFFFFF));
3508
3545hipError_t hipStreamWaitValue64(hipStream_t stream, void* ptr, uint64_t value, unsigned int flags,
3546 uint64_t mask __dparm(0xFFFFFFFFFFFFFFFF));
3547
3568hipError_t hipStreamWriteValue32(hipStream_t stream, void* ptr, uint32_t value, unsigned int flags);
3589hipError_t hipStreamWriteValue64(hipStream_t stream, void* ptr, uint64_t value, unsigned int flags);
3590
3610hipError_t hipStreamBatchMemOp(hipStream_t stream, unsigned int count,
3611 hipStreamBatchMemOpParams* paramArray, unsigned int flags);
3612
3631 const hipGraphNode_t* dependencies, size_t numDependencies,
3632 const hipBatchMemOpNodeParams* nodeParams);
3633
3655 hipBatchMemOpNodeParams* nodeParams_out);
3656
3675 hipBatchMemOpNodeParams* nodeParams);
3676
3697 const hipBatchMemOpNodeParams* nodeParams);
3698
3699// end doxygen Stream Memory Operations
3785 unsigned int flags __dparm(0));
3816#ifdef __cplusplus
3818#else
3820#endif
3903// end doxygen Events
3935 hipDeviceptr_t ptr);
3936
3937
3989hipError_t hipDrvPointerGetAttributes(unsigned int numAttributes, hipPointer_attribute* attributes,
3990 void** data, hipDeviceptr_t ptr);
4015 const hipExternalSemaphoreHandleDesc* semHandleDesc);
4032 const hipExternalSemaphoreSignalParams* paramsArray,
4033 unsigned int numExtSems, hipStream_t stream);
4050 const hipExternalSemaphoreWaitParams* paramsArray,
4051 unsigned int numExtSems, hipStream_t stream);
4066
4079 const hipExternalMemoryHandleDesc* memHandleDesc);
4092 const hipExternalMemoryBufferDesc* bufferDesc);
4118 hipMipmappedArray_t* mipmap, hipExternalMemory_t extMem,
4119 const hipExternalMemoryMipmappedArrayDesc* mipmapDesc);
4120// end of external resource
4137hipError_t hipMalloc(void** ptr, size_t size);
4157hipError_t hipExtMallocWithFlags(void** ptr, size_t sizeBytes, unsigned int flags);
4158
4159
4182HIP_DEPRECATED("use hipHostMalloc instead")
4183hipError_t hipMallocHost(void** ptr, size_t size);
4196HIP_DEPRECATED("use hipHostMalloc instead")
4197hipError_t hipMemAllocHost(void** ptr, size_t size);
4198// end doxygen deprecated management memory
4235hipError_t hipHostMalloc(void** ptr, size_t size, unsigned int flags);
4270hipError_t hipMallocManaged(void** dev_ptr, size_t size,
4271 unsigned int flags __dparm(hipMemAttachGlobal));
4284hipError_t hipMemPrefetchAsync(const void* dev_ptr, size_t count, int device,
4285 hipStream_t stream __dparm(0));
4299hipError_t hipMemPrefetchAsync_v2(const void* dev_ptr, size_t count, hipMemLocation location,
4300 unsigned int flags, hipStream_t stream __dparm(0));
4301
4318hipError_t hipMemPrefetchBatchAsync(void** dev_ptrs, size_t* sizes, size_t count,
4319 hipMemLocation* prefetch_locs, size_t* prefetch_loc_idxs,
4320 size_t num_prefetch_locs, unsigned long long flags,
4321 hipStream_t stream);
4346hipError_t hipMemDiscardBatchAsync(void** dev_ptrs, size_t* sizes, size_t count,
4347 unsigned long long flags, hipStream_t stream);
4368hipError_t hipDrvMemDiscardBatchAsync(hipDeviceptr_t* dptrs, size_t* sizes, size_t count,
4369 unsigned long long flags, hipStream_t stream);
4399hipError_t hipMemDiscardAndPrefetchBatchAsync(void** dptrs, size_t* sizes, size_t count,
4400 hipMemLocation* prefetchLocs,
4401 size_t* prefetchLocIdxs,
4402 size_t numPrefetchLocs,
4403 unsigned long long flags, hipStream_t stream);
4423 hipMemLocation* prefetchLocs,
4424 size_t* prefetchLocIdxs,
4425 size_t numPrefetchLocs,
4426 unsigned long long flags, hipStream_t stream);
4427
4428// Deprecated since 800. Introduced in 700.
4429#if (HIP_FORCE_API_VERSION >= 700 && HIP_FORCE_API_VERSION < 800) || defined(HIP_ABI_IMPL)
4430
4450hipError_t hipMemAdvise_v2(const void* dev_ptr, size_t count, hipMemoryAdvise advice,
4451 hipMemLocation location);
4452
4453#endif
4454
4455// Deprecated since 800.
4456#if HIP_FORCE_API_VERSION < 800 || defined(HIP_ABI_IMPL)
4457
4477hipError_t hipMemAdvise(const void* dev_ptr, size_t count, hipMemoryAdvise advice, int device);
4478
4479#endif
4480
4481// Latest
4482#if HIP_FORCE_API_VERSION >= 800 && !defined(HIP_ABI_IMPL)
4483
4484hipError_t hipMemAdvise_v2(const void* dev_ptr, size_t count, hipMemoryAdvise advice,
4485 hipMemLocation location);
4486
4507static inline hipError_t hipMemAdvise(const void* dev_ptr, size_t count, hipMemoryAdvise advice,
4508 hipMemLocation location) {
4509 return hipMemAdvise_v2(dev_ptr, count, advice, location);
4510}
4511
4512#endif
4513
4528hipError_t hipMemRangeGetAttribute(void* data, size_t data_size, hipMemRangeAttribute attribute,
4529 const void* dev_ptr, size_t count);
4546hipError_t hipMemRangeGetAttributes(void** data, size_t* data_sizes,
4547 hipMemRangeAttribute* attributes, size_t num_attributes,
4548 const void* dev_ptr, size_t count);
4564hipError_t hipStreamAttachMemAsync(hipStream_t stream, void* dev_ptr, size_t length __dparm(0),
4565 unsigned int flags __dparm(hipMemAttachSingle));
4566// end doxygen Managed Memory
4626hipError_t hipMallocAsync(void** dev_ptr, size_t size, hipStream_t stream);
4651hipError_t hipFreeAsync(void* dev_ptr, hipStream_t stream);
4679hipError_t hipMemPoolTrimTo(hipMemPool_t mem_pool, size_t min_bytes_to_hold);
4778 size_t count);
4799 hipMemLocation* location);
4888hipError_t hipMallocFromPoolAsync(void** dev_ptr, size_t size, hipMemPool_t mem_pool,
4889 hipStream_t stream);
4917 hipMemAllocationHandleType handle_type,
4918 unsigned int flags);
4943 hipMemAllocationHandleType handle_type,
4944 unsigned int flags);
4994 hipMemPoolPtrExportData* export_data);
5008
5022
5023// Doxygen end of Stream Ordered Memory Allocator
5047hipError_t hipHostAlloc(void** ptr, size_t size, unsigned int flags);
5059hipError_t hipHostGetDevicePointer(void** devPtr, void* hstPtr, unsigned int flags);
5069hipError_t hipHostGetFlags(unsigned int* flagsPtr, void* hostPtr);
5119hipError_t hipHostRegister(void* hostPtr, size_t sizeBytes, unsigned int flags);
5147hipError_t hipMallocPitch(void** ptr, size_t* pitch, size_t width, size_t height);
5170hipError_t hipMemAllocPitch(hipDeviceptr_t* dptr, size_t* pitch, size_t widthInBytes, size_t height,
5171 unsigned int elementSizeBytes);
5244hipError_t hipMemcpy(void* dst, const void* src, size_t sizeBytes, hipMemcpyKind kind);
5262hipError_t hipMemcpyWithStream(void* dst, const void* src, size_t sizeBytes, hipMemcpyKind kind,
5263 hipStream_t stream);
5281hipError_t hipMemcpyHtoD(hipDeviceptr_t dst, const void* src, size_t sizeBytes);
5299hipError_t hipMemcpyDtoH(void* dst, hipDeviceptr_t src, size_t sizeBytes);
5336hipError_t hipMemcpyAtoD(hipDeviceptr_t dstDevice, hipArray_t srcArray, size_t srcOffset,
5337 size_t ByteCount);
5356hipError_t hipMemcpyDtoA(hipArray_t dstArray, size_t dstOffset, hipDeviceptr_t srcDevice,
5357 size_t ByteCount);
5358
5378hipError_t hipMemcpyAtoA(hipArray_t dstArray, size_t dstOffset, hipArray_t srcArray,
5379 size_t srcOffset, size_t ByteCount);
5398hipError_t hipMemcpyHtoDAsync(hipDeviceptr_t dst, const void* src, size_t sizeBytes,
5399 hipStream_t stream);
5418hipError_t hipMemcpyDtoHAsync(void* dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream);
5438 hipStream_t stream);
5458hipError_t hipMemcpyAtoHAsync(void* dstHost, hipArray_t srcArray, size_t srcOffset,
5459 size_t ByteCount, hipStream_t stream);
5479hipError_t hipMemcpyHtoAAsync(hipArray_t dstArray, size_t dstOffset, const void* srcHost,
5480 size_t ByteCount, hipStream_t stream);
5500 const char* name);
5501
5511hipError_t hipGetSymbolAddress(void** devPtr, const void* symbol);
5512
5513
5523hipError_t hipGetSymbolSize(size_t* size, const void* symbol);
5524
5544hipError_t hipGetProcAddress(const char* symbol, void** pfn, int hipVersion, uint64_t flags,
5545 hipDriverProcAddressQueryResult* symbolStatus);
5546
5568hipError_t hipMemcpyToSymbol(const void* symbol, const void* src, size_t sizeBytes,
5569 size_t offset __dparm(0),
5571
5585hipError_t hipMemcpyToSymbolAsync(const void* symbol, const void* src, size_t sizeBytes,
5586 size_t offset, hipMemcpyKind kind, hipStream_t stream __dparm(0));
5587
5600hipError_t hipMemcpyFromSymbol(void* dst, const void* symbol, size_t sizeBytes,
5601 size_t offset __dparm(0),
5603
5617hipError_t hipMemcpyFromSymbolAsync(void* dst, const void* symbol, size_t sizeBytes, size_t offset,
5618 hipMemcpyKind kind, hipStream_t stream __dparm(0));
5647hipError_t hipMemcpyAsync(void* dst, const void* src, size_t sizeBytes, hipMemcpyKind kind,
5648 hipStream_t stream __dparm(0));
5658hipError_t hipMemset(void* dst, int value, size_t sizeBytes);
5668hipError_t hipMemsetD8(hipDeviceptr_t dest, unsigned char value, size_t count);
5684hipError_t hipMemsetD8Async(hipDeviceptr_t dest, unsigned char value, size_t count,
5685 hipStream_t stream __dparm(0));
5695hipError_t hipMemsetD16(hipDeviceptr_t dest, unsigned short value, size_t count);
5711hipError_t hipMemsetD16Async(hipDeviceptr_t dest, unsigned short value, size_t count,
5712 hipStream_t stream __dparm(0));
5722hipError_t hipMemsetD32(hipDeviceptr_t dest, int value, size_t count);
5738hipError_t hipMemsetAsync(void* dst, int value, size_t sizeBytes, hipStream_t stream __dparm(0));
5754hipError_t hipMemsetD32Async(hipDeviceptr_t dst, int value, size_t count,
5755 hipStream_t stream __dparm(0));
5766hipError_t hipMemset2D(void* dst, size_t pitch, int value, size_t width, size_t height);
5778hipError_t hipMemset2DAsync(void* dst, size_t pitch, int value, size_t width, size_t height,
5779 hipStream_t stream __dparm(0));
5788hipError_t hipMemset3D(hipPitchedPtr pitchedDevPtr, int value, hipExtent extent);
5798hipError_t hipMemset3DAsync(hipPitchedPtr pitchedDevPtr, int value, hipExtent extent,
5799 hipStream_t stream __dparm(0));
5800
5812hipError_t hipMemsetD2D8(hipDeviceptr_t dst, size_t dstPitch, unsigned char value, size_t width,
5813 size_t height);
5826hipError_t hipMemsetD2D8Async(hipDeviceptr_t dst, size_t dstPitch, unsigned char value,
5827 size_t width, size_t height, hipStream_t stream __dparm(0));
5828
5840hipError_t hipMemsetD2D16(hipDeviceptr_t dst, size_t dstPitch, unsigned short value, size_t width,
5841 size_t height);
5854hipError_t hipMemsetD2D16Async(hipDeviceptr_t dst, size_t dstPitch, unsigned short value,
5855 size_t width, size_t height, hipStream_t stream __dparm(0));
5867hipError_t hipMemsetD2D32(hipDeviceptr_t dst, size_t dstPitch, unsigned int value, size_t width,
5868 size_t height);
5881hipError_t hipMemsetD2D32Async(hipDeviceptr_t dst, size_t dstPitch, unsigned int value,
5882 size_t width, size_t height, hipStream_t stream __dparm(0));
5883
5900hipError_t hipMemGetInfo(size_t* free, size_t* total);
5901
5927 size_t height __dparm(0), unsigned int flags __dparm(hipArrayDefault));
5992 struct hipExtent extent, unsigned int flags);
6077hipError_t hipMemcpy2D(void* dst, size_t dpitch, const void* src, size_t spitch, size_t width,
6078 size_t height, hipMemcpyKind kind);
6140hipError_t hipMemcpy2DAsync(void* dst, size_t dpitch, const void* src, size_t spitch, size_t width,
6141 size_t height, hipMemcpyKind kind, hipStream_t stream __dparm(0));
6159hipError_t hipMemcpy2DToArray(hipArray_t dst, size_t wOffset, size_t hOffset, const void* src,
6160 size_t spitch, size_t width, size_t height, hipMemcpyKind kind);
6179hipError_t hipMemcpy2DToArrayAsync(hipArray_t dst, size_t wOffset, size_t hOffset, const void* src,
6180 size_t spitch, size_t width, size_t height, hipMemcpyKind kind,
6181 hipStream_t stream __dparm(0));
6200hipError_t hipMemcpy2DArrayToArray(hipArray_t dst, size_t wOffsetDst, size_t hOffsetDst,
6201 hipArray_const_t src, size_t wOffsetSrc, size_t hOffsetSrc,
6202 size_t width, size_t height, hipMemcpyKind kind);
6222hipError_t hipMemcpyToArray(hipArray_t dst, size_t wOffset, size_t hOffset, const void* src,
6223 size_t count, hipMemcpyKind kind);
6243hipError_t hipMemcpyFromArray(void* dst, hipArray_const_t srcArray, size_t wOffset, size_t hOffset,
6244 size_t count, hipMemcpyKind kind);
6262hipError_t hipMemcpy2DFromArray(void* dst, size_t dpitch, hipArray_const_t src, size_t wOffset,
6263 size_t hOffset, size_t width, size_t height, hipMemcpyKind kind);
6282hipError_t hipMemcpy2DFromArrayAsync(void* dst, size_t dpitch, hipArray_const_t src, size_t wOffset,
6283 size_t hOffset, size_t width, size_t height,
6284 hipMemcpyKind kind, hipStream_t stream __dparm(0));
6298hipError_t hipMemcpyAtoH(void* dst, hipArray_t srcArray, size_t srcOffset, size_t count);
6312hipError_t hipMemcpyHtoA(hipArray_t dstArray, size_t dstOffset, const void* srcHost, size_t count);
6372
6388hipError_t hipMemcpyBatchAsync(void** dsts, void** srcs, size_t* sizes, size_t count,
6389 hipMemcpyAttributes* attrs, size_t* attrsIdxs, size_t numAttrs,
6390 size_t* failIdx, hipStream_t stream __dparm(0));
6391
6404hipError_t hipMemcpy3DBatchAsync(size_t numOps, struct hipMemcpy3DBatchOp* opList, size_t* failIdx,
6405 unsigned long long flags, hipStream_t stream __dparm(0));
6406
6416
6426
6443 hipMipmappedArray_t mipmap, hipDevice_t device);
6444// doxygen end Memory
6479hipError_t hipDeviceCanAccessPeer(int* canAccessPeer, int deviceId, int peerDeviceId);
6494hipError_t hipDeviceEnablePeerAccess(int peerDeviceId, unsigned int flags);
6506
6518hipError_t hipMemcpyPeer(void* dst, int dstDeviceId, const void* src, int srcDeviceId,
6519 size_t sizeBytes);
6532hipError_t hipMemcpyPeerAsync(void* dst, int dstDeviceId, const void* src, int srcDevice,
6533 size_t sizeBytes, hipStream_t stream __dparm(0));
6534
6535// doxygen end PeerToPeer
6557 hipDevResourceType type);
6558
6575 const hipDevResource* input, hipDevResource* remainder,
6576 unsigned int flags, unsigned int minCount);
6577
6594hipError_t hipDevSmResourceSplit(hipDevResource* result, unsigned int nbGroups,
6595 const hipDevResource* input, hipDevResource* remainder,
6596 unsigned int flags,
6597 hipDevSmResourceGroupParams* groupParams);
6598
6610 unsigned int nbResources);
6611
6624 unsigned int flags);
6625
6634
6644
6656 unsigned int flags, int priority);
6657
6668 hipDevResourceType type);
6669
6679
6688hipError_t hipExecutionCtxGetId(hipExecutionCtx_t ctx, unsigned long long* ctxId);
6689
6700 hipDevResourceType type);
6701
6711
6720
6772hipError_t hipCtxCreate(hipCtx_t* ctx, unsigned int flags, hipDevice_t device);
6884hipError_t hipCtxGetApiVersion(hipCtx_t ctx, unsigned int* apiVersion);
6987hipError_t hipCtxGetFlags(unsigned int* flags);
7011hipError_t hipCtxEnablePeerAccess(hipCtx_t peerCtx, unsigned int flags);
7033
7050hipError_t hipDevicePrimaryCtxGetState(hipDevice_t dev, unsigned int* flags, int* active);
7115// doxygen end Context Management
7139hipError_t hipModuleLoadFatBinary(hipModule_t* module, const void* fatbin);
7153hipError_t hipModuleLoad(hipModule_t* module, const char* fname);
7174hipError_t hipModuleGetFunction(hipFunction_t* function, hipModule_t module, const char* kname);
7175
7186
7197hipError_t hipModuleEnumerateFunctions(hipFunction_t* functions, unsigned int numFunctions,
7198 hipModule_t mod);
7199
7228 hipDevice_t dev);
7229
7243hipError_t hipLibraryLoadData(hipLibrary_t* library, const void* code, hipJitOption* jitOptions,
7244 void** jitOptionsValues, unsigned int numJitOptions,
7245 hipLibraryOption* libraryOptions, void** libraryOptionValues,
7246 unsigned int numLibraryOptions);
7247
7261hipError_t hipLibraryLoadFromFile(hipLibrary_t* library, const char* fileName,
7262 hipJitOption* jitOptions, void** jitOptionsValues,
7263 unsigned int numJitOptions, hipLibraryOption* libraryOptions,
7264 void** libraryOptionValues, unsigned int numLibraryOptions);
7265
7273
7282hipError_t hipLibraryGetKernel(hipKernel_t* pKernel, hipLibrary_t library, const char* name);
7283
7292
7307hipError_t hipLibraryGetGlobal(void** dptr, size_t* bytes, hipLibrary_t library,
7308 const char* name);
7309
7326hipError_t hipLibraryGetManaged(void** dptr, size_t* bytes, hipLibrary_t library,
7327 const char* name);
7328
7337hipError_t hipLibraryEnumerateKernels(hipKernel_t* kernels, unsigned int numKernels,
7338 hipLibrary_t library);
7339
7348
7356hipError_t hipKernelGetName(const char** name, hipKernel_t kernel);
7357
7368hipError_t hipKernelGetParamInfo(hipKernel_t kernel, size_t paramIndex, size_t* paramOffset,
7369 size_t* paramSize);
7370
7379hipError_t hipFuncGetAttributes(struct hipFuncAttributes* attr, const void* func);
7399hipError_t hipGetFuncBySymbol(hipFunction_t* functionPtr, const void* symbolPtr);
7411hipError_t hipGetDriverEntryPoint(const char* symbol, void** funcPtr, unsigned long long flags,
7412 hipDriverEntryPointQueryResult* driverStatus);
7446hipError_t hipModuleLoadData(hipModule_t* module, const void* image);
7459hipError_t hipModuleLoadDataEx(hipModule_t* module, const void* image, unsigned int numOptions,
7460 hipJitOption* options, void** optionValues);
7480 const char* name, unsigned int numOptions, hipJitOption* options,
7481 void** optionValues);
7482
7500 unsigned int numOptions, hipJitOption* options, void** optionValues);
7501
7516hipError_t hipLinkComplete(hipLinkState_t state, void** hipBinOut, size_t* sizeOut);
7517
7529hipError_t hipLinkCreate(unsigned int numOptions, hipJitOption* options, void** optionValues,
7530 hipLinkState_t* stateOut);
7540
7569hipError_t hipModuleLaunchKernel(hipFunction_t f, unsigned int gridDimX, unsigned int gridDimY,
7570 unsigned int gridDimZ, unsigned int blockDimX,
7571 unsigned int blockDimY, unsigned int blockDimZ,
7572 unsigned int sharedMemBytes, hipStream_t stream,
7573 void** kernelParams, void** extra);
7603 unsigned int gridDimY, unsigned int gridDimZ,
7604 unsigned int blockDimX, unsigned int blockDimY,
7605 unsigned int blockDimZ, unsigned int sharedMemBytes,
7606 hipStream_t stream, void** kernelParams);
7622 unsigned int numDevices, unsigned int flags);
7643hipError_t hipLaunchCooperativeKernel(const void* f, dim3 gridDim, dim3 blockDimX,
7644 void** kernelParams, unsigned int sharedMemBytes,
7645 hipStream_t stream);
7658 unsigned int flags);
7659
7660// Doxygen end group ModuleCooperativeG
7675 unsigned int flags);
7689hipError_t hipLaunchKernelExC(const hipLaunchConfig_t* config, const void* fPtr, void** args);
7706 void** extra);
7722 hipMemRangeHandleType handleType,
7723 unsigned long long flags);
7724// doxygen end Module
7752// TODO - Match CUoccupancyB2DSize
7754 size_t dynSharedMemPerBlk, int blockSizeLimit);
7770// TODO - Match CUoccupancyB2DSize
7772 hipFunction_t f,
7773 size_t dynSharedMemPerBlk,
7774 int blockSizeLimit, unsigned int flags);
7785 int blockSize,
7786 size_t dynSharedMemPerBlk);
7798 int* numBlocks, hipFunction_t f, int blockSize, size_t dynSharedMemPerBlk, unsigned int flags);
7809 int blockSize, size_t dynSharedMemPerBlk);
7821 int* numBlocks, const void* f, int blockSize, size_t dynSharedMemPerBlk,
7822 unsigned int flags __dparm(hipOccupancyDefault));
7837hipError_t hipOccupancyMaxPotentialBlockSize(int* gridSize, int* blockSize, const void* f,
7838 size_t dynSharedMemPerBlk, int blockSizeLimit);
7854hipError_t hipOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, const void* f,
7855 int numBlocks, int blockSize);
7866hipError_t hipOccupancyMaxActiveClusters(int* numClusters, const void* f,
7867 const hipLaunchConfig_t* config);
7878hipError_t hipOccupancyMaxPotentialClusterSize(int* clusterSize, const void* f,
7879 const hipLaunchConfig_t* config);
7880
7881// doxygen end Occupancy
7895// TODO - expand descriptions:
7902HIP_DEPRECATED("use roctracer/rocTX instead")
7910HIP_DEPRECATED("use roctracer/rocTX instead")
7912// doxygen end profiler
7939hipError_t hipConfigureCall(dim3 gridDim, dim3 blockDim, size_t sharedMem __dparm(0),
7940 hipStream_t stream __dparm(0));
7951hipError_t hipSetupArgument(const void* arg, size_t size, size_t offset);
7960hipError_t hipLaunchByPtr(const void* func);
7977hipError_t __hipPushCallConfiguration(dim3 gridDim, dim3 blockDim, size_t sharedMem __dparm(0),
7978 hipStream_t stream __dparm(0));
7998hipError_t __hipPopCallConfiguration(dim3* gridDim, dim3* blockDim, size_t* sharedMem,
7999 hipStream_t* stream);
8016hipError_t hipLaunchKernel(const void* function_address, dim3 numBlocks, dim3 dimBlocks,
8017 void** args, size_t sharedMemBytes __dparm(0),
8018 hipStream_t stream __dparm(0));
8019
8047
8056// TODO: Move this to hip_ext.h
8078hipError_t hipExtLaunchKernel(const void* function_address, dim3 numBlocks, dim3 dimBlocks,
8079 void** args, size_t sharedMemBytes, hipStream_t stream,
8080 hipEvent_t startEvent, hipEvent_t stopEvent, int flags);
8081// doxygen end Clang launch
8108 const hipTextureDesc* pTexDesc,
8109 const struct hipResourceViewDesc* pResViewDesc);
8110
8120
8131
8142 hipTextureObject_t textureObject);
8143
8154 hipTextureObject_t textureObject);
8155
8166 hipTextureObject_t textureObject);
8167
8180 const HIP_TEXTURE_DESC* pTexDesc,
8181 const HIP_RESOURCE_VIEW_DESC* pResViewDesc);
8182
8192
8203
8214 hipTextureObject_t texObject);
8215
8226
8242 const struct hipChannelFormatDesc* desc, struct hipExtent extent,
8243 unsigned int numLevels, unsigned int flags __dparm(0));
8244
8256
8270 hipMipmappedArray_const_t mipmappedArray, unsigned int level);
8271
8283hipError_t hipMipmappedArrayCreate(hipMipmappedArray_t* pHandle,
8284 HIP_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc,
8285 unsigned int numMipmapLevels);
8286
8297hipError_t hipMipmappedArrayDestroy(hipMipmappedArray_t hMipmappedArray);
8298
8311hipError_t hipMipmappedArrayGetLevel(hipArray_t* pLevelArray, hipMipmappedArray_t hMipMappedArray,
8312 unsigned int level);
8313
8335 const hipChannelFormatDesc* desc);
8336
8348hipError_t hipGetTextureReference(const textureReference** texref, const void* symbol);
8349
8361hipError_t hipTexRefGetBorderColor(float* pBorderColor, const textureReference* texRef);
8362
8376
8390 enum hipTextureAddressMode am);
8430hipError_t hipTexRefSetFlags(textureReference* texRef, unsigned int Flags);
8445 int NumPackedComponents);
8461hipError_t hipBindTexture(size_t* offset, const textureReference* tex, const void* devPtr,
8462 const hipChannelFormatDesc* desc, size_t size __dparm(UINT_MAX));
8480hipError_t hipBindTexture2D(size_t* offset, const textureReference* tex, const void* devPtr,
8481 const hipChannelFormatDesc* desc, size_t width, size_t height,
8482 size_t pitch);
8497 const hipChannelFormatDesc* desc);
8550 int dim);
8576hipError_t hipTexRefGetFlags(unsigned int* pFlags, const textureReference* texRef);
8591 const textureReference* texRef);
8618 const textureReference* texRef);
8645hipError_t hipTexRefGetMipmapLevelClamp(float* pminMipmapLevelClamp, float* pmaxMipmapLevelClamp,
8646 const textureReference* texRef);
8659hipError_t hipTexRefGetMipMappedArray(hipMipmappedArray_t* pArray, const textureReference* texRef);
8675 size_t bytes);
8691 hipDeviceptr_t dptr, size_t Pitch);
8758 float maxMipMapLevelClamp);
8773 struct hipMipmappedArray* mipmappedArray, unsigned int Flags);
8774
8775// doxygen end deprecated texture management
8780// doxygen end Texture management
8792// This group is for HIPrtc
8793
8794// doxygen end Runtime
8813const char* hipApiName(uint32_t id);
8822const char* hipKernelNameRef(const hipFunction_t f);
8832const char* hipKernelNameRefByPtr(const void* hostFunction, hipStream_t stream);
8842
8843// doxygen end Callback
8866
8887 const hipGraphNode_t* dependencies,
8888 const hipGraphEdgeData* dependencyData,
8889 size_t numDependencies, hipStreamCaptureMode mode);
8890
8902
8914 unsigned long long* pId);
8915
8931 unsigned long long* id_out __dparm(0),
8932 hipGraph_t* graph_out __dparm(0),
8933 const hipGraphNode_t** dependencies_out __dparm(0),
8934 size_t* numDependencies_out __dparm(0));
8935
8946
8960 size_t numDependencies,
8961 unsigned int flags __dparm(0));
8962
8971
8981hipError_t hipGraphCreate(hipGraph_t* pGraph, unsigned int flags);
8982
8992
9004 const hipGraphNode_t* to, size_t numDependencies);
9005
9017 const hipGraphNode_t* to, size_t numDependencies);
9018
9035 size_t* numEdges);
9036
9051hipError_t hipGraphGetNodes(hipGraph_t graph, hipGraphNode_t* nodes, size_t* numNodes);
9052
9068 size_t* pNumRootNodes);
9069
9085 size_t* pNumDependencies);
9086
9103 size_t* pNumDependentNodes);
9104
9114
9123
9132hipError_t hipGraphClone(hipGraph_t* pGraphClone, hipGraph_t originalGraph);
9133
9144 hipGraph_t clonedGraph);
9145
9160 hipGraphNode_t* pErrorNode, char* pLogBuffer, size_t bufferSize);
9161
9173 unsigned long long flags);
9174
9185 hipGraphInstantiateParams* instantiateParams);
9195
9205
9218 const hipGraphNode_t* pDependencies, size_t numDependencies,
9219 hipGraphNodeParams* nodeParams);
9220
9229hipError_t hipGraphExecGetFlags(hipGraphExec_t graphExec, unsigned long long* flags);
9230
9241
9253 hipGraphNodeParams* nodeParams);
9254
9264
9265// Check whether an executable graph can be updated with a graph and perform the update if possible.
9278 hipGraphNode_t* hErrorNode_out,
9279 hipGraphExecUpdateResult* updateResult_out);
9280
9293 const hipGraphNode_t* pDependencies, size_t numDependencies,
9294 const hipKernelNodeParams* pNodeParams);
9295
9305
9315
9326 const hipKernelNodeParams* pNodeParams);
9327
9341 const hipGraphNode_t* dependencies, size_t numDependencies,
9342 const HIP_MEMCPY3D* copyParams, hipCtx_t ctx);
9355 const hipGraphNode_t* pDependencies, size_t numDependencies,
9356 const hipMemcpy3DParms* pCopyParams);
9366
9376
9387 const hipKernelNodeAttrValue* value);
9398 hipKernelNodeAttrValue* value);
9409 hipMemcpy3DParms* pNodeParams);
9410
9426 const hipGraphNode_t* pDependencies, size_t numDependencies,
9427 void* dst, const void* src, size_t count, hipMemcpyKind kind);
9428
9441 size_t count, hipMemcpyKind kind);
9442
9457 void* dst, const void* src, size_t count,
9458 hipMemcpyKind kind);
9459
9476 const hipGraphNode_t* pDependencies,
9477 size_t numDependencies, void* dst, const void* symbol,
9478 size_t count, size_t offset, hipMemcpyKind kind);
9479
9493 size_t count, size_t offset, hipMemcpyKind kind);
9494
9510 void* dst, const void* symbol, size_t count,
9511 size_t offset, hipMemcpyKind kind);
9512
9529 const hipGraphNode_t* pDependencies,
9530 size_t numDependencies, const void* symbol,
9531 const void* src, size_t count, size_t offset,
9532 hipMemcpyKind kind);
9533
9547 const void* src, size_t count, size_t offset,
9548 hipMemcpyKind kind);
9549
9550
9565 const void* symbol, const void* src,
9566 size_t count, size_t offset, hipMemcpyKind kind);
9567
9580 const hipGraphNode_t* pDependencies, size_t numDependencies,
9581 const hipMemsetParams* pMemsetParams);
9582
9592
9602
9613 const hipMemsetParams* pNodeParams);
9614
9627 const hipGraphNode_t* pDependencies, size_t numDependencies,
9628 const hipHostNodeParams* pNodeParams);
9629
9639
9649
9660 const hipHostNodeParams* pNodeParams);
9661
9674 const hipGraphNode_t* pDependencies, size_t numDependencies,
9675 hipGraph_t childGraph);
9676
9686
9697 hipGraph_t childGraph);
9698
9710 const hipGraphNode_t* pDependencies, size_t numDependencies);
9711
9712
9725 const hipGraphNode_t* pDependencies, size_t numDependencies,
9726 hipEvent_t event);
9727
9737
9747
9758 hipEvent_t event);
9759
9772 const hipGraphNode_t* pDependencies, size_t numDependencies,
9773 hipEvent_t event);
9774
9775
9785
9795
9806 hipEvent_t event);
9807
9821 const hipGraphNode_t* pDependencies, size_t numDependencies,
9822 hipMemAllocNodeParams* pNodeParams);
9823
9833
9846 const hipGraphNode_t* pDependencies, size_t numDependencies,
9847 void* dev_ptr);
9848
9858
9869
9880
9889
9902 unsigned int initialRefcount, unsigned int flags);
9903
9913
9923
9935 unsigned int count __dparm(1), unsigned int flags __dparm(0));
9936
9947 unsigned int count __dparm(1));
9948
9958hipError_t hipGraphDebugDotPrint(hipGraph_t graph, const char* path, unsigned int flags);
9959
9974
9997 unsigned int isEnabled);
10018 unsigned int* isEnabled);
10019
10032 hipGraphNode_t* pGraphNode, hipGraph_t graph, const hipGraphNode_t* pDependencies,
10033 size_t numDependencies, const hipExternalSemaphoreWaitNodeParams* nodeParams);
10034
10047 hipGraphNode_t* pGraphNode, hipGraph_t graph, const hipGraphNode_t* pDependencies,
10048 size_t numDependencies, const hipExternalSemaphoreSignalNodeParams* nodeParams);
10058 hipGraphNode_t hNode, const hipExternalSemaphoreSignalNodeParams* nodeParams);
10068 hipGraphNode_t hNode, const hipExternalSemaphoreWaitNodeParams* nodeParams);
10099 hipGraphExec_t hGraphExec, hipGraphNode_t hNode,
10100 const hipExternalSemaphoreSignalNodeParams* nodeParams);
10111 hipGraphExec_t hGraphExec, hipGraphNode_t hNode,
10112 const hipExternalSemaphoreWaitNodeParams* nodeParams);
10113
10123
10133
10147 const hipGraphNode_t* dependencies, size_t numDependencies,
10148 const hipMemsetParams* memsetParams, hipCtx_t ctx);
10149
10162 const hipGraphNode_t* dependencies, size_t numDependencies,
10163 hipDeviceptr_t dptr);
10164
10176 const HIP_MEMCPY3D* copyParams, hipCtx_t ctx);
10177
10189 const hipMemsetParams* memsetParams, hipCtx_t ctx);
10190
10191// doxygen end graph API
10221
10234hipError_t hipMemAddressReserve(void** ptr, size_t size, size_t alignment, void* addr,
10235 unsigned long long flags);
10236
10255 const hipMemAllocationProp* prop, unsigned long long flags);
10256
10270 hipMemAllocationHandleType handleType,
10271 unsigned long long flags);
10272
10283hipError_t hipMemGetAccess(unsigned long long* flags, const hipMemLocation* location, void* ptr);
10284
10298
10310
10322 hipMemAllocationHandleType shHandleType);
10323
10336hipError_t hipMemMap(void* ptr, size_t size, size_t offset, hipMemGenericAllocationHandle_t handle,
10337 unsigned long long flags);
10338
10347hipError_t hipMemMapArrayAsync(hipArrayMapInfo* mapInfoList, unsigned int count,
10348 hipStream_t stream);
10349
10360
10371
10384hipError_t hipMemSetAccess(void* ptr, size_t size, const hipMemAccessDesc* desc, size_t count);
10385
10395hipError_t hipMemUnmap(void* ptr, size_t size);
10396
10397// doxygen end virtual memory management API
10420 hipStream_t stream __dparm(0));
10435 unsigned int arrayIndex, unsigned int mipLevel);
10447 hipGraphicsResource_t resource);
10459 hipStream_t stream __dparm(0));
10469// doxygen end GraphicsInterop
10504// end of surface
10505
10506
10543hipError_t hipExtSetLoggingParams(size_t log_level, size_t log_size, size_t log_mask);
10544
10548#ifdef __cplusplus
10549} /* extern "c" */
10550#endif
10551#ifdef __cplusplus
10552#if defined(__clang__) && defined(__HIP__)
10553template <typename T> static hipError_t __host__ inline hipOccupancyMaxPotentialBlockSize(
10554 int* gridSize, int* blockSize, T f, size_t dynSharedMemPerBlk = 0, int blockSizeLimit = 0) {
10555 return hipOccupancyMaxPotentialBlockSize(gridSize, blockSize, reinterpret_cast<const void*>(f),
10556 dynSharedMemPerBlk, blockSizeLimit);
10557}
10558template <typename T> static hipError_t __host__ inline hipOccupancyMaxPotentialBlockSizeWithFlags(
10559 int* gridSize, int* blockSize, T f, size_t dynSharedMemPerBlk = 0, int blockSizeLimit = 0,
10560 unsigned int flags = 0) {
10561 (void)flags;
10562 return hipOccupancyMaxPotentialBlockSize(gridSize, blockSize, reinterpret_cast<const void*>(f),
10563 dynSharedMemPerBlk, blockSizeLimit);
10564}
10565#endif // defined(__clang__) && defined(__HIP__)
10566
10576template <typename T> hipError_t hipGetSymbolAddress(void** devPtr, const T& symbol) {
10577 return ::hipGetSymbolAddress(devPtr, (const void*)&symbol);
10578}
10589template <typename T> hipError_t hipGetSymbolSize(size_t* size, const T& symbol) {
10590 return ::hipGetSymbolSize(size, (const void*)&symbol);
10591}
10592
10601template <typename T>
10602hipError_t hipMemcpyToSymbol(const T& symbol, const void* src, size_t sizeBytes,
10603 size_t offset __dparm(0),
10605 return ::hipMemcpyToSymbol((const void*)&symbol, src, sizeBytes, offset, kind);
10606}
10615template <typename T>
10616hipError_t hipMemcpyToSymbolAsync(const T& symbol, const void* src, size_t sizeBytes, size_t offset,
10617 hipMemcpyKind kind, hipStream_t stream __dparm(0)) {
10618 return ::hipMemcpyToSymbolAsync((const void*)&symbol, src, sizeBytes, offset, kind, stream);
10619}
10627template <typename T>
10628hipError_t hipMemcpyFromSymbol(void* dst, const T& symbol, size_t sizeBytes,
10629 size_t offset __dparm(0),
10631 return ::hipMemcpyFromSymbol(dst, (const void*)&symbol, sizeBytes, offset, kind);
10632}
10640template <typename T>
10641hipError_t hipMemcpyFromSymbolAsync(void* dst, const T& symbol, size_t sizeBytes, size_t offset,
10642 hipMemcpyKind kind, hipStream_t stream __dparm(0)) {
10643 return ::hipMemcpyFromSymbolAsync(dst, (const void*)&symbol, sizeBytes, offset, kind, stream);
10644}
10645
10657template <class T>
10658inline hipError_t hipOccupancyMaxActiveBlocksPerMultiprocessor(int* numBlocks, T f, int blockSize,
10659 size_t dynSharedMemPerBlk) {
10660 return hipOccupancyMaxActiveBlocksPerMultiprocessor(numBlocks, reinterpret_cast<const void*>(f),
10661 blockSize, dynSharedMemPerBlk);
10662}
10677 int* numBlocks, T f, int blockSize, size_t dynSharedMemPerBlk, unsigned int flags) {
10679 numBlocks, reinterpret_cast<const void*>(f), blockSize, dynSharedMemPerBlk, flags);
10680}
10703template <typename UnaryFunction, class T>
10704static hipError_t __host__ inline hipOccupancyMaxPotentialBlockSizeVariableSMemWithFlags(
10705 int* min_grid_size, int* block_size, T func, UnaryFunction block_size_to_dynamic_smem_size,
10706 int block_size_limit = 0, unsigned int flags = 0) {
10707 if (min_grid_size == nullptr || block_size == nullptr ||
10708 reinterpret_cast<const void*>(func) == nullptr) {
10709 return hipErrorInvalidValue;
10710 }
10711
10712 int dev;
10713 hipError_t status;
10714 if ((status = hipGetDevice(&dev)) != hipSuccess) {
10715 return status;
10716 }
10717
10718 int max_threads_per_cu;
10719 if ((status = hipDeviceGetAttribute(&max_threads_per_cu,
10721 hipSuccess) {
10722 return status;
10723 }
10724
10725 int warp_size;
10726 if ((status = hipDeviceGetAttribute(&warp_size, hipDeviceAttributeWarpSize, dev)) != hipSuccess) {
10727 return status;
10728 }
10729
10730 int max_cu_count;
10731 if ((status = hipDeviceGetAttribute(&max_cu_count, hipDeviceAttributeMultiprocessorCount, dev)) !=
10732 hipSuccess) {
10733 return status;
10734 }
10735
10736 struct hipFuncAttributes attr;
10737 if ((status = hipFuncGetAttributes(&attr, reinterpret_cast<const void*>(func))) != hipSuccess) {
10738 return status;
10739 }
10740
10741 // Initial limits for the execution
10742 const int func_max_threads_per_block = attr.maxThreadsPerBlock;
10743 if (block_size_limit == 0) {
10744 block_size_limit = func_max_threads_per_block;
10745 }
10746
10747 if (func_max_threads_per_block < block_size_limit) {
10748 block_size_limit = func_max_threads_per_block;
10749 }
10750
10751 const int block_size_limit_aligned =
10752 ((block_size_limit + (warp_size - 1)) / warp_size) * warp_size;
10753
10754 // For maximum search
10755 int max_threads = 0;
10756 int max_block_size{};
10757 int max_num_blocks{};
10758 for (int block_size_check_aligned = block_size_limit_aligned; block_size_check_aligned > 0;
10759 block_size_check_aligned -= warp_size) {
10760 // Make sure the logic uses the requested limit and not aligned
10761 int block_size_check =
10762 (block_size_limit < block_size_check_aligned) ? block_size_limit : block_size_check_aligned;
10763
10764 size_t dyn_smem_size = block_size_to_dynamic_smem_size(block_size_check);
10765 int optimal_blocks;
10767 &optimal_blocks, func, block_size_check, dyn_smem_size, flags)) != hipSuccess) {
10768 return status;
10769 }
10770
10771 int total_threads = block_size_check * optimal_blocks;
10772 if (total_threads > max_threads) {
10773 max_block_size = block_size_check;
10774 max_num_blocks = optimal_blocks;
10775 max_threads = total_threads;
10776 }
10777
10778 // Break if the logic reached possible maximum
10779 if (max_threads_per_cu == max_threads) {
10780 break;
10781 }
10782 }
10783
10784 // Grid size is the number of blocks per CU * CU count
10785 *min_grid_size = max_num_blocks * max_cu_count;
10786 *block_size = max_block_size;
10787
10788 return status;
10789}
10790
10812template <typename UnaryFunction, class T>
10813static hipError_t __host__ inline hipOccupancyMaxPotentialBlockSizeVariableSMem(
10814 int* min_grid_size, int* block_size, T func, UnaryFunction block_size_to_dynamic_smem_size,
10815 int block_size_limit = 0) {
10816 return hipOccupancyMaxPotentialBlockSizeVariableSMemWithFlags(
10817 min_grid_size, block_size, func, block_size_to_dynamic_smem_size, block_size_limit);
10818}
10834template <typename F> inline hipError_t hipOccupancyMaxPotentialBlockSize(int* gridSize,
10835 int* blockSize, F kernel,
10836 size_t dynSharedMemPerBlk,
10837 uint32_t blockSizeLimit) {
10838 return hipOccupancyMaxPotentialBlockSize(gridSize, blockSize, (hipFunction_t)kernel,
10839 dynSharedMemPerBlk, blockSizeLimit);
10840}
10841
10857template <typename F>
10858inline hipError_t hipOccupancyAvailableDynamicSMemPerBlock(size_t* dynamicSmemSize, F f,
10859 int numBlocks, int blockSize) {
10860 return hipOccupancyAvailableDynamicSMemPerBlock(dynamicSmemSize, reinterpret_cast<const void*>(f),
10861 numBlocks, blockSize);
10862}
10884template <class T>
10885inline hipError_t hipLaunchCooperativeKernel(T f, dim3 gridDim, dim3 blockDim, void** kernelParams,
10886 unsigned int sharedMemBytes, hipStream_t stream) {
10887 return hipLaunchCooperativeKernel(reinterpret_cast<const void*>(f), gridDim, blockDim,
10888 kernelParams, sharedMemBytes, stream);
10889}
10905template <class T>
10907 unsigned int numDevices,
10908 unsigned int flags = 0) {
10909 return hipLaunchCooperativeKernelMultiDevice(launchParamsList, numDevices, flags);
10910}
10923template <class T>
10925 unsigned int numDevices,
10926 unsigned int flags = 0) {
10927 return hipExtLaunchMultiKernelMultiDevice(launchParamsList, numDevices, flags);
10928}
10942template <class T, int dim, enum hipTextureReadMode readMode> HIP_DEPRECATED(HIP_DEPRECATED_MSG)
10943static inline hipError_t hipBindTexture(size_t* offset, const struct texture<T, dim, readMode>& tex,
10944 const void* devPtr, size_t size = UINT_MAX) {
10945 return hipBindTexture(offset, &tex, devPtr, &tex.channelDesc, size);
10946}
10961template <class T, int dim, enum hipTextureReadMode readMode> HIP_DEPRECATED(HIP_DEPRECATED_MSG)
10962static inline hipError_t
10963 hipBindTexture(size_t* offset, const struct texture<T, dim, readMode>& tex, const void* devPtr,
10964 const struct hipChannelFormatDesc& desc, size_t size = UINT_MAX) {
10965 return hipBindTexture(offset, &tex, devPtr, &desc, size);
10966}
10982template <class T, int dim, enum hipTextureReadMode readMode> HIP_DEPRECATED(HIP_DEPRECATED_MSG)
10983static inline hipError_t
10984 hipBindTexture2D(size_t* offset, const struct texture<T, dim, readMode>& tex,
10985 const void* devPtr, size_t width, size_t height, size_t pitch) {
10986 return hipBindTexture2D(offset, &tex, devPtr, &tex.channelDesc, width, height, pitch);
10987}
11004template <class T, int dim, enum hipTextureReadMode readMode> HIP_DEPRECATED(HIP_DEPRECATED_MSG)
11005static inline hipError_t
11006 hipBindTexture2D(size_t* offset, const struct texture<T, dim, readMode>& tex,
11007 const void* devPtr, const struct hipChannelFormatDesc& desc, size_t width,
11008 size_t height, size_t pitch) {
11009 return hipBindTexture2D(offset, &tex, devPtr, &desc, width, height, pitch);
11010}
11022template <class T, int dim, enum hipTextureReadMode readMode> HIP_DEPRECATED(HIP_DEPRECATED_MSG)
11023static inline hipError_t
11028}
11041template <class T, int dim, enum hipTextureReadMode readMode> HIP_DEPRECATED(HIP_DEPRECATED_MSG)
11042static inline hipError_t
11044 const struct hipChannelFormatDesc& desc) {
11045 return hipBindTextureToArray(&tex, array, &desc);
11046}
11058template <class T, int dim, enum hipTextureReadMode readMode> HIP_DEPRECATED(HIP_DEPRECATED_MSG)
11064 if (err != hipSuccess) {
11065 return err;
11066 }
11069}
11082template <class T, int dim, enum hipTextureReadMode readMode> HIP_DEPRECATED(HIP_DEPRECATED_MSG)
11085 const struct hipChannelFormatDesc& desc) {
11087}
11098template <class T, int dim, enum hipTextureReadMode readMode> HIP_DEPRECATED(HIP_DEPRECATED_MSG)
11099static inline hipError_t hipUnbindTexture(const struct texture<T, dim, readMode>& tex) {
11100 return hipUnbindTexture(&tex);
11101}
11125static inline hipError_t hipMallocAsync(void** dev_ptr, size_t size, hipMemPool_t mem_pool,
11126 hipStream_t stream) {
11127 return hipMallocFromPoolAsync(dev_ptr, size, mem_pool, stream);
11128}
11139template <class T> static inline hipError_t hipMallocAsync(T** dev_ptr, size_t size,
11140 hipMemPool_t mem_pool,
11141 hipStream_t stream) {
11142 return hipMallocFromPoolAsync(reinterpret_cast<void**>(dev_ptr), size, mem_pool, stream);
11143}
11154template <class T>
11155static inline hipError_t hipMallocAsync(T** dev_ptr, size_t size, hipStream_t stream) {
11156 return hipMallocAsync(reinterpret_cast<void**>(dev_ptr), size, stream);
11157}
11168template <class T> static inline hipError_t hipMallocFromPoolAsync(T** dev_ptr, size_t size,
11169 hipMemPool_t mem_pool,
11170 hipStream_t stream) {
11171 return hipMallocFromPoolAsync(reinterpret_cast<void**>(dev_ptr), size, mem_pool, stream);
11172}
11186template <typename... KernelArgs, typename... Params>
11187static inline __host__ hipError_t hipLaunchKernelEx(const hipLaunchConfig_t* config,
11188 void (*kernel)(KernelArgs...),
11189 Params&&... args) {
11190 return [&](KernelArgs... convertedArgs) {
11191 void* pArgs[] = {&convertedArgs...};
11192 return ::hipLaunchKernelExC(config, reinterpret_cast<void*>(kernel), pArgs);
11193 }(std::forward<Params>(args)...);
11194}
11200#endif // __cplusplus
11201
11202#ifdef __GNUC__
11203#pragma GCC visibility pop
11204#endif
11205
11206
11207#elif !defined(__HIP_PLATFORM_AMD__) && defined(__HIP_PLATFORM_NVIDIA__)
11208#include "hip/nvidia_detail/nvidia_hip_runtime_api.h"
11209#else
11210#error ("Must define exactly one of __HIP_PLATFORM_AMD__ or __HIP_PLATFORM_NVIDIA__");
11211#endif
11212
11213
11225#if defined(__cplusplus) && !defined(__HIP_DISABLE_CPP_FUNCTIONS__)
11226template <class T> static inline hipError_t hipMalloc(T** devPtr, size_t size) {
11227 return hipMalloc((void**)devPtr, size);
11228}
11240template <class T>
11241static inline hipError_t hipMallocPitch(T** devPtr, size_t* pitch, size_t width, size_t height) {
11242 return hipMallocPitch((void**)devPtr, pitch, width, height);
11243}
11256template <class T>
11257static inline hipError_t hipHostMalloc(T** ptr, size_t size,
11258 unsigned int flags = hipHostMallocDefault) {
11259 return hipHostMalloc((void**)ptr, size, flags);
11260}
11273template <class T> static inline hipError_t hipHostAlloc(T** ptr, size_t size,
11274 unsigned int flags = hipHostAllocDefault) {
11275 return hipHostAlloc((void**)ptr, size, flags);
11276}
11291template <class T>
11292static inline hipError_t hipMallocManaged(T** devPtr, size_t size,
11293 unsigned int flags = hipMemAttachGlobal) {
11294 return hipMallocManaged((void**)devPtr, size, flags);
11295}
11296
11297#endif
11298#endif
11299// doxygen end HIP API
11303#include <hip/amd_detail/amd_hip_runtime_pt_api.h>
11304
11305#if USE_PROF_API
11306#include <hip/amd_detail/hip_prof_str.h>
11307#endif
hipError_t err
Definition hip_runtime_api.h:11026
const struct texture< T, dim, readMode > & tex
Definition hip_runtime_api.h:10943
const struct texture< T, dim, readMode > const void size_t size
Definition hip_runtime_api.h:10944
const struct texture< T, dim, readMode > const void size_t int enum hipTextureReadMode readMode const struct texture< T, dim, readMode > const void const struct hipChannelFormatDesc size_t int enum hipTextureReadMode readMode const struct texture< T, dim, readMode > const void size_t size_t size_t pitch
Definition hip_runtime_api.h:10985
hipArray_t levelArray
Definition hip_runtime_api.h:11062
const struct texture< T, dim, readMode > const void size_t int dim
Definition hip_runtime_api.h:10961
readMode hipMipmappedArray_const_t mipmappedArray
Definition hip_runtime_api.h:11060
const struct texture< T, dim, readMode > const void size_t int enum hipTextureReadMode readMode const struct texture< T, dim, readMode > const void const struct hipChannelFormatDesc size_t int enum hipTextureReadMode readMode const struct texture< T, dim, readMode > const void size_t size_t height
Definition hip_runtime_api.h:10985
const struct texture< T, dim, readMode > const void * devPtr
Definition hip_runtime_api.h:10944
const struct texture< T, dim, readMode > const void size_t int enum hipTextureReadMode readMode const struct texture< T, dim, readMode > const void const struct hipChannelFormatDesc & desc
Definition hip_runtime_api.h:10964
readMode hipArray_const_t array
Definition hip_runtime_api.h:11024
const struct texture< T, dim, readMode > const void size_t int enum hipTextureReadMode readMode const struct texture< T, dim, readMode > const void const struct hipChannelFormatDesc size_t int enum hipTextureReadMode readMode const struct texture< T, dim, readMode > const void size_t width
Definition hip_runtime_api.h:10985
const char * hipApiName(uint32_t id)
Returns HIP API name by ID.
const char * hipKernelNameRef(const hipFunction_t f)
Returns kernel name reference by function name.
const char * hipKernelNameRefByPtr(const void *hostFunction, hipStream_t stream)
Retrives kernel for a given host pointer, unless stated otherwise.
int hipGetStreamDeviceId(hipStream_t stream)
Returns device ID on the stream.
hipError_t hipSetupArgument(const void *arg, size_t size, size_t offset)
Set a kernel argument.
hipError_t __hipPopCallConfiguration(dim3 *gridDim, dim3 *blockDim, size_t *sharedMem, hipStream_t *stream)
Pop configuration of a kernel launch.
hipError_t hipLaunchHostFunc(hipStream_t stream, hipHostFn_t fn, void *userData)
Enqueues a host function call in a stream.
hipError_t hipLaunchKernel(const void *function_address, dim3 numBlocks, dim3 dimBlocks, void **args, size_t sharedMemBytes, hipStream_t stream)
C compliant kernel launch API.
hipError_t hipExtLaunchKernel(const void *function_address, dim3 numBlocks, dim3 dimBlocks, void **args, size_t sharedMemBytes, hipStream_t stream, hipEvent_t startEvent, hipEvent_t stopEvent, int flags)
Launches kernel from the pointer address, with arguments and shared memory on stream.
hipError_t __hipPushCallConfiguration(dim3 gridDim, dim3 blockDim, size_t sharedMem, hipStream_t stream)
Push configuration of a kernel launch.
hipError_t hipLaunchByPtr(const void *func)
Launch a kernel.
hipError_t hipDrvMemcpy2DUnaligned(const hip_Memcpy2D *pCopy)
hipError_t hipConfigureCall(dim3 gridDim, dim3 blockDim, size_t sharedMem, hipStream_t stream)
Configure a kernel launch.
hipError_t hipCtxGetFlags(unsigned int *flags)
Return flags used for creating default context [Deprecated].
hipError_t hipCtxGetApiVersion(hipCtx_t ctx, unsigned int *apiVersion)
Returns the approximate HIP api version.
hipError_t hipCtxPopCurrent(hipCtx_t *ctx)
Pop the current/default context and return the popped context [Deprecated].
hipError_t hipCtxGetSharedMemConfig(hipSharedMemConfig *pConfig)
Get Shared memory bank configuration [Deprecated].
hipError_t hipDevicePrimaryCtxSetFlags(hipDevice_t dev, unsigned int flags)
Set flags for the primary context [Deprecated].
hipError_t hipDevicePrimaryCtxGetState(hipDevice_t dev, unsigned int *flags, int *active)
Get the state of the primary context [Deprecated].
hipError_t hipCtxGetCurrent(hipCtx_t *ctx)
Get the handle of the current/ default context [Deprecated].
hipError_t hipDevicePrimaryCtxRelease(hipDevice_t dev)
Release the primary context on the GPU.
hipError_t hipCtxSetCacheConfig(hipFuncCache_t cacheConfig)
Set L1/Shared cache partition [Deprecated].
hipError_t hipCtxSetCurrent(hipCtx_t ctx)
Set the passed context as current/default [Deprecated].
hipError_t hipCtxEnablePeerAccess(hipCtx_t peerCtx, unsigned int flags)
Enables direct access to memory allocations in a peer context [Deprecated].
hipError_t hipCtxGetDevice(hipDevice_t *device)
Get the handle of the device associated with current/default context [Deprecated].
hipError_t hipCtxDestroy(hipCtx_t ctx)
Destroy a HIP context [Deprecated].
hipError_t hipCtxPushCurrent(hipCtx_t ctx)
Push the context to be set as current/ default context [Deprecated].
hipError_t hipCtxGetCacheConfig(hipFuncCache_t *cacheConfig)
Get Cache configuration for a specific function [Deprecated].
hipError_t hipCtxCreate(hipCtx_t *ctx, unsigned int flags, hipDevice_t device)
Create a context and set it as current/default context.
hipError_t hipDevicePrimaryCtxRetain(hipCtx_t *pctx, hipDevice_t dev)
Retain the primary context on the GPU [Deprecated].
hipError_t hipDevicePrimaryCtxReset(hipDevice_t dev)
Resets the primary context on the GPU [Deprecated].
hipError_t hipCtxSynchronize(void)
Blocks until the default context has completed all preceding requested tasks [Deprecated].
hipError_t hipCtxSetSharedMemConfig(hipSharedMemConfig config)
Set Shared memory bank configuration [Deprecated].
hipError_t hipCtxDisablePeerAccess(hipCtx_t peerCtx)
Disable direct access from current context's virtual address space to memory allocations physically l...
hipError_t hipInitDevice(int device, unsigned int deviceFlags, unsigned int flags)
Initialize the specified device to be used for GPU executions.
hipError_t hipGetDeviceFlags(unsigned int *flags)
Gets the flags set for current device.
hipError_t hipIpcGetEventHandle(hipIpcEventHandle_t *handle, hipEvent_t event)
Gets an opaque interprocess handle for an event.
hipError_t hipDeviceGetDefaultMemPool(hipMemPool_t *mem_pool, int device)
Returns the default memory pool of the specified device.
hipError_t hipDeviceGetSharedMemConfig(hipSharedMemConfig *pConfig)
Returns bank width of shared memory for current device.
hipError_t hipDeviceSetMemPool(int device, hipMemPool_t mem_pool)
Sets the current memory pool of a device.
hipError_t hipIpcOpenMemHandle(void **devPtr, hipIpcMemHandle_t handle, unsigned int flags)
Opens an interprocess memory handle exported from another process and returns a device pointer usable...
hipError_t hipDeviceGetCacheConfig(hipFuncCache_t *cacheConfig)
Get Cache configuration for a specific Device.
hipError_t hipSetDevice(int deviceId)
Set default device to be used for subsequent hip API calls from this thread.
hipError_t hipDeviceFlushGPUDirectRDMAWrites(enum hipFlushGPUDirectRDMAWritesTarget target, enum hipFlushGPUDirectRDMAWritesScope scope)
Blocks until remote writes are visible to the specified scope.
hipError_t hipExtGetLinkTypeAndHopCount(int device1, int device2, uint32_t *linktype, uint32_t *hopcount)
Returns the link type and hop count between two devices.
hipError_t hipDeviceGetTexture1DLinearMaxWidth(size_t *max_width, const hipChannelFormatDesc *desc, int device)
Gets the maximum width for 1D linear textures on the specified device.
hipError_t hipSetDeviceFlags(unsigned flags)
The current device behavior is changed according to the flags passed.
hipError_t hipDeviceGetAttribute(int *pi, hipDeviceAttribute_t attr, int deviceId)
Query for a specific device attribute.
hipError_t hipGetDevice(int *deviceId)
Return the default device id for the calling host thread.
hipError_t hipGetDeviceCount(int *count)
Return number of compute-capable devices.
hipError_t hipDeviceGetMemPool(hipMemPool_t *mem_pool, int device)
Gets the current memory pool for the specified device.
hipError_t hipDeviceReset(void)
The state of current device is discarded and updated to a fresh state.
hipError_t hipDeviceGetLimit(size_t *pValue, enum hipLimit_t limit)
Gets resource limits of current device.
hipError_t hipDeviceSetSharedMemConfig(hipSharedMemConfig config)
The bank width of shared memory on current device is set.
hipError_t hipDeviceSetLimit(enum hipLimit_t limit, size_t value)
Sets resource limits of current device.
hipError_t hipDeviceSetCacheConfig(hipFuncCache_t cacheConfig)
Set L1/Shared cache partition.
hipError_t hipIpcCloseMemHandle(void *devPtr)
Close memory mapped with hipIpcOpenMemHandle.
hipError_t hipSetValidDevices(int *device_arr, int len)
Set a list of devices that can be used.
hipError_t hipGetDevicePropertiesR0600(hipDeviceProp_tR0600 *prop, int deviceId)
hipError_t hipIpcOpenEventHandle(hipEvent_t *event, hipIpcEventHandle_t handle)
Opens an interprocess event handles.
hipError_t hipDeviceSynchronize(void)
Waits on all active streams on current device.
hipError_t hipChooseDeviceR0600(int *device, const hipDeviceProp_tR0600 *prop)
hipError_t hipIpcGetMemHandle(hipIpcMemHandle_t *handle, void *devPtr)
Gets an interprocess memory handle for an existing device memory allocation.
hipError_t hipInit(unsigned int flags)
Explicitly initializes the HIP runtime.
hipError_t hipDeviceComputeCapability(int *major, int *minor, hipDevice_t device)
Returns the compute capability of the device.
hipError_t hipDeviceGetName(char *name, int len, hipDevice_t device)
Returns an identifer string for the device.
hipError_t hipDeviceGetByPCIBusId(int *device, const char *pciBusId)
Returns a handle to a compute device.
hipError_t hipDeviceGetUuid(hipUUID *uuid, hipDevice_t device)
Returns an UUID for the device.[BETA].
hipError_t hipDeviceTotalMem(size_t *bytes, hipDevice_t device)
Returns the total amount of memory on the device.
hipError_t hipDeviceGetPCIBusId(char *pciBusId, int len, int device)
Returns a PCI Bus Id string for the device, overloaded to take int device ID.
hipError_t hipDeviceGet(hipDevice_t *device, int ordinal)
Returns a handle to a compute device.
hipError_t hipDeviceGetLuid(char *luid, unsigned int *deviceNodeMask, hipDevice_t device)
Returns an LUID and device node mask for the device.
hipError_t hipRuntimeGetVersion(int *runtimeVersion)
Returns the approximate HIP Runtime version.
hipError_t hipDeviceGetP2PAttribute(int *value, hipDeviceP2PAttr attr, int srcDevice, int dstDevice)
Returns a value for attribute of link between two devices.
hipError_t hipDriverGetVersion(int *driverVersion)
Returns the approximate HIP driver version.
hipMemcpyKind
Definition driver_types.h:357
hipPointer_attribute
Definition driver_types.h:631
struct hipArray * hipArray_t
Definition driver_types.h:59
void * hipDeviceptr_t
Definition driver_types.h:30
hipFunction_attribute
Definition driver_types.h:604
const struct hipArray * hipArray_const_t
Definition driver_types.h:60
hipArray_Format
Definition driver_types.h:64
hipResourceType
Definition driver_types.h:143
@ hipMemcpyDeviceToHost
Device-to-Host Copy.
Definition driver_types.h:360
@ hipMemcpyHostToDevice
Host-to-Device Copy.
Definition driver_types.h:359
Definition driver_types.h:87
Definition driver_types.h:77
Definition driver_types.h:408
Definition driver_types.h:297
Definition driver_types.h:342
Definition driver_types.h:175
Definition driver_types.h:99
Definition driver_types.h:43
Definition driver_types.h:378
Definition driver_types.h:450
Definition driver_types.h:533
Definition driver_types.h:395
Definition driver_types.h:541
Definition driver_types.h:487
Definition driver_types.h:121
Definition driver_types.h:369
Definition driver_types.h:270
Definition driver_types.h:329
const char * hipGetErrorString(hipError_t hipError)
Return handy text string message to explain the error which occurred.
hipError_t hipPeekAtLastError(void)
Return last error returned by any HIP runtime API call.
hipError_t hipDrvGetErrorString(hipError_t hipError, const char **errorString)
Return handy text string message to explain the error which occurred.
hipError_t hipGetLastError(void)
Return last error returned by any HIP runtime API call and resets the stored error code to hipSuccess...
hipError_t hipExtGetLastError(void)
Return last error returned by any HIP runtime API call and resets the stored error code to hipSuccess...
hipError_t hipDrvGetErrorName(hipError_t hipError, const char **errorString)
Return hip error as text string form.
const char * hipGetErrorName(hipError_t hip_error)
Return hip error as text string form.
hipError_t hipEventSynchronize(hipEvent_t event)
Wait for an event to complete.
hipError_t hipEventQuery(hipEvent_t event)
Query event status.
hipError_t hipEventCreate(hipEvent_t *event)
hipError_t hipEventDestroy(hipEvent_t event)
Destroy the specified event.
hipError_t hipEventRecordWithFlags(hipEvent_t event, hipStream_t stream, unsigned int flags)
Record an event in the specified stream.
hipError_t hipEventRecord(hipEvent_t event, hipStream_t stream=NULL)
Record an event in the specified stream.
hipError_t hipEventElapsedTime(float *ms, hipEvent_t start, hipEvent_t stop)
Return the elapsed time between two events.
hipError_t hipEventCreateWithFlags(hipEvent_t *event, unsigned flags)
Create an event with the specified flags.
hipError_t hipDeviceGetExecutionCtx(hipExecutionCtx_t *ctx, int device)
Returns the default execution context for a device.
hipError_t hipExecutionCtxStreamCreate(hipStream_t *stream, hipExecutionCtx_t greenctx, unsigned int flags, int priority)
Creates a stream on an execution context with specified flags and priority.
hipError_t hipGreenCtxCreate(hipExecutionCtx_t *ctx, hipDevResourceDesc_t desc, int device, unsigned int flags)
Creates a green context from a resource descriptor.
hipError_t hipExecutionCtxGetDevice(int *device, hipExecutionCtx_t ctx)
Returns the device associated with an execution context.
hipError_t hipExecutionCtxWaitEvent(hipExecutionCtx_t ctx, hipEvent_t event)
Makes an execution context wait on an event.
hipError_t hipExecutionCtxSynchronize(hipExecutionCtx_t ctx)
Blocks until all work on an execution context has completed.
hipError_t hipDevResourceGenerateDesc(hipDevResourceDesc_t *phDesc, hipDevResource *resources, unsigned int nbResources)
Generates a resource descriptor from one or more device resources.
hipError_t hipExecutionCtxRecordEvent(hipExecutionCtx_t ctx, hipEvent_t event)
Records an event on an execution context.
hipError_t hipExecutionCtxDestroy(hipExecutionCtx_t ctx)
Destroys an execution context.
hipError_t hipDevSmResourceSplitByCount(hipDevResource *result, unsigned int *nbGroups, const hipDevResource *input, hipDevResource *remainder, unsigned int flags, unsigned int minCount)
Splits SM resources into groups containing the specified number of SMs.
hipError_t hipDeviceGetDevResource(hipDevice_t device, hipDevResource *resource, hipDevResourceType type)
Gets device resource of a given type for a device.
hipError_t hipExecutionCtxGetDevResource(hipExecutionCtx_t ctx, hipDevResource *resource, hipDevResourceType type)
Returns the device resource of a given type for an execution context.
hipError_t hipStreamGetDevResource(hipStream_t hStream, hipDevResource *resource, hipDevResourceType type)
Returns the device resource of a given type for a stream.
hipError_t hipDevSmResourceSplit(hipDevResource *result, unsigned int nbGroups, const hipDevResource *input, hipDevResource *remainder, unsigned int flags, hipDevSmResourceGroupParams *groupParams)
Splits SM resources into structured groups.
hipError_t hipExecutionCtxGetId(hipExecutionCtx_t ctx, unsigned long long *ctxId)
Returns a unique identifier for an execution context.
hipError_t hipFuncGetAttributes(struct hipFuncAttributes *attr, const void *func)
Find out attributes for a given function.
hipError_t hipLaunchKernelExC(const hipLaunchConfig_t *config, const void *fPtr, void **args)
Launches a HIP kernel using a generic function pointer and the specified configuration.
hipError_t hipExtLaunchMultiKernelMultiDevice(hipLaunchParams *launchParamsList, int numDevices, unsigned int flags)
Launches kernels on multiple devices and guarantees all specified kernels are dispatched on respectiv...
hipError_t hipKernelGetFunction(hipFunction_t *pFunc, hipKernel_t kernel)
Function will be extracted for specific kernel.
hipError_t hipModuleLaunchKernel(hipFunction_t f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, hipStream_t stream, void **kernelParams, void **extra)
launches kernel f with launch parameters and shared memory on stream with arguments passed to kernelp...
hipError_t hipFuncSetSharedMemConfig(const void *func, hipSharedMemConfig config)
Set shared memory configuation for a specific function.
hipError_t hipFuncGetAttribute(int *value, hipFunction_attribute attrib, hipFunction_t hfunc)
Find out a specific attribute for a given function.
hipError_t hipKernelSetAttributeForDevice(hipKernel_t kernel, hipFuncAttribute attr, int value, int device)
Set a device-wide attribute for a kernel on a specific device.
hipError_t hipFuncSetAttribute(const void *func, hipFuncAttribute attr, int value)
Set attribute for a specific function.
hipError_t hipDrvLaunchKernelEx(const HIP_LAUNCH_CONFIG *config, hipFunction_t f, void **params, void **extra)
Launches a HIP kernel using the driver API with the specified configuration.
hipError_t hipKernelSetAttribute(hipFunction_attribute attrib, int value, hipKernel_t kernel, hipDevice_t dev)
Set attribute for a specific kernel.
hipError_t hipFuncSetCacheConfig(const void *func, hipFuncCache_t config)
Set Cache configuration for a specific function.
hipError_t hipDestroyExternalMemory(hipExternalMemory_t extMem)
Destroys an external memory object.
hipError_t hipImportExternalSemaphore(hipExternalSemaphore_t *extSem_out, const hipExternalSemaphoreHandleDesc *semHandleDesc)
Imports an external semaphore.
hipError_t hipImportExternalMemory(hipExternalMemory_t *extMem_out, const hipExternalMemoryHandleDesc *memHandleDesc)
Imports an external memory object.
hipError_t hipDestroyExternalSemaphore(hipExternalSemaphore_t extSem)
Destroys an external semaphore object and releases any references to the underlying resource....
hipError_t hipWaitExternalSemaphoresAsync(const hipExternalSemaphore_t *extSemArray, const hipExternalSemaphoreWaitParams *paramsArray, unsigned int numExtSems, hipStream_t stream)
Waits on a set of external semaphore objects.
hipError_t hipSignalExternalSemaphoresAsync(const hipExternalSemaphore_t *extSemArray, const hipExternalSemaphoreSignalParams *paramsArray, unsigned int numExtSems, hipStream_t stream)
Signals a set of external semaphore objects.
hipError_t hipExternalMemoryGetMappedMipmappedArray(hipMipmappedArray_t *mipmap, hipExternalMemory_t extMem, const hipExternalMemoryMipmappedArrayDesc *mipmapDesc)
Maps a mipmapped array onto an external memory object.
hipError_t hipExternalMemoryGetMappedBuffer(void **devPtr, hipExternalMemory_t extMem, const hipExternalMemoryBufferDesc *bufferDesc)
Maps a buffer onto an imported memory object.
hipStreamBatchMemOpType operation
Definition hip_runtime_api.h:1156
unsigned hasSharedInt64Atomics
64-bit integer atomics for shared memory.
Definition hip_runtime_api.h:63
int ECCEnabled
Device has ECC support enabled.
Definition hip_runtime_api.h:320
hipDeviceptr_t address
Definition hip_runtime_api.h:1167
int ipcEventSupported
Device supports IPC events.
Definition hip_runtime_api.h:374
hipGraphNodeType type
Definition hip_runtime_api.h:2140
int computePreemptionSupported
Is compute preemption supported on the device.
Definition hip_runtime_api.h:346
unsigned int flags
Definition hip_runtime_api.h:1496
unsigned int flags
Definition hip_runtime_api.h:1535
int maxTexture1DLinear
Maximum size for 1D textures bound to linear memory.
Definition hip_runtime_api.h:299
int reserved0[3]
Definition hip_runtime_api.h:2141
int priority
Definition hip_runtime_api.h:1803
unsigned int gridDimX
Width(X) of grid in blocks.
Definition hip_runtime_api.h:1465
unsigned int blockDimX
X dimension of each thread block.
Definition hip_runtime_api.h:1468
void * win32HandleMetaData
Metadata for Win32 handles.
Definition hip_runtime_api.h:1989
int timelineSemaphoreInteropSupported
Indicates external timeline semaphore support.
Definition hip_runtime_api.h:364
int device
Definition hip_runtime_api.h:435
hipMemAllocationType type
Memory allocation type.
Definition hip_runtime_api.h:1983
int pciBusID
PCI Bus ID.
Definition hip_runtime_api.h:321
unsigned int flags
flags for future use, must be zero now.
Definition hip_runtime_api.h:2094
unsigned hasSharedInt32Atomics
32-bit integer atomics for shared memory.
Definition hip_runtime_api.h:57
int maxTexture1D
Maximum number of elements in 1D images.
Definition hip_runtime_api.h:297
hipAccessProperty hitProp
hipAccessProperty set for hit
Definition hip_runtime_api.h:1689
void * hostPointer
Definition hip_runtime_api.h:437
hipDeviceptr_t address
Definition hip_runtime_api.h:1157
hipAccessProperty missProp
hipAccessProperty set for miss
Definition hip_runtime_api.h:1691
int memoryBusWidth
Global memory bus width in bits.
Definition hip_runtime_api.h:328
int maxTexture2DMipmap[2]
Maximum number of elements in 2D array mipmap of images.
Definition hip_runtime_api.h:301
hipDevWorkqueueConfigScope sharingScope
Definition hip_runtime_api.h:787
int clockRate
Max clock frequency of the multiProcessors in khz.
Definition hip_runtime_api.h:274
hipExtent extent
Definition hip_runtime_api.h:1508
size_t maxSize
Maximum pool size. When set to 0, defaults to a system dependent value.
Definition hip_runtime_api.h:1394
char pad[64]
64 byte padding
Definition hip_runtime_api.h:1798
unsigned int flags
Definition hip_runtime_api.h:781
unsigned int flags
Definition hip_runtime_api.h:810
unsigned hasFloatAtomicAdd
32-bit float atomic add in global and shared memory.
Definition hip_runtime_api.h:59
int maxThreadsPerMultiProcessor
Maximum resident threads per multi-processor.
Definition hip_runtime_api.h:331
int l2CacheSize
L2 cache size.
Definition hip_runtime_api.h:329
int deferredMappingHipArraySupported
Definition hip_runtime_api.h:372
size_t size
Definition hip_runtime_api.h:2243
int asyncEngineCount
Number of async engines.
Definition hip_runtime_api.h:325
void * dst
Definition hip_runtime_api.h:1656
int accessPolicyMaxWindowSize
Max value of access policy window.
Definition hip_runtime_api.h:358
enum hipMemoryType type
Definition hip_runtime_api.h:434
unsigned int flags
Definition hip_runtime_api.h:1177
size_t totalConstMem
Definition hip_runtime_api.h:275
int memoryPoolsSupported
Indicates if device supports hipMallocAsync and hipMemPool APIs.
Definition hip_runtime_api.h:365
dim3 blockDim
Block dimensions.
Definition hip_runtime_api.h:2215
dim3 gridDim
Definition hip_runtime_api.h:1651
const hipExternalSemaphoreSignalParams * paramsArray
Total number of handles and parameters contained in extSemArray and paramsArray.
Definition hip_runtime_api.h:2004
void * address
Base address (must be cache-line aligned)
Definition hip_runtime_api.h:1747
struct hipDevResource_st * nextResource
Definition hip_runtime_api.h:803
hipHostFn_t fn
Definition hip_runtime_api.h:1644
int unifiedFunctionPointers
Indicates device supports unified function pointers.
Definition hip_runtime_api.h:376
unsigned hasDoubles
Double-precision floating point.
Definition hip_runtime_api.h:66
int maxTexture2DGather[2]
Maximum 2D tex dimensions if gather has to be performed.
Definition hip_runtime_api.h:303
hipStreamBatchMemOpType operation
Definition hip_runtime_api.h:1154
int cacheModeCA
Definition hip_runtime_api.h:851
size_t memPitch
Definition hip_runtime_api.h:269
hipExtDynDataPrefetchRegion regions[HIP_EXT_DYN_DATA_PREFETCH_MAX_REGIONS]
Prefetch regions.
Definition hip_runtime_api.h:1773
hipMemAccessFlags flags
Accessibility flags to set.
Definition hip_runtime_api.h:1354
unsigned int numRegions
Number of valid regions (1-max)
Definition hip_runtime_api.h:1771
hipGraph_t graph
Definition hip_runtime_api.h:2111
int gpuDirectRDMAWritesOrdering
value of hipGPUDirectRDMAWritesOrdering
Definition hip_runtime_api.h:369
unsigned int value
Definition hip_runtime_api.h:1660
unsigned hasWarpVote
Warp vote instructions (__any, __all).
Definition hip_runtime_api.h:69
unsigned int smCount
Definition hip_runtime_api.h:778
hipUUID uuid
UUID of a device.
Definition hip_runtime_api.h:262
unsigned int numLevels
Definition hip_runtime_api.h:1510
unsigned int sharedMemBytes
Definition hip_runtime_api.h:1653
union hipArrayMapInfo::@38 subresource
unsigned int gridDimZ
Grid depth in blocks.
Definition hip_runtime_api.h:2228
unsigned char remote
Definition hip_runtime_api.h:1700
size_t sharedMemPerBlock
Size of shared memory per block (in bytes).
Definition hip_runtime_api.h:266
float hitRatio
hitRatio specifies percentage of lines assigned hitProp
Definition hip_runtime_api.h:1690
unsigned int gpuDirectRDMAFlushWritesOptions
Definition hip_runtime_api.h:367
unsigned hasWarpShuffle
Warp shuffle operations. (__shfl_*).
Definition hip_runtime_api.h:71
size_t surfaceAlignment
Alignment requirement for surface.
Definition hip_runtime_api.h:318
size_t width
Width of each row in bytes (must be a multiple of cache line size)
Definition hip_runtime_api.h:1749
int reserved[63]
CUDA Reserved.
Definition hip_runtime_api.h:377
int maxTexture2DLayered[3]
Maximum number of elements in 2D array images.
Definition hip_runtime_api.h:309
unsigned char reserved[56]
Reserved for future use, must be 0.
Definition hip_runtime_api.h:1395
hipArraySparseSubresourceType subresourceType
Sparse subresource type.
Definition hip_runtime_api.h:2066
int streamPrioritiesSupported
Device supports stream priority.
Definition hip_runtime_api.h:332
unsigned char to_port
Currently no node types define non-zero ports. This field must be set to zero.
Definition hip_runtime_api.h:2193
unsigned int numExtSems
Definition hip_runtime_api.h:2018
hipGraphInstantiateResult result_out
Definition hip_runtime_api.h:1973
unsigned int wqConcurrencyLimit
Definition hip_runtime_api.h:786
hipFunction_t function
Kernel to launch.
Definition hip_runtime_api.h:1464
unsigned int sharedMemBytes
Dynamic shared-memory size in bytes per block.
Definition hip_runtime_api.h:2232
const hipExtDynDataPrefetchConfig * dynDataPrefetch
Value of launch attribute hipLaunchAttributeExtDynDataPrefetch.
Definition hip_runtime_api.h:1832
dim3 blockDim
Definition hip_runtime_api.h:1648
int cooperativeMultiDeviceLaunch
Definition hip_runtime_api.h:350
int hostRegisterSupported
Device supports hipHostRegister.
Definition hip_runtime_api.h:360
unsigned int flags
Definition hip_runtime_api.h:1509
dim3 gridDim
Grid dimensions.
Definition hip_runtime_api.h:2214
unsigned int numAttrs
Number of attributes.
Definition hip_runtime_api.h:2219
unsigned int smCoscheduledAlignment
Definition hip_runtime_api.h:780
hipDeviceptr_t alias
Not valid for AMD backend. Initial value is unimportant.
Definition hip_runtime_api.h:1163
int binaryVersion
Definition hip_runtime_api.h:850
unsigned int flags
Definition hip_runtime_api.h:1553
void * userData
Definition hip_runtime_api.h:1645
hipLaunchMemSyncDomain memSyncDomain
Value of launch attribute hipLaunchAttributeMemSyncDomain.
Definition hip_runtime_api.h:1811
size_t alignment
Definition hip_runtime_api.h:2242
int pageableMemoryAccess
Definition hip_runtime_api.h:342
char name[256]
Device name.
Definition hip_runtime_api.h:261
unsigned char reserved[64]
Definition hip_runtime_api.h:1401
size_t textureAlignment
Alignment requirement for textures.
Definition hip_runtime_api.h:286
hipStreamBatchMemOpType operation
Definition hip_runtime_api.h:1176
unsigned int flags
Definition hip_runtime_api.h:1181
hipExternalSemaphoreHandleType type
Definition hip_runtime_api.h:1526
int globalL1CacheSupported
Indicates globals are cached in L1.
Definition hip_runtime_api.h:333
size_t constSizeBytes
Definition hip_runtime_api.h:852
const hipMemAccessDesc * accessDescs
The number of memory access descriptors.
Definition hip_runtime_api.h:1667
int hostNativeAtomicSupported
Link between host and device supports native atomics.
Definition hip_runtime_api.h:340
hipResourceType resourceType
Resource type.
Definition hip_runtime_api.h:2061
int maxSurfaceCubemapLayered[2]
Maximum cubemap layered surface size.
Definition hip_runtime_api.h:317
int isManaged
Definition hip_runtime_api.h:438
unsigned long long size
Definition hip_runtime_api.h:1495
int maxTextureCubemapLayered[2]
Maximum cubemaps layered texture dims.
Definition hip_runtime_api.h:310
size_t sharedMemPerBlockOptin
Per device m ax shared mem per block usable by special opt in.
Definition hip_runtime_api.h:352
size_t sharedMemPerMultiprocessor
Amount of shared memory available per multiprocessor.
Definition hip_runtime_api.h:335
int singleToDoublePrecisionPerfRatio
Deprecated. CUDA only.
Definition hip_runtime_api.h:341
hipMemOperationType memOperationType
Memory operation type.
Definition hip_runtime_api.h:2087
unsigned int blockDimY
Thread block dimension in Y.
Definition hip_runtime_api.h:2230
int maxSurface2D[2]
Maximum 2D surface size.
Definition hip_runtime_api.h:312
int memoryClockRate
Max global memory clock frequency in khz.
Definition hip_runtime_api.h:327
hipEvent_t event
Event to wait on.
Definition hip_runtime_api.h:2119
int maxTexture2DLinear[3]
Maximum 2D tex dimensions if tex are bound to pitched memory.
Definition hip_runtime_api.h:302
int sparseHipArraySupported
Indicates if device supports sparse hip arrays.
Definition hip_runtime_api.h:361
unsigned int reserved[2]
Reserved for future use, must be zero now.
Definition hip_runtime_api.h:2095
unsigned int minSmPartitionSize
Definition hip_runtime_api.h:779
hipMemLocation location
Location on which the accessibility has to change.
Definition hip_runtime_api.h:1353
int clockInstructionRate
Definition hip_runtime_api.h:384
hipMemLocation location
Location where allocations should reside.
Definition hip_runtime_api.h:1389
int localL1CacheSupported
Locals are cahced in L1.
Definition hip_runtime_api.h:334
int regsPerMultiprocessor
registers available per multiprocessor
Definition hip_runtime_api.h:336
int regsPerBlock
Registers per block.
Definition hip_runtime_api.h:267
hipStream_t stream
Stream identifier.
Definition hip_runtime_api.h:2217
size_t bytesize
The size of the requested allocation in bytes.
Definition hip_runtime_api.h:1670
int reserved[3]
Must be zero.
Definition hip_runtime_api.h:2103
unsigned int preferredCoscheduledSmCount
Definition hip_runtime_api.h:809
const hipExternalSemaphoreWaitParams * paramsArray
Total number of handles and parameters contained in extSemArray and paramsArray.
Definition hip_runtime_api.h:2016
int maxTexture2D[2]
Maximum dimensions (width, height) of 2D images, in image elements.
Definition hip_runtime_api.h:300
int preferredShmemCarveout
Definition hip_runtime_api.h:857
int cooperativeLaunch
HIP device supports cooperative launch.
Definition hip_runtime_api.h:349
int maxTexture3D[3]
Definition hip_runtime_api.h:304
hipMemAllocationHandleType handleTypes
Handle types that will be supported by allocations from the pool.
Definition hip_runtime_api.h:1388
int directManagedMemAccessFromHost
Definition hip_runtime_api.h:355
hipStream_t hStream
HIP stream identifier.
Definition hip_runtime_api.h:2233
hipStreamBatchMemOpParams * paramArray
Definition hip_runtime_api.h:1216
hipLaunchAttribute * attrs
Attribute list.
Definition hip_runtime_api.h:2234
int cooperativeMultiDeviceUnmatchedFunc
Definition hip_runtime_api.h:389
hipMemAllocationType allocType
Allocation type. Currently must be specified as hipMemAllocationTypePinned.
Definition hip_runtime_api.h:1386
int deviceOverlap
Deprecated. Use asyncEngineCount instead.
Definition hip_runtime_api.h:288
int pageableMemoryAccessUsesHostPageTables
Definition hip_runtime_api.h:353
int cooperative
Definition hip_runtime_api.h:1801
hipExternalSemaphore_t * extSemArray
< Array containing external semaphore handles.
Definition hip_runtime_api.h:2014
void ** kernelParams
Definition hip_runtime_api.h:1652
unsigned int * hdpRegFlushCntl
Addres of HDP_REG_COHERENCY_FLUSH_CNTL register.
Definition hip_runtime_api.h:388
unsigned hasGlobalInt32Atomics
32-bit integer atomics for global memory.
Definition hip_runtime_api.h:55
hipAccessPolicyWindow accessPolicyWindow
Value of launch attribute hipLaunchAttributeAccessPolicyWindow.
Definition hip_runtime_api.h:1800
size_t dynamicSmemBytes
Dynamic shared-memory size per thread block.
Definition hip_runtime_api.h:2216
int maxThreadsDim[3]
Max number of threads in each dimension (XYZ) of a block.
Definition hip_runtime_api.h:272
unsigned hasGlobalFloatAtomicExch
32-bit float atomic exch for global memory.
Definition hip_runtime_api.h:56
int unifiedAddressing
Does device and host share unified address space.
Definition hip_runtime_api.h:326
unsigned hasDynamicParallelism
Dynamic parallelism.
Definition hip_runtime_api.h:81
hipStream_t hStream
Stream identifier.
Definition hip_runtime_api.h:1472
hipMemHandleType memHandleType
Memory handle type.
Definition hip_runtime_api.h:2088
unsigned char reserved[5]
These bytes are unused and must be zeroed.
Definition hip_runtime_api.h:2191
unsigned long long offset
Definition hip_runtime_api.h:1506
struct hipLaunchAttributeValue::@33 clusterDim
Specifies the desired cluster dimensions for a kernel launch.
size_t sharedMem
Shared memory.
Definition hip_runtime_api.h:1457
hipEvent_t event
The event to be recorded when node executes.
Definition hip_runtime_api.h:2126
int multiGpuBoardGroupID
Unique identifier for a group of devices on same multiboard GPU.
Definition hip_runtime_api.h:339
hipStream_t uploadStream
Definition hip_runtime_api.h:1975
int isMultiGpuBoard
1 if device is on a multi-GPU board, 0 if not.
Definition hip_runtime_api.h:338
hipMemPoolProps poolProps
Definition hip_runtime_api.h:1665
unsigned int smCount
Definition hip_runtime_api.h:807
size_t sharedSizeBytes
Definition hip_runtime_api.h:859
size_t accessDescCount
Definition hip_runtime_api.h:1668
int maxDynamicSharedSizeBytes
Definition hip_runtime_api.h:854
unsigned int blockDimY
Y dimension of each thread block.
Definition hip_runtime_api.h:1469
int canUseHostPointerForRegisteredMem
Definition hip_runtime_api.h:347
unsigned char type
This should be populated with a value from hipGraphDependencyType.
Definition hip_runtime_api.h:2194
unsigned hasSurfaceFuncs
Surface functions.
Definition hip_runtime_api.h:79
int maxTexture1DLayered[2]
Maximum number of elements in 1D array images.
Definition hip_runtime_api.h:308
hipGraphNode_t errNode_out
Definition hip_runtime_api.h:1971
int pciDomainID
PCI Domain ID.
Definition hip_runtime_api.h:323
hipExternalSemaphore_t * extSemArray
< Array containing external semaphore handles.
Definition hip_runtime_api.h:2002
unsigned int coscheduledSmCount
Definition hip_runtime_api.h:808
size_t maxSharedMemoryPerMultiProcessor
Maximum Shared Memory Per CU. HIP Only.
Definition hip_runtime_api.h:383
int device
Definition hip_runtime_api.h:785
hipMemLocation location
Memory location.
Definition hip_runtime_api.h:1988
hipExtDynDataPrefetchTemporal temporal
Cache retention policy for prefetched data.
Definition hip_runtime_api.h:1772
int maxTextureCubemap
Maximum cubemap texture dims.
Definition hip_runtime_api.h:307
unsigned int blockDimZ
Thread block dimension in Z.
Definition hip_runtime_api.h:2231
unsigned has3dGrid
Grid and group dims are 3D (rather than 2D).
Definition hip_runtime_api.h:80
unsigned int numExtSems
Definition hip_runtime_api.h:2006
hipExternalMemoryHandleType type
Definition hip_runtime_api.h:1486
int ptxVersion
Definition hip_runtime_api.h:858
void ** extra
Definition hip_runtime_api.h:1649
unsigned long long flags
Definition hip_runtime_api.h:1972
unsigned int count
Definition hip_runtime_api.h:1215
unsigned int numAttrs
Number of attributes.
Definition hip_runtime_api.h:2235
unsigned hasFunnelShift
Funnel two words into one with shift&mask caps.
Definition hip_runtime_api.h:72
int hipReserved[32]
Reserved for adding new entries for HIP/CUDA.
Definition hip_runtime_api.h:379
void * dptr
Returned device address of the allocation.
Definition hip_runtime_api.h:1671
hipDeviceptr_t alias
Not valid for AMD backend. Initial value is unimportant.
Definition hip_runtime_api.h:1173
unsigned int elementSize
Definition hip_runtime_api.h:1657
int cooperativeMultiDeviceUnmatchedGridDim
Definition hip_runtime_api.h:392
unsigned int flags
Definition hip_runtime_api.h:1574
int gpuDirectRDMASupported
Indicates device support of RDMA APIs.
Definition hip_runtime_api.h:366
union hipArrayMapInfo::@37 resource
unsigned int gridDimX
Grid width in blocks.
Definition hip_runtime_api.h:2226
int minor
Definition hip_runtime_api.h:281
char gcnArchName[256]
AMD GCN Arch Name. HIP Only.
Definition hip_runtime_api.h:382
void * devicePointer
Definition hip_runtime_api.h:436
char luid[8]
8-byte unique identifier. Only valid on windows
Definition hip_runtime_api.h:263
hipLaunchAttribute * attrs
Attributes list.
Definition hip_runtime_api.h:2218
int kernelExecTimeoutEnabled
Run time limit for kernels executed on the device.
Definition hip_runtime_api.h:293
void * func
Definition hip_runtime_api.h:1650
unsigned int memoryPoolSupportedHandleTypes
Bitmask of handle types support with mempool based IPC.
Definition hip_runtime_api.h:371
unsigned int * hdpMemFlushCntl
Addres of HDP_MEM_COHERENCY_FLUSH_CNTL register.
Definition hip_runtime_api.h:387
int concurrentManagedAccess
Definition hip_runtime_api.h:344
int integrated
APU vs dGPU.
Definition hip_runtime_api.h:294
int canMapHostMemory
Check whether HIP can map host memory.
Definition hip_runtime_api.h:295
unsigned hasThreadFenceSystem
__threadfence_system.
Definition hip_runtime_api.h:75
int flags
Must be zero.
Definition hip_runtime_api.h:2102
size_t reservedSharedMemPerBlock
Shared memory reserved by driver per block.
Definition hip_runtime_api.h:359
hipDevResourceType type
Definition hip_runtime_api.h:795
int maxSurfaceCubemap
Maximum cubemap surface size.
Definition hip_runtime_api.h:316
int maxSurface3D[3]
Maximum 3D surface size.
Definition hip_runtime_api.h:313
void ** args
Arguments.
Definition hip_runtime_api.h:1456
int asicRevision
Revision of the GPU in this device.
Definition hip_runtime_api.h:402
unsigned char from_port
Definition hip_runtime_api.h:2184
dim3 blockDim
Block dimensions.
Definition hip_runtime_api.h:1455
hipLaunchAttributeID id
Identifier of the launch attribute.
Definition hip_runtime_api.h:2202
unsigned int deviceBitMask
Device ordinal bit mask.
Definition hip_runtime_api.h:2093
unsigned int gridDimY
Height(Y) of grid in blocks.
Definition hip_runtime_api.h:1466
size_t totalGlobalMem
Size of global memory region (in bytes).
Definition hip_runtime_api.h:265
size_t width
Definition hip_runtime_api.h:1661
int cooperativeMultiDeviceUnmatchedBlockDim
Definition hip_runtime_api.h:395
unsigned int gridDimZ
Depth(Z) of grid in blocks.
Definition hip_runtime_api.h:1467
unsigned allocationFlags
Definition hip_runtime_api.h:439
hipStreamBatchMemOpType operation
Definition hip_runtime_api.h:1166
unsigned int sharedMemBytes
Shared memory.
Definition hip_runtime_api.h:1471
unsigned int flags
Definition hip_runtime_api.h:1217
int maxSurface1DLayered[2]
Maximum 1D layered surface size.
Definition hip_runtime_api.h:314
unsigned hasGlobalInt64Atomics
64-bit integer atomics for global memory.
Definition hip_runtime_api.h:62
int persistingL2CacheMaxSize
Device's max L2 persisting lines in bytes.
Definition hip_runtime_api.h:330
int maxSurface1D
Maximum 1D surface size.
Definition hip_runtime_api.h:311
unsigned int flags
Definition hip_runtime_api.h:1172
int concurrentKernels
Device can possibly execute multiple kernels concurrently.
Definition hip_runtime_api.h:319
int isLargeBar
1: if it is a large PCI bar device, else 0
Definition hip_runtime_api.h:401
int clusterLaunch
Device supports cluster launch.
Definition hip_runtime_api.h:375
int numRegs
Definition hip_runtime_api.h:856
int maxTexture1DMipmap
Maximum 1D mipmap texture size.
Definition hip_runtime_api.h:298
int multiProcessorCount
Definition hip_runtime_api.h:289
struct hipMemAllocationProp::@36 allocFlags
long long reserved2
Definition hip_runtime_api.h:2157
unsigned hasSyncThreadsExt
__syncthreads_count, syncthreads_and, syncthreads_or.
Definition hip_runtime_api.h:76
unsigned int flags
Definition hip_runtime_api.h:1502
unsigned char reserved[HIP_RESOURCE_ABI_BYTES]
Definition hip_runtime_api.h:791
int maxTexture3DAlt[3]
Maximum alternate 3D texture dims.
Definition hip_runtime_api.h:306
void * dptr
the pointer to be freed
Definition hip_runtime_api.h:2133
int maxGridSize[3]
Max grid dimensions (XYZ).
Definition hip_runtime_api.h:273
void * base_ptr
Starting address of the access policy window.
Definition hip_runtime_api.h:1688
int pciDeviceID
PCI Device ID.
Definition hip_runtime_api.h:322
int maxBlocksPerMultiProcessor
Max number of blocks on CU.
Definition hip_runtime_api.h:357
hipStreamBatchMemOpType operation
Definition hip_runtime_api.h:1180
int computeMode
Compute mode.
Definition hip_runtime_api.h:296
hipSynchronizationPolicy syncPolicy
Definition hip_runtime_api.h:1806
void * win32SecurityAttributes
Definition hip_runtime_api.h:1393
unsigned int blockDimZ
Z dimension of each thread block.
Definition hip_runtime_api.h:1470
size_t height
Number of rows to prefetch.
Definition hip_runtime_api.h:1750
hipClusterSchedulingPolicy clusterSchedulingPolicyPreference
Definition hip_runtime_api.h:1830
int maxSurface2DLayered[3]
Maximum 2D layared surface size.
Definition hip_runtime_api.h:315
int major
Definition hip_runtime_api.h:277
union hipArrayMapInfo::@39 memHandle
unsigned char default_
Definition hip_runtime_api.h:1699
hipCtx_t ctx
Definition hip_runtime_api.h:1214
dim3 gridDim
Grid dimensions.
Definition hip_runtime_api.h:1454
void * func
Device function symbol.
Definition hip_runtime_api.h:1453
hipMemcpy3DParms copyParams
Params set for the memory copy.
Definition hip_runtime_api.h:2104
unsigned int flags
Definition hip_runtime_api.h:1162
unsigned hasWarpBallot
Warp ballot instructions (__ballot).
Definition hip_runtime_api.h:70
unsigned int gridDimY
Grid height in blocks.
Definition hip_runtime_api.h:2227
unsigned long long offset
Definition hip_runtime_api.h:1500
int warpSize
Warp size.
Definition hip_runtime_api.h:268
int tccDriver
1:If device is Tesla device using TCC driver, else 0
Definition hip_runtime_api.h:324
unsigned int luidDeviceNodeMask
LUID node mask.
Definition hip_runtime_api.h:264
size_t pitch
Definition hip_runtime_api.h:1659
hipChannelFormatDesc formatDesc
Definition hip_runtime_api.h:1507
size_t height
Definition hip_runtime_api.h:1658
void ** kernelParams
Kernel parameters.
Definition hip_runtime_api.h:1473
int hostRegisterReadOnlySupported
Definition hip_runtime_api.h:362
size_t localSizeBytes
Definition hip_runtime_api.h:853
unsigned long long size
Definition hip_runtime_api.h:1501
unsigned int blockDimX
Thread block dimension in X.
Definition hip_runtime_api.h:2229
int cooperativeMultiDeviceUnmatchedSharedMem
Definition hip_runtime_api.h:398
unsigned long long offset
Offset within the memory.
Definition hip_runtime_api.h:2092
hipStream_t stream
Stream identifier.
Definition hip_runtime_api.h:1458
int maxThreadsPerBlock
Definition hip_runtime_api.h:855
size_t stride
Stride between row starts in bytes.
Definition hip_runtime_api.h:1748
int maxThreadsPerBlock
Max work items per work group or workgroup max size.
Definition hip_runtime_api.h:271
size_t num_bytes
Size in bytes of the window policy.
Definition hip_runtime_api.h:1692
hipDeviceArch_t arch
Architectural feature flags. New for HIP.
Definition hip_runtime_api.h:386
hipLaunchMemSyncDomainMap memSyncDomainMap
Value of launch attribute hipLaunchAttributeMemSyncDomainMap.
Definition hip_runtime_api.h:1809
int managedMemory
Device supports allocating managed memory on this system.
Definition hip_runtime_api.h:337
unsigned hasSharedFloatAtomicExch
32-bit float atomic exch for shared memory.
Definition hip_runtime_api.h:58
size_t texturePitchAlignment
Pitch alignment requirement for texture references bound to.
Definition hip_runtime_api.h:287
hipLimit_t
Definition hip_runtime_api.h:869
hipMemRangeHandleType
Definition hip_runtime_api.h:2249
struct ihipExecutionCtx_t * hipExecutionCtx_t
Definition hip_runtime_api.h:754
hipMemAllocationHandleType
Definition hip_runtime_api.h:1373
hipGraphicsResource * hipGraphicsResource_t
Definition hip_runtime_api.h:1599
enum __HIP_NODISCARD hipError_t UINT32_BASE hipError_t
struct ihipCtx_t * hipCtx_t
Definition hip_runtime_api.h:753
#define __dparm(x)
Definition hip_runtime_api.h:735
struct ihipStream_t * hipStream_t
Definition hip_runtime_api.h:827
hipGraphInstantiateResult
Definition hip_runtime_api.h:1955
int hipDevice_t
Definition hip_runtime_api.h:815
hipAccessProperty
Definition hip_runtime_api.h:1677
hipFlushGPUDirectRDMAWritesScope
Definition hip_runtime_api.h:703
struct ihipLinkState_t * hipLinkState_t
Definition hip_runtime_api.h:841
hipGraphDependencyType
Definition hip_runtime_api.h:2177
hipMemRangeAttribute
Definition hip_runtime_api.h:1266
#define hipMemAttachSingle
Definition hip_runtime_api.h:1022
hipMemoryAdvise
Definition hip_runtime_api.h:1233
#define hipArrayDefault
Definition hip_runtime_api.h:1083
hipSharedMemConfig
Definition hip_runtime_api.h:1430
#define hipKernelNodeAttrValue
Definition hip_runtime_api.h:1858
hipComputeMode
Definition hip_runtime_api.h:671
struct ihipEvent_t * hipEvent_t
Definition hip_runtime_api.h:861
hipStreamCaptureMode
Definition hip_runtime_api.h:1887
hipStreamBatchMemOpType
Definition hip_runtime_api.h:1108
hipDriverProcAddressQueryResult
Definition hip_runtime_api.h:665
#define HIP_DEPRECATED_MSG
Definition hip_runtime_api.h:727
hipLaunchAttributeID
Definition hip_runtime_api.h:1779
struct ihipKernel_t * hipKernel_t
Definition hip_runtime_api.h:843
hipSynchronizationPolicy
Definition hip_runtime_api.h:1715
hipGraphNodeType
Definition hip_runtime_api.h:1623
hipExternalMemoryHandleType
Definition hip_runtime_api.h:1475
#define hipMemAttachGlobal
Definition hip_runtime_api.h:1016
struct ihipLibrary_t * hipLibrary_t
Definition hip_runtime_api.h:842
hipFuncAttribute
Definition hip_runtime_api.h:1407
hipExternalSemaphoreHandleType
Definition hip_runtime_api.h:1513
hipLaunchMemSyncDomain
Definition hip_runtime_api.h:1706
struct ihipDevResourceDesc_t * hipDevResourceDesc_t
Definition hip_runtime_api.h:755
hipDeviceP2PAttr
Definition hip_runtime_api.h:816
hipGraphDebugDotFlags
Definition hip_runtime_api.h:1933
hipDevSmResourceGroup_flags
Definition hip_runtime_api.h:762
hipUserObjectRetainFlags
Definition hip_runtime_api.h:1918
#define hipStreamAttrID
Definition hip_runtime_api.h:1838
#define hipHostAllocDefault
Definition hip_runtime_api.h:958
void(* hipHostFn_t)(void *userData)
Definition hip_runtime_api.h:1642
#define hipOccupancyDefault
Definition hip_runtime_api.h:1088
hipStreamUpdateCaptureDependenciesFlags
Definition hip_runtime_api.h:1899
struct ihipGraph * hipGraph_t
Definition hip_runtime_api.h:1604
hipMemHandleType
Definition hip_runtime_api.h:2037
hipFlushGPUDirectRDMAWritesOptions
Definition hip_runtime_api.h:678
hipFuncCache_t
Definition hip_runtime_api.h:1421
hipUserObjectFlags
Definition hip_runtime_api.h:1914
#define __HIP_NODISCARD
Definition hip_runtime_api.h:96
hipDevWorkqueueConfigScope
Definition hip_runtime_api.h:770
hipGraphMemAttributeType
Definition hip_runtime_api.h:1904
hipMemPoolAttr
Definition hip_runtime_api.h:1281
hipDriverEntryPointQueryResult
Definition hip_runtime_api.h:822
hipMemRangeFlags
Definition hip_runtime_api.h:2257
hipDevSmResourceSplitByCount_flags
Definition hip_runtime_api.h:766
void __hipGetPCH(const char **pch, unsigned int *size)
#define HIP_RESOURCE_ABI_BYTES
Definition hip_runtime_api.h:775
#define UINT32_BASE
Definition hip_runtime_api.h:102
struct ihipModule_t * hipModule_t
Definition hip_runtime_api.h:839
struct hipUserObject * hipUserObject_t
Definition hip_runtime_api.h:1617
hipMemOperationType
Definition hip_runtime_api.h:2044
void * hipExternalSemaphore_t
Definition hip_runtime_api.h:1538
hipGraphicsRegisterFlags
Definition hip_runtime_api.h:1587
#define HIP_EXT_DYN_DATA_PREFETCH_MAX_REGIONS
Definition hip_runtime_api.h:1758
#define hipStreamAttrValue
Definition hip_runtime_api.h:1845
hipMemRangeCoherencyMode
Definition hip_runtime_api.h:1254
hipMemAccessFlags
Definition hip_runtime_api.h:1341
hipMemAllocationGranularity_flags
Definition hip_runtime_api.h:2029
hipExtDynDataPrefetchTemporal
Temporal locality hint for dynamic data prefetch.
Definition hip_runtime_api.h:1733
struct hipGraphExec * hipGraphExec_t
Definition hip_runtime_api.h:1612
hipGraphExecUpdateResult
Definition hip_runtime_api.h:1872
struct ihipModuleSymbol_t * hipFunction_t
Definition hip_runtime_api.h:840
#define hipKernelNodeAttrID
Definition hip_runtime_api.h:1850
void * hipExternalMemory_t
Definition hip_runtime_api.h:1512
hipStreamCaptureStatus
Definition hip_runtime_api.h:1892
hipDeviceAttribute_t
Definition hip_runtime_api.h:447
hipGPUDirectRDMAWritesOrdering
Definition hip_runtime_api.h:683
hipDeviceProp_t hipDeviceProp_tR0600
Definition hip_runtime_api.h:406
#define hipHostMallocDefault
Definition hip_runtime_api.h:962
#define HIP_DEPRECATED(msg)
Definition hip_runtime_api.h:724
struct _hipGraphicsResource hipGraphicsResource
Definition hip_runtime_api.h:1597
hipMemAllocationType
Definition hip_runtime_api.h:1359
struct hipGraphNode * hipGraphNode_t
Definition hip_runtime_api.h:1608
struct ihipMemGenericAllocationHandle * hipMemGenericAllocationHandle_t
Definition hip_runtime_api.h:2024
hipClusterSchedulingPolicy
Definition hip_runtime_api.h:1723
hipMemoryType
Definition hip_runtime_api.h:416
hipGraphInstantiateFlags
Definition hip_runtime_api.h:1922
#define HIP_IPC_HANDLE_SIZE
Definition hip_runtime_api.h:829
struct ihipMemPoolHandle_t * hipMemPool_t
Definition hip_runtime_api.h:847
hipDevResourceType
Definition hip_runtime_api.h:756
hipArraySparseSubresourceType
Definition hip_runtime_api.h:2052
hipFlushGPUDirectRDMAWritesTarget
Definition hip_runtime_api.h:692
@ hipExtLimitScratchMin
Definition hip_runtime_api.h:877
@ hipLimitMallocHeapSize
Definition hip_runtime_api.h:875
@ hipLimitStackSize
Definition hip_runtime_api.h:870
@ hipLimitRange
Supported limit range.
Definition hip_runtime_api.h:885
@ hipLimitPrintfFifoSize
Definition hip_runtime_api.h:873
@ hipExtLimitScratchMax
Definition hip_runtime_api.h:879
@ hipExtLimitScratchCurrent
Definition hip_runtime_api.h:881
@ hipMemRangeHandleTypeMax
Definition hip_runtime_api.h:2251
@ hipMemRangeHandleTypeDmaBufFd
Definition hip_runtime_api.h:2250
@ hipMemHandleTypeWin32
Allows a Win32 NT handle for exporting. (HANDLE)
Definition hip_runtime_api.h:1377
@ hipMemHandleTypeWin32Kmt
Allows a Win32 KMT handle for exporting. (D3DKMT_HANDLE)
Definition hip_runtime_api.h:1378
@ hipMemHandleTypeNone
Does not allow any export mechanism.
Definition hip_runtime_api.h:1374
@ hipMemHandleTypePosixFileDescriptor
Allows a file descriptor for exporting. Permitted only on POSIX systems.
Definition hip_runtime_api.h:1375
@ hipMemHandleTypeFabric
Allows a fabric handle to be used for exporting.
Definition hip_runtime_api.h:1379
@ hipGraphInstantiateNodeOperationNotSupported
Definition hip_runtime_api.h:1961
@ hipGraphInstantiateMultipleDevicesNotSupported
Definition hip_runtime_api.h:1963
@ hipGraphInstantiateError
Definition hip_runtime_api.h:1957
@ hipGraphInstantiateInvalidStructure
Definition hip_runtime_api.h:1959
@ hipGraphInstantiateSuccess
Definition hip_runtime_api.h:1956
@ hipAccessPropertyNormal
Normal cache persistence.
Definition hip_runtime_api.h:1678
@ hipAccessPropertyPersisting
Persisting access is more likely to persist in cache.
Definition hip_runtime_api.h:1680
@ hipAccessPropertyStreaming
Streaming access is less likely to persist from cache.
Definition hip_runtime_api.h:1679
@ hipFlushGPUDirectRDMAWritesToAllDevices
Visible to all HIP devices.
Definition hip_runtime_api.h:705
@ hipFlushGPUDirectRDMAWritesToOwner
Visible to the device owning the memory.
Definition hip_runtime_api.h:704
@ hipGraphDependencyTypeDefault
Definition hip_runtime_api.h:2178
@ hipGraphDependencyTypeProgrammatic
Definition hip_runtime_api.h:2179
@ hipMemRangeAttributeLastPrefetchLocation
Definition hip_runtime_api.h:1272
@ hipMemRangeAttributePreferredLocation
The preferred location of the range.
Definition hip_runtime_api.h:1269
@ hipMemRangeAttributeAccessedBy
Definition hip_runtime_api.h:1270
@ hipMemRangeAttributeReadMostly
Definition hip_runtime_api.h:1267
@ hipMemRangeAttributeCoherencyMode
Definition hip_runtime_api.h:1274
@ hipMemAdviseUnsetAccessedBy
Definition hip_runtime_api.h:1242
@ hipMemAdviseUnsetCoarseGrain
Restores cache coherency policy back to fine-grain.
Definition hip_runtime_api.h:1249
@ hipMemAdviseSetCoarseGrain
Definition hip_runtime_api.h:1244
@ hipMemAdviseUnsetPreferredLocation
Clear the preferred location for the data.
Definition hip_runtime_api.h:1239
@ hipMemAdviseSetAccessedBy
Definition hip_runtime_api.h:1240
@ hipMemAdviseSetPreferredLocation
Definition hip_runtime_api.h:1237
@ hipMemAdviseSetReadMostly
Definition hip_runtime_api.h:1234
@ hipMemAdviseUnsetReadMostly
Undo the effect of hipMemAdviseSetReadMostly.
Definition hip_runtime_api.h:1236
@ hipSharedMemBankSizeFourByte
Definition hip_runtime_api.h:1432
@ hipSharedMemBankSizeEightByte
Definition hip_runtime_api.h:1434
@ hipSharedMemBankSizeDefault
The compiler selects a device-specific value for the banking.
Definition hip_runtime_api.h:1431
@ hipComputeModeProhibited
Definition hip_runtime_api.h:674
@ hipComputeModeExclusive
Definition hip_runtime_api.h:673
@ hipComputeModeDefault
Definition hip_runtime_api.h:672
@ hipComputeModeExclusiveProcess
Definition hip_runtime_api.h:675
@ hipStreamCaptureModeRelaxed
Definition hip_runtime_api.h:1890
@ hipStreamCaptureModeThreadLocal
Definition hip_runtime_api.h:1889
@ hipStreamCaptureModeGlobal
Definition hip_runtime_api.h:1888
@ hipStreamMemOpWriteValue64
Definition hip_runtime_api.h:1112
@ hipStreamMemOpBarrier
Currently not supported.
Definition hip_runtime_api.h:1113
@ hipStreamMemOpWriteValue32
Definition hip_runtime_api.h:1110
@ hipStreamMemOpWaitValue32
Definition hip_runtime_api.h:1109
@ hipStreamMemOpWaitValue64
Definition hip_runtime_api.h:1111
@ hipStreamMemOpFlushRemoteWrites
Currently not supported.
Definition hip_runtime_api.h:1114
@ HIP_GET_PROC_ADDRESS_SYMBOL_NOT_FOUND
Definition hip_runtime_api.h:667
@ HIP_GET_PROC_ADDRESS_SUCCESS
Definition hip_runtime_api.h:666
@ HIP_GET_PROC_ADDRESS_VERSION_NOT_SUFFICIENT
Definition hip_runtime_api.h:668
@ hipLaunchAttributePriority
Valid for graph node, streams, launches.
Definition hip_runtime_api.h:1786
@ hipLaunchAttributeMax
Definition hip_runtime_api.h:1790
@ hipLaunchAttributeClusterDimension
Valid for graph nodes, launches.
Definition hip_runtime_api.h:1784
@ hipLaunchAttributeMemSyncDomain
Valid for streams, graph nodes, launches.
Definition hip_runtime_api.h:1788
@ hipLaunchAttributeMemSyncDomainMap
Valid for streams, graph nodes, launches.
Definition hip_runtime_api.h:1787
@ hipLaunchAttributeIgnore
Ignored entry.
Definition hip_runtime_api.h:1780
@ hipLaunchAttributeSynchronizationPolicy
Valid for streams.
Definition hip_runtime_api.h:1783
@ hipLaunchAttributeExtDynDataPrefetch
Valid for launches. Prefetch data into L2 before kernel execution.
Definition hip_runtime_api.h:1789
@ hipLaunchAttributeClusterSchedulingPolicyPreference
Valid for graph nodes, launches.
Definition hip_runtime_api.h:1785
@ hipLaunchAttributeAccessPolicyWindow
Valid for Streams, graph nodes, launches.
Definition hip_runtime_api.h:1781
@ hipLaunchAttributeCooperative
Valid for graph nodes, launches.
Definition hip_runtime_api.h:1782
@ hipSyncPolicyYield
Definition hip_runtime_api.h:1718
@ hipSyncPolicyBlockingSync
Definition hip_runtime_api.h:1719
@ hipSyncPolicyAuto
Definition hip_runtime_api.h:1716
@ hipSyncPolicySpin
Definition hip_runtime_api.h:1717
@ hipGraphNodeTypeBatchMemOp
BatchMemOp node.
Definition hip_runtime_api.h:1638
@ hipGraphNodeTypeGraph
Node which executes an embedded graph.
Definition hip_runtime_api.h:1628
@ hipGraphNodeTypeMemset
Memset node.
Definition hip_runtime_api.h:1626
@ hipGraphNodeTypeEventRecord
External event record node.
Definition hip_runtime_api.h:1631
@ hipGraphNodeTypeExtSemaphoreSignal
External Semaphore signal node.
Definition hip_runtime_api.h:1632
@ hipGraphNodeTypeMemcpy
Memcpy node.
Definition hip_runtime_api.h:1625
@ hipGraphNodeTypeWaitEvent
External event wait node.
Definition hip_runtime_api.h:1630
@ hipGraphNodeTypeCount
Definition hip_runtime_api.h:1639
@ hipGraphNodeTypeKernel
GPU kernel node.
Definition hip_runtime_api.h:1624
@ hipGraphNodeTypeHost
Host (executable) node.
Definition hip_runtime_api.h:1627
@ hipGraphNodeTypeMemAlloc
Memory alloc node.
Definition hip_runtime_api.h:1634
@ hipGraphNodeTypeMemFree
Memory free node.
Definition hip_runtime_api.h:1635
@ hipGraphNodeTypeMemcpyFromSymbol
MemcpyFromSymbol node.
Definition hip_runtime_api.h:1636
@ hipGraphNodeTypeMemcpyToSymbol
MemcpyToSymbol node.
Definition hip_runtime_api.h:1637
@ hipGraphNodeTypeEmpty
Empty (no-op) node.
Definition hip_runtime_api.h:1629
@ hipGraphNodeTypeExtSemaphoreWait
External Semaphore wait node.
Definition hip_runtime_api.h:1633
@ hipExternalMemoryHandleTypeD3D11Resource
Definition hip_runtime_api.h:1481
@ hipExternalMemoryHandleTypeD3D12Resource
Definition hip_runtime_api.h:1480
@ hipExternalMemoryHandleTypeNvSciBuf
Definition hip_runtime_api.h:1483
@ hipExternalMemoryHandleTypeOpaqueFd
Definition hip_runtime_api.h:1476
@ hipExternalMemoryHandleTypeD3D12Heap
Definition hip_runtime_api.h:1479
@ hipExternalMemoryHandleTypeOpaqueWin32Kmt
Definition hip_runtime_api.h:1478
@ hipExternalMemoryHandleTypeOpaqueWin32
Definition hip_runtime_api.h:1477
@ hipExternalMemoryHandleTypeD3D11ResourceKmt
Definition hip_runtime_api.h:1482
@ hipFuncAttributeClusterSchedulingPolicyPreference
The block scheduling policy of a function.
Definition hip_runtime_api.h:1415
@ hipFuncAttributePreferredSharedMemoryCarveout
Sets the percentage of total shared memory allocated as the shared memory carveout.
Definition hip_runtime_api.h:1409
@ hipFuncAttributeRequiredClusterWidth
The required cluster width in blocks.
Definition hip_runtime_api.h:1411
@ hipFuncAttributeMaxDynamicSharedMemorySize
The maximum number of bytes requested for dynamically allocated shared memory.
Definition hip_runtime_api.h:1408
@ hipFuncAttributeMax
Definition hip_runtime_api.h:1416
@ hipFuncAttributeRequiredClusterDepth
The required cluster depth in blocks.
Definition hip_runtime_api.h:1413
@ hipFuncAttributeRequiredClusterHeight
The required cluster height in blocks.
Definition hip_runtime_api.h:1412
@ hipFuncAttributeClusterDimMustBeSet
The kernel must launch with a valid cluster size specified.
Definition hip_runtime_api.h:1410
@ hipFuncAttributeNonPortableClusterSizeAllowed
Is the function allowed to launch with non-portable cluster size.
Definition hip_runtime_api.h:1414
@ hipExternalSemaphoreHandleTypeNvSciSync
Definition hip_runtime_api.h:1519
@ hipExternalSemaphoreHandleTypeKeyedMutexKmt
Definition hip_runtime_api.h:1521
@ hipExternalSemaphoreHandleTypeOpaqueWin32Kmt
Definition hip_runtime_api.h:1516
@ hipExternalSemaphoreHandleTypeKeyedMutex
Definition hip_runtime_api.h:1520
@ hipExternalSemaphoreHandleTypeD3D11Fence
Definition hip_runtime_api.h:1518
@ hipExternalSemaphoreHandleTypeTimelineSemaphoreWin32
Definition hip_runtime_api.h:1523
@ hipExternalSemaphoreHandleTypeOpaqueFd
Definition hip_runtime_api.h:1514
@ hipExternalSemaphoreHandleTypeOpaqueWin32
Definition hip_runtime_api.h:1515
@ hipExternalSemaphoreHandleTypeTimelineSemaphoreFd
Definition hip_runtime_api.h:1522
@ hipExternalSemaphoreHandleTypeD3D12Fence
Definition hip_runtime_api.h:1517
@ hipLaunchMemSyncDomainRemote
Definition hip_runtime_api.h:1708
@ hipLaunchMemSyncDomainDefault
Definition hip_runtime_api.h:1707
@ hipDevP2PAttrAccessSupported
Definition hip_runtime_api.h:818
@ hipDevP2PAttrHipArrayAccessSupported
Definition hip_runtime_api.h:820
@ hipDevP2PAttrNativeAtomicSupported
Definition hip_runtime_api.h:819
@ hipDevP2PAttrPerformanceRank
Definition hip_runtime_api.h:817
@ hipGraphDebugDotFlagsKernelNodeAttributes
Definition hip_runtime_api.h:1946
@ hipGraphDebugDotFlagsMemsetNodeParams
Definition hip_runtime_api.h:1938
@ hipGraphDebugDotFlagsKernelNodeParams
Definition hip_runtime_api.h:1936
@ hipGraphDebugDotFlagsExtSemasWaitNodeParams
Definition hip_runtime_api.h:1944
@ hipGraphDebugDotFlagsHandles
Definition hip_runtime_api.h:1948
@ hipGraphDebugDotFlagsExtSemasSignalNodeParams
Definition hip_runtime_api.h:1942
@ hipGraphDebugDotFlagsHostNodeParams
Definition hip_runtime_api.h:1939
@ hipGraphDebugDotFlagsEventNodeParams
Definition hip_runtime_api.h:1940
@ hipGraphDebugDotFlagsVerbose
Definition hip_runtime_api.h:1934
@ hipGraphDebugDotFlagsMemcpyNodeParams
Definition hip_runtime_api.h:1937
@ hipDevSmResourceGroupBackfill
Definition hip_runtime_api.h:764
@ hipDevSmResourceGroupDefault
Definition hip_runtime_api.h:763
@ hipGraphUserObjectMove
Add new reference or retain.
Definition hip_runtime_api.h:1919
@ hipStreamAddCaptureDependencies
Add new nodes to the dependency set.
Definition hip_runtime_api.h:1900
@ hipStreamSetCaptureDependencies
Replace the dependency set with the new nodes.
Definition hip_runtime_api.h:1901
@ hipMemHandleTypeGeneric
Generic handle type.
Definition hip_runtime_api.h:2038
@ hipFlushGPUDirectRDMAWritesOptionHost
Definition hip_runtime_api.h:679
@ hipFlushGPUDirectRDMAWritesOptionMemOps
Definition hip_runtime_api.h:680
@ hipFuncCachePreferNone
no preference for shared memory or L1 (default)
Definition hip_runtime_api.h:1422
@ hipFuncCachePreferEqual
prefer equal size L1 cache and shared memory
Definition hip_runtime_api.h:1425
@ hipFuncCachePreferL1
prefer larger L1 cache and smaller shared memory
Definition hip_runtime_api.h:1424
@ hipFuncCachePreferShared
prefer larger shared memory and smaller L1 cache
Definition hip_runtime_api.h:1423
@ hipUserObjectNoDestructorSync
Destructor execution is not synchronized.
Definition hip_runtime_api.h:1915
@ hipDevWorkqueueConfigScopeDeviceCtx
Definition hip_runtime_api.h:771
@ hipDevWorkqueueConfigScopeGreenCtxBalanced
Definition hip_runtime_api.h:772
@ hipGraphMemAttrReservedMemHigh
Definition hip_runtime_api.h:1911
@ hipGraphMemAttrUsedMemCurrent
Amount of memory, in bytes, currently associated with graphs.
Definition hip_runtime_api.h:1905
@ hipGraphMemAttrUsedMemHigh
Definition hip_runtime_api.h:1907
@ hipGraphMemAttrReservedMemCurrent
Definition hip_runtime_api.h:1909
@ hipMemPoolAttrUsedMemCurrent
Definition hip_runtime_api.h:1328
@ hipMemPoolAttrReservedMemHigh
Definition hip_runtime_api.h:1323
@ hipMemPoolAttrReservedMemCurrent
Definition hip_runtime_api.h:1317
@ hipMemPoolAttrReleaseThreshold
Definition hip_runtime_api.h:1312
@ hipMemPoolAttrUsedMemHigh
Definition hip_runtime_api.h:1334
@ hipMemPoolReuseAllowInternalDependencies
Definition hip_runtime_api.h:1303
@ hipMemPoolReuseFollowEventDependencies
Definition hip_runtime_api.h:1290
@ hipMemPoolReuseAllowOpportunistic
Definition hip_runtime_api.h:1296
@ hipDriverEntryPointSuccess
Definition hip_runtime_api.h:823
@ hipDriverEntryPointSymbolNotFound
Definition hip_runtime_api.h:824
@ hipDriverEntryPointVersionNotSufficent
Definition hip_runtime_api.h:825
@ hipMemRangeFlagsMax
Definition hip_runtime_api.h:2259
@ hipMemRangeFlagDmaBufMappingTypePcie
Definition hip_runtime_api.h:2258
@ hipDevSmResourceSplitMaxPotentialClusterSize
Definition hip_runtime_api.h:768
@ hipDevSmResourceSplitIgnoreSmCoscheduling
Definition hip_runtime_api.h:767
@ hipMemOperationTypeMap
Map operation.
Definition hip_runtime_api.h:2045
@ hipMemOperationTypeUnmap
Unmap operation.
Definition hip_runtime_api.h:2046
@ hipGraphicsRegisterFlagsReadOnly
HIP will not write to this registered resource, read only.
Definition hip_runtime_api.h:1589
@ hipGraphicsRegisterFlagsTextureGather
HIP will perform texture gather operations on this registered resource, read and write or read only.
Definition hip_runtime_api.h:1593
@ hipGraphicsRegisterFlagsWriteDiscard
HIP will only write and will not read from this registered resource, write only.
Definition hip_runtime_api.h:1590
@ hipGraphicsRegisterFlagsNone
Definition hip_runtime_api.h:1588
@ hipGraphicsRegisterFlagsSurfaceLoadStore
HIP will bind this resource to a surface, read and write.
Definition hip_runtime_api.h:1592
@ hipMemRangeCoherencyModeFineGrain
Definition hip_runtime_api.h:1255
@ hipMemRangeCoherencyModeIndeterminate
Definition hip_runtime_api.h:1259
@ hipMemRangeCoherencyModeCoarseGrain
Definition hip_runtime_api.h:1257
@ hipMemAccessFlagsProtRead
Set the address range read accessible.
Definition hip_runtime_api.h:1343
@ hipMemAccessFlagsProtNone
Default, make the address range not accessible.
Definition hip_runtime_api.h:1342
@ hipMemAccessFlagsProtReadWrite
Set the address range read-write accessible.
Definition hip_runtime_api.h:1344
@ hipMemAllocationGranularityMinimum
Minimum granularity.
Definition hip_runtime_api.h:2030
@ hipMemAllocationGranularityRecommended
Recommended granularity for performance.
Definition hip_runtime_api.h:2031
@ hipExtDynDataPrefetchTemporalRegular
Regular temporal locality.
Definition hip_runtime_api.h:1734
@ hipExtDynDataPrefetchTemporalHigh
High temporal locality (prefer caching)
Definition hip_runtime_api.h:1735
@ hipGraphExecUpdateErrorNotSupported
The update failed because something about the node is not supported.
Definition hip_runtime_api.h:1882
@ hipGraphExecUpdateErrorNodeTypeChanged
The update failed because a node type changed.
Definition hip_runtime_api.h:1877
@ hipGraphExecUpdateErrorTopologyChanged
The update failed because the topology changed.
Definition hip_runtime_api.h:1876
@ hipGraphExecUpdateErrorUnsupportedFunctionChange
Definition hip_runtime_api.h:1884
@ hipGraphExecUpdateError
Definition hip_runtime_api.h:1874
@ hipGraphExecUpdateErrorFunctionChanged
The update failed because the function of a kernel node changed.
Definition hip_runtime_api.h:1878
@ hipGraphExecUpdateSuccess
The update succeeded.
Definition hip_runtime_api.h:1873
@ hipGraphExecUpdateErrorParametersChanged
The update failed because the parameters changed in a way that is not supported.
Definition hip_runtime_api.h:1880
@ hipStreamCaptureStatusInvalidated
Definition hip_runtime_api.h:1895
@ hipStreamCaptureStatusNone
Stream is not capturing.
Definition hip_runtime_api.h:1893
@ hipStreamCaptureStatusActive
Stream is actively capturing.
Definition hip_runtime_api.h:1894
@ hipDeviceAttributeDirectManagedMemAccessFromHost
Definition hip_runtime_api.h:472
@ hipDeviceAttributeSurfaceAlignment
Alignment requirement for surfaces.
Definition hip_runtime_api.h:562
@ hipDeviceAttributeMaxGridDimX
Max grid size in width.
Definition hip_runtime_api.h:493
@ hipDeviceAttributeMaxSurfaceCubemapLayered
Definition hip_runtime_api.h:502
@ hipDeviceAttributeMaxSurface3D
Maximum dimension (width, height, depth) of 3D surface.
Definition hip_runtime_api.h:500
@ hipDeviceAttributeMaxPitch
Maximum pitch in bytes allowed by memory copies.
Definition hip_runtime_api.h:527
@ hipDeviceAttributeTccDriver
Cuda only. Whether device is a Tesla device using TCC driver.
Definition hip_runtime_api.h:563
@ hipDeviceAttributeHostNativeAtomicSupported
Definition hip_runtime_api.h:475
@ hipDeviceAttributePageableMemoryAccessUsesHostPageTables
Definition hip_runtime_api.h:540
@ hipDeviceAttributeUnused5
Previously hipDeviceAttributeGcnArchName.
Definition hip_runtime_api.h:607
@ hipDeviceAttributeMaxBlockDimY
Max block size in height.
Definition hip_runtime_api.h:491
@ hipDeviceAttributeMaxSurfaceCubemap
Cuda only. Maximum dimensions of Cubemap surface.
Definition hip_runtime_api.h:501
@ hipDeviceAttributePageableMemoryAccess
Definition hip_runtime_api.h:538
@ hipDeviceAttributeClockRate
Peak clock frequency in kilohertz.
Definition hip_runtime_api.h:460
@ hipDeviceAttributeCudaCompatibleEnd
Definition hip_runtime_api.h:598
@ hipDeviceAttributeMaxTexture1DMipmap
Maximum size of 1D mipmapped texture.
Definition hip_runtime_api.h:509
@ hipDeviceAttributeComputeCapabilityMajor
Major compute capability version number.
Definition hip_runtime_api.h:487
@ hipDeviceAttributeGlobalL1CacheSupported
Device supports caching globals in L1.
Definition hip_runtime_api.h:474
@ hipDeviceAttributeCooperativeMultiDeviceUnmatchedSharedMem
Definition hip_runtime_api.h:619
@ hipDeviceAttributeAccessPolicyMaxWindowSize
Definition hip_runtime_api.h:452
@ hipDeviceAttributeMaxTexture3DHeight
Maximum dimension height of 3D texture.
Definition hip_runtime_api.h:519
@ hipDeviceAttributeComputeCapabilityMinor
Minor compute capability version number.
Definition hip_runtime_api.h:530
@ hipDeviceAttributeNumberOfXccs
Definition hip_runtime_api.h:631
@ hipDeviceAttributeMaxTextureCubemap
Maximum dimensions of Cubemap texture.
Definition hip_runtime_api.h:522
@ hipDeviceAttributeGPUDirectRDMASupported
Device supports GPUDirect RDMA APIs.
Definition hip_runtime_api.h:588
@ hipDeviceAttributeDeviceOverlap
Definition hip_runtime_api.h:470
@ hipDeviceAttributeMaxTexture2DLinear
Definition hip_runtime_api.h:515
@ hipDeviceAttributeHostAllocDmaBufSupported
Device supports host-allocated DMABuf buffer sharing.
Definition hip_runtime_api.h:587
@ hipDeviceAttributeMaxSurface2D
Maximum dimension (width, height) of 2D surface.
Definition hip_runtime_api.h:498
@ hipDeviceAttributeGPUDirectRDMAFlushWritesOptions
Definition hip_runtime_api.h:589
@ hipDeviceAttributeMaxSurface1DLayered
Cuda only. Maximum dimensions of 1D layered surface.
Definition hip_runtime_api.h:497
@ hipDeviceAttributeHdpRegFlushCntl
Address of the HDP_REG_COHERENCY_FLUSH_CNTL register.
Definition hip_runtime_api.h:609
@ hipDeviceAttributeMaxAvailableVgprsPerThread
Definition hip_runtime_api.h:638
@ hipDeviceAttributeComputeMode
Compute mode that device is currently in.
Definition hip_runtime_api.h:461
@ hipDeviceAttributeCooperativeMultiDeviceUnmatchedFunc
Definition hip_runtime_api.h:610
@ hipDeviceAttributeAsicRevision
Revision of the GPU in this device.
Definition hip_runtime_api.h:623
@ hipDeviceAttributeUnused4
Previously hipDeviceAttributeGcnArch.
Definition hip_runtime_api.h:606
@ hipDeviceAttributeCooperativeMultiDeviceLaunch
Definition hip_runtime_api.h:468
@ hipDeviceAttributeMaxTexture2DHeight
Maximum dimension hight of 2D texture.
Definition hip_runtime_api.h:511
@ hipDeviceAttributePersistingL2CacheMaxSize
Maximum l2 persisting lines capacity in bytes.
Definition hip_runtime_api.h:547
@ hipDeviceAttributeEccEnabled
Whether ECC support is enabled.
Definition hip_runtime_api.h:450
@ hipDeviceAttributeDmaBufSupported
Device supports DMABuf buffer sharing.
Definition hip_runtime_api.h:582
@ hipDeviceAttributeExpertSchedMode
Definition hip_runtime_api.h:642
@ hipDeviceAttributeCanUseHostPointerForRegisteredMem
Definition hip_runtime_api.h:457
@ hipDeviceAttributePciBusId
PCI Bus ID.
Definition hip_runtime_api.h:542
@ hipDeviceAttributeL2CacheSize
Definition hip_runtime_api.h:480
@ hipDeviceAttributeKernelExecTimeout
Run time limit for kernels executed on the device.
Definition hip_runtime_api.h:479
@ hipDeviceAttributeMaxThreadsDim
Maximum dimension of a block.
Definition hip_runtime_api.h:524
@ hipDeviceAttributeSingleToDoublePrecisionPerfRatio
Definition hip_runtime_api.h:559
@ hipDeviceAttributeMaxGridDimY
Max grid size in height.
Definition hip_runtime_api.h:494
@ hipDeviceAttributeMultiprocessorCount
Definition hip_runtime_api.h:533
@ hipDeviceAttributeAmdSpecificBegin
Definition hip_runtime_api.h:599
@ hipDeviceAttributeMaxRegistersPerMultiprocessor
32-bit registers available per block.
Definition hip_runtime_api.h:551
@ hipDeviceAttributeIsMultiGpuBoard
Multiple GPU devices.
Definition hip_runtime_api.h:478
@ hipDeviceAttributeSharedMemPerBlockOptin
Definition hip_runtime_api.h:556
@ hipDeviceAttributeMaxSurface2DLayered
Cuda only. Maximum dimensions of 2D layered surface.
Definition hip_runtime_api.h:499
@ hipDeviceAttributeAmdSpecificEnd
Definition hip_runtime_api.h:647
@ hipDeviceAttributeMemoryClockRate
Peak memory clock frequency in kilohertz.
Definition hip_runtime_api.h:529
@ hipDeviceAttributeMaxGridDimZ
Max grid size in depth.
Definition hip_runtime_api.h:495
@ hipDeviceAttributeHdpMemFlushCntl
Address of the HDP_MEM_COHERENCY_FLUSH_CNTL register.
Definition hip_runtime_api.h:608
@ hipDeviceAttributeUnused2
Previously hipDeviceAttributeUuid.
Definition hip_runtime_api.h:571
@ hipDeviceAttributeFineGrainSupport
'1' if Device supports fine grain, '0' otherwise
Definition hip_runtime_api.h:629
@ hipDeviceAttributeCooperativeLaunch
Support cooperative launch.
Definition hip_runtime_api.h:467
@ hipDeviceAttributeUnifiedAddressing
Definition hip_runtime_api.h:569
@ hipDeviceAttributeAsyncEngineCount
Asynchronous engines number.
Definition hip_runtime_api.h:454
@ hipDeviceAttributeMultiGpuBoardGroupID
Definition hip_runtime_api.h:531
@ hipDeviceAttributeStreamPrioritiesSupported
Whether to support stream priorities.
Definition hip_runtime_api.h:561
@ hipDeviceAttributeMaxSharedMemoryPerBlock
Definition hip_runtime_api.h:554
@ hipDeviceAttributeLocalL1CacheSupported
caching locals in L1 is supported
Definition hip_runtime_api.h:482
@ hipDeviceAttributeCanUseStreamWaitValue
Definition hip_runtime_api.h:624
@ hipDeviceAttributeMaxRegistersPerBlock
Definition hip_runtime_api.h:548
@ hipDeviceAttributeMaxThreadsPerBlock
Maximum number of threads per block.
Definition hip_runtime_api.h:525
@ hipDeviceAttributePciDomainId
PCI Domain Id.
Definition hip_runtime_api.h:544
@ hipDeviceAttributeMemoryBusWidth
Global memory bus width in bits.
Definition hip_runtime_api.h:528
@ hipDeviceAttributeMemoryPoolSupportedHandleTypes
Definition hip_runtime_api.h:578
@ hipDeviceAttributeComputePreemptionSupported
Device supports Compute Preemption.
Definition hip_runtime_api.h:462
@ hipDeviceAttributeMaxSurface1D
Maximum size of 1D surface.
Definition hip_runtime_api.h:496
@ hipDeviceAttributeUnused1
Previously hipDeviceAttributeName.
Definition hip_runtime_api.h:537
@ hipDeviceAttributeMaxTexture3DAlt
Maximum dimensions of alternate 3D texture.
Definition hip_runtime_api.h:521
@ hipDeviceAttributeMaxTexture1DLinear
Definition hip_runtime_api.h:506
@ hipDeviceAttributeMaxTexture2DGather
Definition hip_runtime_api.h:512
@ hipDeviceAttributeWallClockRate
Constant frequency of wall clock in kilohertz.
Definition hip_runtime_api.h:630
@ hipDeviceAttributePciDeviceId
PCI Device ID. Returns pcie slot id.
Definition hip_runtime_api.h:543
@ hipDeviceAttributeCanMapHostMemory
Definition hip_runtime_api.h:455
@ hipDeviceAttributeMaxTexture1DWidth
Maximum size of 1D texture.
Definition hip_runtime_api.h:504
@ hipDeviceAttributeConcurrentManagedAccess
Definition hip_runtime_api.h:465
@ hipDeviceAttributeVendorSpecificBegin
Definition hip_runtime_api.h:648
@ hipDeviceAttributeManagedMemory
Device supports allocating managed memory on this system.
Definition hip_runtime_api.h:488
@ hipDeviceAttributeHostNumaId
Definition hip_runtime_api.h:580
@ hipDeviceAttributeIntegrated
Device is integrated GPU.
Definition hip_runtime_api.h:477
@ hipDeviceAttributeMaxTexture2DLayered
Maximum dimensions of 2D layered texture.
Definition hip_runtime_api.h:514
@ hipDeviceAttributeCooperativeMultiDeviceUnmatchedGridDim
Definition hip_runtime_api.h:613
@ hipDeviceAttributeMaxTexture3DDepth
Maximum dimension depth of 3D texture.
Definition hip_runtime_api.h:520
@ hipDeviceAttributePciChipId
GPU Manufacturer device id.
Definition hip_runtime_api.h:641
@ hipDeviceAttributeImageSupport
'1' if Device supports image, '0' otherwise.
Definition hip_runtime_api.h:626
@ hipDeviceAttributeTotalGlobalMem
Global memory available on devicice.
Definition hip_runtime_api.h:568
@ hipDeviceAttributeMaxBlocksPerMultiProcessor
Max block size per multiprocessor.
Definition hip_runtime_api.h:489
@ hipDeviceAttributeHandleTypeFabricSupported
Device supports exporting memory to a fabric handle.
Definition hip_runtime_api.h:586
@ hipDeviceAttributeGPUDirectRDMAWritesOrdering
Definition hip_runtime_api.h:593
@ hipDeviceAttributeIsLargeBar
Whether it is LargeBar.
Definition hip_runtime_api.h:622
@ hipDeviceAttributeMaxTexture2DWidth
Maximum dimension width of 2D texture.
Definition hip_runtime_api.h:510
@ hipDeviceAttributeMaxBlockDimX
Max block size in width.
Definition hip_runtime_api.h:490
@ hipDeviceAttributeMaxTexture3DWidth
Maximum dimension width of 3D texture.
Definition hip_runtime_api.h:518
@ hipDeviceAttributeUnused3
Previously hipDeviceAttributeArch.
Definition hip_runtime_api.h:604
@ hipDeviceAttributeTotalConstantMemory
Constant memory size in bytes.
Definition hip_runtime_api.h:567
@ hipDeviceAttributeTextureAlignment
Alignment requirement for textures.
Definition hip_runtime_api.h:564
@ hipDeviceAttributeMaxTexture1DLayered
Maximum dimensions of 1D layered texture.
Definition hip_runtime_api.h:505
@ hipDeviceAttributeMaxSharedMemoryPerMultiprocessor
Maximum Shared Memory PerMultiprocessor.
Definition hip_runtime_api.h:605
@ hipDeviceAttributeGPUDirectRDMAWithHipVMMSupported
Definition hip_runtime_api.h:583
@ hipDeviceAttributeReservedSharedMemPerBlock
Definition hip_runtime_api.h:552
@ hipDeviceAttributeCudaCompatibleBegin
Definition hip_runtime_api.h:448
@ hipDeviceAttributeConcurrentKernels
Definition hip_runtime_api.h:463
@ hipDeviceAttributeLuid
Definition hip_runtime_api.h:483
@ hipDeviceAttributePciDomainID
PCI Domain ID, for backward compatibility.
Definition hip_runtime_api.h:545
@ hipDeviceAttributeMaxThreadsPerMultiProcessor
Maximum resident threads per multiprocessor.
Definition hip_runtime_api.h:526
@ hipDeviceAttributeTexturePitchAlignment
Definition hip_runtime_api.h:565
@ hipDeviceAttributePhysicalMultiProcessorCount
Definition hip_runtime_api.h:627
@ hipDeviceAttributeHostRegisterSupported
Definition hip_runtime_api.h:576
@ hipDeviceAttributeSharedMemPerMultiprocessor
Shared memory available per multiprocessor.
Definition hip_runtime_api.h:558
@ hipDeviceAttributeLuidDeviceNodeMask
Definition hip_runtime_api.h:485
@ hipDeviceAttributeMaxTextureCubemapLayered
Maximum dimensions of Cubemap layered texture.
Definition hip_runtime_api.h:523
@ hipDeviceAttributeCooperativeMultiDeviceUnmatchedBlockDim
Definition hip_runtime_api.h:616
@ hipDeviceAttributeVirtualMemoryManagementSupported
Definition hip_runtime_api.h:574
@ hipDeviceAttributeMemoryPoolsSupported
Device supports HIP Stream Ordered Memory Allocator.
Definition hip_runtime_api.h:573
@ hipDeviceAttributeClockInstructionRate
Definition hip_runtime_api.h:601
@ hipDeviceAttributeMaxTexture2DMipmap
Maximum dimensions of 2D mipmapped texture.
Definition hip_runtime_api.h:517
@ hipDeviceAttributeMaxDynDataPrefetchRegions
Definition hip_runtime_api.h:644
@ hipDeviceAttributeMaxBlockDimZ
Max block size in depth.
Definition hip_runtime_api.h:492
@ hipDeviceAttributeWarpSize
Warp size in threads.
Definition hip_runtime_api.h:572
@ hipGPUDirectRDMAWritesOrderingOwner
Definition hip_runtime_api.h:685
@ hipGPUDirectRDMAWritesOrderingNone
Definition hip_runtime_api.h:684
@ hipGPUDirectRDMAWritesOrderingAllDevices
Definition hip_runtime_api.h:686
@ hipMemAllocationTypeManaged
Definition hip_runtime_api.h:1365
@ hipMemAllocationTypeMax
Definition hip_runtime_api.h:1367
@ hipMemAllocationTypePinned
Definition hip_runtime_api.h:1364
@ hipMemAllocationTypeUncached
Definition hip_runtime_api.h:1366
@ hipMemAllocationTypeInvalid
Definition hip_runtime_api.h:1360
@ hipClusterSchedulingPolicyDefault
the default scheduling policy
Definition hip_runtime_api.h:1724
@ hipClusterSchedulingPolicyLoadBalancing
Dynamically balance block assignment to optimize resource usage.
Definition hip_runtime_api.h:1726
@ hipClusterSchedulingPolicySpread
distribute blocks evenly across cluster's CUs
Definition hip_runtime_api.h:1725
@ hipMemoryTypeDevice
Definition hip_runtime_api.h:419
@ hipMemoryTypeHost
Memory is physically located on host.
Definition hip_runtime_api.h:418
@ hipMemoryTypeUnregistered
Unregistered memory.
Definition hip_runtime_api.h:417
@ hipMemoryTypeArray
Definition hip_runtime_api.h:424
@ hipMemoryTypeManaged
Definition hip_runtime_api.h:421
@ hipMemoryTypeUnified
unified address space
Definition hip_runtime_api.h:426
@ hipGraphInstantiateFlagAutoFreeOnLaunch
Automatically free memory allocated in a graph before relaunching.
Definition hip_runtime_api.h:1923
@ hipGraphInstantiateFlagUseNodePriority
Definition hip_runtime_api.h:1928
@ hipGraphInstantiateFlagUpload
Automatically upload the graph after instantiation.
Definition hip_runtime_api.h:1925
@ hipGraphInstantiateFlagDeviceLaunch
Instantiate the graph to be launched from the device.
Definition hip_runtime_api.h:1926
@ hipDevResourceTypeWorkqueue
Definition hip_runtime_api.h:760
@ hipDevResourceTypeSm
Definition hip_runtime_api.h:758
@ hipDevResourceTypeInvalid
Definition hip_runtime_api.h:757
@ hipDevResourceTypeWorkqueueConfig
Definition hip_runtime_api.h:759
@ hipArraySparseSubresourceTypeSparseLevel
Sparse level.
Definition hip_runtime_api.h:2053
@ hipArraySparseSubresourceTypeMiptail
Miptail.
Definition hip_runtime_api.h:2054
@ hipFlushGPUDirectRDMAWritesTargetCurrentDevice
Memory of the current HIP device.
Definition hip_runtime_api.h:693
Definition hip_runtime_api.h:2225
Definition hip_runtime_api.h:1687
Definition hip_runtime_api.h:2060
Definition hip_runtime_api.h:2241
Structure representing node parameters for batch memory operations in HIP graphs.
Definition hip_runtime_api.h:1213
Definition hip_runtime_api.h:2110
Definition hip_runtime_api.h:794
Definition hip_runtime_api.h:777
Definition hip_runtime_api.h:806
Definition hip_runtime_api.h:784
Definition hip_runtime_api.h:790
Definition hip_runtime_api.h:53
Definition hip_runtime_api.h:260
Definition hip_runtime_api.h:2125
Definition hip_runtime_api.h:2118
Configuration for dynamic data prefetch.
Definition hip_runtime_api.h:1770
Describes one 2D memory region to prefetch into L2 cache.
Definition hip_runtime_api.h:1746
Definition hip_runtime_api.h:1499
Definition hip_runtime_api.h:1485
Definition hip_runtime_api.h:1505
Definition hip_runtime_api.h:1525
Definition hip_runtime_api.h:2000
Definition hip_runtime_api.h:1539
Definition hip_runtime_api.h:2012
Definition hip_runtime_api.h:1559
Definition hip_runtime_api.h:849
Definition hip_runtime_api.h:1463
Definition hip_runtime_api.h:2182
Definition hip_runtime_api.h:1970
Definition hip_runtime_api.h:2139
Definition hip_runtime_api.h:1643
Definition hip_runtime_api.h:833
Definition hip_runtime_api.h:830
Definition hip_runtime_api.h:1647
Definition hip_runtime_api.h:2201
Definition hip_runtime_api.h:2213
Definition hip_runtime_api.h:1698
Definition hip_runtime_api.h:1452
Definition hip_runtime_api.h:1352
Definition hip_runtime_api.h:1664
Definition hip_runtime_api.h:1982
Definition hip_runtime_api.h:836
Definition hip_runtime_api.h:2132
Definition hip_runtime_api.h:1384
Definition hip_runtime_api.h:1400
Definition hip_runtime_api.h:2101
Definition hip_runtime_api.h:1655
Definition hip_runtime_api.h:433
Definition hip_runtime_api.h:84
Definition hip_runtime_api.h:1797
Union representing batch memory operation parameters for HIP streams.
Definition hip_runtime_api.h:1153
hipError_t hipGraphKernelNodeSetParams(hipGraphNode_t node, const hipKernelNodeParams *pNodeParams)
Sets a kernel node's parameters.
hipError_t hipGraphMemFreeNodeGetParams(hipGraphNode_t node, void *dev_ptr)
Returns parameters for memory free node.
hipError_t hipDrvGraphExecMemsetNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, const hipMemsetParams *memsetParams, hipCtx_t ctx)
Sets the parameters for a memset node in the given graphExec.
hipError_t hipGraphNodeGetDependencies(hipGraphNode_t node, hipGraphNode_t *pDependencies, size_t *pNumDependencies)
Returns a node's dependencies.
hipError_t hipGraphCreate(hipGraph_t *pGraph, unsigned int flags)
Creates a graph.
hipError_t hipGraphAddMemcpyNode1D(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, void *dst, const void *src, size_t count, hipMemcpyKind kind)
Creates a 1D memcpy node and adds it to a graph.
hipError_t hipDrvGraphMemcpyNodeGetParams(hipGraphNode_t hNode, HIP_MEMCPY3D *nodeParams)
Gets a memcpy node's parameters.
hipError_t hipDeviceSetGraphMemAttribute(int device, hipGraphMemAttributeType attr, void *value)
Set the mem attribute for graphs.
hipError_t hipGraphMemcpyNodeSetParams(hipGraphNode_t node, const hipMemcpy3DParms *pNodeParams)
Sets a memcpy node's parameters.
hipError_t hipUserObjectCreate(hipUserObject_t *object_out, void *ptr, hipHostFn_t destroy, unsigned int initialRefcount, unsigned int flags)
Create an instance of userObject to manage lifetime of a resource.
hipError_t hipGraphExecUpdate(hipGraphExec_t hGraphExec, hipGraph_t hGraph, hipGraphNode_t *hErrorNode_out, hipGraphExecUpdateResult *updateResult_out)
Check whether an executable graph can be updated with a graph and perform the update if * possible.
hipError_t hipGraphNodeFindInClone(hipGraphNode_t *pNode, hipGraphNode_t originalNode, hipGraph_t clonedGraph)
Finds a cloned version of a node.
hipError_t hipGraphAddEventWaitNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, hipEvent_t event)
Creates an event wait node and adds it to a graph.
hipError_t hipGraphMemcpyNodeSetParamsToSymbol(hipGraphNode_t node, const void *symbol, const void *src, size_t count, size_t offset, hipMemcpyKind kind)
Sets a memcpy node's parameters to copy to a symbol on the device.
hipError_t hipStreamIsCapturing(hipStream_t stream, hipStreamCaptureStatus *pCaptureStatus)
Get stream's capture state.
hipError_t hipGraphNodeGetEnabled(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, unsigned int *isEnabled)
Query whether a node in the given graphExec is enabled.
hipError_t hipGraphAddChildGraphNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, hipGraph_t childGraph)
Creates a child graph node and adds it to a graph.
hipError_t hipGraphExternalSemaphoresSignalNodeSetParams(hipGraphNode_t hNode, const hipExternalSemaphoreSignalNodeParams *nodeParams)
Updates node parameters in the external semaphore signal node.
hipError_t hipGraphDestroyNode(hipGraphNode_t node)
Remove a node from the graph.
hipError_t hipGraphMemcpyNodeSetParamsFromSymbol(hipGraphNode_t node, void *dst, const void *symbol, size_t count, size_t offset, hipMemcpyKind kind)
Sets a memcpy node's parameters to copy from a symbol on the device.
hipError_t hipGraphReleaseUserObject(hipGraph_t graph, hipUserObject_t object, unsigned int count)
Release user object from graphs.
hipError_t hipDrvGraphAddMemcpyNode(hipGraphNode_t *phGraphNode, hipGraph_t hGraph, const hipGraphNode_t *dependencies, size_t numDependencies, const HIP_MEMCPY3D *copyParams, hipCtx_t ctx)
Creates a memcpy node and adds it to a graph.
hipError_t hipGraphRemoveDependencies(hipGraph_t graph, const hipGraphNode_t *from, const hipGraphNode_t *to, size_t numDependencies)
Removes dependency edges from a graph.
hipError_t hipGraphMemcpyNodeSetParams1D(hipGraphNode_t node, void *dst, const void *src, size_t count, hipMemcpyKind kind)
Sets a memcpy node's parameters to perform a 1-dimensional copy.
hipError_t hipGraphExecMemcpyNodeSetParams1D(hipGraphExec_t hGraphExec, hipGraphNode_t node, void *dst, const void *src, size_t count, hipMemcpyKind kind)
Sets the parameters for a memcpy node in the given graphExec to perform a 1-dimensional copy.
hipError_t hipGraphExecDestroy(hipGraphExec_t graphExec)
Destroys an executable graph.
hipError_t hipGraphAddExternalSemaphoresSignalNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, const hipExternalSemaphoreSignalNodeParams *nodeParams)
Creates a external semaphor signal node and adds it to a graph.
hipError_t hipGraphExecExternalSemaphoresWaitNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, const hipExternalSemaphoreWaitNodeParams *nodeParams)
Updates node parameters in the external semaphore wait node in the given graphExec.
hipError_t hipGraphExecHostNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node, const hipHostNodeParams *pNodeParams)
Sets the parameters for a host node in the given graphExec.
hipError_t hipGraphExecChildGraphNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node, hipGraph_t childGraph)
Updates node parameters in the child graph node in the given graphExec.
hipError_t hipStreamGetCaptureInfo(hipStream_t stream, hipStreamCaptureStatus *pCaptureStatus, unsigned long long *pId)
Get capture status of a stream.
hipError_t hipGraphAddDependencies(hipGraph_t graph, const hipGraphNode_t *from, const hipGraphNode_t *to, size_t numDependencies)
Adds dependency edges to a graph.
hipError_t hipDrvGraphAddMemFreeNode(hipGraphNode_t *phGraphNode, hipGraph_t hGraph, const hipGraphNode_t *dependencies, size_t numDependencies, hipDeviceptr_t dptr)
Creates a memory free node and adds it to a graph.
hipError_t hipGraphExecKernelNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node, const hipKernelNodeParams *pNodeParams)
Sets the parameters for a kernel node in the given graphExec.
hipError_t hipGraphNodeGetDependentNodes(hipGraphNode_t node, hipGraphNode_t *pDependentNodes, size_t *pNumDependentNodes)
Returns a node's dependent nodes.
hipError_t hipDeviceGetGraphMemAttribute(int device, hipGraphMemAttributeType attr, void *value)
Get the mem attribute for graphs.
hipError_t hipGraphHostNodeGetParams(hipGraphNode_t node, hipHostNodeParams *pNodeParams)
Returns a host node's parameters.
hipError_t hipGraphInstantiateWithFlags(hipGraphExec_t *pGraphExec, hipGraph_t graph, unsigned long long flags)
Creates an executable graph from a graph.
hipError_t hipGraphExternalSemaphoresSignalNodeGetParams(hipGraphNode_t hNode, hipExternalSemaphoreSignalNodeParams *params_out)
Returns external semaphore signal node params.
hipError_t hipGraphUpload(hipGraphExec_t graphExec, hipStream_t stream)
Uploads an executable graph to a stream.
hipError_t hipDrvGraphAddMemsetNode(hipGraphNode_t *phGraphNode, hipGraph_t hGraph, const hipGraphNode_t *dependencies, size_t numDependencies, const hipMemsetParams *memsetParams, hipCtx_t ctx)
Creates a memset node and adds it to a graph.
hipError_t hipGraphExecExternalSemaphoresSignalNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, const hipExternalSemaphoreSignalNodeParams *nodeParams)
Updates node parameters in the external semaphore signal node in the given graphExec.
hipError_t hipGraphExecMemcpyNodeSetParamsToSymbol(hipGraphExec_t hGraphExec, hipGraphNode_t node, const void *symbol, const void *src, size_t count, size_t offset, hipMemcpyKind kind)
Sets the parameters for a memcpy node in the given graphExec to copy to a symbol on the device.
hipError_t hipUserObjectRelease(hipUserObject_t object, unsigned int count)
Release number of references to resource.
hipError_t hipGraphKernelNodeGetParams(hipGraphNode_t node, hipKernelNodeParams *pNodeParams)
Gets kernel node's parameters.
hipError_t hipGraphAddMemcpyNodeFromSymbol(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, void *dst, const void *symbol, size_t count, size_t offset, hipMemcpyKind kind)
Creates a memcpy node to copy from a symbol on the device and adds it to a graph.
hipError_t hipGraphKernelNodeCopyAttributes(hipGraphNode_t hSrc, hipGraphNode_t hDst)
Copies attributes from source node to destination node.
hipError_t hipGraphAddMemFreeNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, void *dev_ptr)
Creates a memory free node and adds it to a graph.
hipError_t hipDrvGraphMemcpyNodeSetParams(hipGraphNode_t hNode, const HIP_MEMCPY3D *nodeParams)
Sets a memcpy node's parameters.
hipError_t hipGraphMemcpyNodeGetParams(hipGraphNode_t node, hipMemcpy3DParms *pNodeParams)
Gets a memcpy node's parameters.
hipError_t hipGraphNodeSetParams(hipGraphNode_t node, hipGraphNodeParams *nodeParams)
Updates parameters of a graph's node.
hipError_t hipGraphAddEventRecordNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, hipEvent_t event)
Creates an event record node and adds it to a graph.
hipError_t hipDrvGraphExecMemcpyNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, const HIP_MEMCPY3D *copyParams, hipCtx_t ctx)
Sets the parameters for a memcpy node in the given graphExec.
hipError_t hipStreamBeginCapture(hipStream_t stream, hipStreamCaptureMode mode)
Begins graph capture on a stream.
hipError_t hipStreamEndCapture(hipStream_t stream, hipGraph_t *pGraph)
Ends capture on a stream, returning the captured graph.
hipError_t hipGraphExecGetFlags(hipGraphExec_t graphExec, unsigned long long *flags)
Return the flags of an executable graph.
hipError_t hipUserObjectRetain(hipUserObject_t object, unsigned int count)
Retain number of references to resource.
hipError_t hipGraphNodeGetType(hipGraphNode_t node, hipGraphNodeType *pType)
Returns a node's type.
hipError_t hipGraphNodeSetEnabled(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, unsigned int isEnabled)
Enables or disables the specified node in the given graphExec.
hipError_t hipGraphExecMemcpyNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node, hipMemcpy3DParms *pNodeParams)
Sets the parameters of a memcpy node in the given graphExec.
hipError_t hipGraphExecNodeSetParams(hipGraphExec_t graphExec, hipGraphNode_t node, hipGraphNodeParams *nodeParams)
Updates parameters of an executable graph's node.
hipError_t hipGraphHostNodeSetParams(hipGraphNode_t node, const hipHostNodeParams *pNodeParams)
Sets a host node's parameters.
hipError_t hipGraphMemAllocNodeGetParams(hipGraphNode_t node, hipMemAllocNodeParams *pNodeParams)
Returns parameters for memory allocation node.
hipError_t hipGraphInstantiateWithParams(hipGraphExec_t *pGraphExec, hipGraph_t graph, hipGraphInstantiateParams *instantiateParams)
Creates an executable graph from a graph.
hipError_t hipGraphExecEventRecordNodeSetEvent(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, hipEvent_t event)
Sets the event for an event record node in the given graphExec.
hipError_t hipGraphExternalSemaphoresWaitNodeSetParams(hipGraphNode_t hNode, const hipExternalSemaphoreWaitNodeParams *nodeParams)
Updates node parameters in the external semaphore wait node.
hipError_t hipGraphMemsetNodeGetParams(hipGraphNode_t node, hipMemsetParams *pNodeParams)
Gets a memset node's parameters.
hipError_t hipGraphChildGraphNodeGetGraph(hipGraphNode_t node, hipGraph_t *pGraph)
Gets a handle to the embedded graph of a child graph node.
hipError_t hipGraphKernelNodeGetAttribute(hipGraphNode_t hNode, hipKernelNodeAttrID attr, hipKernelNodeAttrValue *value)
Gets a node's attribute.
hipError_t hipThreadExchangeStreamCaptureMode(hipStreamCaptureMode *mode)
Swaps the stream capture mode of a thread.
hipError_t hipGraphLaunch(hipGraphExec_t graphExec, hipStream_t stream)
Launches an executable graph in the specified stream.
hipError_t hipGraphDebugDotPrint(hipGraph_t graph, const char *path, unsigned int flags)
Write a DOT file describing graph structure.
hipError_t hipGraphExecMemsetNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node, const hipMemsetParams *pNodeParams)
Sets the parameters for a memset node in the given graphExec.
hipError_t hipGraphGetEdges(hipGraph_t graph, hipGraphNode_t *from, hipGraphNode_t *to, size_t *numEdges)
Returns a graph's dependency edges.
hipError_t hipGraphAddKernelNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, const hipKernelNodeParams *pNodeParams)
Creates a kernel execution node and adds it to a graph.
hipError_t hipGraphExecEventWaitNodeSetEvent(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, hipEvent_t event)
Sets the event for an event record node in the given graphExec.
hipError_t hipStreamGetCaptureInfo_v2(hipStream_t stream, hipStreamCaptureStatus *captureStatus_out, unsigned long long *id_out, hipGraph_t *graph_out, const hipGraphNode_t **dependencies_out, size_t *numDependencies_out)
Get stream's capture state.
hipError_t hipStreamBeginCaptureToGraph(hipStream_t stream, hipGraph_t graph, const hipGraphNode_t *dependencies, const hipGraphEdgeData *dependencyData, size_t numDependencies, hipStreamCaptureMode mode)
Begins graph capture on a stream to an existing graph.
hipError_t hipGraphAddExternalSemaphoresWaitNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, const hipExternalSemaphoreWaitNodeParams *nodeParams)
Creates a external semaphor wait node and adds it to a graph.
hipError_t hipGraphEventWaitNodeSetEvent(hipGraphNode_t node, hipEvent_t event)
Sets an event wait node's event.
hipError_t hipGraphEventRecordNodeSetEvent(hipGraphNode_t node, hipEvent_t event)
Sets an event record node's event.
hipError_t hipGraphEventWaitNodeGetEvent(hipGraphNode_t node, hipEvent_t *event_out)
Returns the event associated with an event wait node.
hipError_t hipGraphKernelNodeSetAttribute(hipGraphNode_t hNode, hipKernelNodeAttrID attr, const hipKernelNodeAttrValue *value)
Sets a node's attribute.
hipError_t hipGraphMemsetNodeSetParams(hipGraphNode_t node, const hipMemsetParams *pNodeParams)
Sets a memset node's parameters.
hipError_t hipGraphEventRecordNodeGetEvent(hipGraphNode_t node, hipEvent_t *event_out)
Returns the event associated with an event record node.
hipError_t hipGraphAddEmptyNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies)
Creates an empty node and adds it to a graph.
hipError_t hipGraphAddMemcpyNodeToSymbol(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, const void *symbol, const void *src, size_t count, size_t offset, hipMemcpyKind kind)
Creates a memcpy node to copy to a symbol on the device and adds it to a graph.
hipError_t hipGraphDestroy(hipGraph_t graph)
Destroys a graph.
hipError_t hipGraphRetainUserObject(hipGraph_t graph, hipUserObject_t object, unsigned int count, unsigned int flags)
Retain user object for graphs.
hipError_t hipGraphExecMemcpyNodeSetParamsFromSymbol(hipGraphExec_t hGraphExec, hipGraphNode_t node, void *dst, const void *symbol, size_t count, size_t offset, hipMemcpyKind kind)
Sets the parameters for a memcpy node in the given graphExec to copy from a symbol on the.
hipError_t hipGraphAddMemAllocNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, hipMemAllocNodeParams *pNodeParams)
Creates a memory allocation node and adds it to a graph.
hipError_t hipGraphAddHostNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, const hipHostNodeParams *pNodeParams)
Creates a host execution node and adds it to a graph.
hipError_t hipGraphAddNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, hipGraphNodeParams *nodeParams)
Creates a kernel execution node and adds it to a graph.
hipError_t hipGraphGetNodes(hipGraph_t graph, hipGraphNode_t *nodes, size_t *numNodes)
Returns a graph's nodes.
hipError_t hipGraphAddMemsetNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, const hipMemsetParams *pMemsetParams)
Creates a memset node and adds it to a graph.
hipError_t hipStreamUpdateCaptureDependencies(hipStream_t stream, hipGraphNode_t *dependencies, size_t numDependencies, unsigned int flags)
Update the set of dependencies in a capturing stream.
hipError_t hipGraphInstantiate(hipGraphExec_t *pGraphExec, hipGraph_t graph, hipGraphNode_t *pErrorNode, char *pLogBuffer, size_t bufferSize)
Creates an executable graph from a graph.
hipError_t hipDeviceGraphMemTrim(int device)
Free unused memory reserved for graphs on a specific device and return it back to the OS.
hipError_t hipGraphExternalSemaphoresWaitNodeGetParams(hipGraphNode_t hNode, hipExternalSemaphoreWaitNodeParams *params_out)
Returns external semaphore wait node params.
hipError_t hipGraphClone(hipGraph_t *pGraphClone, hipGraph_t originalGraph)
Clones a graph.
hipError_t hipGraphGetRootNodes(hipGraph_t graph, hipGraphNode_t *pRootNodes, size_t *pNumRootNodes)
Returns a graph's root nodes.
hipError_t hipGraphAddMemcpyNode(hipGraphNode_t *pGraphNode, hipGraph_t graph, const hipGraphNode_t *pDependencies, size_t numDependencies, const hipMemcpy3DParms *pCopyParams)
Creates a memcpy node and adds it to a graph.
hipError_t hipGraphicsUnregisterResource(hipGraphicsResource_t resource)
Unregisters a graphics resource.
hipError_t hipGraphicsUnmapResources(int count, hipGraphicsResource_t *resources, hipStream_t stream)
Unmaps graphics resources.
hipError_t hipGraphicsSubResourceGetMappedArray(hipArray_t *array, hipGraphicsResource_t resource, unsigned int arrayIndex, unsigned int mipLevel)
Get an array through which to access a subresource of a mapped graphics resource.
hipError_t hipGraphicsResourceGetMappedPointer(void **devPtr, size_t *size, hipGraphicsResource_t resource)
Gets device accessible address of a graphics resource.
hipError_t hipGraphicsMapResources(int count, hipGraphicsResource_t *resources, hipStream_t stream)
Maps a graphics resource for access.
hipLibraryOption
Definition linker_types.h:108
hipJitOption
Definition linker_types.h:31
hipJitInputType
Definition linker_types.h:76
hipError_t hipHostFree(void *ptr)
Free memory allocated by the HIP-Clang hip host memory allocation API This API performs an implicit h...
hipError_t hipMallocHost(void **ptr, size_t size)
Allocate pinned host memory [Deprecated].
hipError_t hipMemcpyToArray(hipArray_t dst, size_t wOffset, size_t hOffset, const void *src, size_t count, hipMemcpyKind kind)
Copies data between host and device [Deprecated].
hipError_t hipMemcpyFromArray(void *dst, hipArray_const_t srcArray, size_t wOffset, size_t hOffset, size_t count, hipMemcpyKind kind)
Copies data between host and device [Deprecated].
hipError_t hipMemAllocHost(void **ptr, size_t size)
Allocate pinned host memory [Deprecated].
hipError_t hipMemcpyAtoA(hipArray_t dstArray, size_t dstOffset, hipArray_t srcArray, size_t srcOffset, size_t ByteCount)
Copies from one 1D array to another.
hipError_t hipHostAlloc(void **ptr, size_t size, unsigned int flags)
Allocate device accessible page locked host memory.
hipError_t hipMemcpy3DBatchAsync(size_t numOps, struct hipMemcpy3DBatchOp *opList, size_t *failIdx, unsigned long long flags, hipStream_t stream)
Perform Batch of 3D copies.
hipError_t hipMemcpy2DArrayToArray(hipArray_t dst, size_t wOffsetDst, size_t hOffsetDst, hipArray_const_t src, size_t wOffsetSrc, size_t hOffsetSrc, size_t width, size_t height, hipMemcpyKind kind)
Copies data between host and device.
hipError_t hipMemsetD8Async(hipDeviceptr_t dest, unsigned char value, size_t count, hipStream_t stream)
Fills the first sizeBytes bytes of the memory area pointed to by dest with the constant byte value va...
hipError_t hipMemcpyAtoHAsync(void *dstHost, hipArray_t srcArray, size_t srcOffset, size_t ByteCount, hipStream_t stream)
Copies from one 1D array to host memory.
hipError_t hipFreeHost(void *ptr)
Frees page-locked memory This API performs an implicit hipDeviceSynchronize() call....
hipError_t hipMemset2DAsync(void *dst, size_t pitch, int value, size_t width, size_t height, hipStream_t stream)
Fills asynchronously the memory area pointed to by dst with the constant value.
hipError_t hipMemGetInfo(size_t *free, size_t *total)
Query memory info.
hipError_t hipExtMallocWithFlags(void **ptr, size_t sizeBytes, unsigned int flags)
Allocate memory on the default accelerator.
hipError_t hipMemcpy3D(const struct hipMemcpy3DParms *p)
Copies data between host and device.
hipError_t hipMalloc3DArray(hipArray_t *array, const struct hipChannelFormatDesc *desc, struct hipExtent extent, unsigned int flags)
Allocate an array on the device.
hipError_t hipArrayCreate(hipArray_t *pHandle, const HIP_ARRAY_DESCRIPTOR *pAllocateArray)
Create an array memory pointer on the device.
hipError_t hipMemset3D(hipPitchedPtr pitchedDevPtr, int value, hipExtent extent)
Fills synchronously the memory area pointed to by pitchedDevPtr with the constant value.
hipError_t hipMemsetD16(hipDeviceptr_t dest, unsigned short value, size_t count)
Fills the first sizeBytes bytes of the memory area pointed to by dest with the constant short value v...
hipError_t hipMemcpyAtoD(hipDeviceptr_t dstDevice, hipArray_t srcArray, size_t srcOffset, size_t ByteCount)
Copies from one 1D array to device memory.
hipError_t hipMalloc(void **ptr, size_t size)
Allocate memory on the default accelerator.
hipError_t hipHostUnregister(void *hostPtr)
Un-register host pointer.
hipError_t hipHostGetFlags(unsigned int *flagsPtr, void *hostPtr)
Return flags associated with host pointer.
hipError_t hipMemcpyFromSymbolAsync(void *dst, const void *symbol, size_t sizeBytes, size_t offset, hipMemcpyKind kind, hipStream_t stream)
Copies data from the given symbol on the device asynchronously.
hipError_t hipMemsetD2D32(hipDeviceptr_t dst, size_t dstPitch, unsigned int value, size_t width, size_t height)
Fills 2D memory range of 'width' 32-bit values synchronously to the specified int value....
hipError_t hipMemsetD32(hipDeviceptr_t dest, int value, size_t count)
Fills the memory area pointed to by dest with the constant integer value for specified number of time...
hipError_t hipMemset3DAsync(hipPitchedPtr pitchedDevPtr, int value, hipExtent extent, hipStream_t stream)
Fills asynchronously the memory area pointed to by pitchedDevPtr with the constant value.
hipError_t hipMemcpyFromSymbol(void *dst, const void *symbol, size_t sizeBytes, size_t offset, hipMemcpyKind kind)
Copies data from the given symbol on the device.
hipError_t hipDrvMemcpy3DAsync(const HIP_MEMCPY3D *pCopy, hipStream_t stream)
Copies data between host and device asynchronously.
hipError_t hipMemsetD2D32Async(hipDeviceptr_t dst, size_t dstPitch, unsigned int value, size_t width, size_t height, hipStream_t stream)
Fills 2D memory range of 'width' 32-bit values asynchronously to the specified int value....
hipError_t hipArray3DGetDescriptor(HIP_ARRAY3D_DESCRIPTOR *pArrayDescriptor, hipArray_t array)
Gets a 3D array descriptor.
hipError_t hipMemcpy2DAsync(void *dst, size_t dpitch, const void *src, size_t spitch, size_t width, size_t height, hipMemcpyKind kind, hipStream_t stream)
Copies data between host and device asynchronously.
hipError_t hipArrayGetDescriptor(HIP_ARRAY_DESCRIPTOR *pArrayDescriptor, hipArray_t array)
Gets a 1D or 2D array descriptor.
hipError_t hipFree(void *ptr)
Free memory allocated by the HIP-Clang hip memory allocation API. This API performs an implicit hipDe...
hipError_t hipMemcpyHtoAAsync(hipArray_t dstArray, size_t dstOffset, const void *srcHost, size_t ByteCount, hipStream_t stream)
Copies from host memory to a 1D array.
hipError_t hipMemsetD16Async(hipDeviceptr_t dest, unsigned short value, size_t count, hipStream_t stream)
Fills the first sizeBytes bytes of the memory area pointed to by dest with the constant short value v...
hipError_t hipGetProcAddress(const char *symbol, void **pfn, int hipVersion, uint64_t flags, hipDriverProcAddressQueryResult *symbolStatus)
Gets the pointer of requested HIP driver function.
hipError_t hipPointerGetAttributes(hipPointerAttribute_t *attributes, const void *ptr)
Returns attributes for the specified pointer.
hipError_t hipMallocPitch(void **ptr, size_t *pitch, size_t width, size_t height)
hipError_t hipMemcpy3DPeer(hipMemcpy3DPeerParms *p)
Performs 3D memory copies between devices This API is asynchronous with respect to host.
hipError_t hipMemcpyDtoD(hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes)
Copy data from Device to Device.
hipError_t hipMallocArray(hipArray_t *array, const hipChannelFormatDesc *desc, size_t width, size_t height, unsigned int flags)
Allocate an array on the device.
hipError_t hipMemcpy2D(void *dst, size_t dpitch, const void *src, size_t spitch, size_t width, size_t height, hipMemcpyKind kind)
Copies data between host and device.
hipError_t hipHostGetDevicePointer(void **devPtr, void *hstPtr, unsigned int flags)
Get Device pointer from Host Pointer allocated through hipHostMalloc.
hipError_t hipMemcpyDtoA(hipArray_t dstArray, size_t dstOffset, hipDeviceptr_t srcDevice, size_t ByteCount)
Copies from device memory to a 1D array.
hipError_t hipMemcpy2DFromArrayAsync(void *dst, size_t dpitch, hipArray_const_t src, size_t wOffset, size_t hOffset, size_t width, size_t height, hipMemcpyKind kind, hipStream_t stream)
Copies data between host and device asynchronously.
hipError_t hipMemsetD2D16Async(hipDeviceptr_t dst, size_t dstPitch, unsigned short value, size_t width, size_t height, hipStream_t stream)
Fills 2D memory range of 'width' 16-bit values asynchronously to the specified short value....
hipError_t hipMemcpy2DFromArray(void *dst, size_t dpitch, hipArray_const_t src, size_t wOffset, size_t hOffset, size_t width, size_t height, hipMemcpyKind kind)
Copies data between host and device.
hipError_t hipMemcpy3DAsync(const struct hipMemcpy3DParms *p, hipStream_t stream)
Copies data between host and device asynchronously.
hipError_t hipArray3DCreate(hipArray_t *array, const HIP_ARRAY3D_DESCRIPTOR *pAllocateArray)
Create a 3D array memory pointer on the device.
hipError_t hipArrayGetInfo(hipChannelFormatDesc *desc, hipExtent *extent, unsigned int *flags, hipArray_t array)
Gets info about the specified array.
hipError_t hipDrvMemcpy3D(const HIP_MEMCPY3D *pCopy)
Copies data between host and device.
hipError_t hipMemcpyParam2D(const hip_Memcpy2D *pCopy)
Copies memory for 2D arrays.
hipError_t hipMemcpyHtoA(hipArray_t dstArray, size_t dstOffset, const void *srcHost, size_t count)
Copies data between host and device.
hipError_t hipMemcpyToSymbolAsync(const void *symbol, const void *src, size_t sizeBytes, size_t offset, hipMemcpyKind kind, hipStream_t stream)
Copies data to the given symbol on the device asynchronously.
hipError_t hipHostMalloc(void **ptr, size_t size, unsigned int flags)
Allocates device accessible page locked (pinned) host memory.
hipError_t hipMemsetD2D8(hipDeviceptr_t dst, size_t dstPitch, unsigned char value, size_t width, size_t height)
Fills 2D memory range of 'width' 8-bit values synchronously to the specified char value....
hipError_t hipMemcpy2DToArrayAsync(hipArray_t dst, size_t wOffset, size_t hOffset, const void *src, size_t spitch, size_t width, size_t height, hipMemcpyKind kind, hipStream_t stream)
Copies data between host and device.
hipError_t hipHostRegister(void *hostPtr, size_t sizeBytes, unsigned int flags)
Register host memory so it can be accessed from the current device.
hipError_t hipMipmappedArrayGetMemoryRequirements(hipArrayMemoryRequirements *memoryRequirements, hipMipmappedArray_t mipmap, hipDevice_t device)
Returns the memory requirements of a HIP mipmapped array.
hipError_t hipMemsetD2D16(hipDeviceptr_t dst, size_t dstPitch, unsigned short value, size_t width, size_t height)
Fills 2D memory range of 'width' 16-bit values synchronously to the specified short value....
hipError_t hipMemcpyBatchAsync(void **dsts, void **srcs, size_t *sizes, size_t count, hipMemcpyAttributes *attrs, size_t *attrsIdxs, size_t numAttrs, size_t *failIdx, hipStream_t stream)
Perform Batch of 1D copies.
hipError_t hipMemcpyAtoH(void *dst, hipArray_t srcArray, size_t srcOffset, size_t count)
Copies data between host and device.
hipError_t hipMemcpyToSymbol(const void *symbol, const void *src, size_t sizeBytes, size_t offset, hipMemcpyKind kind)
Copies data to the given symbol on the device. Symbol HIP APIs allow a kernel to define a device-side...
hipError_t hipMemcpy(void *dst, const void *src, size_t sizeBytes, hipMemcpyKind kind)
Copy data from src to dst.
hipError_t hipMemset(void *dst, int value, size_t sizeBytes)
Fills the first sizeBytes bytes of the memory area pointed to by dest with the constant byte value va...
hipError_t hipMemGetAddressRange(hipDeviceptr_t *pbase, size_t *psize, hipDeviceptr_t dptr)
Get information on memory allocations.
hipError_t hipMemcpy2DToArray(hipArray_t dst, size_t wOffset, size_t hOffset, const void *src, size_t spitch, size_t width, size_t height, hipMemcpyKind kind)
Copies data between host and device.
hipError_t hipMemcpyParam2DAsync(const hip_Memcpy2D *pCopy, hipStream_t stream)
Copies memory for 2D arrays.
hipError_t hipDrvPointerGetAttributes(unsigned int numAttributes, hipPointer_attribute *attributes, void **data, hipDeviceptr_t ptr)
Returns information about the specified pointer.[BETA].
hipError_t hipMalloc3D(hipPitchedPtr *pitchedDevPtr, hipExtent extent)
Create a 3D memory pointer on the device.
hipError_t hipPointerSetAttribute(const void *value, hipPointer_attribute attribute, hipDeviceptr_t ptr)
Sets information on the specified pointer.[BETA].
hipError_t hipMemcpyDtoDAsync(hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream)
Copy data from Device to Device asynchronously.
hipError_t hipMemAllocPitch(hipDeviceptr_t *dptr, size_t *pitch, size_t widthInBytes, size_t height, unsigned int elementSizeBytes)
hipError_t hipMemsetD8(hipDeviceptr_t dest, unsigned char value, size_t count)
Fills the first sizeBytes bytes of the memory area pointed to by dest with the constant byte value va...
hipError_t hipMemcpyAsync(void *dst, const void *src, size_t sizeBytes, hipMemcpyKind kind, hipStream_t stream)
Copies data from src to dst asynchronously.
hipError_t hipMemcpyDtoHAsync(void *dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream)
Copy data from Device to Host asynchronously.
hipError_t hipFreeArray(hipArray_t array)
Frees an array on the device.
hipError_t hipMemcpyHtoD(hipDeviceptr_t dst, const void *src, size_t sizeBytes)
Copy data from Host to Device.
hipError_t hipMemsetD32Async(hipDeviceptr_t dst, int value, size_t count, hipStream_t stream)
Fills the memory area pointed to by dev with the constant integer value for specified number of times...
hipError_t hipMemset2D(void *dst, size_t pitch, int value, size_t width, size_t height)
Fills the memory area pointed to by dst with the constant value.
hipError_t hipGetSymbolSize(size_t *size, const void *symbol)
Gets the size of the given symbol on the device.
hipError_t hipMemcpyDtoH(void *dst, hipDeviceptr_t src, size_t sizeBytes)
Copy data from Device to Host.
hipError_t hipMemcpyHtoDAsync(hipDeviceptr_t dst, const void *src, size_t sizeBytes, hipStream_t stream)
Copy data from Host to Device asynchronously.
hipError_t hipMemsetAsync(void *dst, int value, size_t sizeBytes, hipStream_t stream)
Fills the first sizeBytes bytes of the memory area pointed to by dev with the constant byte value val...
hipError_t hipMemcpyWithStream(void *dst, const void *src, size_t sizeBytes, hipMemcpyKind kind, hipStream_t stream)
Memory copy on the stream. It allows single or multiple devices to do memory copy on single or multip...
hipError_t hipGetSymbolAddress(void **devPtr, const void *symbol)
Gets device pointer associated with symbol on the device.
hipError_t hipPointerGetAttribute(void *data, hipPointer_attribute attribute, hipDeviceptr_t ptr)
Returns information about the specified pointer.[BETA].
hipError_t hipMemsetD2D8Async(hipDeviceptr_t dst, size_t dstPitch, unsigned char value, size_t width, size_t height, hipStream_t stream)
Fills 2D memory range of 'width' 8-bit values asynchronously to the specified char value....
hipError_t hipMemcpy3DPeerAsync(hipMemcpy3DPeerParms *p, hipStream_t stream)
Performs 3D memory copies between devices asynchronously.
hipError_t hipMemPtrGetInfo(void *ptr, size_t *size)
Get allocated memory size via memory pointer.
hipError_t hipArrayDestroy(hipArray_t array)
Destroy an array memory pointer on the device.
hipError_t hipMemPrefetchAsync(const void *dev_ptr, size_t count, int device, hipStream_t stream)
Prefetches memory to the specified destination device using HIP.
hipError_t hipMemPrefetchBatchAsync(void **dev_ptrs, size_t *sizes, size_t count, hipMemLocation *prefetch_locs, size_t *prefetch_loc_idxs, size_t num_prefetch_locs, unsigned long long flags, hipStream_t stream)
Prefetches a batch of memory ranges to the specified locations using HIP.
hipError_t hipMemPrefetchAsync_v2(const void *dev_ptr, size_t count, hipMemLocation location, unsigned int flags, hipStream_t stream)
Prefetches memory to the specified destination device using HIP.
hipError_t hipDrvMemDiscardBatchAsync(hipDeviceptr_t *dptrs, size_t *sizes, size_t count, unsigned long long flags, hipStream_t stream)
Discards a batch of memory ranges asynchronously (driver API variant).
hipError_t hipMemRangeGetAttributes(void **data, size_t *data_sizes, hipMemRangeAttribute *attributes, size_t num_attributes, const void *dev_ptr, size_t count)
Query attributes of a given memory range in HIP.
hipError_t hipMemDiscardAndPrefetchBatchAsync(void **dptrs, size_t *sizes, size_t count, hipMemLocation *prefetchLocs, size_t *prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, hipStream_t stream)
Discards and prefetches a batch of memory ranges asynchronously.
hipError_t hipDrvMemDiscardAndPrefetchBatchAsync(hipDeviceptr_t *dptrs, size_t *sizes, size_t count, hipMemLocation *prefetchLocs, size_t *prefetchLocIdxs, size_t numPrefetchLocs, unsigned long long flags, hipStream_t stream)
Discards and prefetches a batch of memory ranges asynchronously (driver API variant).
hipError_t hipMemRangeGetAttribute(void *data, size_t data_size, hipMemRangeAttribute attribute, const void *dev_ptr, size_t count)
Query an attribute of a given memory range in HIP.
hipError_t hipMallocManaged(void **dev_ptr, size_t size, unsigned int flags)
Allocates memory that will be automatically managed by HIP.
hipError_t hipStreamAttachMemAsync(hipStream_t stream, void *dev_ptr, size_t length, unsigned int flags)
Attach memory to a stream asynchronously in HIP.
hipError_t hipMemDiscardBatchAsync(void **dev_ptrs, size_t *sizes, size_t count, unsigned long long flags, hipStream_t stream)
Discards a batch of memory ranges asynchronously.
hipError_t hipMemAdvise_v2(const void *dev_ptr, size_t count, hipMemoryAdvise advice, hipMemLocation location)
hipError_t hipModuleLaunchCooperativeKernelMultiDevice(hipFunctionLaunchParams *launchParamsList, unsigned int numDevices, unsigned int flags)
Launches kernels on multiple devices where thread blocks can cooperate and synchronize as they execut...
hipError_t hipLaunchCooperativeKernelMultiDevice(hipLaunchParams *launchParamsList, int numDevices, unsigned int flags)
Launches kernels on multiple devices where thread blocks can cooperate and synchronize as they execut...
hipError_t hipModuleLaunchCooperativeKernel(hipFunction_t f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY, unsigned int blockDimZ, unsigned int sharedMemBytes, hipStream_t stream, void **kernelParams)
launches kernel f with launch parameters and shared memory on stream with arguments passed to kernelP...
hipError_t hipLaunchCooperativeKernel(const void *f, dim3 gridDim, dim3 blockDimX, void **kernelParams, unsigned int sharedMemBytes, hipStream_t stream)
Launches kernel f with launch parameters and shared memory on stream with arguments passed to kernelp...
hipError_t hipModuleEnumerateFunctions(hipFunction_t *functions, unsigned int numFunctions, hipModule_t mod)
Returns the function handles within a module.
hipError_t hipModuleGetTexRef(textureReference **texRef, hipModule_t hmod, const char *name)
returns the handle of the texture reference with the name from the module.
hipError_t hipLinkComplete(hipLinkState_t state, void **hipBinOut, size_t *sizeOut)
Completes the linking of the given program.
hipError_t hipModuleGetFunctionCount(unsigned int *count, hipModule_t mod)
Returns the number of functions within a module.
hipError_t hipModuleLoad(hipModule_t *module, const char *fname)
Loads code object from file into a module the currrent context.
hipError_t hipModuleGetGlobal(hipDeviceptr_t *dptr, size_t *bytes, hipModule_t hmod, const char *name)
Returns a global pointer from a module.
hipError_t hipModuleLoadDataEx(hipModule_t *module, const void *image, unsigned int numOptions, hipJitOption *options, void **optionValues)
builds module from code object which resides in host memory. Image is pointer to that location....
hipError_t hipLibraryUnload(hipLibrary_t library)
Unload HIP Library.
hipError_t hipLinkAddFile(hipLinkState_t state, hipJitInputType type, const char *path, unsigned int numOptions, hipJitOption *options, void **optionValues)
Adds a file with bitcode to be linked with options.
hipError_t hipGetFuncBySymbol(hipFunction_t *functionPtr, const void *symbolPtr)
Gets pointer to device entry function that matches entry function symbolPtr.
hipError_t hipLinkDestroy(hipLinkState_t state)
Deletes the linker instance.
hipError_t hipLibraryLoadFromFile(hipLibrary_t *library, const char *fileName, hipJitOption *jitOptions, void **jitOptionsValues, unsigned int numJitOptions, hipLibraryOption *libraryOptions, void **libraryOptionValues, unsigned int numLibraryOptions)
Load hip Library from file.
hipError_t hipMemGetHandleForAddressRange(void *handle, hipDeviceptr_t dptr, size_t size, hipMemRangeHandleType handleType, unsigned long long flags)
Returns a handle for the address range requested.
hipError_t hipLibraryEnumerateKernels(hipKernel_t *kernels, unsigned int numKernels, hipLibrary_t library)
Retrieve kernel handles within a library.
hipError_t hipLibraryGetKernel(hipKernel_t *pKernel, hipLibrary_t library, const char *name)
Get Kernel object from library.
hipError_t hipKernelGetName(const char **name, hipKernel_t kernel)
Returns a Kernel Name.
hipError_t hipModuleGetFunction(hipFunction_t *function, hipModule_t module, const char *kname)
Function with kname will be extracted if present in module.
hipError_t hipLinkCreate(unsigned int numOptions, hipJitOption *options, void **optionValues, hipLinkState_t *stateOut)
Creates a linker instance with options.
hipError_t hipLibraryGetGlobal(void **dptr, size_t *bytes, hipLibrary_t library, const char *name)
Get device pointer to a __device__ global variable defined in a library.
hipError_t hipGetDriverEntryPoint(const char *symbol, void **funcPtr, unsigned long long flags, hipDriverEntryPointQueryResult *driverStatus)
Gets function pointer of a requested HIP API.
hipError_t hipModuleLoadData(hipModule_t *module, const void *image)
builds module from code object data which resides in host memory.
hipError_t hipLibraryGetKernelCount(unsigned int *count, hipLibrary_t library)
Get Kernel count in library.
hipError_t hipKernelGetParamInfo(hipKernel_t kernel, size_t paramIndex, size_t *paramOffset, size_t *paramSize)
Returns the offset and size of a kernel parameter.
hipError_t hipKernelGetAttribute(int *pi, hipFunction_attribute attrib, hipKernel_t kernel, hipDevice_t dev)
Returns information about a kernel.
hipError_t hipModuleLoadFatBinary(hipModule_t *module, const void *fatbin)
Loads fatbin object.
hipError_t hipLibraryLoadData(hipLibrary_t *library, const void *code, hipJitOption *jitOptions, void **jitOptionsValues, unsigned int numJitOptions, hipLibraryOption *libraryOptions, void **libraryOptionValues, unsigned int numLibraryOptions)
Load hip Library from inmemory object.
hipError_t hipModuleUnload(hipModule_t module)
Frees the module.
hipError_t hipKernelGetLibrary(hipLibrary_t *library, hipKernel_t kernel)
Returns a Library Handle.
hipError_t hipLibraryGetManaged(void **dptr, size_t *bytes, hipLibrary_t library, const char *name)
Get host pointer to a __managed__ variable defined in a library.
hipError_t hipLinkAddData(hipLinkState_t state, hipJitInputType type, void *data, size_t size, const char *name, unsigned int numOptions, hipJitOption *options, void **optionValues)
Adds bitcode data to be linked with options.
hipError_t hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int *numBlocks, const void *f, int blockSize, size_t dynSharedMemPerBlk, unsigned int flags)
Returns occupancy for a device function.
hipError_t hipOccupancyAvailableDynamicSMemPerBlock(size_t *dynamicSmemSize, const void *f, int numBlocks, int blockSize)
Returns dynamic shared memory available per block when launching numBlocks blocks on SM.
hipError_t hipModuleOccupancyMaxPotentialBlockSize(int *gridSize, int *blockSize, hipFunction_t f, size_t dynSharedMemPerBlk, int blockSizeLimit)
determine the grid and block sizes to achieves maximum occupancy for a kernel
hipError_t hipOccupancyMaxActiveBlocksPerMultiprocessor(int *numBlocks, const void *f, int blockSize, size_t dynSharedMemPerBlk)
Returns occupancy for a device function.
hipError_t hipOccupancyMaxPotentialBlockSize(int *gridSize, int *blockSize, const void *f, size_t dynSharedMemPerBlk, int blockSizeLimit)
determine the grid and block sizes to achieves maximum occupancy for a kernel
hipError_t hipOccupancyMaxActiveClusters(int *numClusters, const void *f, const hipLaunchConfig_t *config)
determines the amount of active kernel clusters can co-exist at the same time in a device
hipError_t hipOccupancyMaxPotentialClusterSize(int *clusterSize, const void *f, const hipLaunchConfig_t *config)
returns the maximum cluster size (in number of blocks) that can run on the device
hipError_t hipModuleOccupancyMaxActiveBlocksPerMultiprocessor(int *numBlocks, hipFunction_t f, int blockSize, size_t dynSharedMemPerBlk)
Returns occupancy for a device function.
hipError_t hipModuleOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int *numBlocks, hipFunction_t f, int blockSize, size_t dynSharedMemPerBlk, unsigned int flags)
Returns occupancy for a device function.
hipError_t hipModuleOccupancyMaxPotentialBlockSizeWithFlags(int *gridSize, int *blockSize, hipFunction_t f, size_t dynSharedMemPerBlk, int blockSizeLimit, unsigned int flags)
determine the grid and block sizes to achieves maximum occupancy for a kernel
hipError_t hipDeviceCanAccessPeer(int *canAccessPeer, int deviceId, int peerDeviceId)
Determines if a device can access a peer device's memory.
hipError_t hipDeviceEnablePeerAccess(int peerDeviceId, unsigned int flags)
Enables direct access to memory allocations on a peer device.
hipError_t hipMemcpyPeer(void *dst, int dstDeviceId, const void *src, int srcDeviceId, size_t sizeBytes)
Copies memory between two peer accessible devices.
hipError_t hipMemcpyPeerAsync(void *dst, int dstDeviceId, const void *src, int srcDevice, size_t sizeBytes, hipStream_t stream)
Copies memory between two peer accessible devices asynchronously.
hipError_t hipDeviceDisablePeerAccess(int peerDeviceId)
Disables direct access to memory allocations on a peer device.
hipError_t hipProfilerStart()
Start recording of profiling information [Deprecated] When using this API, start the profiler with pr...
hipError_t hipProfilerStop()
Stop recording of profiling information [Deprecated] When using this API, start the profiler with pro...
hipError_t hipStreamGetId(hipStream_t stream, unsigned long long *streamId)
Queries the Id of a stream.
hipError_t hipDeviceGetStreamPriorityRange(int *leastPriority, int *greatestPriority)
Returns numerical values that correspond to the least and greatest stream priority.
hipError_t hipStreamDestroy(hipStream_t stream)
Destroys the specified stream.
hipError_t hipStreamGetFlags(hipStream_t stream, unsigned int *flags)
Returns flags associated with this stream.
hipError_t hipStreamAddCallback(hipStream_t stream, hipStreamCallback_t callback, void *userData, unsigned int flags)
Adds a callback to be called on the host after all currently enqueued items in the stream have comple...
hipError_t hipStreamCopyAttributes(hipStream_t dst, hipStream_t src)
Copies attributes from source stream to destination stream.
void(* hipStreamCallback_t)(hipStream_t stream, hipError_t status, void *userData)
Definition hip_runtime_api.h:3411
hipError_t hipStreamGetDevice(hipStream_t stream, hipDevice_t *device)
Gets the device associated with the stream.
hipError_t hipStreamQuery(hipStream_t stream)
Returns hipSuccess if all of the operations in the specified stream have completed,...
hipError_t hipStreamSynchronize(hipStream_t stream)
Waits for all commands in the stream to complete.
hipError_t hipStreamSetAttribute(hipStream_t stream, hipStreamAttrID attr, const hipStreamAttrValue *value)
Sets stream attribute. Updated attribute is applied to work submitted to the stream.
hipError_t hipStreamWaitEvent(hipStream_t stream, hipEvent_t event, unsigned int flags)
Makes the specified compute stream wait for the specified event.
hipError_t hipStreamCreateWithPriority(hipStream_t *stream, unsigned int flags, int priority)
Creates an asynchronous stream with the specified priority.
hipError_t hipExtStreamCreateWithCUMask(hipStream_t *stream, uint32_t cuMaskSize, const uint32_t *cuMask)
Creates an asynchronous stream with the specified CU mask.
hipError_t hipStreamGetPriority(hipStream_t stream, int *priority)
Queries the priority of a stream.
hipError_t hipExtStreamGetCUMask(hipStream_t stream, uint32_t cuMaskSize, uint32_t *cuMask)
Gets CU mask associated with an asynchronous stream.
hipError_t hipStreamGetAttribute(hipStream_t stream, hipStreamAttrID attr, hipStreamAttrValue *value_out)
queries stream attribute.
hipError_t hipStreamCreateWithFlags(hipStream_t *stream, unsigned int flags)
Creates an asynchronous stream with flag.
hipError_t hipStreamCreate(hipStream_t *stream)
Creates an asynchronous stream.
hipError_t hipStreamWriteValue64(hipStream_t stream, void *ptr, uint64_t value, unsigned int flags)
Enqueues a write command to the stream.[BETA].
hipError_t hipStreamWriteValue32(hipStream_t stream, void *ptr, uint32_t value, unsigned int flags)
Enqueues a write command to the stream.[BETA].
hipError_t hipGraphExecBatchMemOpNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, const hipBatchMemOpNodeParams *nodeParams)
Sets the parameters for a batch mem op node in the given graphExec.[BETA].
hipError_t hipGraphAddBatchMemOpNode(hipGraphNode_t *phGraphNode, hipGraph_t hGraph, const hipGraphNode_t *dependencies, size_t numDependencies, const hipBatchMemOpNodeParams *nodeParams)
Creates a batch memory operation node and adds it to a graph.[BETA].
hipError_t hipStreamWaitValue64(hipStream_t stream, void *ptr, uint64_t value, unsigned int flags, uint64_t mask)
Enqueues a wait command to the stream.[BETA].
hipError_t hipGraphBatchMemOpNodeGetParams(hipGraphNode_t hNode, hipBatchMemOpNodeParams *nodeParams_out)
Returns a batch mem op node's parameters.[BETA].
hipError_t hipStreamBatchMemOp(hipStream_t stream, unsigned int count, hipStreamBatchMemOpParams *paramArray, unsigned int flags)
Enqueues an array of stream memory operations in the stream.[BETA].
hipError_t hipGraphBatchMemOpNodeSetParams(hipGraphNode_t hNode, hipBatchMemOpNodeParams *nodeParams)
Sets the batch mem op node's parameters.[BETA].
hipError_t hipStreamWaitValue32(hipStream_t stream, void *ptr, uint32_t value, unsigned int flags, uint32_t mask)
Enqueues a wait command to the stream.[BETA].
hipError_t hipMemPoolImportPointer(void **dev_ptr, hipMemPool_t mem_pool, hipMemPoolPtrExportData *export_data)
Import a memory pool allocation from another process.
hipError_t hipMemPoolImportFromShareableHandle(hipMemPool_t *mem_pool, void *shared_handle, hipMemAllocationHandleType handle_type, unsigned int flags)
Imports a memory pool from a shared handle.
hipError_t hipMallocFromPoolAsync(void **dev_ptr, size_t size, hipMemPool_t mem_pool, hipStream_t stream)
Allocates memory from a specified pool with stream ordered semantics.
hipError_t hipMemGetDefaultMemPool(hipMemPool_t *memPool, hipMemLocation *location, hipMemAllocationType type)
Returns the default memory pool for a given location and allocation type.
hipError_t hipMemSetMemPool(hipMemLocation *location, hipMemAllocationType type, hipMemPool_t pool)
Sets memory pool for memory location and allocation type.
hipError_t hipFreeAsync(void *dev_ptr, hipStream_t stream)
Frees memory with stream ordered semantics.
hipError_t hipMemPoolTrimTo(hipMemPool_t mem_pool, size_t min_bytes_to_hold)
Releases freed memory back to the OS.
hipError_t hipMemPoolCreate(hipMemPool_t *mem_pool, const hipMemPoolProps *pool_props)
Creates a memory pool.
hipError_t hipMemPoolSetAccess(hipMemPool_t mem_pool, const hipMemAccessDesc *desc_list, size_t count)
Controls visibility of the specified pool between devices.
hipError_t hipMemPoolDestroy(hipMemPool_t mem_pool)
Destroys the specified memory pool.
hipError_t hipMemPoolSetAttribute(hipMemPool_t mem_pool, hipMemPoolAttr attr, void *value)
Sets attributes of a memory pool.
hipError_t hipMemPoolGetAttribute(hipMemPool_t mem_pool, hipMemPoolAttr attr, void *value)
Gets attributes of a memory pool.
hipError_t hipMemPoolExportToShareableHandle(void *shared_handle, hipMemPool_t mem_pool, hipMemAllocationHandleType handle_type, unsigned int flags)
Exports a memory pool to the requested handle type.
hipError_t hipMemPoolExportPointer(hipMemPoolPtrExportData *export_data, void *dev_ptr)
Export data to share a memory pool allocation between processes.
hipError_t hipMallocAsync(void **dev_ptr, size_t size, hipStream_t stream)
Allocates memory with stream ordered semantics.
hipError_t hipMemPoolGetAccess(hipMemAccessFlags *flags, hipMemPool_t mem_pool, hipMemLocation *location)
Returns the accessibility of a pool from a device.
hipError_t hipMemGetMemPool(hipMemPool_t *pool, hipMemLocation *location, hipMemAllocationType type)
Retrieves memory pool for memory location and allocation type.
hipError_t hipDestroySurfaceObject(hipSurfaceObject_t surfaceObject)
Destroy a surface object.
hipError_t hipExtEnableLogging()
Enable HIP runtime logging.
hipError_t hipCreateSurfaceObject(hipSurfaceObject_t *pSurfObject, const hipResourceDesc *pResDesc)
Create a surface object.
hipError_t hipExtDisableLogging()
Disable HIP runtime logging.
hipError_t hipExtSetLoggingParams(size_t log_level, size_t log_size, size_t log_mask)
Set HIP runtime logging parameters.
hipError_t hipTexRefGetFilterMode(enum hipTextureFilterMode *pfm, const textureReference *texRef)
Gets filter mode for a texture reference [Deprecated].
hipError_t hipBindTextureToMipmappedArray(const textureReference *tex, hipMipmappedArray_const_t mipmappedArray, const hipChannelFormatDesc *desc)
Binds a mipmapped array to a texture [Deprecated].
hipError_t hipTexRefGetMipmapLevelClamp(float *pminMipmapLevelClamp, float *pmaxMipmapLevelClamp, const textureReference *texRef)
Gets the minimum and maximum mipmap level clamps for a texture reference [Deprecated].
hipError_t hipTexRefGetAddressMode(enum hipTextureAddressMode *pam, const textureReference *texRef, int dim)
Gets the address mode for a texture reference [Deprecated].
hipError_t hipTexRefGetFlags(unsigned int *pFlags, const textureReference *texRef)
Gets flags for a texture reference [Deprecated].
hipError_t hipTexRefSetAddress(size_t *ByteOffset, textureReference *texRef, hipDeviceptr_t dptr, size_t bytes)
Sets an bound address for a texture reference [Deprecated].
hipError_t hipTexRefSetFilterMode(textureReference *texRef, enum hipTextureFilterMode fm)
Set filter mode for a texture reference [Deprecated].
hipError_t hipTexRefSetMipmappedArray(textureReference *texRef, struct hipMipmappedArray *mipmappedArray, unsigned int Flags)
Binds mipmapped array to a texture reference [Deprecated].
hipError_t hipTexRefGetMipmapFilterMode(enum hipTextureFilterMode *pfm, const textureReference *texRef)
Gets the mipmap filter mode for a texture reference [Deprecated].
hipError_t hipGetTextureAlignmentOffset(size_t *offset, const textureReference *texref)
Get the offset of the alignment in a texture [Deprecated].
hipError_t hipBindTexture2D(size_t *offset, const textureReference *tex, const void *devPtr, const hipChannelFormatDesc *desc, size_t width, size_t height, size_t pitch)
Binds a 2D memory area to a texture [Deprecated].
hipError_t hipTexRefGetMaxAnisotropy(int *pmaxAnsio, const textureReference *texRef)
Gets the maximum anisotropy for a texture reference [Deprecated].
hipError_t hipBindTexture(size_t *offset, const textureReference *tex, const void *devPtr, const hipChannelFormatDesc *desc, size_t size)
Binds a memory area to a texture [Deprecated].
hipError_t hipUnbindTexture(const textureReference *tex)
Unbinds a texture [Deprecated].
hipError_t hipTexRefGetBorderColor(float *pBorderColor, const textureReference *texRef)
Gets the border color used by a texture reference [Deprecated].
hipError_t hipTexRefSetFormat(textureReference *texRef, hipArray_Format fmt, int NumPackedComponents)
Set format for a texture reference [Deprecated].
hipError_t hipTexRefGetAddress(hipDeviceptr_t *dev_ptr, const textureReference *texRef)
Gets the address for a texture reference [Deprecated].
hipError_t hipTexRefGetArray(hipArray_t *pArray, const textureReference *texRef)
Gets the array bound to a texture reference [Deprecated].
hipError_t hipTexRefSetFlags(textureReference *texRef, unsigned int Flags)
Set flags for a texture reference [Deprecated].
hipError_t hipTexRefSetAddressMode(textureReference *texRef, int dim, enum hipTextureAddressMode am)
Sets address mode for a texture reference [Deprecated].
hipError_t hipTexRefGetMipMappedArray(hipMipmappedArray_t *pArray, const textureReference *texRef)
Gets the mipmapped array bound to a texture reference [Deprecated].
hipError_t hipTexRefSetMaxAnisotropy(textureReference *texRef, unsigned int maxAniso)
Sets the maximum anisotropy for a texture reference [Deprecated].
hipError_t hipTexRefSetMipmapLevelClamp(textureReference *texRef, float minMipMapLevelClamp, float maxMipMapLevelClamp)
Sets mipmap level clamp for a texture reference [Deprecated].
hipError_t hipTexRefSetBorderColor(textureReference *texRef, float *pBorderColor)
Sets border color for a texture reference [Deprecated].
hipError_t hipTexRefSetArray(textureReference *tex, hipArray_const_t array, unsigned int flags)
Binds an array as a texture reference [Deprecated].
hipError_t hipTexRefSetMipmapLevelBias(textureReference *texRef, float bias)
Sets mipmap level bias for a texture reference [Deprecated].
hipError_t hipTexRefGetMipmapLevelBias(float *pbias, const textureReference *texRef)
Gets the mipmap level bias for a texture reference [Deprecated].
hipError_t hipBindTextureToArray(const textureReference *tex, hipArray_const_t array, const hipChannelFormatDesc *desc)
Binds a memory area to a texture [Deprecated].
hipError_t hipGetTextureReference(const textureReference **texref, const void *symbol)
Gets the texture reference related with the symbol [Deprecated].
hipError_t hipTexRefSetAddress2D(textureReference *texRef, const HIP_ARRAY_DESCRIPTOR *desc, hipDeviceptr_t dptr, size_t Pitch)
Set a bind an address as a 2D texture reference [Deprecated].
hipError_t hipTexRefSetMipmapFilterMode(textureReference *texRef, enum hipTextureFilterMode fm)
Sets mipmap filter mode for a texture reference [Deprecated].
hipError_t hipTexRefGetFormat(hipArray_Format *pFormat, int *pNumChannels, const textureReference *texRef)
Gets texture format for a texture reference [Deprecated].
hipError_t hipFreeMipmappedArray(hipMipmappedArray_t mipmappedArray)
Frees a mipmapped array on the device.
hipError_t hipGetMipmappedArrayLevel(hipArray_t *levelArray, hipMipmappedArray_const_t mipmappedArray, unsigned int level)
Gets a mipmap level of a HIP mipmapped array.
hipError_t hipMipmappedArrayGetLevel(hipArray_t *pLevelArray, hipMipmappedArray_t hMipMappedArray, unsigned int level)
Get a mipmapped array on a mipmapped level.
hipError_t hipMipmappedArrayDestroy(hipMipmappedArray_t hMipmappedArray)
Destroy a mipmapped array.
hipError_t hipTexObjectCreate(hipTextureObject_t *pTexObject, const HIP_RESOURCE_DESC *pResDesc, const HIP_TEXTURE_DESC *pTexDesc, const HIP_RESOURCE_VIEW_DESC *pResViewDesc)
Creates a texture object.
hipError_t hipGetTextureObjectResourceDesc(hipResourceDesc *pResDesc, hipTextureObject_t textureObject)
Gets resource descriptor for the texture object.
hipError_t hipGetTextureObjectResourceViewDesc(struct hipResourceViewDesc *pResViewDesc, hipTextureObject_t textureObject)
Gets resource view descriptor for the texture object.
hipError_t hipTexObjectGetTextureDesc(HIP_TEXTURE_DESC *pTexDesc, hipTextureObject_t texObject)
Gets texture descriptor of a texture object.
hipError_t hipCreateTextureObject(hipTextureObject_t *pTexObject, const hipResourceDesc *pResDesc, const hipTextureDesc *pTexDesc, const struct hipResourceViewDesc *pResViewDesc)
Creates a texture object.
hipError_t hipTexObjectDestroy(hipTextureObject_t texObject)
Destroys a texture object.
hipError_t hipMipmappedArrayCreate(hipMipmappedArray_t *pHandle, HIP_ARRAY3D_DESCRIPTOR *pMipmappedArrayDesc, unsigned int numMipmapLevels)
Create a mipmapped array.
hipError_t hipGetChannelDesc(hipChannelFormatDesc *desc, hipArray_const_t array)
Gets the channel descriptor in an array.
hipError_t hipTexObjectGetResourceDesc(HIP_RESOURCE_DESC *pResDesc, hipTextureObject_t texObject)
Gets resource descriptor of a texture object.
hipError_t hipTexObjectGetResourceViewDesc(HIP_RESOURCE_VIEW_DESC *pResViewDesc, hipTextureObject_t texObject)
Gets resource view descriptor of a texture object.
hipError_t hipMallocMipmappedArray(hipMipmappedArray_t *mipmappedArray, const struct hipChannelFormatDesc *desc, struct hipExtent extent, unsigned int numLevels, unsigned int flags)
Allocate a mipmapped array on the device.
hipError_t hipDestroyTextureObject(hipTextureObject_t textureObject)
Destroys a texture object.
hipError_t hipGetTextureObjectTextureDesc(hipTextureDesc *pTexDesc, hipTextureObject_t textureObject)
Gets texture descriptor for the texture object.
hipError_t hipMemAddressFree(void *devPtr, size_t size)
Frees an address range reservation made via hipMemAddressReserve.
hipError_t hipMemExportToShareableHandle(void *shareableHandle, hipMemGenericAllocationHandle_t handle, hipMemAllocationHandleType handleType, unsigned long long flags)
Exports an allocation to a requested shareable handle type.
hipError_t hipMemGetAccess(unsigned long long *flags, const hipMemLocation *location, void *ptr)
Get the access flags set for the given location and ptr.
hipError_t hipMemSetAccess(void *ptr, size_t size, const hipMemAccessDesc *desc, size_t count)
Set the access flags for each location specified in desc for the given virtual address range.
hipError_t hipMemRelease(hipMemGenericAllocationHandle_t handle)
Release a memory handle representing a memory allocation which was previously allocated through hipMe...
hipError_t hipMemUnmap(void *ptr, size_t size)
Unmap memory allocation of a given address range.
hipError_t hipMemGetAllocationGranularity(size_t *granularity, const hipMemAllocationProp *prop, hipMemAllocationGranularity_flags option)
Calculates either the minimal or recommended granularity.
hipError_t hipMemRetainAllocationHandle(hipMemGenericAllocationHandle_t *handle, void *addr)
Returns the allocation handle of the backing memory allocation given the address.
hipError_t hipMemCreate(hipMemGenericAllocationHandle_t *handle, size_t size, const hipMemAllocationProp *prop, unsigned long long flags)
Creates a memory handle for the allocation described by the properties and given size.
hipError_t hipMemMap(void *ptr, size_t size, size_t offset, hipMemGenericAllocationHandle_t handle, unsigned long long flags)
Maps an allocation handle to a reserved virtual address range.
hipError_t hipMemAddressReserve(void **ptr, size_t size, size_t alignment, void *addr, unsigned long long flags)
Reserves an address range.
hipError_t hipMemGetAllocationPropertiesFromHandle(hipMemAllocationProp *prop, hipMemGenericAllocationHandle_t handle)
Retrieve the property structure of the given handle.
hipError_t hipMemMapArrayAsync(hipArrayMapInfo *mapInfoList, unsigned int count, hipStream_t stream)
Maps or unmaps subregions of sparse HIP arrays and sparse HIP mipmapped arrays.
hipError_t hipMemImportFromShareableHandle(hipMemGenericAllocationHandle_t *handle, void *osHandle, hipMemAllocationHandleType shHandleType)
Imports an allocation from a requested shareable handle type.
Definition hip_deprecated.h:13
hipErrorStreamDetached
The stream is detached.
Definition hip_runtime_api.h:222
hipErrorIllegalAddress
Definition hip_runtime_api.h:172
hipErrorMemoryAllocation
Memory allocation error.
Definition hip_runtime_api.h:118
hipErrorNotFound
Not found.
Definition hip_runtime_api.h:167
hipErrorProfilerDisabled
Definition hip_runtime_api.h:123
hipErrorInvalidDevicePointer
Invalid Device Pointer.
Definition hip_runtime_api.h:130
@ HIP_ERROR_LAUNCH_OUT_OF_RESOURCES
Definition hip_runtime_api.h:41
@ HIP_ERROR_INVALID_VALUE
Definition hip_runtime_api.h:39
@ HIP_SUCCESS
Definition hip_runtime_api.h:38
@ HIP_ERROR_NOT_INITIALIZED
Definition hip_runtime_api.h:40
hipErrorRuntimeMemory
Definition hip_runtime_api.h:225
hipErrorInvalidImage
Invalid image.
Definition hip_runtime_api.h:138
hipErrorPeerAccessUnsupported
Definition hip_runtime_api.h:155
hipErrorArrayIsMapped
Definition hip_runtime_api.h:145
hipErrorStreamCaptureIsolation
Definition hip_runtime_api.h:200
hipErrorInvalidKernelFile
In CUDA DRV, it is CUDA_ERROR_INVALID_PTX.
Definition hip_runtime_api.h:156
hipErrorNotMapped
Definition hip_runtime_api.h:149
hipErrorInvalidClusterSize
calculations
Definition hip_runtime_api.h:229
hipErrorGraphExecUpdateFailure
Definition hip_runtime_api.h:213
hipErrorNotInitialized
Invalid not initialized.
Definition hip_runtime_api.h:119
hipErrorInvalidResourceHandle
Resource handle (hipEvent_t or hipStream_t) invalid.
Definition hip_runtime_api.h:165
hipErrorSharedObjectInitFailed
Failed to initialize shared object.
Definition hip_runtime_api.h:161
hipErrorInvalidPitchValue
Invalid pitch value.
Definition hip_runtime_api.h:128
hipErrorNoBinaryForGpu
Definition hip_runtime_api.h:147
hipErrorInvalidContext
Produced when input context is invalid.
Definition hip_runtime_api.h:139
hipErrorStreamCaptureUnsupported
Definition hip_runtime_api.h:191
hipErrorPeerAccessNotEnabled
Peer access was never enabled from the current device.
Definition hip_runtime_api.h:177
hipErrorOperatingSystem
Not the correct operating system.
Definition hip_runtime_api.h:162
hipErrorStreamCaptureUnjoined
Definition hip_runtime_api.h:198
hipErrorInitializationError
Definition hip_runtime_api.h:121
hipErrorNotMappedAsPointer
Definition hip_runtime_api.h:151
hipErrorPriorLaunchFailure
Definition hip_runtime_api.h:134
hipErrorContextIsDestroyed
The context is already destroyed.
Definition hip_runtime_api.h:179
hipErrorInvalidValue
Definition hip_runtime_api.h:114
hipErrorLaunchTimeOut
Timeout for the launch.
Definition hip_runtime_api.h:174
hipErrorUnmapFailed
Definition hip_runtime_api.h:144
hipErrorSetOnActiveProcess
The process is active.
Definition hip_runtime_api.h:178
hipErrorFileNotFound
the file is not found.
Definition hip_runtime_api.h:159
hipErrorLaunchFailure
An exception occurred on the device while executing a kernel.
Definition hip_runtime_api.h:185
hipErrorInvalidDevice
DeviceID must be in range from 0 to compute-devices.
Definition hip_runtime_api.h:137
hipErrorUnsupportedLimit
Unsupported limit.
Definition hip_runtime_api.h:153
hipErrorMapBufferObjectFailed
Produced when the IPC memory attach failed from ROCr.
Definition hip_runtime_api.h:143
hipErrorHostMemoryAlreadyRegistered
Definition hip_runtime_api.h:181
hipErrorMissingConfiguration
Definition hip_runtime_api.h:133
hipErrorSharedObjectSymbolNotFound
Definition hip_runtime_api.h:160
hipErrorECCNotCorrectable
Definition hip_runtime_api.h:152
hipErrorStreamCaptureWrongThread
Definition hip_runtime_api.h:209
hipErrorAssert
Produced when the kernel calls assert.
Definition hip_runtime_api.h:180
hipErrorContextAlreadyInUse
The context is already in use.
Definition hip_runtime_api.h:154
hipErrorNotReady
Definition hip_runtime_api.h:168
hipErrorInvalidSource
Invalid source.
Definition hip_runtime_api.h:158
hipErrorLaunchOutOfResources
Out of resources error.
Definition hip_runtime_api.h:173
hipErrorInvalidDeviceFunction
Invalid device function.
Definition hip_runtime_api.h:135
hipErrorCooperativeLaunchTooLarge
Definition hip_runtime_api.h:186
hipErrorAlreadyMapped
Definition hip_runtime_api.h:146
hipErrorInvalidResourceType
Resource type is not valid for the operation.
Definition hip_runtime_api.h:219
hipErrorProfilerNotInitialized
Definition hip_runtime_api.h:124
hipErrorProfilerAlreadyStarted
Definition hip_runtime_api.h:125
hipErrorInvalidChannelDescriptor
Invalid channel descriptor.
Definition hip_runtime_api.h:217
hipErrorNoDevice
Call to hipGetDeviceCount returned 0 devices.
Definition hip_runtime_api.h:136
hipErrorMapFailed
Definition hip_runtime_api.h:141
hipErrorStreamCaptureInvalidated
Definition hip_runtime_api.h:193
hipErrorProfilerAlreadyStopped
Definition hip_runtime_api.h:126
hipErrorDeinitialized
Deinitialized.
Definition hip_runtime_api.h:122
hipErrorPeerAccessAlreadyEnabled
Definition hip_runtime_api.h:175
hipErrorNotMappedAsArray
Definition hip_runtime_api.h:150
hipErrorNotSupported
Produced when the hip API is not supported/implemented.
Definition hip_runtime_api.h:190
hipErrorInvalidConfiguration
Invalide configuration.
Definition hip_runtime_api.h:127
hipErrorStreamCaptureImplicit
Definition hip_runtime_api.h:204
hipErrorStreamCaptureMerge
Definition hip_runtime_api.h:195
hipErrorInvalidGraphicsContext
Definition hip_runtime_api.h:157
hipErrorIllegalState
Resource required is not in a valid state to perform operation.
Definition hip_runtime_api.h:166
hipErrorOutOfMemory
out of memory range.
Definition hip_runtime_api.h:116
hipErrorInvalidSymbol
Invalid symbol.
Definition hip_runtime_api.h:129
hipSuccess
Successful completion.
Definition hip_runtime_api.h:113
hipErrorUnknown
Unknown error.
Definition hip_runtime_api.h:223
hipErrorInvalidHandle
Invalide handle.
Definition hip_runtime_api.h:163
hipErrorStreamCaptureUnmatched
The capture was not initiated in this stream.
Definition hip_runtime_api.h:197
hipErrorCapturedEvent
Definition hip_runtime_api.h:207
hipErrorAlreadyAcquired
Definition hip_runtime_api.h:148
hipErrorInsufficientDriver
Definition hip_runtime_api.h:132
hipErrorHostMemoryNotRegistered
Definition hip_runtime_api.h:183
hipErrorInvalidTexture
Invalid texture.
Definition hip_runtime_api.h:218
hipErrorRuntimeOther
Definition hip_runtime_api.h:227
hipErrorContextAlreadyCurrent
Definition hip_runtime_api.h:140
hipErrorInvalidMemcpyDirection
Invalid memory copy direction.
Definition hip_runtime_api.h:131
hipErrorInvalidResourceConfiguration
Definition hip_runtime_api.h:220
Definition hip_runtime_api.h:743
hipError_t hip_init()
Definition hip_runtime_api.h:1440
uint32_t y
y
Definition hip_runtime_api.h:1442
uint32_t z
z
Definition hip_runtime_api.h:1443
uint32_t x
x
Definition hip_runtime_api.h:1441
constexpr dim3(uint32_t _x=1, uint32_t _y=1, uint32_t _z=1)
Definition hip_runtime_api.h:1445
Definition texture_types.h:131
Definition texture_types.h:79
Defines surface types for HIP runtime.
struct __hip_surface * hipSurfaceObject_t
Definition surface_types.h:28
struct __hip_texture * hipTextureObject_t
Definition texture_types.h:54
hipTextureAddressMode
Definition texture_types.h:59
hipTextureFilterMode
Definition texture_types.h:69
Definition texture_types.h:100