/home/docs/checkouts/readthedocs.org/user_builds/advanced-micro-devices-hip/checkouts/docs-6.0.2/include/hip/hip_runtime_api.h Source File

• include
• hip

hip_runtime_api.h

Go to the documentation of this file.

1/*

2Copyright (c) 2015 - 2023 Advanced Micro Devices, Inc. All rights reserved.

3

4Permission is hereby granted, free of charge, to any person obtaining a copy

5of this software and associated documentation files (the "Software"), to deal

6in the Software without restriction, including without limitation the rights

7to use, copy, modify, merge, publish, distribute, sublicense, and/or sell

8copies of the Software, and to permit persons to whom the Software is

9furnished to do so, subject to the following conditions:

10

11The above copyright notice and this permission notice shall be included in

12all copies or substantial portions of the Software.

13

14THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR

15IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,

16FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE

17AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER

18LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,

19OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN

20THE SOFTWARE.

21*/

22

30#ifndef HIP_INCLUDE_HIP_HIP_RUNTIME_API_H

31#define HIP_INCLUDE_HIP_HIP_RUNTIME_API_H

32

33#include <string.h> // for getDeviceProp

34#include <hip/hip_version.h>

35#include <hip/hip_common.h>

36

37enum {

38 HIP_SUCCESS = 0,

39 HIP_ERROR_INVALID_VALUE,

40 HIP_ERROR_NOT_INITIALIZED,

41 HIP_ERROR_LAUNCH_OUT_OF_RESOURCES

42};

43// hack to get these to show up in Doxygen:

53typedef struct {

54 // 32-bit Atomics

55 unsigned hasGlobalInt32Atomics : 1;

56 unsigned hasGlobalFloatAtomicExch : 1;

57 unsigned hasSharedInt32Atomics : 1;

58 unsigned hasSharedFloatAtomicExch : 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;

82} hipDeviceArch_t;

83

84typedef struct hipUUID_t {

85 char bytes[16];

86} hipUUID;

87

88//---

89// Common headers for both NVCC and HCC paths:

90

91#define hipGetDeviceProperties hipGetDevicePropertiesR0600

92#define hipDeviceProp_t hipDeviceProp_tR0600

93#define hipChooseDevice hipChooseDeviceR0600

94

99typedef struct hipDeviceProp_t {

100 char name[256];

101 hipUUID uuid;

102 char luid[8];

103 unsigned int luidDeviceNodeMask;

104 size_t totalGlobalMem;

105 size_t sharedMemPerBlock;

106 int regsPerBlock;

107 int warpSize;

108 size_t memPitch;

110 int maxThreadsPerBlock;

111 int maxThreadsDim[3];

112 int maxGridSize[3];

113 int clockRate;

114 size_t totalConstMem;

115 int major;

118 int minor;

121 size_t textureAlignment;

122 size_t texturePitchAlignment;

123 int deviceOverlap;

124 int multiProcessorCount;

125 int kernelExecTimeoutEnabled;

126 int integrated;

127 int canMapHostMemory;

128 int computeMode;

129 int maxTexture1D;

130 int maxTexture1DMipmap;

131 int maxTexture1DLinear;

132 int maxTexture2D[2];

133 int maxTexture2DMipmap[2];

134 int maxTexture2DLinear[3];

135 int maxTexture2DGather[2];

136 int maxTexture3D[3];

138 int maxTexture3DAlt[3];

139 int maxTextureCubemap;

140 int maxTexture1DLayered[2];

141 int maxTexture2DLayered[3];

142 int maxTextureCubemapLayered[2];

143 int maxSurface1D;

144 int maxSurface2D[2];

145 int maxSurface3D[3];

146 int maxSurface1DLayered[2];

147 int maxSurface2DLayered[3];

148 int maxSurfaceCubemap;

149 int maxSurfaceCubemapLayered[2];

150 size_t surfaceAlignment;

151 int concurrentKernels;

152 int ECCEnabled;

153 int pciBusID;

154 int pciDeviceID;

155 int pciDomainID;

156 int tccDriver;

157 int asyncEngineCount;

158 int unifiedAddressing;

159 int memoryClockRate;

160 int memoryBusWidth;

161 int l2CacheSize;

162 int persistingL2CacheMaxSize;

163 int maxThreadsPerMultiProcessor;

164 int streamPrioritiesSupported;

165 int globalL1CacheSupported;

166 int localL1CacheSupported;

167 size_t sharedMemPerMultiprocessor;

168 int regsPerMultiprocessor;

169 int managedMemory;

170 int isMultiGpuBoard;

171 int multiGpuBoardGroupID;

172 int hostNativeAtomicSupported;

173 int singleToDoublePrecisionPerfRatio;

174 int pageableMemoryAccess;

176 int concurrentManagedAccess;

178 int computePreemptionSupported;

179 int canUseHostPointerForRegisteredMem;

181 int cooperativeLaunch;

182 int cooperativeMultiDeviceLaunch;

184 size_t

185 sharedMemPerBlockOptin;

186 int pageableMemoryAccessUsesHostPageTables;

188 int directManagedMemAccessFromHost;

190 int maxBlocksPerMultiProcessor;

191 int accessPolicyMaxWindowSize;

192 size_t reservedSharedMemPerBlock;

193 int hostRegisterSupported;

194 int sparseHipArraySupported;

195 int hostRegisterReadOnlySupported;

197 int timelineSemaphoreInteropSupported;

198 int memoryPoolsSupported;

199 int gpuDirectRDMASupported;

200 unsigned int gpuDirectRDMAFlushWritesOptions;

202 int gpuDirectRDMAWritesOrdering;

203 unsigned int

204 memoryPoolSupportedHandleTypes;

205 int deferredMappingHipArraySupported;

207 int ipcEventSupported;

208 int clusterLaunch;

209 int unifiedFunctionPointers;

210 int reserved[63];

211

212 int hipReserved[32];

213

214 /* HIP Only struct members */

215 char gcnArchName[256];

216 size_t maxSharedMemoryPerMultiProcessor;

217 int clockInstructionRate;

219 hipDeviceArch_t arch;

220 unsigned int* hdpMemFlushCntl;

221 unsigned int* hdpRegFlushCntl;

222 int cooperativeMultiDeviceUnmatchedFunc;

225 int cooperativeMultiDeviceUnmatchedGridDim;

228 int cooperativeMultiDeviceUnmatchedBlockDim;

231 int cooperativeMultiDeviceUnmatchedSharedMem;

234 int isLargeBar;

235 int asicRevision;

236} hipDeviceProp_t;

237

244typedef enum hipMemoryType {

245 hipMemoryTypeUnregistered = 0,

246 hipMemoryTypeHost = 1,

247 hipMemoryTypeDevice = 2,

249 hipMemoryTypeManaged = 3,

252 hipMemoryTypeArray = 10,

254 hipMemoryTypeUnified = 11

255

256} hipMemoryType;

257

261typedef struct hipPointerAttribute_t {

262 enum hipMemoryType type;

263 int device;

264 void* devicePointer;

265 void* hostPointer;

266 int isManaged;

267 unsigned allocationFlags; /* flags specified when memory was allocated*/

268 /* peers? */

269} hipPointerAttribute_t;

270

271// Ignoring error-code return values from hip APIs is discouraged. On C++17,

272// we can make that yield a warning

273#if __cplusplus >= 201703L

274#define __HIP_NODISCARD [[nodiscard]]

275#else

276#define __HIP_NODISCARD

277#endif

278

283// Developer note - when updating these, update the hipErrorName and hipErrorString functions in

284// NVCC and HCC paths Also update the hipCUDAErrorTohipError function in NVCC path.

285

286typedef enum __HIP_NODISCARD hipError_t {

287 hipSuccess = 0,

288 hipErrorInvalidValue = 1,

290 hipErrorOutOfMemory = 2,

291 // Deprecated

292 hipErrorMemoryAllocation = 2,

293 hipErrorNotInitialized = 3,

294 // Deprecated

295 hipErrorInitializationError = 3,

296 hipErrorDeinitialized = 4,

297 hipErrorProfilerDisabled = 5,

298 hipErrorProfilerNotInitialized = 6,

299 hipErrorProfilerAlreadyStarted = 7,

300 hipErrorProfilerAlreadyStopped = 8,

301 hipErrorInvalidConfiguration = 9,

302 hipErrorInvalidPitchValue = 12,

303 hipErrorInvalidSymbol = 13,

304 hipErrorInvalidDevicePointer = 17,

305 hipErrorInvalidMemcpyDirection = 21,

306 hipErrorInsufficientDriver = 35,

307 hipErrorMissingConfiguration = 52,

308 hipErrorPriorLaunchFailure = 53,

309 hipErrorInvalidDeviceFunction = 98,

310 hipErrorNoDevice = 100,

311 hipErrorInvalidDevice = 101,

312 hipErrorInvalidImage = 200,

313 hipErrorInvalidContext = 201,

314 hipErrorContextAlreadyCurrent = 202,

315 hipErrorMapFailed = 205,

316 // Deprecated

317 hipErrorMapBufferObjectFailed = 205,

318 hipErrorUnmapFailed = 206,

319 hipErrorArrayIsMapped = 207,

320 hipErrorAlreadyMapped = 208,

321 hipErrorNoBinaryForGpu = 209,

322 hipErrorAlreadyAcquired = 210,

323 hipErrorNotMapped = 211,

324 hipErrorNotMappedAsArray = 212,

325 hipErrorNotMappedAsPointer = 213,

326 hipErrorECCNotCorrectable = 214,

327 hipErrorUnsupportedLimit = 215,

328 hipErrorContextAlreadyInUse = 216,

329 hipErrorPeerAccessUnsupported = 217,

330 hipErrorInvalidKernelFile = 218,

331 hipErrorInvalidGraphicsContext = 219,

332 hipErrorInvalidSource = 300,

333 hipErrorFileNotFound = 301,

334 hipErrorSharedObjectSymbolNotFound = 302,

335 hipErrorSharedObjectInitFailed = 303,

336 hipErrorOperatingSystem = 304,

337 hipErrorInvalidHandle = 400,

338 // Deprecated

339 hipErrorInvalidResourceHandle = 400,

340 hipErrorIllegalState = 401,

341 hipErrorNotFound = 500,

342 hipErrorNotReady = 600,

346 hipErrorIllegalAddress = 700,

347 hipErrorLaunchOutOfResources = 701,

348 hipErrorLaunchTimeOut = 702,

349 hipErrorPeerAccessAlreadyEnabled =

350 704,

351 hipErrorPeerAccessNotEnabled =

352 705,

353 hipErrorSetOnActiveProcess = 708,

354 hipErrorContextIsDestroyed = 709,

355 hipErrorAssert = 710,

356 hipErrorHostMemoryAlreadyRegistered =

357 712,

358 hipErrorHostMemoryNotRegistered =

359 713,

360 hipErrorLaunchFailure =

361 719,

362 hipErrorCooperativeLaunchTooLarge =

363 720,

366 hipErrorNotSupported = 801,

367 hipErrorStreamCaptureUnsupported = 900,

369 hipErrorStreamCaptureInvalidated = 901,

371 hipErrorStreamCaptureMerge = 902,

373 hipErrorStreamCaptureUnmatched = 903,

374 hipErrorStreamCaptureUnjoined = 904,

376 hipErrorStreamCaptureIsolation = 905,

380 hipErrorStreamCaptureImplicit = 906,

383 hipErrorCapturedEvent = 907,

385 hipErrorStreamCaptureWrongThread = 908,

389 hipErrorGraphExecUpdateFailure = 910,

393 hipErrorUnknown = 999,

394 // HSA Runtime Error Codes start here.

395 hipErrorRuntimeMemory = 1052,

397 hipErrorRuntimeOther = 1053,

399 hipErrorTbd

400} hipError_t;

401

402#undef __HIP_NODISCARD

403

408typedef enum hipDeviceAttribute_t {

409 hipDeviceAttributeCudaCompatibleBegin = 0,

410

411 hipDeviceAttributeEccEnabled = hipDeviceAttributeCudaCompatibleBegin,

412 hipDeviceAttributeAccessPolicyMaxWindowSize,

413 hipDeviceAttributeAsyncEngineCount,

414 hipDeviceAttributeCanMapHostMemory,

415 hipDeviceAttributeCanUseHostPointerForRegisteredMem,

417 hipDeviceAttributeClockRate,

418 hipDeviceAttributeComputeMode,

419 hipDeviceAttributeComputePreemptionSupported,

420 hipDeviceAttributeConcurrentKernels,

421 hipDeviceAttributeConcurrentManagedAccess,

422 hipDeviceAttributeCooperativeLaunch,

423 hipDeviceAttributeCooperativeMultiDeviceLaunch,

424 hipDeviceAttributeDeviceOverlap,

426 hipDeviceAttributeDirectManagedMemAccessFromHost,

428 hipDeviceAttributeGlobalL1CacheSupported,

429 hipDeviceAttributeHostNativeAtomicSupported,

430 hipDeviceAttributeIntegrated,

431 hipDeviceAttributeIsMultiGpuBoard,

432 hipDeviceAttributeKernelExecTimeout,

433 hipDeviceAttributeL2CacheSize,

434 hipDeviceAttributeLocalL1CacheSupported,

435 hipDeviceAttributeLuid,

436 hipDeviceAttributeLuidDeviceNodeMask,

437 hipDeviceAttributeComputeCapabilityMajor,

438 hipDeviceAttributeManagedMemory,

439 hipDeviceAttributeMaxBlocksPerMultiProcessor,

440 hipDeviceAttributeMaxBlockDimX,

441 hipDeviceAttributeMaxBlockDimY,

442 hipDeviceAttributeMaxBlockDimZ,

443 hipDeviceAttributeMaxGridDimX,

444 hipDeviceAttributeMaxGridDimY,

445 hipDeviceAttributeMaxGridDimZ,

446 hipDeviceAttributeMaxSurface1D,

447 hipDeviceAttributeMaxSurface1DLayered,

448 hipDeviceAttributeMaxSurface2D,

449 hipDeviceAttributeMaxSurface2DLayered,

450 hipDeviceAttributeMaxSurface3D,

451 hipDeviceAttributeMaxSurfaceCubemap,

452 hipDeviceAttributeMaxSurfaceCubemapLayered,

453 hipDeviceAttributeMaxTexture1DWidth,

454 hipDeviceAttributeMaxTexture1DLayered,

455 hipDeviceAttributeMaxTexture1DLinear,

457 hipDeviceAttributeMaxTexture1DMipmap,

458 hipDeviceAttributeMaxTexture2DWidth,

459 hipDeviceAttributeMaxTexture2DHeight,

460 hipDeviceAttributeMaxTexture2DGather,

461 hipDeviceAttributeMaxTexture2DLayered,

462 hipDeviceAttributeMaxTexture2DLinear,

463 hipDeviceAttributeMaxTexture2DMipmap,

464 hipDeviceAttributeMaxTexture3DWidth,

465 hipDeviceAttributeMaxTexture3DHeight,

466 hipDeviceAttributeMaxTexture3DDepth,

467 hipDeviceAttributeMaxTexture3DAlt,

468 hipDeviceAttributeMaxTextureCubemap,

469 hipDeviceAttributeMaxTextureCubemapLayered,

470 hipDeviceAttributeMaxThreadsDim,

471 hipDeviceAttributeMaxThreadsPerBlock,

472 hipDeviceAttributeMaxThreadsPerMultiProcessor,

473 hipDeviceAttributeMaxPitch,

474 hipDeviceAttributeMemoryBusWidth,

475 hipDeviceAttributeMemoryClockRate,

476 hipDeviceAttributeComputeCapabilityMinor,

477 hipDeviceAttributeMultiGpuBoardGroupID,

478 hipDeviceAttributeMultiprocessorCount,

479 hipDeviceAttributeUnused1,

480 hipDeviceAttributePageableMemoryAccess,

482 hipDeviceAttributePageableMemoryAccessUsesHostPageTables,

483 hipDeviceAttributePciBusId,

484 hipDeviceAttributePciDeviceId,

485 hipDeviceAttributePciDomainID,

486 hipDeviceAttributePersistingL2CacheMaxSize,

487 hipDeviceAttributeMaxRegistersPerBlock,

489 hipDeviceAttributeMaxRegistersPerMultiprocessor,

490 hipDeviceAttributeReservedSharedMemPerBlock,

491 hipDeviceAttributeMaxSharedMemoryPerBlock,

492 hipDeviceAttributeSharedMemPerBlockOptin,

493 hipDeviceAttributeSharedMemPerMultiprocessor,

494 hipDeviceAttributeSingleToDoublePrecisionPerfRatio,

495 hipDeviceAttributeStreamPrioritiesSupported,

496 hipDeviceAttributeSurfaceAlignment,

497 hipDeviceAttributeTccDriver,

498 hipDeviceAttributeTextureAlignment,

499 hipDeviceAttributeTexturePitchAlignment,

500 hipDeviceAttributeTotalConstantMemory,

501 hipDeviceAttributeTotalGlobalMem,

502 hipDeviceAttributeUnifiedAddressing,

503 hipDeviceAttributeUnused2,

504 hipDeviceAttributeWarpSize,

505 hipDeviceAttributeMemoryPoolsSupported,

506 hipDeviceAttributeVirtualMemoryManagementSupported,

507 hipDeviceAttributeHostRegisterSupported,

508 hipDeviceAttributeMemoryPoolSupportedHandleTypes,

509

510 hipDeviceAttributeCudaCompatibleEnd = 9999,

511 hipDeviceAttributeAmdSpecificBegin = 10000,

512

513 hipDeviceAttributeClockInstructionRate = hipDeviceAttributeAmdSpecificBegin,

514 hipDeviceAttributeUnused3,

515 hipDeviceAttributeMaxSharedMemoryPerMultiprocessor,

516 hipDeviceAttributeUnused4,

517 hipDeviceAttributeUnused5,

518 hipDeviceAttributeHdpMemFlushCntl,

519 hipDeviceAttributeHdpRegFlushCntl,

520 hipDeviceAttributeCooperativeMultiDeviceUnmatchedFunc,

522 hipDeviceAttributeCooperativeMultiDeviceUnmatchedGridDim,

524 hipDeviceAttributeCooperativeMultiDeviceUnmatchedBlockDim,

526 hipDeviceAttributeCooperativeMultiDeviceUnmatchedSharedMem,

528 hipDeviceAttributeIsLargeBar,

529 hipDeviceAttributeAsicRevision,

530 hipDeviceAttributeCanUseStreamWaitValue,

532 hipDeviceAttributeImageSupport,

533 hipDeviceAttributePhysicalMultiProcessorCount,

535 hipDeviceAttributeFineGrainSupport,

536 hipDeviceAttributeWallClockRate,

537

538 hipDeviceAttributeAmdSpecificEnd = 19999,

539 hipDeviceAttributeVendorSpecificBegin = 20000,

540 // Extended attributes for vendors

541} hipDeviceAttribute_t;

542

543typedef enum hipDriverProcAddressQueryResult {

544 HIP_GET_PROC_ADDRESS_SUCCESS = 0,

545 HIP_GET_PROC_ADDRESS_SYMBOL_NOT_FOUND = 1,

546 HIP_GET_PROC_ADDRESS_VERSION_NOT_SUFFICIENT = 2

547} hipDriverProcAddressQueryResult;

548

549enum hipComputeMode {

550 hipComputeModeDefault = 0,

551 hipComputeModeExclusive = 1,

552 hipComputeModeProhibited = 2,

553 hipComputeModeExclusiveProcess = 3

554};

555

556enum hipFlushGPUDirectRDMAWritesOptions {

557 hipFlushGPUDirectRDMAWritesOptionHost = 1 << 0,

558 hipFlushGPUDirectRDMAWritesOptionMemOps = 1 << 1

559};

560

561enum hipGPUDirectRDMAWritesOrdering {

562 hipGPUDirectRDMAWritesOrderingNone = 0,

563 hipGPUDirectRDMAWritesOrderingOwner = 100,

564 hipGPUDirectRDMAWritesOrderingAllDevices = 200

565};

566

567#if defined(__HIP_PLATFORM_AMD__) && !defined(__HIP_PLATFORM_NVIDIA__)

568

569#include <stdint.h>

570#include <stddef.h>

571#ifndef GENERIC_GRID_LAUNCH

572#define GENERIC_GRID_LAUNCH 1

573#endif

574#include <hip/amd_detail/host_defines.h>

575#include <hip/driver_types.h>

576#include <hip/texture_types.h>

577#include <hip/surface_types.h>

578#if defined(_MSC_VER)

579#define DEPRECATED(msg) __declspec(deprecated(msg))

580#else // !defined(_MSC_VER)

581#define DEPRECATED(msg) __attribute__ ((deprecated(msg)))

582#endif // !defined(_MSC_VER)

583#define DEPRECATED_MSG "This API is marked as deprecated and may not be supported in future releases. For more details please refer https://github.com/ROCm-Developer-Tools/HIP/blob/master/docs/markdown/hip_deprecated_api_list.md"

584#define HIP_LAUNCH_PARAM_BUFFER_POINTER ((void*)0x01)

585#define HIP_LAUNCH_PARAM_BUFFER_SIZE ((void*)0x02)

586#define HIP_LAUNCH_PARAM_END ((void*)0x03)

587#ifdef __cplusplus

588 #define __dparm(x) \

589 = x

590#else

591 #define __dparm(x)

592#endif

593#ifdef __GNUC__

594#pragma GCC visibility push (default)

595#endif

596#ifdef __cplusplus

597namespace hip_impl {

598hipError_t hip_init();

599} // namespace hip_impl

600#endif

601// Structure definitions:

602#ifdef __cplusplus

603extern "C" {

604#endif

605//---

606// API-visible structures

607typedef struct ihipCtx_t* hipCtx_t;

608// Note many APIs also use integer deviceIds as an alternative to the device pointer:

609typedef int hipDevice_t;

610typedef enum hipDeviceP2PAttr {

611 hipDevP2PAttrPerformanceRank = 0,

612 hipDevP2PAttrAccessSupported,

613 hipDevP2PAttrNativeAtomicSupported,

614 hipDevP2PAttrHipArrayAccessSupported

615} hipDeviceP2PAttr;

616typedef struct ihipStream_t* hipStream_t;

617#define hipIpcMemLazyEnablePeerAccess 0x01

618#define HIP_IPC_HANDLE_SIZE 64

619typedef struct hipIpcMemHandle_st {

620 char reserved[HIP_IPC_HANDLE_SIZE];

621} hipIpcMemHandle_t;

622typedef struct hipIpcEventHandle_st {

623 char reserved[HIP_IPC_HANDLE_SIZE];

624} hipIpcEventHandle_t;

625typedef struct ihipModule_t* hipModule_t;

626typedef struct ihipModuleSymbol_t* hipFunction_t;

630typedef struct ihipMemPoolHandle_t* hipMemPool_t;

631

632typedef struct hipFuncAttributes {

633 int binaryVersion;

634 int cacheModeCA;

635 size_t constSizeBytes;

636 size_t localSizeBytes;

637 int maxDynamicSharedSizeBytes;

638 int maxThreadsPerBlock;

639 int numRegs;

640 int preferredShmemCarveout;

641 int ptxVersion;

642 size_t sharedSizeBytes;

643} hipFuncAttributes;

644typedef struct ihipEvent_t* hipEvent_t;

645

652enum hipLimit_t {

653 hipLimitStackSize = 0x0,

656 hipLimitPrintfFifoSize = 0x01,

658 hipLimitMallocHeapSize = 0x02,

660 hipLimitRange

661};

665//Flags that can be used with hipStreamCreateWithFlags.

667#define hipStreamDefault 0x00

668

670#define hipStreamNonBlocking 0x01

671

672//Flags that can be used with hipEventCreateWithFlags.

674#define hipEventDefault 0x0

675

677#define hipEventBlockingSync 0x1

678

680#define hipEventDisableTiming 0x2

681

683#define hipEventInterprocess 0x4

684

693#define hipEventDisableSystemFence 0x20000000

694

697#define hipEventReleaseToDevice 0x40000000

698

701#define hipEventReleaseToSystem 0x80000000

702

703//Flags that can be used with hipHostMalloc.

705#define hipHostMallocDefault 0x0

706

708#define hipHostMallocPortable 0x1

709

712#define hipHostMallocMapped 0x2

713

717#define hipHostMallocWriteCombined 0x4

718

723#define hipHostMallocNumaUser 0x20000000

724

726#define hipHostMallocCoherent 0x40000000

727

729#define hipHostMallocNonCoherent 0x80000000

730

732#define hipMemAttachGlobal 0x01

733

735#define hipMemAttachHost 0x02

736

738#define hipMemAttachSingle 0x04

739

740#define hipDeviceMallocDefault 0x0

741

743#define hipDeviceMallocFinegrained 0x1

744

746#define hipMallocSignalMemory 0x2

747

749#define hipDeviceMallocUncached 0x3

750

751//Flags that can be used with hipHostRegister.

753#define hipHostRegisterDefault 0x0

754

756#define hipHostRegisterPortable 0x1

757

760#define hipHostRegisterMapped 0x2

761

763#define hipHostRegisterIoMemory 0x4

764

766#define hipHostRegisterReadOnly 0x08

767

769#define hipExtHostRegisterCoarseGrained 0x8

770

772#define hipDeviceScheduleAuto 0x0

773

776#define hipDeviceScheduleSpin 0x1

777

780#define hipDeviceScheduleYield 0x2

781#define hipDeviceScheduleBlockingSync 0x4

782#define hipDeviceScheduleMask 0x7

783#define hipDeviceMapHost 0x8

784#define hipDeviceLmemResizeToMax 0x10

786#define hipArrayDefault 0x00

787#define hipArrayLayered 0x01

788#define hipArraySurfaceLoadStore 0x02

789#define hipArrayCubemap 0x04

790#define hipArrayTextureGather 0x08

791#define hipOccupancyDefault 0x00

792#define hipOccupancyDisableCachingOverride 0x01

793#define hipCooperativeLaunchMultiDeviceNoPreSync 0x01

794#define hipCooperativeLaunchMultiDeviceNoPostSync 0x02

795#define hipCpuDeviceId ((int)-1)

796#define hipInvalidDeviceId ((int)-2)

797//Flags that can be used with hipExtLaunch Set of APIs.

799#define hipExtAnyOrderLaunch 0x01

800// Flags to be used with hipStreamWaitValue32 and hipStreamWaitValue64.

801#define hipStreamWaitValueGte 0x0

802#define hipStreamWaitValueEq 0x1

803#define hipStreamWaitValueAnd 0x2

804#define hipStreamWaitValueNor 0x3

805// Stream per thread

807#define hipStreamPerThread ((hipStream_t)2)

808

809// Indicates that the external memory object is a dedicated resource

810#define hipExternalMemoryDedicated 0x1

816typedef enum hipMemoryAdvise {

817 hipMemAdviseSetReadMostly = 1,

819 hipMemAdviseUnsetReadMostly = 2,

820 hipMemAdviseSetPreferredLocation = 3,

822 hipMemAdviseUnsetPreferredLocation = 4,

823 hipMemAdviseSetAccessedBy = 5,

825 hipMemAdviseUnsetAccessedBy = 6,

827 hipMemAdviseSetCoarseGrain = 100,

832 hipMemAdviseUnsetCoarseGrain = 101

833} hipMemoryAdvise;

837typedef enum hipMemRangeCoherencyMode {

838 hipMemRangeCoherencyModeFineGrain = 0,

840 hipMemRangeCoherencyModeCoarseGrain = 1,

842 hipMemRangeCoherencyModeIndeterminate = 2

845} hipMemRangeCoherencyMode;

849typedef enum hipMemRangeAttribute {

850 hipMemRangeAttributeReadMostly = 1,

852 hipMemRangeAttributePreferredLocation = 2,

853 hipMemRangeAttributeAccessedBy = 3,

855 hipMemRangeAttributeLastPrefetchLocation = 4,

857 hipMemRangeAttributeCoherencyMode = 100,

859} hipMemRangeAttribute;

860

864typedef enum hipMemPoolAttr

865{

874 hipMemPoolReuseFollowEventDependencies = 0x1,

880 hipMemPoolReuseAllowOpportunistic = 0x2,

887 hipMemPoolReuseAllowInternalDependencies = 0x3,

896 hipMemPoolAttrReleaseThreshold = 0x4,

901 hipMemPoolAttrReservedMemCurrent = 0x5,

907 hipMemPoolAttrReservedMemHigh = 0x6,

912 hipMemPoolAttrUsedMemCurrent = 0x7,

918 hipMemPoolAttrUsedMemHigh = 0x8

919} hipMemPoolAttr;

923 typedef enum hipMemLocationType {

924 hipMemLocationTypeInvalid = 0,

925 hipMemLocationTypeDevice = 1

926} hipMemLocationType;

932typedef struct hipMemLocation {

933 hipMemLocationType type;

934 int id;

935} hipMemLocation;

940typedef enum hipMemAccessFlags {

941 hipMemAccessFlagsProtNone = 0,

942 hipMemAccessFlagsProtRead = 1,

943 hipMemAccessFlagsProtReadWrite = 3

944} hipMemAccessFlags;

948typedef struct hipMemAccessDesc {

949 hipMemLocation location;

950 hipMemAccessFlags flags;

951} hipMemAccessDesc;

955typedef enum hipMemAllocationType {

956 hipMemAllocationTypeInvalid = 0x0,

960 hipMemAllocationTypePinned = 0x1,

961 hipMemAllocationTypeMax = 0x7FFFFFFF

962} hipMemAllocationType;

967typedef enum hipMemAllocationHandleType {

968 hipMemHandleTypeNone = 0x0,

969 hipMemHandleTypePosixFileDescriptor = 0x1,

970 hipMemHandleTypeWin32 = 0x2,

971 hipMemHandleTypeWin32Kmt = 0x4

972} hipMemAllocationHandleType;

976typedef struct hipMemPoolProps {

977 hipMemAllocationType allocType;

978 hipMemAllocationHandleType handleTypes;

979 hipMemLocation location;

983 void* win32SecurityAttributes;

984 unsigned char reserved[64];

985} hipMemPoolProps;

989typedef struct hipMemPoolPtrExportData {

990 unsigned char reserved[64];

991} hipMemPoolPtrExportData;

992

996typedef enum hipJitOption {

997 hipJitOptionMaxRegisters = 0,

998 hipJitOptionThreadsPerBlock,

999 hipJitOptionWallTime,

1000 hipJitOptionInfoLogBuffer,

1001 hipJitOptionInfoLogBufferSizeBytes,

1002 hipJitOptionErrorLogBuffer,

1003 hipJitOptionErrorLogBufferSizeBytes,

1004 hipJitOptionOptimizationLevel,

1005 hipJitOptionTargetFromContext,

1006 hipJitOptionTarget,

1007 hipJitOptionFallbackStrategy,

1008 hipJitOptionGenerateDebugInfo,

1009 hipJitOptionLogVerbose,

1010 hipJitOptionGenerateLineInfo,

1011 hipJitOptionCacheMode,

1012 hipJitOptionSm3xOpt,

1013 hipJitOptionFastCompile,

1014 hipJitOptionNumOptions

1015} hipJitOption;

1019typedef enum hipFuncAttribute {

1020 hipFuncAttributeMaxDynamicSharedMemorySize = 8,

1021 hipFuncAttributePreferredSharedMemoryCarveout = 9,

1022 hipFuncAttributeMax

1023} hipFuncAttribute;

1027typedef enum hipFuncCache_t {

1028 hipFuncCachePreferNone,

1029 hipFuncCachePreferShared,

1030 hipFuncCachePreferL1,

1031 hipFuncCachePreferEqual,

1032} hipFuncCache_t;

1036typedef enum hipSharedMemConfig {

1037 hipSharedMemBankSizeDefault,

1038 hipSharedMemBankSizeFourByte,

1040 hipSharedMemBankSizeEightByte

1042} hipSharedMemConfig;

1046typedef struct dim3 {

1047 uint32_t x;

1048 uint32_t y;

1049 uint32_t z;

1050#ifdef __cplusplus

1051 constexpr __host__ __device__ dim3(uint32_t _x = 1, uint32_t _y = 1, uint32_t _z = 1) : x(_x), y(_y), z(_z){};

1052#endif

1053} dim3;

1057typedef struct hipLaunchParams_t {

1058 void* func;

1059 dim3 gridDim;

1060 dim3 blockDim;

1061 void **args;

1062 size_t sharedMem;

1063 hipStream_t stream;

1064} hipLaunchParams;

1068typedef struct hipFunctionLaunchParams_t {

1069 hipFunction_t function;

1070 unsigned int gridDimX;

1071 unsigned int gridDimY;

1072 unsigned int gridDimZ;

1073 unsigned int blockDimX;

1074 unsigned int blockDimY;

1075 unsigned int blockDimZ;

1076 unsigned int sharedMemBytes;

1077 hipStream_t hStream;

1078 void **kernelParams;

1079} hipFunctionLaunchParams;

1080typedef enum hipExternalMemoryHandleType_enum {

1081 hipExternalMemoryHandleTypeOpaqueFd = 1,

1082 hipExternalMemoryHandleTypeOpaqueWin32 = 2,

1083 hipExternalMemoryHandleTypeOpaqueWin32Kmt = 3,

1084 hipExternalMemoryHandleTypeD3D12Heap = 4,

1085 hipExternalMemoryHandleTypeD3D12Resource = 5,

1086 hipExternalMemoryHandleTypeD3D11Resource = 6,

1087 hipExternalMemoryHandleTypeD3D11ResourceKmt = 7,

1088 hipExternalMemoryHandleTypeNvSciBuf = 8

1089} hipExternalMemoryHandleType;

1090typedef struct hipExternalMemoryHandleDesc_st {

1091 hipExternalMemoryHandleType type;

1092 union {

1093 int fd;

1094 struct {

1095 void *handle;

1096 const void *name;

1097 } win32;

1098 const void *nvSciBufObject;

1099 } handle;

1100 unsigned long long size;

1101 unsigned int flags;

1102 unsigned int reserved[16];

1103} hipExternalMemoryHandleDesc;

1104typedef struct hipExternalMemoryBufferDesc_st {

1105 unsigned long long offset;

1106 unsigned long long size;

1107 unsigned int flags;

1108 unsigned int reserved[16];

1109} hipExternalMemoryBufferDesc;

1110typedef struct hipExternalMemoryMipmappedArrayDesc_st {

1111 unsigned long long offset;

1112 hipChannelFormatDesc formatDesc;

1113 hipExtent extent;

1114 unsigned int flags;

1115 unsigned int numLevels;

1116} hipExternalMemoryMipmappedArrayDesc;

1117typedef void* hipExternalMemory_t;

1118typedef enum hipExternalSemaphoreHandleType_enum {

1119 hipExternalSemaphoreHandleTypeOpaqueFd = 1,

1120 hipExternalSemaphoreHandleTypeOpaqueWin32 = 2,

1121 hipExternalSemaphoreHandleTypeOpaqueWin32Kmt = 3,

1122 hipExternalSemaphoreHandleTypeD3D12Fence = 4,

1123 hipExternalSemaphoreHandleTypeD3D11Fence = 5,

1124 hipExternalSemaphoreHandleTypeNvSciSync = 6,

1125 hipExternalSemaphoreHandleTypeKeyedMutex = 7,

1126 hipExternalSemaphoreHandleTypeKeyedMutexKmt = 8,

1127 hipExternalSemaphoreHandleTypeTimelineSemaphoreFd = 9,

1128 hipExternalSemaphoreHandleTypeTimelineSemaphoreWin32 = 10

1129} hipExternalSemaphoreHandleType;

1130typedef struct hipExternalSemaphoreHandleDesc_st {

1131 hipExternalSemaphoreHandleType type;

1132 union {

1133 int fd;

1134 struct {

1135 void* handle;

1136 const void* name;

1137 } win32;

1138 const void* NvSciSyncObj;

1139 } handle;

1140 unsigned int flags;

1141 unsigned int reserved[16];

1142} hipExternalSemaphoreHandleDesc;

1143typedef void* hipExternalSemaphore_t;

1144typedef struct hipExternalSemaphoreSignalParams_st {

1145 struct {

1146 struct {

1147 unsigned long long value;

1148 } fence;

1149 union {

1150 void *fence;

1151 unsigned long long reserved;

1152 } nvSciSync;

1153 struct {

1154 unsigned long long key;

1155 } keyedMutex;

1156 unsigned int reserved[12];

1157 } params;

1158 unsigned int flags;

1159 unsigned int reserved[16];

1160} hipExternalSemaphoreSignalParams;

1164typedef struct hipExternalSemaphoreWaitParams_st {

1165 struct {

1166 struct {

1167 unsigned long long value;

1168 } fence;

1169 union {

1170 void *fence;

1171 unsigned long long reserved;

1172 } nvSciSync;

1173 struct {

1174 unsigned long long key;

1175 unsigned int timeoutMs;

1176 } keyedMutex;

1177 unsigned int reserved[10];

1178 } params;

1179 unsigned int flags;

1180 unsigned int reserved[16];

1181} hipExternalSemaphoreWaitParams;

1182

1183#if __HIP_HAS_GET_PCH

1188 void __hipGetPCH(const char** pch, unsigned int*size);

1189#endif

1190

1194typedef enum hipGraphicsRegisterFlags {

1195 hipGraphicsRegisterFlagsNone = 0,

1196 hipGraphicsRegisterFlagsReadOnly = 1,

1197 hipGraphicsRegisterFlagsWriteDiscard =

1198 2,

1199 hipGraphicsRegisterFlagsSurfaceLoadStore = 4,

1200 hipGraphicsRegisterFlagsTextureGather =

1201 8

1202} hipGraphicsRegisterFlags;

1203

1204typedef struct _hipGraphicsResource hipGraphicsResource;

1205

1206typedef hipGraphicsResource* hipGraphicsResource_t;

1207

1211typedef struct ihipGraph* hipGraph_t;

1215typedef struct hipGraphNode* hipGraphNode_t;

1219typedef struct hipGraphExec* hipGraphExec_t;

1220

1224typedef struct hipUserObject* hipUserObject_t;

1225

1226

1230typedef enum hipGraphNodeType {

1231 hipGraphNodeTypeKernel = 0,

1232 hipGraphNodeTypeMemcpy = 1,

1233 hipGraphNodeTypeMemset = 2,

1234 hipGraphNodeTypeHost = 3,

1235 hipGraphNodeTypeGraph = 4,

1236 hipGraphNodeTypeEmpty = 5,

1237 hipGraphNodeTypeWaitEvent = 6,

1238 hipGraphNodeTypeEventRecord = 7,

1239 hipGraphNodeTypeExtSemaphoreSignal = 8,

1240 hipGraphNodeTypeExtSemaphoreWait = 9,

1241 hipGraphNodeTypeMemAlloc = 10,

1242 hipGraphNodeTypeMemFree = 11,

1243 hipGraphNodeTypeMemcpyFromSymbol = 12,

1244 hipGraphNodeTypeMemcpyToSymbol = 13,

1245 hipGraphNodeTypeCount

1246} hipGraphNodeType;

1247

1248typedef void (*hipHostFn_t)(void* userData);

1249typedef struct hipHostNodeParams {

1250 hipHostFn_t fn;

1251 void* userData;

1252} hipHostNodeParams;

1253typedef struct hipKernelNodeParams {

1254 dim3 blockDim;

1255 void** extra;

1256 void* func;

1257 dim3 gridDim;

1258 void** kernelParams;

1259 unsigned int sharedMemBytes;

1260} hipKernelNodeParams;

1261typedef struct hipMemsetParams {

1262 void* dst;

1263 unsigned int elementSize;

1264 size_t height;

1265 size_t pitch;

1266 unsigned int value;

1267 size_t width;

1268} hipMemsetParams;

1269

1270typedef struct hipMemAllocNodeParams {

1271 hipMemPoolProps poolProps;

1273 const hipMemAccessDesc* accessDescs;

1275 size_t accessDescCount;

1276 size_t bytesize;

1277 void* dptr;

1278} hipMemAllocNodeParams;

1279

1283typedef enum hipKernelNodeAttrID {

1284 hipKernelNodeAttributeAccessPolicyWindow = 1,

1285 hipKernelNodeAttributeCooperative = 2,

1286 hipLaunchAttributePriority = 8,

1287} hipKernelNodeAttrID;

1288typedef enum hipAccessProperty {

1289 hipAccessPropertyNormal = 0,

1290 hipAccessPropertyStreaming = 1,

1291 hipAccessPropertyPersisting = 2,

1292} hipAccessProperty;

1293typedef struct hipAccessPolicyWindow {

1294 void* base_ptr;

1295 hipAccessProperty hitProp;

1296 float hitRatio;

1297 hipAccessProperty missProp;

1298 size_t num_bytes;

1299} hipAccessPolicyWindow;

1300typedef union hipKernelNodeAttrValue {

1301 hipAccessPolicyWindow accessPolicyWindow;

1302 int cooperative;

1303 int priority;

1304} hipKernelNodeAttrValue;

1305

1309typedef struct HIP_MEMSET_NODE_PARAMS {

1310 hipDeviceptr_t dst;

1311 size_t pitch;

1312 unsigned int value;

1313 unsigned int elementSize;

1314 size_t width;

1315 size_t height;

1316} HIP_MEMSET_NODE_PARAMS;

1317

1321typedef enum hipGraphExecUpdateResult {

1322 hipGraphExecUpdateSuccess = 0x0,

1323 hipGraphExecUpdateError = 0x1,

1325 hipGraphExecUpdateErrorTopologyChanged = 0x2,

1326 hipGraphExecUpdateErrorNodeTypeChanged = 0x3,

1327 hipGraphExecUpdateErrorFunctionChanged =

1328 0x4,

1329 hipGraphExecUpdateErrorParametersChanged =

1330 0x5,

1331 hipGraphExecUpdateErrorNotSupported =

1332 0x6,

1333 hipGraphExecUpdateErrorUnsupportedFunctionChange = 0x7

1334} hipGraphExecUpdateResult;

1335

1336typedef enum hipStreamCaptureMode {

1337 hipStreamCaptureModeGlobal = 0,

1338 hipStreamCaptureModeThreadLocal,

1339 hipStreamCaptureModeRelaxed

1340} hipStreamCaptureMode;

1341typedef enum hipStreamCaptureStatus {

1342 hipStreamCaptureStatusNone = 0,

1343 hipStreamCaptureStatusActive,

1344 hipStreamCaptureStatusInvalidated

1346} hipStreamCaptureStatus;

1347

1348typedef enum hipStreamUpdateCaptureDependenciesFlags {

1349 hipStreamAddCaptureDependencies = 0,

1350 hipStreamSetCaptureDependencies,

1351} hipStreamUpdateCaptureDependenciesFlags;

1352

1353typedef enum hipGraphMemAttributeType {

1354 hipGraphMemAttrUsedMemCurrent = 0,

1355 hipGraphMemAttrUsedMemHigh,

1356 hipGraphMemAttrReservedMemCurrent,

1357 hipGraphMemAttrReservedMemHigh,

1358}hipGraphMemAttributeType;

1359typedef enum hipUserObjectFlags {

1360 hipUserObjectNoDestructorSync = 0x1,

1361} hipUserObjectFlags;

1362

1363typedef enum hipUserObjectRetainFlags {

1364 hipGraphUserObjectMove = 0x1,

1365} hipUserObjectRetainFlags;

1366

1367typedef enum hipGraphInstantiateFlags {

1368 hipGraphInstantiateFlagAutoFreeOnLaunch =

1369 1,

1370 hipGraphInstantiateFlagUpload =

1371 2,

1372 hipGraphInstantiateFlagDeviceLaunch =

1373 4,

1374 hipGraphInstantiateFlagUseNodePriority =

1375 8,

1376} hipGraphInstantiateFlags;

1377

1378enum hipGraphDebugDotFlags {

1379 hipGraphDebugDotFlagsVerbose = 1

1380 << 0,

1381 hipGraphDebugDotFlagsKernelNodeParams = 1 << 2,

1382 hipGraphDebugDotFlagsMemcpyNodeParams = 1 << 3,

1383 hipGraphDebugDotFlagsMemsetNodeParams = 1 << 4,

1384 hipGraphDebugDotFlagsHostNodeParams = 1 << 5,

1385 hipGraphDebugDotFlagsEventNodeParams = 1

1386 << 6,

1387 hipGraphDebugDotFlagsExtSemasSignalNodeParams = 1

1388 << 7,

1389 hipGraphDebugDotFlagsExtSemasWaitNodeParams = 1

1390 << 8,

1391 hipGraphDebugDotFlagsKernelNodeAttributes = 1

1392 << 9,

1393 hipGraphDebugDotFlagsHandles = 1

1394 << 10

1395};

1396

1400typedef enum hipGraphInstantiateResult {

1401 hipGraphInstantiateSuccess = 0,

1402 hipGraphInstantiateError = 1,

1404 hipGraphInstantiateInvalidStructure = 2,

1406 hipGraphInstantiateNodeOperationNotSupported = 3,

1408 hipGraphInstantiateMultipleDevicesNotSupported = 4,

1410}hipGraphInstantiateResult;

1411

1415typedef struct hipGraphInstantiateParams {

1416 hipGraphNode_t errNode_out;

1417 unsigned long long flags;

1418 hipGraphInstantiateResult result_out;

1420 hipStream_t uploadStream;

1421} hipGraphInstantiateParams;

1422

1423

1427typedef struct hipMemAllocationProp {

1428 hipMemAllocationType type;

1429 hipMemAllocationHandleType requestedHandleType;

1430 hipMemLocation location;

1431 void* win32HandleMetaData;

1432 struct {

1433 unsigned char compressionType;

1434 unsigned char gpuDirectRDMACapable;

1435 unsigned short usage;

1436 } allocFlags;

1437} hipMemAllocationProp;

1438

1442typedef struct hipExternalSemaphoreSignalNodeParams {

1444 hipExternalSemaphore_t* extSemArray;

1446 const hipExternalSemaphoreSignalParams* paramsArray;

1448 unsigned int numExtSems;

1449} hipExternalSemaphoreSignalNodeParams;

1450

1454typedef struct hipExternalSemaphoreWaitNodeParams {

1456 hipExternalSemaphore_t* extSemArray;

1458 const hipExternalSemaphoreWaitParams* paramsArray;

1460 unsigned int numExtSems;

1461} hipExternalSemaphoreWaitNodeParams;

1462

1466typedef struct ihipMemGenericAllocationHandle* hipMemGenericAllocationHandle_t;

1467

1471typedef enum hipMemAllocationGranularity_flags {

1472 hipMemAllocationGranularityMinimum = 0x0,

1473 hipMemAllocationGranularityRecommended = 0x1

1474} hipMemAllocationGranularity_flags;

1475

1479typedef enum hipMemHandleType {

1480 hipMemHandleTypeGeneric = 0x0

1481} hipMemHandleType;

1482

1486typedef enum hipMemOperationType {

1487 hipMemOperationTypeMap = 0x1,

1488 hipMemOperationTypeUnmap = 0x2

1489} hipMemOperationType;

1490

1494typedef enum hipArraySparseSubresourceType {

1495 hipArraySparseSubresourceTypeSparseLevel = 0x0,

1496 hipArraySparseSubresourceTypeMiptail = 0x1

1497} hipArraySparseSubresourceType;

1498

1502typedef struct hipArrayMapInfo {

1503 hipResourceType resourceType;

1504 union {

1505 hipMipmappedArray mipmap;

1506 hipArray_t array;

1507 } resource;

1508 hipArraySparseSubresourceType subresourceType;

1509 union {

1510 struct {

1511 unsigned int level;

1512 unsigned int layer;

1513 unsigned int offsetX;

1514 unsigned int offsetY;

1515 unsigned int offsetZ;

1516 unsigned int extentWidth;

1517 unsigned int extentHeight;

1518 unsigned int extentDepth;

1519 } sparseLevel;

1520 struct {

1521 unsigned int layer;

1522 unsigned long long offset;

1523 unsigned long long size;

1524 } miptail;

1525 } subresource;

1526 hipMemOperationType memOperationType;

1527 hipMemHandleType memHandleType;

1528 union {

1529 hipMemGenericAllocationHandle_t memHandle;

1530 } memHandle;

1531 unsigned long long offset;

1532 unsigned int deviceBitMask;

1533 unsigned int flags;

1534 unsigned int reserved[2];

1535} hipArrayMapInfo;

1536

1540typedef struct hipMemcpyNodeParams {

1541 int flags;

1542 int reserved[3];

1543 hipMemcpy3DParms copyParams;

1544} hipMemcpyNodeParams;

1545

1549typedef struct hipChildGraphNodeParams {

1550 hipGraph_t graph;

1552} hipChildGraphNodeParams;

1553

1557typedef struct hipEventWaitNodeParams {

1558 hipEvent_t event;

1559} hipEventWaitNodeParams;

1560

1564typedef struct hipEventRecordNodeParams {

1565 hipEvent_t event;

1566} hipEventRecordNodeParams;

1567

1571typedef struct hipMemFreeNodeParams {

1572 void *dptr;

1573} hipMemFreeNodeParams;

1574

1578typedef struct hipGraphNodeParams {

1579 hipGraphNodeType type;

1580 int reserved0[3];

1581 union {

1582 long long reserved1[29];

1583 hipKernelNodeParams kernel;

1584 hipMemcpyNodeParams memcpy;

1585 hipMemsetParams memset;

1586 hipHostNodeParams host;

1587 hipChildGraphNodeParams graph;

1588 hipEventWaitNodeParams eventWait;

1589 hipEventRecordNodeParams eventRecord;

1590 hipExternalSemaphoreSignalNodeParams extSemSignal;

1591 hipExternalSemaphoreWaitNodeParams extSemWait;

1592 hipMemAllocNodeParams alloc;

1593 hipMemFreeNodeParams free;

1594 };

1595

1596 long long reserved2;

1597} hipGraphNodeParams;

1598// Doxygen end group GlobalDefs

1624// TODO-ctx - more description on error codes.

1625hipError_t hipInit(unsigned int flags);

1626

1642hipError_t hipDriverGetVersion(int* driverVersion);

1657hipError_t hipRuntimeGetVersion(int* runtimeVersion);

1665hipError_t hipDeviceGet(hipDevice_t* device, int ordinal);

1666

1675hipError_t hipDeviceComputeCapability(int* major, int* minor, hipDevice_t device);

1684hipError_t hipDeviceGetName(char* name, int len, hipDevice_t device);

1696hipError_t hipDeviceGetUuid(hipUUID* uuid, hipDevice_t device);

1706hipError_t hipDeviceGetP2PAttribute(int* value, hipDeviceP2PAttr attr,

1707 int srcDevice, int dstDevice);

1716hipError_t hipDeviceGetPCIBusId(char* pciBusId, int len, int device);

1724hipError_t hipDeviceGetByPCIBusId(int* device, const char* pciBusId);

1732hipError_t hipDeviceTotalMem(size_t* bytes, hipDevice_t device);

1733// doxygen end initialization

1752hipError_t hipDeviceSynchronize(void);

1764hipError_t hipDeviceReset(void);

1796hipError_t hipSetDevice(int deviceId);

1810hipError_t hipGetDevice(int* deviceId);

1823hipError_t hipGetDeviceCount(int* count);

1833hipError_t hipDeviceGetAttribute(int* pi, hipDeviceAttribute_t attr, int deviceId);

1848hipError_t hipDeviceGetDefaultMemPool(hipMemPool_t* mem_pool, int device);

1870hipError_t hipDeviceSetMemPool(int device, hipMemPool_t mem_pool);

1890hipError_t hipDeviceGetMemPool(hipMemPool_t* mem_pool, int device);

1904hipError_t hipGetDeviceProperties(hipDeviceProp_t* prop, int deviceId);

1916hipError_t hipDeviceSetCacheConfig(hipFuncCache_t cacheConfig);

1927hipError_t hipDeviceGetCacheConfig(hipFuncCache_t* cacheConfig);

1941hipError_t hipDeviceGetLimit(size_t* pValue, enum hipLimit_t limit);

1961hipError_t hipDeviceSetLimit ( enum hipLimit_t limit, size_t value );

1973hipError_t hipDeviceGetSharedMemConfig(hipSharedMemConfig* pConfig);

1981hipError_t hipGetDeviceFlags(unsigned int* flags);

1993hipError_t hipDeviceSetSharedMemConfig(hipSharedMemConfig config);

2018hipError_t hipSetDeviceFlags(unsigned flags);

2027hipError_t hipChooseDevice(int* device, const hipDeviceProp_t* prop);

2040hipError_t hipExtGetLinkTypeAndHopCount(int device1, int device2, uint32_t* linktype, uint32_t* hopcount);

2041// TODO: implement IPC apis

2065hipError_t hipIpcGetMemHandle(hipIpcMemHandle_t* handle, void* devPtr);

2101hipError_t hipIpcOpenMemHandle(void** devPtr, hipIpcMemHandle_t handle, unsigned int flags);

2119hipError_t hipIpcCloseMemHandle(void* devPtr);

2120

2137hipError_t hipIpcGetEventHandle(hipIpcEventHandle_t* handle, hipEvent_t event);

2138

2156hipError_t hipIpcOpenEventHandle(hipEvent_t* event, hipIpcEventHandle_t handle);

2157

2158// end doxygen Device

2182hipError_t hipFuncSetAttribute(const void* func, hipFuncAttribute attr, int value);

2194hipError_t hipFuncSetCacheConfig(const void* func, hipFuncCache_t config);

2207hipError_t hipFuncSetSharedMemConfig(const void* func, hipSharedMemConfig config);

2208//doxygen end execution

2230hipError_t hipGetLastError(void);

2231

2243hipError_t hipExtGetLastError(void);

2244

2255hipError_t hipPeekAtLastError(void);

2264const char* hipGetErrorName(hipError_t hip_error);

2273const char* hipGetErrorString(hipError_t hipError);

2283hipError_t hipDrvGetErrorName(hipError_t hipError, const char** errorString);

2293hipError_t hipDrvGetErrorString(hipError_t hipError, const char** errorString);

2294// end doxygen Error

2324hipError_t hipStreamCreate(hipStream_t* stream);

2341hipError_t hipStreamCreateWithFlags(hipStream_t* stream, unsigned int flags);

2359hipError_t hipStreamCreateWithPriority(hipStream_t* stream, unsigned int flags, int priority);

2374hipError_t hipDeviceGetStreamPriorityRange(int* leastPriority, int* greatestPriority);

2392hipError_t hipStreamDestroy(hipStream_t stream);

2408hipError_t hipStreamQuery(hipStream_t stream);

2429hipError_t hipStreamSynchronize(hipStream_t stream);

2449hipError_t hipStreamWaitEvent(hipStream_t stream, hipEvent_t event, unsigned int flags __dparm(0));

2463hipError_t hipStreamGetFlags(hipStream_t stream, unsigned int* flags);

2477hipError_t hipStreamGetPriority(hipStream_t stream, int* priority);

2488hipError_t hipStreamGetDevice(hipStream_t stream, hipDevice_t* device);

2508hipError_t hipExtStreamCreateWithCUMask(hipStream_t* stream, uint32_t cuMaskSize, const uint32_t* cuMask);

2521hipError_t hipExtStreamGetCUMask(hipStream_t stream, uint32_t cuMaskSize, uint32_t* cuMask);

2525typedef void (*hipStreamCallback_t)(hipStream_t stream, hipError_t status, void* userData);

2541hipError_t hipStreamAddCallback(hipStream_t stream, hipStreamCallback_t callback, void* userData,

2542 unsigned int flags);

2543// end doxygen Stream

2586hipError_t hipStreamWaitValue32(hipStream_t stream, void* ptr, uint32_t value, unsigned int flags,

2587 uint32_t mask __dparm(0xFFFFFFFF));

2620hipError_t hipStreamWaitValue64(hipStream_t stream, void* ptr, uint64_t value, unsigned int flags,

2621 uint64_t mask __dparm(0xFFFFFFFFFFFFFFFF));

2641hipError_t hipStreamWriteValue32(hipStream_t stream, void* ptr, uint32_t value, unsigned int flags);

2661hipError_t hipStreamWriteValue64(hipStream_t stream, void* ptr, uint64_t value, unsigned int flags);

2662// end doxygen Stream Memory Operations

2698hipError_t hipEventCreateWithFlags(hipEvent_t* event, unsigned flags);

2710hipError_t hipEventCreate(hipEvent_t* event);

2741#ifdef __cplusplus

2742hipError_t hipEventRecord(hipEvent_t event, hipStream_t stream = NULL);

2743#else

2744hipError_t hipEventRecord(hipEvent_t event, hipStream_t stream);

2745#endif

2762hipError_t hipEventDestroy(hipEvent_t event);

2782hipError_t hipEventSynchronize(hipEvent_t event);

2811hipError_t hipEventElapsedTime(float* ms, hipEvent_t start, hipEvent_t stop);

2828hipError_t hipEventQuery(hipEvent_t event);

2829// end doxygen Events

2860hipError_t hipPointerSetAttribute(const void* value, hipPointer_attribute attribute,

2861 hipDeviceptr_t ptr);

2862

2863

2881hipError_t hipPointerGetAttributes(hipPointerAttribute_t* attributes, const void* ptr);

2896hipError_t hipPointerGetAttribute(void* data, hipPointer_attribute attribute,

2897 hipDeviceptr_t ptr);

2914hipError_t hipDrvPointerGetAttributes(unsigned int numAttributes, hipPointer_attribute* attributes,

2915 void** data, hipDeviceptr_t ptr);

2936hipError_t hipImportExternalSemaphore(hipExternalSemaphore_t* extSem_out,

2937 const hipExternalSemaphoreHandleDesc* semHandleDesc);

2950hipError_t hipSignalExternalSemaphoresAsync(const hipExternalSemaphore_t* extSemArray,

2951 const hipExternalSemaphoreSignalParams* paramsArray,

2952 unsigned int numExtSems, hipStream_t stream);

2965hipError_t hipWaitExternalSemaphoresAsync(const hipExternalSemaphore_t* extSemArray,

2966 const hipExternalSemaphoreWaitParams* paramsArray,

2967 unsigned int numExtSems, hipStream_t stream);

2977hipError_t hipDestroyExternalSemaphore(hipExternalSemaphore_t extSem);

2978

2989hipError_t hipImportExternalMemory(hipExternalMemory_t* extMem_out, const hipExternalMemoryHandleDesc* memHandleDesc);

3001hipError_t hipExternalMemoryGetMappedBuffer(void **devPtr, hipExternalMemory_t extMem, const hipExternalMemoryBufferDesc *bufferDesc);

3011hipError_t hipDestroyExternalMemory(hipExternalMemory_t extMem);

3025hipError_t hipExternalMemoryGetMappedMipmappedArray(hipMipmappedArray_t* mipmap, hipExternalMemory_t extMem,

3026 const hipExternalMemoryMipmappedArrayDesc* mipmapDesc);

3027 // end of external resource

3044hipError_t hipMalloc(void** ptr, size_t size);

3064hipError_t hipExtMallocWithFlags(void** ptr, size_t sizeBytes, unsigned int flags);

3077DEPRECATED("use hipHostMalloc instead")

3078hipError_t hipMallocHost(void** ptr, size_t size);

3091DEPRECATED("use hipHostMalloc instead")

3092hipError_t hipMemAllocHost(void** ptr, size_t size);

3124hipError_t hipHostMalloc(void** ptr, size_t size, unsigned int flags);

3157hipError_t hipMallocManaged(void** dev_ptr,

3158 size_t size,

3159 unsigned int flags __dparm(hipMemAttachGlobal));

3172hipError_t hipMemPrefetchAsync(const void* dev_ptr,

3173 size_t count,

3174 int device,

3175 hipStream_t stream __dparm(0));

3195hipError_t hipMemAdvise(const void* dev_ptr,

3196 size_t count,

3197 hipMemoryAdvise advice,

3198 int device);

3213hipError_t hipMemRangeGetAttribute(void* data,

3214 size_t data_size,

3215 hipMemRangeAttribute attribute,

3216 const void* dev_ptr,

3217 size_t count);

3234hipError_t hipMemRangeGetAttributes(void** data,

3235 size_t* data_sizes,

3236 hipMemRangeAttribute* attributes,

3237 size_t num_attributes,

3238 const void* dev_ptr,

3239 size_t count);

3254hipError_t hipStreamAttachMemAsync(hipStream_t stream,

3255 void* dev_ptr,

3256 size_t length __dparm(0),

3257 unsigned int flags __dparm(hipMemAttachSingle));

3258// end doxygen Managed Memory

3318hipError_t hipMallocAsync(void** dev_ptr, size_t size, hipStream_t stream);

3343hipError_t hipFreeAsync(void* dev_ptr, hipStream_t stream);

3371hipError_t hipMemPoolTrimTo(hipMemPool_t mem_pool, size_t min_bytes_to_hold);

3410hipError_t hipMemPoolSetAttribute(hipMemPool_t mem_pool, hipMemPoolAttr attr, void* value);

3449hipError_t hipMemPoolGetAttribute(hipMemPool_t mem_pool, hipMemPoolAttr attr, void* value);

3467hipError_t hipMemPoolSetAccess(hipMemPool_t mem_pool, const hipMemAccessDesc* desc_list, size_t count);

3487hipError_t hipMemPoolGetAccess(hipMemAccessFlags* flags, hipMemPool_t mem_pool, hipMemLocation* location);

3511hipError_t hipMemPoolCreate(hipMemPool_t* mem_pool, const hipMemPoolProps* pool_props);

3538hipError_t hipMemPoolDestroy(hipMemPool_t mem_pool);

3572hipError_t hipMallocFromPoolAsync(void** dev_ptr, size_t size, hipMemPool_t mem_pool, hipStream_t stream);

3599hipError_t hipMemPoolExportToShareableHandle(

3600 void* shared_handle,

3601 hipMemPool_t mem_pool,

3602 hipMemAllocationHandleType handle_type,

3603 unsigned int flags);

3627hipError_t hipMemPoolImportFromShareableHandle(

3628 hipMemPool_t* mem_pool,

3629 void* shared_handle,

3630 hipMemAllocationHandleType handle_type,

3631 unsigned int flags);

3651hipError_t hipMemPoolExportPointer(hipMemPoolPtrExportData* export_data, void* dev_ptr);

3680hipError_t hipMemPoolImportPointer(

3681 void** dev_ptr,

3682 hipMemPool_t mem_pool,

3683 hipMemPoolPtrExportData* export_data);

3684// Doxygen end of ordered memory allocator

3702DEPRECATED("use hipHostMalloc instead")

3703hipError_t hipHostAlloc(void** ptr, size_t size, unsigned int flags);

3715hipError_t hipHostGetDevicePointer(void** devPtr, void* hstPtr, unsigned int flags);

3725hipError_t hipHostGetFlags(unsigned int* flagsPtr, void* hostPtr);

3762hipError_t hipHostRegister(void* hostPtr, size_t sizeBytes, unsigned int flags);

3771hipError_t hipHostUnregister(void* hostPtr);

3790hipError_t hipMallocPitch(void** ptr, size_t* pitch, size_t width, size_t height);

3813hipError_t hipMemAllocPitch(hipDeviceptr_t* dptr, size_t* pitch, size_t widthInBytes, size_t height,

3814 unsigned int elementSizeBytes);

3828hipError_t hipFree(void* ptr);

3839DEPRECATED("use hipHostFree instead")

3840hipError_t hipFreeHost(void* ptr);

3854hipError_t hipHostFree(void* ptr);

3884hipError_t hipMemcpy(void* dst, const void* src, size_t sizeBytes, hipMemcpyKind kind);

3899hipError_t hipMemcpyWithStream(void* dst, const void* src, size_t sizeBytes,

3900 hipMemcpyKind kind, hipStream_t stream);

3918hipError_t hipMemcpyHtoD(hipDeviceptr_t dst, void* src, size_t sizeBytes);

3936hipError_t hipMemcpyDtoH(void* dst, hipDeviceptr_t src, size_t sizeBytes);

3954hipError_t hipMemcpyDtoD(hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes);

3973hipError_t hipMemcpyHtoDAsync(hipDeviceptr_t dst, void* src, size_t sizeBytes, hipStream_t stream);

3992hipError_t hipMemcpyDtoHAsync(void* dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream);

4011hipError_t hipMemcpyDtoDAsync(hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes,

4012 hipStream_t stream);

4013

4028hipError_t hipModuleGetGlobal(hipDeviceptr_t* dptr, size_t* bytes,

4029 hipModule_t hmod, const char* name);

4030

4040hipError_t hipGetSymbolAddress(void** devPtr, const void* symbol);

4041

4042

4043

4053hipError_t hipGetSymbolSize(size_t* size, const void* symbol);

4054

4065hipError_t hipGetProcAddress(const char* symbol, void** pfn, int hipVersion, uint64_t flags,

4066 hipDriverProcAddressQueryResult* symbolStatus);

4067

4086hipError_t hipMemcpyToSymbol(const void* symbol, const void* src,

4087 size_t sizeBytes, size_t offset __dparm(0),

4088 hipMemcpyKind kind __dparm(hipMemcpyHostToDevice));

4089

4103hipError_t hipMemcpyToSymbolAsync(const void* symbol, const void* src,

4104 size_t sizeBytes, size_t offset,

4105 hipMemcpyKind kind, hipStream_t stream __dparm(0));

4106

4119hipError_t hipMemcpyFromSymbol(void* dst, const void* symbol,

4120 size_t sizeBytes, size_t offset __dparm(0),

4121 hipMemcpyKind kind __dparm(hipMemcpyDeviceToHost));

4122

4136hipError_t hipMemcpyFromSymbolAsync(void* dst, const void* symbol,

4137 size_t sizeBytes, size_t offset,

4138 hipMemcpyKind kind,

4139 hipStream_t stream __dparm(0));

4169hipError_t hipMemcpyAsync(void* dst, const void* src, size_t sizeBytes, hipMemcpyKind kind,

4170 hipStream_t stream __dparm(0));

4180hipError_t hipMemset(void* dst, int value, size_t sizeBytes);

4190hipError_t hipMemsetD8(hipDeviceptr_t dest, unsigned char value, size_t count);

4206hipError_t hipMemsetD8Async(hipDeviceptr_t dest, unsigned char value, size_t count, hipStream_t stream __dparm(0));

4216hipError_t hipMemsetD16(hipDeviceptr_t dest, unsigned short value, size_t count);

4232hipError_t hipMemsetD16Async(hipDeviceptr_t dest, unsigned short value, size_t count, hipStream_t stream __dparm(0));

4242hipError_t hipMemsetD32(hipDeviceptr_t dest, int value, size_t count);

4258hipError_t hipMemsetAsync(void* dst, int value, size_t sizeBytes, hipStream_t stream __dparm(0));

4274hipError_t hipMemsetD32Async(hipDeviceptr_t dst, int value, size_t count,

4275 hipStream_t stream __dparm(0));

4286hipError_t hipMemset2D(void* dst, size_t pitch, int value, size_t width, size_t height);

4298hipError_t hipMemset2DAsync(void* dst, size_t pitch, int value, size_t width, size_t height,hipStream_t stream __dparm(0));

4307hipError_t hipMemset3D(hipPitchedPtr pitchedDevPtr, int value, hipExtent extent );

4317hipError_t hipMemset3DAsync(hipPitchedPtr pitchedDevPtr, int value, hipExtent extent ,hipStream_t stream __dparm(0));

4334hipError_t hipMemGetInfo(size_t* free, size_t* total);

4335

4347hipError_t hipMemPtrGetInfo(void* ptr, size_t* size);

4360hipError_t hipMallocArray(hipArray_t* array, const hipChannelFormatDesc* desc, size_t width,

4361 size_t height __dparm(0), unsigned int flags __dparm(hipArrayDefault));

4372hipError_t hipArrayCreate(hipArray_t* pHandle, const HIP_ARRAY_DESCRIPTOR* pAllocateArray);

4382hipError_t hipArrayDestroy(hipArray_t array);

4393hipError_t hipArray3DCreate(hipArray_t* array, const HIP_ARRAY3D_DESCRIPTOR* pAllocateArray);

4404hipError_t hipMalloc3D(hipPitchedPtr* pitchedDevPtr, hipExtent extent);

4413hipError_t hipFreeArray(hipArray_t array);

4425hipError_t hipMalloc3DArray(hipArray_t* array, const struct hipChannelFormatDesc* desc,

4426 struct hipExtent extent, unsigned int flags);

4439hipError_t hipArrayGetInfo(hipChannelFormatDesc* desc, hipExtent* extent, unsigned int* flags,

4440 hipArray_t array);

4458hipError_t hipArrayGetDescriptor(HIP_ARRAY_DESCRIPTOR* pArrayDescriptor, hipArray_t array);

4476hipError_t hipArray3DGetDescriptor(HIP_ARRAY3D_DESCRIPTOR* pArrayDescriptor, hipArray_t array);

4493hipError_t hipMemcpy2D(void* dst, size_t dpitch, const void* src, size_t spitch, size_t width,

4494 size_t height, hipMemcpyKind kind);

4504hipError_t hipMemcpyParam2D(const hip_Memcpy2D* pCopy);

4515hipError_t hipMemcpyParam2DAsync(const hip_Memcpy2D* pCopy, hipStream_t stream __dparm(0));

4533hipError_t hipMemcpy2DAsync(void* dst, size_t dpitch, const void* src, size_t spitch, size_t width,

4534 size_t height, hipMemcpyKind kind, hipStream_t stream __dparm(0));

4552hipError_t hipMemcpy2DToArray(hipArray_t dst, size_t wOffset, size_t hOffset, const void* src,

4553 size_t spitch, size_t width, size_t height, hipMemcpyKind kind);

4572hipError_t hipMemcpy2DToArrayAsync(hipArray_t dst, size_t wOffset, size_t hOffset, const void* src,

4573 size_t spitch, size_t width, size_t height, hipMemcpyKind kind,

4574 hipStream_t stream __dparm(0));

4591DEPRECATED(DEPRECATED_MSG)

4592hipError_t hipMemcpyToArray(hipArray_t dst, size_t wOffset, size_t hOffset, const void* src,

4593 size_t count, hipMemcpyKind kind);

4610DEPRECATED(DEPRECATED_MSG)

4611hipError_t hipMemcpyFromArray(void* dst, hipArray_const_t srcArray, size_t wOffset, size_t hOffset,

4612 size_t count, hipMemcpyKind kind);

4630hipError_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);

4649hipError_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 __dparm(0));

4663hipError_t hipMemcpyAtoH(void* dst, hipArray_t srcArray, size_t srcOffset, size_t count);

4677hipError_t hipMemcpyHtoA(hipArray_t dstArray, size_t dstOffset, const void* srcHost, size_t count);

4688hipError_t hipMemcpy3D(const struct hipMemcpy3DParms* p);

4700hipError_t hipMemcpy3DAsync(const struct hipMemcpy3DParms* p, hipStream_t stream __dparm(0));

4711hipError_t hipDrvMemcpy3D(const HIP_MEMCPY3D* pCopy);

4723hipError_t hipDrvMemcpy3DAsync(const HIP_MEMCPY3D* pCopy, hipStream_t stream);

4724// doxygen end Memory

4752hipError_t hipDeviceCanAccessPeer(int* canAccessPeer, int deviceId, int peerDeviceId);

4769hipError_t hipDeviceEnablePeerAccess(int peerDeviceId, unsigned int flags);

4781hipError_t hipDeviceDisablePeerAccess(int peerDeviceId);

4794hipError_t hipMemGetAddressRange(hipDeviceptr_t* pbase, size_t* psize, hipDeviceptr_t dptr);

4795#ifndef USE_PEER_NON_UNIFIED

4796#define USE_PEER_NON_UNIFIED 1

4797#endif

4798#if USE_PEER_NON_UNIFIED == 1

4810hipError_t hipMemcpyPeer(void* dst, int dstDeviceId, const void* src, int srcDeviceId,

4811 size_t sizeBytes);

4824hipError_t hipMemcpyPeerAsync(void* dst, int dstDeviceId, const void* src, int srcDevice,

4825 size_t sizeBytes, hipStream_t stream __dparm(0));

4826#endif

4827// doxygen end PeerToPeer

4859DEPRECATED(DEPRECATED_MSG)

4860hipError_t hipCtxCreate(hipCtx_t* ctx, unsigned int flags, hipDevice_t device);

4873DEPRECATED(DEPRECATED_MSG)

4874hipError_t hipCtxDestroy(hipCtx_t ctx);

4887DEPRECATED(DEPRECATED_MSG)

4888hipError_t hipCtxPopCurrent(hipCtx_t* ctx);

4901DEPRECATED(DEPRECATED_MSG)

4902hipError_t hipCtxPushCurrent(hipCtx_t ctx);

4915DEPRECATED(DEPRECATED_MSG)

4916hipError_t hipCtxSetCurrent(hipCtx_t ctx);

4929DEPRECATED(DEPRECATED_MSG)

4930hipError_t hipCtxGetCurrent(hipCtx_t* ctx);

4943DEPRECATED(DEPRECATED_MSG)

4944hipError_t hipCtxGetDevice(hipDevice_t* device);

4964DEPRECATED(DEPRECATED_MSG)

4965hipError_t hipCtxGetApiVersion(hipCtx_t ctx, int* apiVersion);

4981DEPRECATED(DEPRECATED_MSG)

4982hipError_t hipCtxGetCacheConfig(hipFuncCache_t* cacheConfig);

4998DEPRECATED(DEPRECATED_MSG)

4999hipError_t hipCtxSetCacheConfig(hipFuncCache_t cacheConfig);

5015DEPRECATED(DEPRECATED_MSG)

5016hipError_t hipCtxSetSharedMemConfig(hipSharedMemConfig config);

5032DEPRECATED(DEPRECATED_MSG)

5033hipError_t hipCtxGetSharedMemConfig(hipSharedMemConfig* pConfig);

5047DEPRECATED(DEPRECATED_MSG)

5048hipError_t hipCtxSynchronize(void);

5061DEPRECATED(DEPRECATED_MSG)

5062hipError_t hipCtxGetFlags(unsigned int* flags);

5084DEPRECATED(DEPRECATED_MSG)

5085hipError_t hipCtxEnablePeerAccess(hipCtx_t peerCtx, unsigned int flags);

5104DEPRECATED(DEPRECATED_MSG)

5105hipError_t hipCtxDisablePeerAccess(hipCtx_t peerCtx);

5106// doxygen end Context deprecated

5122hipError_t hipDevicePrimaryCtxGetState(hipDevice_t dev, unsigned int* flags, int* active);

5135hipError_t hipDevicePrimaryCtxRelease(hipDevice_t dev);

5148hipError_t hipDevicePrimaryCtxRetain(hipCtx_t* pctx, hipDevice_t dev);

5159hipError_t hipDevicePrimaryCtxReset(hipDevice_t dev);

5171hipError_t hipDevicePrimaryCtxSetFlags(hipDevice_t dev, unsigned int flags);

5172// doxygen end Context Management

5199hipError_t hipModuleLoad(hipModule_t* module, const char* fname);

5209hipError_t hipModuleUnload(hipModule_t module);

5220hipError_t hipModuleGetFunction(hipFunction_t* function, hipModule_t module, const char* kname);

5229hipError_t hipFuncGetAttributes(struct hipFuncAttributes* attr, const void* func);

5239hipError_t hipFuncGetAttribute(int* value, hipFunction_attribute attrib, hipFunction_t hfunc);

5249hipError_t hipModuleGetTexRef(textureReference** texRef, hipModule_t hmod, const char* name);

5259hipError_t hipModuleLoadData(hipModule_t* module, const void* image);

5272hipError_t hipModuleLoadDataEx(hipModule_t* module, const void* image, unsigned int numOptions,

5273 hipJitOption* options, void** optionValues);

5302hipError_t hipModuleLaunchKernel(hipFunction_t f, unsigned int gridDimX, unsigned int gridDimY,

5303 unsigned int gridDimZ, unsigned int blockDimX,

5304 unsigned int blockDimY, unsigned int blockDimZ,

5305 unsigned int sharedMemBytes, hipStream_t stream,

5306 void** kernelParams, void** extra);

5332hipError_t hipModuleLaunchCooperativeKernel(hipFunction_t f, unsigned int gridDimX,

5333 unsigned int gridDimY, unsigned int gridDimZ,

5334 unsigned int blockDimX, unsigned int blockDimY,

5335 unsigned int blockDimZ, unsigned int sharedMemBytes,

5336 hipStream_t stream, void** kernelParams);

5351hipError_t hipModuleLaunchCooperativeKernelMultiDevice(hipFunctionLaunchParams* launchParamsList,

5352 unsigned int numDevices,

5353 unsigned int flags);

5372hipError_t hipLaunchCooperativeKernel(const void* f, dim3 gridDim, dim3 blockDimX,

5373 void** kernelParams, unsigned int sharedMemBytes,

5374 hipStream_t stream);

5386hipError_t hipLaunchCooperativeKernelMultiDevice(hipLaunchParams* launchParamsList,

5387 int numDevices, unsigned int flags);

5399hipError_t hipExtLaunchMultiKernelMultiDevice(hipLaunchParams* launchParamsList,

5400 int numDevices, unsigned int flags);

5401// doxygen end Module

5428//TODO - Match CUoccupancyB2DSize

5429hipError_t hipModuleOccupancyMaxPotentialBlockSize(int* gridSize, int* blockSize,

5430 hipFunction_t f, size_t dynSharedMemPerBlk,

5431 int blockSizeLimit);

5447//TODO - Match CUoccupancyB2DSize

5448hipError_t hipModuleOccupancyMaxPotentialBlockSizeWithFlags(int* gridSize, int* blockSize,

5449 hipFunction_t f, size_t dynSharedMemPerBlk,

5450 int blockSizeLimit, unsigned int flags);

5460hipError_t hipModuleOccupancyMaxActiveBlocksPerMultiprocessor(

5461 int* numBlocks, hipFunction_t f, int blockSize, size_t dynSharedMemPerBlk);

5472hipError_t hipModuleOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(

5473 int* numBlocks, hipFunction_t f, int blockSize, size_t dynSharedMemPerBlk, unsigned int flags);

5483hipError_t hipOccupancyMaxActiveBlocksPerMultiprocessor(

5484 int* numBlocks, const void* f, int blockSize, size_t dynSharedMemPerBlk);

5495hipError_t hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(

5496 int* numBlocks, const void* f, int blockSize, size_t dynSharedMemPerBlk, unsigned int flags __dparm(hipOccupancyDefault));

5511hipError_t hipOccupancyMaxPotentialBlockSize(int* gridSize, int* blockSize,

5512 const void* f, size_t dynSharedMemPerBlk,

5513 int blockSizeLimit);

5514// doxygen end Occupancy

5528// TODO - expand descriptions:

5535DEPRECATED("use roctracer/rocTX instead")

5536hipError_t hipProfilerStart();

5543DEPRECATED("use roctracer/rocTX instead")

5544hipError_t hipProfilerStop();

5545// doxygen end profiler

5572hipError_t hipConfigureCall(dim3 gridDim, dim3 blockDim, size_t sharedMem __dparm(0), hipStream_t stream __dparm(0));

5583hipError_t hipSetupArgument(const void* arg, size_t size, size_t offset);

5592hipError_t hipLaunchByPtr(const void* func);

5609hipError_t __hipPushCallConfiguration(dim3 gridDim,

5610 dim3 blockDim,

5611 size_t sharedMem __dparm(0),

5612 hipStream_t stream __dparm(0));

5632hipError_t __hipPopCallConfiguration(dim3 *gridDim,

5633 dim3 *blockDim,

5634 size_t *sharedMem,

5635 hipStream_t *stream);

5651hipError_t hipLaunchKernel(const void* function_address,

5652 dim3 numBlocks,

5653 dim3 dimBlocks,

5654 void** args,

5655 size_t sharedMemBytes __dparm(0),

5656 hipStream_t stream __dparm(0));

5657

5669hipError_t hipLaunchHostFunc(hipStream_t stream, hipHostFn_t fn, void* userData);

5670

5678hipError_t hipDrvMemcpy2DUnaligned(const hip_Memcpy2D* pCopy);

5679//TODO: Move this to hip_ext.h

5700hipError_t hipExtLaunchKernel(const void* function_address, dim3 numBlocks, dim3 dimBlocks,

5701 void** args, size_t sharedMemBytes, hipStream_t stream,

5702 hipEvent_t startEvent, hipEvent_t stopEvent, int flags);

5703// doxygen end Clang launch

5729hipError_t hipCreateTextureObject(

5730 hipTextureObject_t* pTexObject,

5731 const hipResourceDesc* pResDesc,

5732 const hipTextureDesc* pTexDesc,

5733 const struct hipResourceViewDesc* pResViewDesc);

5734

5743hipError_t hipDestroyTextureObject(hipTextureObject_t textureObject);

5744

5754hipError_t hipGetChannelDesc(

5755 hipChannelFormatDesc* desc,

5756 hipArray_const_t array);

5757

5767hipError_t hipGetTextureObjectResourceDesc(

5768 hipResourceDesc* pResDesc,

5769 hipTextureObject_t textureObject);

5770

5780hipError_t hipGetTextureObjectResourceViewDesc(

5781 struct hipResourceViewDesc* pResViewDesc,

5782 hipTextureObject_t textureObject);

5783

5793hipError_t hipGetTextureObjectTextureDesc(

5794 hipTextureDesc* pTexDesc,

5795 hipTextureObject_t textureObject);

5796

5808hipError_t hipTexObjectCreate(

5809 hipTextureObject_t* pTexObject,

5810 const HIP_RESOURCE_DESC* pResDesc,

5811 const HIP_TEXTURE_DESC* pTexDesc,

5812 const HIP_RESOURCE_VIEW_DESC* pResViewDesc);

5813

5822hipError_t hipTexObjectDestroy(

5823 hipTextureObject_t texObject);

5824

5834hipError_t hipTexObjectGetResourceDesc(

5835 HIP_RESOURCE_DESC* pResDesc,

5836 hipTextureObject_t texObject);

5837

5847hipError_t hipTexObjectGetResourceViewDesc(

5848 HIP_RESOURCE_VIEW_DESC* pResViewDesc,

5849 hipTextureObject_t texObject);

5850

5860hipError_t hipTexObjectGetTextureDesc(

5861 HIP_TEXTURE_DESC* pTexDesc,

5862 hipTextureObject_t texObject);

5863

5878hipError_t hipMallocMipmappedArray(

5879 hipMipmappedArray_t *mipmappedArray,

5880 const struct hipChannelFormatDesc* desc,

5881 struct hipExtent extent,

5882 unsigned int numLevels,

5883 unsigned int flags __dparm(0));

5884

5895hipError_t hipFreeMipmappedArray(hipMipmappedArray_t mipmappedArray);

5896

5909hipError_t hipGetMipmappedArrayLevel(

5910 hipArray_t *levelArray,

5911 hipMipmappedArray_const_t mipmappedArray,

5912 unsigned int level);

5913

5925hipError_t hipMipmappedArrayCreate(

5926 hipMipmappedArray_t* pHandle,

5927 HIP_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc,

5928 unsigned int numMipmapLevels);

5929

5940hipError_t hipMipmappedArrayDestroy(hipMipmappedArray_t hMipmappedArray);

5941

5954hipError_t hipMipmappedArrayGetLevel(

5955 hipArray_t* pLevelArray,

5956 hipMipmappedArray_t hMipMappedArray,

5957 unsigned int level);

5958

5977DEPRECATED(DEPRECATED_MSG)

5978hipError_t hipBindTextureToMipmappedArray(

5979 const textureReference* tex,

5980 hipMipmappedArray_const_t mipmappedArray,

5981 const hipChannelFormatDesc* desc);

5982

5993DEPRECATED(DEPRECATED_MSG)

5994hipError_t hipGetTextureReference(

5995 const textureReference** texref,

5996 const void* symbol);

6008DEPRECATED(DEPRECATED_MSG)

6009hipError_t hipTexRefSetAddressMode(

6010 textureReference* texRef,

6011 int dim,

6012 enum hipTextureAddressMode am);

6025DEPRECATED(DEPRECATED_MSG)

6026hipError_t hipTexRefSetArray(

6027 textureReference* tex,

6028 hipArray_const_t array,

6029 unsigned int flags);

6041DEPRECATED(DEPRECATED_MSG)

6042hipError_t hipTexRefSetFilterMode(

6043 textureReference* texRef,

6044 enum hipTextureFilterMode fm);

6056DEPRECATED(DEPRECATED_MSG)

6057hipError_t hipTexRefSetFlags(

6058 textureReference* texRef,

6059 unsigned int Flags);

6072DEPRECATED(DEPRECATED_MSG)

6073hipError_t hipTexRefSetFormat(

6074 textureReference* texRef,

6075 hipArray_Format fmt,

6076 int NumPackedComponents);

6091DEPRECATED(DEPRECATED_MSG)

6092hipError_t hipBindTexture(

6093 size_t* offset,

6094 const textureReference* tex,

6095 const void* devPtr,

6096 const hipChannelFormatDesc* desc,

6097 size_t size __dparm(UINT_MAX));

6114DEPRECATED(DEPRECATED_MSG)

6115hipError_t hipBindTexture2D(

6116 size_t* offset,

6117 const textureReference* tex,

6118 const void* devPtr,

6119 const hipChannelFormatDesc* desc,

6120 size_t width,

6121 size_t height,

6122 size_t pitch);

6135DEPRECATED(DEPRECATED_MSG)

6136hipError_t hipBindTextureToArray(

6137 const textureReference* tex,

6138 hipArray_const_t array,

6139 const hipChannelFormatDesc* desc);

6151DEPRECATED(DEPRECATED_MSG)

6152hipError_t hipGetTextureAlignmentOffset(

6153 size_t* offset,

6154 const textureReference* texref);

6165DEPRECATED(DEPRECATED_MSG)

6166hipError_t hipUnbindTexture(const textureReference* tex);

6178DEPRECATED(DEPRECATED_MSG)

6179hipError_t hipTexRefGetAddress(

6180 hipDeviceptr_t* dev_ptr,

6181 const textureReference* texRef);

6194DEPRECATED(DEPRECATED_MSG)

6195hipError_t hipTexRefGetAddressMode(

6196 enum hipTextureAddressMode* pam,

6197 const textureReference* texRef,

6198 int dim);

6210DEPRECATED(DEPRECATED_MSG)

6211hipError_t hipTexRefGetFilterMode(

6212 enum hipTextureFilterMode* pfm,

6213 const textureReference* texRef);

6225DEPRECATED(DEPRECATED_MSG)

6226hipError_t hipTexRefGetFlags(

6227 unsigned int* pFlags,

6228 const textureReference* texRef);

6241DEPRECATED(DEPRECATED_MSG)

6242hipError_t hipTexRefGetFormat(

6243 hipArray_Format* pFormat,

6244 int* pNumChannels,

6245 const textureReference* texRef);

6257DEPRECATED(DEPRECATED_MSG)

6258hipError_t hipTexRefGetMaxAnisotropy(

6259 int* pmaxAnsio,

6260 const textureReference* texRef);

6272DEPRECATED(DEPRECATED_MSG)

6273hipError_t hipTexRefGetMipmapFilterMode(

6274 enum hipTextureFilterMode* pfm,

6275 const textureReference* texRef);

6287DEPRECATED(DEPRECATED_MSG)

6288hipError_t hipTexRefGetMipmapLevelBias(

6289 float* pbias,

6290 const textureReference* texRef);

6303DEPRECATED(DEPRECATED_MSG)

6304hipError_t hipTexRefGetMipmapLevelClamp(

6305 float* pminMipmapLevelClamp,

6306 float* pmaxMipmapLevelClamp,

6307 const textureReference* texRef);

6319DEPRECATED(DEPRECATED_MSG)

6320hipError_t hipTexRefGetMipMappedArray(

6321 hipMipmappedArray_t* pArray,

6322 const textureReference* texRef);

6336DEPRECATED(DEPRECATED_MSG)

6337hipError_t hipTexRefSetAddress(

6338 size_t* ByteOffset,

6339 textureReference* texRef,

6340 hipDeviceptr_t dptr,

6341 size_t bytes);

6355DEPRECATED(DEPRECATED_MSG)

6356hipError_t hipTexRefSetAddress2D(

6357 textureReference* texRef,

6358 const HIP_ARRAY_DESCRIPTOR* desc,

6359 hipDeviceptr_t dptr,

6360 size_t Pitch);

6372DEPRECATED(DEPRECATED_MSG)

6373hipError_t hipTexRefSetMaxAnisotropy(

6374 textureReference* texRef,

6375 unsigned int maxAniso);

6387DEPRECATED(DEPRECATED_MSG)

6388hipError_t hipTexRefSetBorderColor(

6389 textureReference* texRef,

6390 float* pBorderColor);

6402DEPRECATED(DEPRECATED_MSG)

6403hipError_t hipTexRefSetMipmapFilterMode(

6404 textureReference* texRef,

6405 enum hipTextureFilterMode fm);

6417DEPRECATED(DEPRECATED_MSG)

6418hipError_t hipTexRefSetMipmapLevelBias(

6419 textureReference* texRef,

6420 float bias);

6433DEPRECATED(DEPRECATED_MSG)

6434hipError_t hipTexRefSetMipmapLevelClamp(

6435 textureReference* texRef,

6436 float minMipMapLevelClamp,

6437 float maxMipMapLevelClamp);

6450DEPRECATED(DEPRECATED_MSG)

6451hipError_t hipTexRefSetMipmappedArray(

6452 textureReference* texRef,

6453 struct hipMipmappedArray* mipmappedArray,

6454 unsigned int Flags);

6455

6456// doxygen end deprecated texture management

6461// doxygen end Texture management

6473// This group is for HIPrtc

6474

6475// doxygen end Runtime

6494const char* hipApiName(uint32_t id);

6503const char* hipKernelNameRef(const hipFunction_t f);

6513const char* hipKernelNameRefByPtr(const void* hostFunction, hipStream_t stream);

6522int hipGetStreamDeviceId(hipStream_t stream);

6523

6524// doxygen end Callback

6549hipError_t hipStreamBeginCapture(hipStream_t stream, hipStreamCaptureMode mode);

6550

6563hipError_t hipStreamEndCapture(hipStream_t stream, hipGraph_t* pGraph);

6564

6578hipError_t hipStreamGetCaptureInfo(hipStream_t stream, hipStreamCaptureStatus* pCaptureStatus,

6579 unsigned long long* pId);

6580

6597hipError_t hipStreamGetCaptureInfo_v2(hipStream_t stream, hipStreamCaptureStatus* captureStatus_out,

6598 unsigned long long* id_out __dparm(0),

6599 hipGraph_t* graph_out __dparm(0),

6600 const hipGraphNode_t** dependencies_out __dparm(0),

6601 size_t* numDependencies_out __dparm(0));

6602

6615hipError_t hipStreamIsCapturing(hipStream_t stream, hipStreamCaptureStatus* pCaptureStatus);

6616

6631hipError_t hipStreamUpdateCaptureDependencies(hipStream_t stream, hipGraphNode_t* dependencies,

6632 size_t numDependencies,

6633 unsigned int flags __dparm(0));

6634

6645hipError_t hipThreadExchangeStreamCaptureMode(hipStreamCaptureMode* mode);

6646

6659hipError_t hipGraphCreate(hipGraph_t* pGraph, unsigned int flags);

6660

6672hipError_t hipGraphDestroy(hipGraph_t graph);

6673

6687hipError_t hipGraphAddDependencies(hipGraph_t graph, const hipGraphNode_t* from,

6688 const hipGraphNode_t* to, size_t numDependencies);

6689

6703hipError_t hipGraphRemoveDependencies(hipGraph_t graph, const hipGraphNode_t* from,

6704 const hipGraphNode_t* to, size_t numDependencies);

6705

6723hipError_t hipGraphGetEdges(hipGraph_t graph, hipGraphNode_t* from, hipGraphNode_t* to,

6724 size_t* numEdges);

6725

6742hipError_t hipGraphGetNodes(hipGraph_t graph, hipGraphNode_t* nodes, size_t* numNodes);

6743

6760hipError_t hipGraphGetRootNodes(hipGraph_t graph, hipGraphNode_t* pRootNodes,

6761 size_t* pNumRootNodes);

6762

6779hipError_t hipGraphNodeGetDependencies(hipGraphNode_t node, hipGraphNode_t* pDependencies,

6780 size_t* pNumDependencies);

6781

6799hipError_t hipGraphNodeGetDependentNodes(hipGraphNode_t node, hipGraphNode_t* pDependentNodes,

6800 size_t* pNumDependentNodes);

6801

6813hipError_t hipGraphNodeGetType(hipGraphNode_t node, hipGraphNodeType* pType);

6814

6825hipError_t hipGraphDestroyNode(hipGraphNode_t node);

6826

6838hipError_t hipGraphClone(hipGraph_t* pGraphClone, hipGraph_t originalGraph);

6839

6852hipError_t hipGraphNodeFindInClone(hipGraphNode_t* pNode, hipGraphNode_t originalNode,

6853 hipGraph_t clonedGraph);

6854

6871hipError_t hipGraphInstantiate(hipGraphExec_t* pGraphExec, hipGraph_t graph,

6872 hipGraphNode_t* pErrorNode, char* pLogBuffer, size_t bufferSize);

6873

6886hipError_t hipGraphInstantiateWithFlags(hipGraphExec_t* pGraphExec, hipGraph_t graph,

6887 unsigned long long flags);

6888

6900hipError_t hipGraphInstantiateWithParams(hipGraphExec_t* pGraphExec, hipGraph_t graph,

6901 hipGraphInstantiateParams *instantiateParams);

6912hipError_t hipGraphLaunch(hipGraphExec_t graphExec, hipStream_t stream);

6913

6924hipError_t hipGraphUpload(hipGraphExec_t graphExec, hipStream_t stream);

6925

6938hipError_t hipGraphAddNode(hipGraphNode_t *pGraphNode, hipGraph_t graph,

6939 const hipGraphNode_t *pDependencies, size_t numDependencies,

6940 hipGraphNodeParams *nodeParams);

6941

6951hipError_t hipGraphExecGetFlags(hipGraphExec_t graphExec, unsigned long long* flags);

6952

6962hipError_t hipGraphNodeSetParams(hipGraphNode_t node, hipGraphNodeParams *nodeParams);

6963

6974hipError_t hipGraphExecNodeSetParams(hipGraphExec_t graphExec, hipGraphNode_t node, hipGraphNodeParams* nodeParams);

6975

6986hipError_t hipGraphExecDestroy(hipGraphExec_t graphExec);

6987

6988// Check whether an executable graph can be updated with a graph and perform the update if possible.

7002hipError_t hipGraphExecUpdate(hipGraphExec_t hGraphExec, hipGraph_t hGraph,

7003 hipGraphNode_t* hErrorNode_out,

7004 hipGraphExecUpdateResult* updateResult_out);

7005

7018hipError_t hipGraphAddKernelNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7019 const hipGraphNode_t* pDependencies, size_t numDependencies,

7020 const hipKernelNodeParams* pNodeParams);

7021

7031hipError_t hipGraphKernelNodeGetParams(hipGraphNode_t node, hipKernelNodeParams* pNodeParams);

7032

7042hipError_t hipGraphKernelNodeSetParams(hipGraphNode_t node, const hipKernelNodeParams* pNodeParams);

7043

7054hipError_t hipGraphExecKernelNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node,

7055 const hipKernelNodeParams* pNodeParams);

7056

7070hipError_t hipDrvGraphAddMemcpyNode(hipGraphNode_t* phGraphNode, hipGraph_t hGraph,

7071 const hipGraphNode_t* dependencies,

7072 size_t numDependencies,

7073 const HIP_MEMCPY3D* copyParams, hipCtx_t ctx);

7086hipError_t hipGraphAddMemcpyNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7087 const hipGraphNode_t* pDependencies, size_t numDependencies,

7088 const hipMemcpy3DParms* pCopyParams);

7098hipError_t hipGraphMemcpyNodeGetParams(hipGraphNode_t node, hipMemcpy3DParms* pNodeParams);

7099

7109hipError_t hipGraphMemcpyNodeSetParams(hipGraphNode_t node, const hipMemcpy3DParms* pNodeParams);

7110

7121hipError_t hipGraphKernelNodeSetAttribute(hipGraphNode_t hNode, hipKernelNodeAttrID attr,

7122 const hipKernelNodeAttrValue* value);

7133hipError_t hipGraphKernelNodeGetAttribute(hipGraphNode_t hNode, hipKernelNodeAttrID attr,

7134 hipKernelNodeAttrValue* value);

7145hipError_t hipGraphExecMemcpyNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node,

7146 hipMemcpy3DParms* pNodeParams);

7147

7163hipError_t hipGraphAddMemcpyNode1D(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7164 const hipGraphNode_t* pDependencies, size_t numDependencies,

7165 void* dst, const void* src, size_t count, hipMemcpyKind kind);

7166

7179hipError_t hipGraphMemcpyNodeSetParams1D(hipGraphNode_t node, void* dst, const void* src,

7180 size_t count, hipMemcpyKind kind);

7181

7196hipError_t hipGraphExecMemcpyNodeSetParams1D(hipGraphExec_t hGraphExec, hipGraphNode_t node,

7197 void* dst, const void* src, size_t count,

7198 hipMemcpyKind kind);

7199

7216hipError_t hipGraphAddMemcpyNodeFromSymbol(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7217 const hipGraphNode_t* pDependencies,

7218 size_t numDependencies, void* dst, const void* symbol,

7219 size_t count, size_t offset, hipMemcpyKind kind);

7220

7234hipError_t hipGraphMemcpyNodeSetParamsFromSymbol(hipGraphNode_t node, void* dst, const void* symbol,

7235 size_t count, size_t offset, hipMemcpyKind kind);

7236

7252hipError_t hipGraphExecMemcpyNodeSetParamsFromSymbol(hipGraphExec_t hGraphExec, hipGraphNode_t node,

7253 void* dst, const void* symbol, size_t count,

7254 size_t offset, hipMemcpyKind kind);

7255

7272hipError_t hipGraphAddMemcpyNodeToSymbol(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7273 const hipGraphNode_t* pDependencies,

7274 size_t numDependencies, const void* symbol,

7275 const void* src, size_t count, size_t offset,

7276 hipMemcpyKind kind);

7277

7291hipError_t hipGraphMemcpyNodeSetParamsToSymbol(hipGraphNode_t node, const void* symbol,

7292 const void* src, size_t count, size_t offset,

7293 hipMemcpyKind kind);

7294

7295

7310hipError_t hipGraphExecMemcpyNodeSetParamsToSymbol(hipGraphExec_t hGraphExec, hipGraphNode_t node,

7311 const void* symbol, const void* src,

7312 size_t count, size_t offset, hipMemcpyKind kind);

7313

7326hipError_t hipGraphAddMemsetNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7327 const hipGraphNode_t* pDependencies, size_t numDependencies,

7328 const hipMemsetParams* pMemsetParams);

7329

7339hipError_t hipGraphMemsetNodeGetParams(hipGraphNode_t node, hipMemsetParams* pNodeParams);

7340

7350hipError_t hipGraphMemsetNodeSetParams(hipGraphNode_t node, const hipMemsetParams* pNodeParams);

7351

7362hipError_t hipGraphExecMemsetNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node,

7363 const hipMemsetParams* pNodeParams);

7364

7377hipError_t hipGraphAddHostNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7378 const hipGraphNode_t* pDependencies, size_t numDependencies,

7379 const hipHostNodeParams* pNodeParams);

7380

7390hipError_t hipGraphHostNodeGetParams(hipGraphNode_t node, hipHostNodeParams* pNodeParams);

7391

7401hipError_t hipGraphHostNodeSetParams(hipGraphNode_t node, const hipHostNodeParams* pNodeParams);

7402

7413hipError_t hipGraphExecHostNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node,

7414 const hipHostNodeParams* pNodeParams);

7415

7428hipError_t hipGraphAddChildGraphNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7429 const hipGraphNode_t* pDependencies, size_t numDependencies,

7430 hipGraph_t childGraph);

7431

7441hipError_t hipGraphChildGraphNodeGetGraph(hipGraphNode_t node, hipGraph_t* pGraph);

7442

7453hipError_t hipGraphExecChildGraphNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node,

7454 hipGraph_t childGraph);

7455

7467hipError_t hipGraphAddEmptyNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7468 const hipGraphNode_t* pDependencies, size_t numDependencies);

7469

7470

7483hipError_t hipGraphAddEventRecordNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7484 const hipGraphNode_t* pDependencies, size_t numDependencies,

7485 hipEvent_t event);

7486

7496hipError_t hipGraphEventRecordNodeGetEvent(hipGraphNode_t node, hipEvent_t* event_out);

7497

7507hipError_t hipGraphEventRecordNodeSetEvent(hipGraphNode_t node, hipEvent_t event);

7508

7519hipError_t hipGraphExecEventRecordNodeSetEvent(hipGraphExec_t hGraphExec, hipGraphNode_t hNode,

7520 hipEvent_t event);

7521

7534hipError_t hipGraphAddEventWaitNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7535 const hipGraphNode_t* pDependencies, size_t numDependencies,

7536 hipEvent_t event);

7537

7538

7548hipError_t hipGraphEventWaitNodeGetEvent(hipGraphNode_t node, hipEvent_t* event_out);

7549

7559hipError_t hipGraphEventWaitNodeSetEvent(hipGraphNode_t node, hipEvent_t event);

7560

7571hipError_t hipGraphExecEventWaitNodeSetEvent(hipGraphExec_t hGraphExec, hipGraphNode_t hNode,

7572 hipEvent_t event);

7573

7586hipError_t hipGraphAddMemAllocNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7587 const hipGraphNode_t* pDependencies, size_t numDependencies, hipMemAllocNodeParams* pNodeParams);

7588

7598hipError_t hipGraphMemAllocNodeGetParams(hipGraphNode_t node, hipMemAllocNodeParams* pNodeParams);

7599

7612hipError_t hipGraphAddMemFreeNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7613 const hipGraphNode_t* pDependencies, size_t numDependencies, void* dev_ptr);

7614

7624hipError_t hipGraphMemFreeNodeGetParams(hipGraphNode_t node, void* dev_ptr);

7625

7636hipError_t hipDeviceGetGraphMemAttribute(int device, hipGraphMemAttributeType attr, void* value);

7637

7648hipError_t hipDeviceSetGraphMemAttribute(int device, hipGraphMemAttributeType attr, void* value);

7649

7659hipError_t hipDeviceGraphMemTrim(int device);

7660

7673hipError_t hipUserObjectCreate(hipUserObject_t* object_out, void* ptr, hipHostFn_t destroy,

7674 unsigned int initialRefcount, unsigned int flags);

7675

7685hipError_t hipUserObjectRelease(hipUserObject_t object, unsigned int count __dparm(1));

7686

7696hipError_t hipUserObjectRetain(hipUserObject_t object, unsigned int count __dparm(1));

7697

7709hipError_t hipGraphRetainUserObject(hipGraph_t graph, hipUserObject_t object,

7710 unsigned int count __dparm(1), unsigned int flags __dparm(0));

7711

7722hipError_t hipGraphReleaseUserObject(hipGraph_t graph, hipUserObject_t object,

7723 unsigned int count __dparm(1));

7724

7735hipError_t hipGraphDebugDotPrint(hipGraph_t graph, const char* path, unsigned int flags);

7736

7751hipError_t hipGraphKernelNodeCopyAttributes(hipGraphNode_t hSrc, hipGraphNode_t hDst);

7752

7775hipError_t hipGraphNodeSetEnabled(hipGraphExec_t hGraphExec, hipGraphNode_t hNode,

7776 unsigned int isEnabled);

7797hipError_t hipGraphNodeGetEnabled(hipGraphExec_t hGraphExec, hipGraphNode_t hNode,

7798 unsigned int* isEnabled);

7799

7812hipError_t hipGraphAddExternalSemaphoresWaitNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7813 const hipGraphNode_t* pDependencies, size_t numDependencies,

7814 const hipExternalSemaphoreWaitNodeParams* nodeParams);

7815

7828hipError_t hipGraphAddExternalSemaphoresSignalNode(hipGraphNode_t* pGraphNode, hipGraph_t graph,

7829 const hipGraphNode_t* pDependencies, size_t numDependencies,

7830 const hipExternalSemaphoreSignalNodeParams* nodeParams);

7840hipError_t hipGraphExternalSemaphoresSignalNodeSetParams(hipGraphNode_t hNode,

7841 const hipExternalSemaphoreSignalNodeParams* nodeParams);

7851hipError_t hipGraphExternalSemaphoresWaitNodeSetParams(hipGraphNode_t hNode,

7852 const hipExternalSemaphoreWaitNodeParams* nodeParams);

7862hipError_t hipGraphExternalSemaphoresSignalNodeGetParams(hipGraphNode_t hNode,

7863 hipExternalSemaphoreSignalNodeParams* params_out);

7873hipError_t hipGraphExternalSemaphoresWaitNodeGetParams(hipGraphNode_t hNode,

7874 hipExternalSemaphoreWaitNodeParams* params_out);

7885hipError_t hipGraphExecExternalSemaphoresSignalNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t hNode,

7886 const hipExternalSemaphoreSignalNodeParams* nodeParams);

7897hipError_t hipGraphExecExternalSemaphoresWaitNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t hNode,

7898 const hipExternalSemaphoreWaitNodeParams* nodeParams);

7899

7909hipError_t hipDrvGraphMemcpyNodeGetParams(hipGraphNode_t hNode, HIP_MEMCPY3D* nodeParams);

7910

7920hipError_t hipDrvGraphMemcpyNodeSetParams(hipGraphNode_t hNode, const HIP_MEMCPY3D* nodeParams);

7921

7935hipError_t hipDrvGraphAddMemsetNode(hipGraphNode_t* phGraphNode, hipGraph_t hGraph,

7936 const hipGraphNode_t* dependencies, size_t numDependencies,

7937 const HIP_MEMSET_NODE_PARAMS* memsetParams, hipCtx_t ctx);

7938

7951hipError_t hipDrvGraphAddMemFreeNode(hipGraphNode_t* phGraphNode, hipGraph_t hGraph,

7952 const hipGraphNode_t* dependencies, size_t numDependencies,

7953 hipDeviceptr_t dptr);

7954

7966hipError_t hipDrvGraphExecMemcpyNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t hNode,

7967 const HIP_MEMCPY3D* copyParams, hipCtx_t ctx);

7968

7980hipError_t hipDrvGraphExecMemsetNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t hNode,

7981 const HIP_MEMSET_NODE_PARAMS* memsetParams, hipCtx_t ctx);

7982

7983// doxygen end graph API

8011hipError_t hipMemAddressFree(void* devPtr, size_t size);

8012

8027hipError_t hipMemAddressReserve(void** ptr, size_t size, size_t alignment, void* addr, unsigned long long flags);

8028

8042hipError_t hipMemCreate(hipMemGenericAllocationHandle_t* handle, size_t size, const hipMemAllocationProp* prop, unsigned long long flags);

8043

8057hipError_t hipMemExportToShareableHandle(void* shareableHandle, hipMemGenericAllocationHandle_t handle, hipMemAllocationHandleType handleType, unsigned long long flags);

8058

8071hipError_t hipMemGetAccess(unsigned long long* flags, const hipMemLocation* location, void* ptr);

8072

8086hipError_t hipMemGetAllocationGranularity(size_t* granularity, const hipMemAllocationProp* prop, hipMemAllocationGranularity_flags option);

8087

8099hipError_t hipMemGetAllocationPropertiesFromHandle(hipMemAllocationProp* prop, hipMemGenericAllocationHandle_t handle);

8100

8113hipError_t hipMemImportFromShareableHandle(hipMemGenericAllocationHandle_t* handle, void* osHandle, hipMemAllocationHandleType shHandleType);

8114

8129hipError_t hipMemMap(void* ptr, size_t size, size_t offset, hipMemGenericAllocationHandle_t handle, unsigned long long flags);

8130

8143hipError_t hipMemMapArrayAsync(hipArrayMapInfo* mapInfoList, unsigned int count, hipStream_t stream);

8144

8155hipError_t hipMemRelease(hipMemGenericAllocationHandle_t handle);

8156

8168hipError_t hipMemRetainAllocationHandle(hipMemGenericAllocationHandle_t* handle, void* addr);

8169

8183hipError_t hipMemSetAccess(void* ptr, size_t size, const hipMemAccessDesc* desc, size_t count);

8184

8196hipError_t hipMemUnmap(void* ptr, size_t size);

8197

8198// doxygen end virtual memory management API

8220hipError_t hipGraphicsMapResources(int count, hipGraphicsResource_t* resources,

8221 hipStream_t stream __dparm(0) );

8235hipError_t hipGraphicsSubResourceGetMappedArray(hipArray_t* array, hipGraphicsResource_t resource,

8236 unsigned int arrayIndex, unsigned int mipLevel);

8247hipError_t hipGraphicsResourceGetMappedPointer(void** devPtr, size_t* size,

8248 hipGraphicsResource_t resource);

8259hipError_t hipGraphicsUnmapResources(int count, hipGraphicsResource_t* resources,

8260 hipStream_t stream __dparm(0));

8269hipError_t hipGraphicsUnregisterResource(hipGraphicsResource_t resource);

8270// doxygen end GL Interop

8296hipError_t hipCreateSurfaceObject(hipSurfaceObject_t* pSurfObject, const hipResourceDesc* pResDesc);

8304hipError_t hipDestroySurfaceObject(hipSurfaceObject_t surfaceObject);

8305// end of surface

8309#ifdef __cplusplus

8310} /* extern "c" */

8311#endif

8312#ifdef __cplusplus

8313#if defined(__clang__) && defined(__HIP__)

8314template <typename T>

8315static hipError_t __host__ inline hipOccupancyMaxPotentialBlockSize(int* gridSize, int* blockSize,

8316 T f, size_t dynSharedMemPerBlk = 0, int blockSizeLimit = 0) {

8317 return hipOccupancyMaxPotentialBlockSize(gridSize, blockSize, reinterpret_cast<const void*>(f),dynSharedMemPerBlk,blockSizeLimit);

8318}

8319template <typename T>

8320static hipError_t __host__ inline hipOccupancyMaxPotentialBlockSizeWithFlags(int* gridSize, int* blockSize,

8321 T f, size_t dynSharedMemPerBlk = 0, int blockSizeLimit = 0, unsigned int flags = 0 ) {

8322 return hipOccupancyMaxPotentialBlockSize(gridSize, blockSize, reinterpret_cast<const void*>(f),dynSharedMemPerBlk,blockSizeLimit);

8323}

8324#endif // defined(__clang__) && defined(__HIP__)

8325

8335template <typename T>

8336hipError_t hipGetSymbolAddress(void** devPtr, const T &symbol) {

8337 return ::hipGetSymbolAddress(devPtr, (const void *)&symbol);

8338}

8349template <typename T>

8350hipError_t hipGetSymbolSize(size_t* size, const T &symbol) {

8351 return ::hipGetSymbolSize(size, (const void *)&symbol);

8352}

8353

8362template <typename T>

8363hipError_t hipMemcpyToSymbol(const T& symbol, const void* src, size_t sizeBytes,

8364 size_t offset __dparm(0),

8365 hipMemcpyKind kind __dparm(hipMemcpyHostToDevice)) {

8366 return ::hipMemcpyToSymbol((const void*)&symbol, src, sizeBytes, offset, kind);

8367}

8376template <typename T>

8377hipError_t hipMemcpyToSymbolAsync(const T& symbol, const void* src, size_t sizeBytes, size_t offset,

8378 hipMemcpyKind kind, hipStream_t stream __dparm(0)) {

8379 return ::hipMemcpyToSymbolAsync((const void*)&symbol, src, sizeBytes, offset, kind, stream);

8380}

8388template <typename T>

8389hipError_t hipMemcpyFromSymbol(void* dst, const T &symbol,

8390 size_t sizeBytes, size_t offset __dparm(0),

8391 hipMemcpyKind kind __dparm(hipMemcpyDeviceToHost)) {

8392 return ::hipMemcpyFromSymbol(dst, (const void*)&symbol, sizeBytes, offset, kind);

8393}

8401template <typename T>

8402hipError_t hipMemcpyFromSymbolAsync(void* dst, const T& symbol, size_t sizeBytes, size_t offset,

8403 hipMemcpyKind kind, hipStream_t stream __dparm(0)) {

8404 return ::hipMemcpyFromSymbolAsync(dst, (const void*)&symbol, sizeBytes, offset, kind, stream);

8405}

8406

8418template <class T>

8419inline hipError_t hipOccupancyMaxActiveBlocksPerMultiprocessor(

8420 int* numBlocks, T f, int blockSize, size_t dynSharedMemPerBlk) {

8421 return hipOccupancyMaxActiveBlocksPerMultiprocessor(

8422 numBlocks, reinterpret_cast<const void*>(f), blockSize, dynSharedMemPerBlk);

8423}

8437template <class T>

8438inline hipError_t hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(

8439 int* numBlocks, T f, int blockSize, size_t dynSharedMemPerBlk, unsigned int flags) {

8440 return hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(

8441 numBlocks, reinterpret_cast<const void*>(f), blockSize, dynSharedMemPerBlk, flags);

8442}

8463template<typename UnaryFunction, class T>

8464static hipError_t __host__ inline hipOccupancyMaxPotentialBlockSizeVariableSMemWithFlags(

8465 int* min_grid_size,

8466 int* block_size,

8467 T func,

8468 UnaryFunction block_size_to_dynamic_smem_size,

8469 int block_size_limit = 0,

8470 unsigned int flags = 0) {

8471 if (min_grid_size == nullptr || block_size == nullptr ||

8472 reinterpret_cast<const void*>(func) == nullptr) {

8473 return hipErrorInvalidValue;

8474 }

8475

8476 int dev;

8477 hipError_t status;

8478 if ((status = hipGetDevice(&dev)) != hipSuccess) {

8479 return status;

8480 }

8481

8482 int max_threads_per_cu;

8483 if ((status = hipDeviceGetAttribute(&max_threads_per_cu,

8484 hipDeviceAttributeMaxThreadsPerMultiProcessor, dev)) != hipSuccess) {

8485 return status;

8486 }

8487

8488 int warp_size;

8489 if ((status = hipDeviceGetAttribute(&warp_size,

8490 hipDeviceAttributeWarpSize, dev)) != hipSuccess) {

8491 return status;

8492 }

8493

8494 int max_cu_count;

8495 if ((status = hipDeviceGetAttribute(&max_cu_count,

8496 hipDeviceAttributeMultiprocessorCount, dev)) != hipSuccess) {

8497 return status;

8498 }

8499

8500 struct hipFuncAttributes attr;

8501 if ((status = hipFuncGetAttributes(&attr, reinterpret_cast<const void*>(func))) != hipSuccess) {

8502 return status;

8503 }

8504

8505 // Initial limits for the execution

8506 const int func_max_threads_per_block = attr.maxThreadsPerBlock;

8507 if (block_size_limit == 0) {

8508 block_size_limit = func_max_threads_per_block;

8509 }

8510

8511 if (func_max_threads_per_block < block_size_limit) {

8512 block_size_limit = func_max_threads_per_block;

8513 }

8514

8515 const int block_size_limit_aligned =

8516 ((block_size_limit + (warp_size - 1)) / warp_size) * warp_size;

8517

8518 // For maximum search

8519 int max_threads = 0;

8520 int max_block_size{};

8521 int max_num_blocks{};

8522 for (int block_size_check_aligned = block_size_limit_aligned;

8523 block_size_check_aligned > 0;

8524 block_size_check_aligned -= warp_size) {

8525 // Make sure the logic uses the requested limit and not aligned

8526 int block_size_check = (block_size_limit < block_size_check_aligned) ?

8527 block_size_limit : block_size_check_aligned;

8528

8529 size_t dyn_smem_size = block_size_to_dynamic_smem_size(block_size_check);

8530 int optimal_blocks;

8531 if ((status = hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(

8532 &optimal_blocks, func, block_size_check, dyn_smem_size, flags)) != hipSuccess) {

8533 return status;

8534 }

8535

8536 int total_threads = block_size_check * optimal_blocks;

8537 if (total_threads > max_threads) {

8538 max_block_size = block_size_check;

8539 max_num_blocks = optimal_blocks;

8540 max_threads = total_threads;

8541 }

8542

8543 // Break if the logic reached possible maximum

8544 if (max_threads_per_cu == max_threads) {

8545 break;

8546 }

8547 }

8548

8549 // Grid size is the number of blocks per CU * CU count

8550 *min_grid_size = max_num_blocks * max_cu_count;

8551 *block_size = max_block_size;

8552

8553 return status;

8554}

8555

8575template<typename UnaryFunction, class T>

8576static hipError_t __host__ inline hipOccupancyMaxPotentialBlockSizeVariableSMem(

8577 int* min_grid_size,

8578 int* block_size,

8579 T func,

8580 UnaryFunction block_size_to_dynamic_smem_size,

8581 int block_size_limit = 0)

8582{

8583 return hipOccupancyMaxPotentialBlockSizeVariableSMemWithFlags(min_grid_size, block_size, func,

8584 block_size_to_dynamic_smem_size, block_size_limit);

8585}

8600template <typename F>

8601inline hipError_t hipOccupancyMaxPotentialBlockSize(int* gridSize, int* blockSize,

8602 F kernel, size_t dynSharedMemPerBlk, uint32_t blockSizeLimit) {

8603return hipOccupancyMaxPotentialBlockSize(gridSize, blockSize,(hipFunction_t)kernel, dynSharedMemPerBlk, blockSizeLimit);

8604}

8621template <class T>

8622inline hipError_t hipLaunchCooperativeKernel(T f, dim3 gridDim, dim3 blockDim,

8623 void** kernelParams, unsigned int sharedMemBytes, hipStream_t stream) {

8624 return hipLaunchCooperativeKernel(reinterpret_cast<const void*>(f), gridDim,

8625 blockDim, kernelParams, sharedMemBytes, stream);

8626}

8641template <class T>

8642inline hipError_t hipLaunchCooperativeKernelMultiDevice(hipLaunchParams* launchParamsList,

8643 unsigned int numDevices, unsigned int flags = 0) {

8644 return hipLaunchCooperativeKernelMultiDevice(launchParamsList, numDevices, flags);

8645}

8660template <class T>

8661inline hipError_t hipExtLaunchMultiKernelMultiDevice(hipLaunchParams* launchParamsList,

8662 unsigned int numDevices, unsigned int flags = 0) {

8663 return hipExtLaunchMultiKernelMultiDevice(launchParamsList, numDevices, flags);

8664}

8678template <class T, int dim, enum hipTextureReadMode readMode>

8679DEPRECATED(DEPRECATED_MSG)

8680static inline hipError_t hipBindTexture(size_t* offset, const struct texture<T, dim, readMode>& tex,

8681 const void* devPtr, size_t size = UINT_MAX) {

8682 return hipBindTexture(offset, &tex, devPtr, &tex.channelDesc, size);

8683}

8698template <class T, int dim, enum hipTextureReadMode readMode>

8699DEPRECATED(DEPRECATED_MSG)

8700static inline hipError_t

8701 hipBindTexture(size_t* offset, const struct texture<T, dim, readMode>& tex, const void* devPtr,

8702 const struct hipChannelFormatDesc& desc, size_t size = UINT_MAX) {

8703 return hipBindTexture(offset, &tex, devPtr, &desc, size);

8704}

8720template<class T, int dim, enum hipTextureReadMode readMode>

8721DEPRECATED(DEPRECATED_MSG)

8722static inline hipError_t hipBindTexture2D(

8723 size_t *offset,

8724 const struct texture<T, dim, readMode> &tex,

8725 const void *devPtr,

8726 size_t width,

8727 size_t height,

8728 size_t pitch)

8729{

8730 return hipBindTexture2D(offset, &tex, devPtr, &tex.channelDesc, width, height, pitch);

8731}

8748template<class T, int dim, enum hipTextureReadMode readMode>

8749DEPRECATED(DEPRECATED_MSG)

8750static inline hipError_t hipBindTexture2D(

8751 size_t *offset,

8752 const struct texture<T, dim, readMode> &tex,

8753 const void *devPtr,

8754 const struct hipChannelFormatDesc &desc,

8755 size_t width,

8756 size_t height,

8757 size_t pitch)

8758{

8759 return hipBindTexture2D(offset, &tex, devPtr, &desc, width, height, pitch);

8760}

8772template<class T, int dim, enum hipTextureReadMode readMode>

8773DEPRECATED(DEPRECATED_MSG)

8774static inline hipError_t hipBindTextureToArray(

8775 const struct texture<T, dim, readMode> &tex,

8776 hipArray_const_t array)

8777{

8778 struct hipChannelFormatDesc desc;

8779 hipError_t err = hipGetChannelDesc(&desc, array);

8780 return (err == hipSuccess) ? hipBindTextureToArray(&tex, array, &desc) : err;

8781}

8794template<class T, int dim, enum hipTextureReadMode readMode>

8795DEPRECATED(DEPRECATED_MSG)

8796static inline hipError_t hipBindTextureToArray(

8797 const struct texture<T, dim, readMode> &tex,

8798 hipArray_const_t array,

8799 const struct hipChannelFormatDesc &desc)

8800{

8801 return hipBindTextureToArray(&tex, array, &desc);

8802}

8814template<class T, int dim, enum hipTextureReadMode readMode>

8815DEPRECATED(DEPRECATED_MSG)

8816static inline hipError_t hipBindTextureToMipmappedArray(

8817 const struct texture<T, dim, readMode> &tex,

8818 hipMipmappedArray_const_t mipmappedArray)

8819{

8820 struct hipChannelFormatDesc desc;

8821 hipArray_t levelArray;

8822 hipError_t err = hipGetMipmappedArrayLevel(&levelArray, mipmappedArray, 0);

8823 if (err != hipSuccess) {

8824 return err;

8825 }

8826 err = hipGetChannelDesc(&desc, levelArray);

8827 return (err == hipSuccess) ? hipBindTextureToMipmappedArray(&tex, mipmappedArray, &desc) : err;

8828}

8841template<class T, int dim, enum hipTextureReadMode readMode>

8842DEPRECATED(DEPRECATED_MSG)

8843static inline hipError_t hipBindTextureToMipmappedArray(

8844 const struct texture<T, dim, readMode> &tex,

8845 hipMipmappedArray_const_t mipmappedArray,

8846 const struct hipChannelFormatDesc &desc)

8847{

8848 return hipBindTextureToMipmappedArray(&tex, mipmappedArray, &desc);

8849}

8860template<class T, int dim, enum hipTextureReadMode readMode>

8861DEPRECATED(DEPRECATED_MSG)

8862static inline hipError_t hipUnbindTexture(

8863 const struct texture<T, dim, readMode> &tex)

8864{

8865 return hipUnbindTexture(&tex);

8866}

8890static inline hipError_t hipMallocAsync(

8891 void** dev_ptr,

8892 size_t size,

8893 hipMemPool_t mem_pool,

8894 hipStream_t stream) {

8895 return hipMallocFromPoolAsync(dev_ptr, size, mem_pool, stream);

8896}

8907template<class T>

8908static inline hipError_t hipMallocAsync(

8909 T** dev_ptr,

8910 size_t size,

8911 hipMemPool_t mem_pool,

8912 hipStream_t stream) {

8913 return hipMallocFromPoolAsync(reinterpret_cast<void**>(dev_ptr), size, mem_pool, stream);

8914}

8925template<class T>

8926static inline hipError_t hipMallocAsync(

8927 T** dev_ptr,

8928 size_t size,

8929 hipStream_t stream) {

8930 return hipMallocAsync(reinterpret_cast<void**>(dev_ptr), size, stream);

8931}

8942template<class T>

8943static inline hipError_t hipMallocFromPoolAsync(

8944 T** dev_ptr,

8945 size_t size,

8946 hipMemPool_t mem_pool,

8947 hipStream_t stream) {

8948 return hipMallocFromPoolAsync(reinterpret_cast<void**>(dev_ptr), size, mem_pool, stream);

8949}

8955#endif // __cplusplus

8956

8957#ifdef __GNUC__

8958#pragma GCC visibility pop

8959#endif

8960

8961

8962#elif !defined(__HIP_PLATFORM_AMD__) && defined(__HIP_PLATFORM_NVIDIA__)

8963#include "hip/nvidia_detail/nvidia_hip_runtime_api.h"

8964#else

8965#error("Must define exactly one of __HIP_PLATFORM_AMD__ or __HIP_PLATFORM_NVIDIA__");

8966#endif

8967

8968

8980#if defined(__cplusplus) && !defined(__HIP_DISABLE_CPP_FUNCTIONS__)

8981template <class T>

8982static inline hipError_t hipMalloc(T** devPtr, size_t size) {

8983 return hipMalloc((void**)devPtr, size);

8984}

8997template <class T>

8998static inline hipError_t hipHostMalloc(T** ptr, size_t size,

8999 unsigned int flags = hipHostMallocDefault) {

9000 return hipHostMalloc((void**)ptr, size, flags);

9001}

9016template <class T>

9017static inline hipError_t hipMallocManaged(T** devPtr, size_t size,

9018 unsigned int flags = hipMemAttachGlobal) {

9019 return hipMallocManaged((void**)devPtr, size, flags);

9020}

9021

9022

9023#endif

9024#endif

9025// doxygen end HIP API

9029#include <hip/amd_detail/amd_hip_runtime_pt_api.h>

9030

9031#if USE_PROF_API

9032#include <hip/amd_detail/hip_prof_str.h>

9033#endif

driver_types.h

hipMemcpyKind

hipMemcpyKind

Definition driver_types.h:333

hipMemcpyDeviceToHost

@ hipMemcpyDeviceToHost

Device-to-Host Copy.

Definition driver_types.h:336

hipMemcpyHostToDevice

@ hipMemcpyHostToDevice

Host-to-Device Copy.

Definition driver_types.h:335

hipPointer_attribute

hipPointer_attribute

Definition driver_types.h:431

hipArray_t

struct hipArray * hipArray_t

Definition driver_types.h:58

hipDeviceptr_t

void * hipDeviceptr_t

Definition driver_types.h:39

hipFunction_attribute

hipFunction_attribute

Definition driver_types.h:417

hipArray_const_t

const struct hipArray * hipArray_const_t

Definition driver_types.h:59

hipArray_Format

hipArray_Format

Definition driver_types.h:60

hipResourceType

hipResourceType

Definition driver_types.h:123

hipApiName

const char * hipApiName(uint32_t id)

Returns HIP API name by ID.

hipKernelNameRef

const char * hipKernelNameRef(const hipFunction_t f)

Returns kernel name reference by function name.

hipKernelNameRefByPtr

const char * hipKernelNameRefByPtr(const void *hostFunction, hipStream_t stream)

Retrives kernel for a given host pointer, unless stated otherwise.

hipGetStreamDeviceId

int hipGetStreamDeviceId(hipStream_t stream)

Returns device ID on the stream.

hipSetupArgument

hipError_t hipSetupArgument(const void *arg, size_t size, size_t offset)

Set a kernel argument.

__hipPopCallConfiguration

hipError_t __hipPopCallConfiguration(dim3 *gridDim, dim3 *blockDim, size_t *sharedMem, hipStream_t *stream)

Pop configuration of a kernel launch.

hipLaunchHostFunc

hipError_t hipLaunchHostFunc(hipStream_t stream, hipHostFn_t fn, void *userData)

Enqueues a host function call in a stream.

hipLaunchKernel

hipError_t hipLaunchKernel(const void *function_address, dim3 numBlocks, dim3 dimBlocks, void **args, size_t sharedMemBytes, hipStream_t stream)

C compliant kernel launch API.

hipExtLaunchKernel

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.

__hipPushCallConfiguration

hipError_t __hipPushCallConfiguration(dim3 gridDim, dim3 blockDim, size_t sharedMem, hipStream_t stream)

Push configuration of a kernel launch.

hipLaunchByPtr

hipError_t hipLaunchByPtr(const void *func)

Launch a kernel.

hipDrvMemcpy2DUnaligned

hipError_t hipDrvMemcpy2DUnaligned(const hip_Memcpy2D *pCopy)

hipConfigureCall

hipError_t hipConfigureCall(dim3 gridDim, dim3 blockDim, size_t sharedMem, hipStream_t stream)

Configure a kernel launch.

hipCtxGetFlags

hipError_t hipCtxGetFlags(unsigned int *flags)

Return flags used for creating default context.

hipCtxPopCurrent

hipError_t hipCtxPopCurrent(hipCtx_t *ctx)

Pop the current/default context and return the popped context.

hipCtxGetSharedMemConfig

hipError_t hipCtxGetSharedMemConfig(hipSharedMemConfig *pConfig)

Get Shared memory bank configuration.

hipCtxGetCurrent

hipError_t hipCtxGetCurrent(hipCtx_t *ctx)

Get the handle of the current/ default context.

hipCtxSetCacheConfig

hipError_t hipCtxSetCacheConfig(hipFuncCache_t cacheConfig)

Set L1/Shared cache partition.

hipCtxSetCurrent

hipError_t hipCtxSetCurrent(hipCtx_t ctx)

Set the passed context as current/default.

hipCtxEnablePeerAccess

hipError_t hipCtxEnablePeerAccess(hipCtx_t peerCtx, unsigned int flags)

Enables direct access to memory allocations in a peer context.

hipCtxGetDevice

hipError_t hipCtxGetDevice(hipDevice_t *device)

Get the handle of the device associated with current/default context.

hipCtxDestroy

hipError_t hipCtxDestroy(hipCtx_t ctx)

Destroy a HIP context.

hipCtxPushCurrent

hipError_t hipCtxPushCurrent(hipCtx_t ctx)

Push the context to be set as current/ default context.

hipCtxGetCacheConfig

hipError_t hipCtxGetCacheConfig(hipFuncCache_t *cacheConfig)

Get Cache configuration for a specific function.

hipCtxCreate

hipError_t hipCtxCreate(hipCtx_t *ctx, unsigned int flags, hipDevice_t device)

Create a context and set it as current/default context.

hipCtxGetApiVersion

hipError_t hipCtxGetApiVersion(hipCtx_t ctx, int *apiVersion)

Returns the approximate HIP api version.

hipCtxSynchronize

hipError_t hipCtxSynchronize(void)

Blocks until the default context has completed all preceding requested tasks.

hipCtxSetSharedMemConfig

hipError_t hipCtxSetSharedMemConfig(hipSharedMemConfig config)

Set Shared memory bank configuration.

hipCtxDisablePeerAccess

hipError_t hipCtxDisablePeerAccess(hipCtx_t peerCtx)

Disable direct access from current context's virtual address space to memory allocations physically l...

hipDevicePrimaryCtxSetFlags

hipError_t hipDevicePrimaryCtxSetFlags(hipDevice_t dev, unsigned int flags)

Set flags for the primary context.

hipDevicePrimaryCtxGetState

hipError_t hipDevicePrimaryCtxGetState(hipDevice_t dev, unsigned int *flags, int *active)

Get the state of the primary context.

hipDevicePrimaryCtxRelease

hipError_t hipDevicePrimaryCtxRelease(hipDevice_t dev)

Release the primary context on the GPU.

hipDevicePrimaryCtxRetain

hipError_t hipDevicePrimaryCtxRetain(hipCtx_t *pctx, hipDevice_t dev)

Retain the primary context on the GPU.

hipDevicePrimaryCtxReset

hipError_t hipDevicePrimaryCtxReset(hipDevice_t dev)

Resets the primary context on the GPU.

hipGetDeviceFlags

hipError_t hipGetDeviceFlags(unsigned int *flags)

Gets the flags set for current device.

hipIpcGetEventHandle

hipError_t hipIpcGetEventHandle(hipIpcEventHandle_t *handle, hipEvent_t event)

Gets an opaque interprocess handle for an event.

hipDeviceGetDefaultMemPool

hipError_t hipDeviceGetDefaultMemPool(hipMemPool_t *mem_pool, int device)

Returns the default memory pool of the specified device.

hipDeviceGetSharedMemConfig

hipError_t hipDeviceGetSharedMemConfig(hipSharedMemConfig *pConfig)

Returns bank width of shared memory for current device.

hipDeviceSetMemPool

hipError_t hipDeviceSetMemPool(int device, hipMemPool_t mem_pool)

Sets the current memory pool of a device.

hipIpcOpenMemHandle

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...

hipDeviceGetCacheConfig

hipError_t hipDeviceGetCacheConfig(hipFuncCache_t *cacheConfig)

Get Cache configuration for a specific Device.

hipSetDevice

hipError_t hipSetDevice(int deviceId)

Set default device to be used for subsequent hip API calls from this thread.

hipExtGetLinkTypeAndHopCount

hipError_t hipExtGetLinkTypeAndHopCount(int device1, int device2, uint32_t *linktype, uint32_t *hopcount)

Returns the link type and hop count between two devices.

hipSetDeviceFlags

hipError_t hipSetDeviceFlags(unsigned flags)

The current device behavior is changed according the flags passed.

hipDeviceGetAttribute

hipError_t hipDeviceGetAttribute(int *pi, hipDeviceAttribute_t attr, int deviceId)

Query for a specific device attribute.

hipGetDevice

hipError_t hipGetDevice(int *deviceId)

Return the default device id for the calling host thread.

hipGetDeviceCount

hipError_t hipGetDeviceCount(int *count)

Return number of compute-capable devices.

hipDeviceGetMemPool

hipError_t hipDeviceGetMemPool(hipMemPool_t *mem_pool, int device)

Gets the current memory pool for the specified device.

hipDeviceReset

hipError_t hipDeviceReset(void)

The state of current device is discarded and updated to a fresh state.

hipDeviceGetLimit

hipError_t hipDeviceGetLimit(size_t *pValue, enum hipLimit_t limit)

Gets resource limits of current device.

hipDeviceSetSharedMemConfig

hipError_t hipDeviceSetSharedMemConfig(hipSharedMemConfig config)

The bank width of shared memory on current device is set.

hipDeviceSetLimit

hipError_t hipDeviceSetLimit(enum hipLimit_t limit, size_t value)

Sets resource limits of current device.

hipDeviceSetCacheConfig

hipError_t hipDeviceSetCacheConfig(hipFuncCache_t cacheConfig)

Set L1/Shared cache partition.

hipIpcCloseMemHandle

hipError_t hipIpcCloseMemHandle(void *devPtr)

Close memory mapped with hipIpcOpenMemHandle.

hipIpcOpenEventHandle

hipError_t hipIpcOpenEventHandle(hipEvent_t *event, hipIpcEventHandle_t handle)

Opens an interprocess event handles.

hipDeviceSynchronize

hipError_t hipDeviceSynchronize(void)

Waits on all active streams on current device.

hipIpcGetMemHandle

hipError_t hipIpcGetMemHandle(hipIpcMemHandle_t *handle, void *devPtr)

Gets an interprocess memory handle for an existing device memory allocation.

hipInit

hipError_t hipInit(unsigned int flags)

Explicitly initializes the HIP runtime.

hipDeviceComputeCapability

hipError_t hipDeviceComputeCapability(int *major, int *minor, hipDevice_t device)

Returns the compute capability of the device.

hipDeviceGetName

hipError_t hipDeviceGetName(char *name, int len, hipDevice_t device)

Returns an identifer string for the device.

hipDeviceGetByPCIBusId

hipError_t hipDeviceGetByPCIBusId(int *device, const char *pciBusId)

Returns a handle to a compute device.

hipDeviceGetUuid

hipError_t hipDeviceGetUuid(hipUUID *uuid, hipDevice_t device)

Returns an UUID for the device.[BETA].

hipDeviceTotalMem

hipError_t hipDeviceTotalMem(size_t *bytes, hipDevice_t device)

Returns the total amount of memory on the device.

hipDeviceGetPCIBusId

hipError_t hipDeviceGetPCIBusId(char *pciBusId, int len, int device)

Returns a PCI Bus Id string for the device, overloaded to take int device ID.

hipDeviceGet

hipError_t hipDeviceGet(hipDevice_t *device, int ordinal)

Returns a handle to a compute device.

hipRuntimeGetVersion

hipError_t hipRuntimeGetVersion(int *runtimeVersion)

Returns the approximate HIP Runtime version.

hipDeviceGetP2PAttribute

hipError_t hipDeviceGetP2PAttribute(int *value, hipDeviceP2PAttr attr, int srcDevice, int dstDevice)

Returns a value for attribute of link between two devices.

hipDriverGetVersion

hipError_t hipDriverGetVersion(int *driverVersion)

Returns the approximate HIP driver version.

hipGetErrorString

const char * hipGetErrorString(hipError_t hipError)

Return handy text string message to explain the error which occurred.

hipPeekAtLastError

hipError_t hipPeekAtLastError(void)

Return last error returned by any HIP runtime API call.

hipDrvGetErrorString

hipError_t hipDrvGetErrorString(hipError_t hipError, const char **errorString)

Return handy text string message to explain the error which occurred.

hipGetLastError

hipError_t hipGetLastError(void)

Return last error returned by any HIP runtime API call and resets the stored error code to hipSuccess...

hipExtGetLastError

hipError_t hipExtGetLastError(void)

Return last error returned by any HIP runtime API call and resets the stored error code to hipSuccess...

hipDrvGetErrorName

hipError_t hipDrvGetErrorName(hipError_t hipError, const char **errorString)

Return hip error as text string form.

hipGetErrorName

const char * hipGetErrorName(hipError_t hip_error)

Return hip error as text string form.

hipEventSynchronize

hipError_t hipEventSynchronize(hipEvent_t event)

Wait for an event to complete.

hipEventRecord

hipError_t hipEventRecord(hipEvent_t event, hipStream_t stream)

Record an event in the specified stream.

hipEventQuery

hipError_t hipEventQuery(hipEvent_t event)

Query event status.

hipEventCreate

hipError_t hipEventCreate(hipEvent_t *event)

hipEventDestroy

hipError_t hipEventDestroy(hipEvent_t event)

Destroy the specified event.

hipEventElapsedTime

hipError_t hipEventElapsedTime(float *ms, hipEvent_t start, hipEvent_t stop)

Return the elapsed time between two events.

hipEventCreateWithFlags

hipError_t hipEventCreateWithFlags(hipEvent_t *event, unsigned flags)

Create an event with the specified flags.

hipFuncSetSharedMemConfig

hipError_t hipFuncSetSharedMemConfig(const void *func, hipSharedMemConfig config)

Set shared memory configuation for a specific function.

hipFuncSetAttribute

hipError_t hipFuncSetAttribute(const void *func, hipFuncAttribute attr, int value)

Set attribute for a specific function.

hipFuncSetCacheConfig

hipError_t hipFuncSetCacheConfig(const void *func, hipFuncCache_t config)

Set Cache configuration for a specific function.

hipDestroyExternalMemory

hipError_t hipDestroyExternalMemory(hipExternalMemory_t extMem)

Destroys an external memory object.

hipImportExternalSemaphore

hipError_t hipImportExternalSemaphore(hipExternalSemaphore_t *extSem_out, const hipExternalSemaphoreHandleDesc *semHandleDesc)

Imports an external semaphore.

hipImportExternalMemory

hipError_t hipImportExternalMemory(hipExternalMemory_t *extMem_out, const hipExternalMemoryHandleDesc *memHandleDesc)

Imports an external memory object.

hipDestroyExternalSemaphore

hipError_t hipDestroyExternalSemaphore(hipExternalSemaphore_t extSem)

Destroys an external semaphore object and releases any references to the underlying resource....

hipWaitExternalSemaphoresAsync

hipError_t hipWaitExternalSemaphoresAsync(const hipExternalSemaphore_t *extSemArray, const hipExternalSemaphoreWaitParams *paramsArray, unsigned int numExtSems, hipStream_t stream)

Waits on a set of external semaphore objects.

hipSignalExternalSemaphoresAsync

hipError_t hipSignalExternalSemaphoresAsync(const hipExternalSemaphore_t *extSemArray, const hipExternalSemaphoreSignalParams *paramsArray, unsigned int numExtSems, hipStream_t stream)

Signals a set of external semaphore objects.

hipExternalMemoryGetMappedMipmappedArray

hipError_t hipExternalMemoryGetMappedMipmappedArray(hipMipmappedArray_t *mipmap, hipExternalMemory_t extMem, const hipExternalMemoryMipmappedArrayDesc *mipmapDesc)

Maps a mipmapped array onto an external memory object.

hipExternalMemoryGetMappedBuffer

hipError_t hipExternalMemoryGetMappedBuffer(void **devPtr, hipExternalMemory_t extMem, const hipExternalMemoryBufferDesc *bufferDesc)

Maps a buffer onto an imported memory object.

hipGraphicsUnregisterResource

hipError_t hipGraphicsUnregisterResource(hipGraphicsResource_t resource)

Unregisters a graphics resource.

hipGraphicsUnmapResources

hipError_t hipGraphicsUnmapResources(int count, hipGraphicsResource_t *resources, hipStream_t stream)

Unmaps graphics resources.

hipGraphicsSubResourceGetMappedArray

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.

hipGraphicsResourceGetMappedPointer

hipError_t hipGraphicsResourceGetMappedPointer(void **devPtr, size_t *size, hipGraphicsResource_t resource)

Gets device accessible address of a graphics resource.

hipGraphicsMapResources

hipError_t hipGraphicsMapResources(int count, hipGraphicsResource_t *resources, hipStream_t stream)

Maps a graphics resource for access.

hipLimit_t

hipLimit_t

Definition hip_runtime_api.h:652

hipMemAllocationHandleType

hipMemAllocationHandleType

Definition hip_runtime_api.h:967

hipGraphicsResource_t

hipGraphicsResource * hipGraphicsResource_t

Definition hip_runtime_api.h:1206

hipCtx_t

struct ihipCtx_t * hipCtx_t

Definition hip_runtime_api.h:607

__dparm

#define __dparm(x)

Definition hip_runtime_api.h:591

hipStream_t

struct ihipStream_t * hipStream_t

Definition hip_runtime_api.h:616

hipGraphInstantiateResult

hipGraphInstantiateResult

Definition hip_runtime_api.h:1400

hipDevice_t

int hipDevice_t

Definition hip_runtime_api.h:609

hipAccessProperty

hipAccessProperty

Definition hip_runtime_api.h:1288

hipMemRangeAttribute

hipMemRangeAttribute

Definition hip_runtime_api.h:849

hipMemAttachSingle

#define hipMemAttachSingle

Definition hip_runtime_api.h:738

hipMemoryAdvise

hipMemoryAdvise

Definition hip_runtime_api.h:816

hipArrayDefault

#define hipArrayDefault

Definition hip_runtime_api.h:786

hipSharedMemConfig

hipSharedMemConfig

Definition hip_runtime_api.h:1036

hipComputeMode

hipComputeMode

Definition hip_runtime_api.h:549

hipEvent_t

struct ihipEvent_t * hipEvent_t

Definition hip_runtime_api.h:644

hipStreamCaptureMode

hipStreamCaptureMode

Definition hip_runtime_api.h:1336

hipDriverProcAddressQueryResult

hipDriverProcAddressQueryResult

Definition hip_runtime_api.h:543

hipGraphNodeType

hipGraphNodeType

Definition hip_runtime_api.h:1230

hipExternalMemoryHandleType

hipExternalMemoryHandleType

Definition hip_runtime_api.h:1080

hipMemAttachGlobal

#define hipMemAttachGlobal

Definition hip_runtime_api.h:732

hipFuncAttribute

hipFuncAttribute

Definition hip_runtime_api.h:1019

hipExternalSemaphoreHandleType

hipExternalSemaphoreHandleType

Definition hip_runtime_api.h:1118

hipJitOption

hipJitOption

Definition hip_runtime_api.h:996

hipDeviceP2PAttr

hipDeviceP2PAttr

Definition hip_runtime_api.h:610

hipGraphDebugDotFlags

hipGraphDebugDotFlags

Definition hip_runtime_api.h:1378

hipUserObjectRetainFlags

hipUserObjectRetainFlags

Definition hip_runtime_api.h:1363

hipError_t

enum __HIP_NODISCARD hipError_t hipError_t

Definition hip_runtime_api.h:286

hipHostFn_t

void(* hipHostFn_t)(void *userData)

Definition hip_runtime_api.h:1248

hipOccupancyDefault

#define hipOccupancyDefault

Definition hip_runtime_api.h:791

hipStreamUpdateCaptureDependenciesFlags

hipStreamUpdateCaptureDependenciesFlags

Definition hip_runtime_api.h:1348

hipGraph_t

struct ihipGraph * hipGraph_t

Definition hip_runtime_api.h:1211

hipChooseDevice

#define hipChooseDevice

Definition hip_runtime_api.h:93

hipMemHandleType

hipMemHandleType

Definition hip_runtime_api.h:1479

hipFlushGPUDirectRDMAWritesOptions

hipFlushGPUDirectRDMAWritesOptions

Definition hip_runtime_api.h:556

hipFuncCache_t

hipFuncCache_t

Definition hip_runtime_api.h:1027

hipUserObjectFlags

hipUserObjectFlags

Definition hip_runtime_api.h:1359

__HIP_NODISCARD

#define __HIP_NODISCARD

Definition hip_runtime_api.h:276

DEPRECATED_MSG

#define DEPRECATED_MSG

Definition hip_runtime_api.h:583

hipGraphMemAttributeType

hipGraphMemAttributeType

Definition hip_runtime_api.h:1353

hipMemPoolAttr

hipMemPoolAttr

Definition hip_runtime_api.h:865

hipDeviceProp_t

#define hipDeviceProp_t

Definition hip_runtime_api.h:92

hipModule_t

struct ihipModule_t * hipModule_t

Definition hip_runtime_api.h:625

hipUserObject_t

struct hipUserObject * hipUserObject_t

Definition hip_runtime_api.h:1224

hipMemOperationType

hipMemOperationType

Definition hip_runtime_api.h:1486

hipExternalSemaphore_t

void * hipExternalSemaphore_t

Definition hip_runtime_api.h:1143

hipGraphicsRegisterFlags

hipGraphicsRegisterFlags

Definition hip_runtime_api.h:1194

hipMemRangeCoherencyMode

hipMemRangeCoherencyMode

Definition hip_runtime_api.h:837

hipMemAccessFlags

hipMemAccessFlags

Definition hip_runtime_api.h:940

hipMemAllocationGranularity_flags

hipMemAllocationGranularity_flags

Definition hip_runtime_api.h:1471

hipGraphExec_t

struct hipGraphExec * hipGraphExec_t

Definition hip_runtime_api.h:1219

hipGraphExecUpdateResult

hipGraphExecUpdateResult

Definition hip_runtime_api.h:1321

hipFunction_t

struct ihipModuleSymbol_t * hipFunction_t

Definition hip_runtime_api.h:626

hipExternalMemory_t

void * hipExternalMemory_t

Definition hip_runtime_api.h:1117

hipStreamCaptureStatus

hipStreamCaptureStatus

Definition hip_runtime_api.h:1341

hipDeviceAttribute_t

hipDeviceAttribute_t

Definition hip_runtime_api.h:408

hipGPUDirectRDMAWritesOrdering

hipGPUDirectRDMAWritesOrdering

Definition hip_runtime_api.h:561

hipGetDeviceProperties

#define hipGetDeviceProperties

Definition hip_runtime_api.h:91

DEPRECATED

#define DEPRECATED(msg)

Definition hip_runtime_api.h:581

hipHostMallocDefault

#define hipHostMallocDefault

Definition hip_runtime_api.h:705

hipGraphicsResource

struct _hipGraphicsResource hipGraphicsResource

Definition hip_runtime_api.h:1204

hipMemAllocationType

hipMemAllocationType

Definition hip_runtime_api.h:955

hipGraphNode_t

struct hipGraphNode * hipGraphNode_t

Definition hip_runtime_api.h:1215

hipMemGenericAllocationHandle_t

struct ihipMemGenericAllocationHandle * hipMemGenericAllocationHandle_t

Definition hip_runtime_api.h:1466

hipMemoryType

hipMemoryType

Definition hip_runtime_api.h:244

hipGraphInstantiateFlags

hipGraphInstantiateFlags

Definition hip_runtime_api.h:1367

hipKernelNodeAttrID

hipKernelNodeAttrID

Definition hip_runtime_api.h:1283

hipMemLocationType

hipMemLocationType

Definition hip_runtime_api.h:923

HIP_IPC_HANDLE_SIZE

#define HIP_IPC_HANDLE_SIZE

Definition hip_runtime_api.h:618

hipMemPool_t

struct ihipMemPoolHandle_t * hipMemPool_t

Definition hip_runtime_api.h:630

hipArraySparseSubresourceType

hipArraySparseSubresourceType

Definition hip_runtime_api.h:1494

hipLimitMallocHeapSize

@ hipLimitMallocHeapSize

Definition hip_runtime_api.h:658

hipLimitStackSize

@ hipLimitStackSize

Definition hip_runtime_api.h:653

hipLimitRange

@ hipLimitRange

Supported limit range.

Definition hip_runtime_api.h:660

hipLimitPrintfFifoSize

@ hipLimitPrintfFifoSize

Definition hip_runtime_api.h:656

hipMemHandleTypeWin32

@ hipMemHandleTypeWin32

Allows a Win32 NT handle for exporting. (HANDLE)

Definition hip_runtime_api.h:970

hipMemHandleTypeWin32Kmt

@ hipMemHandleTypeWin32Kmt

Allows a Win32 KMT handle for exporting. (D3DKMT_HANDLE)

Definition hip_runtime_api.h:971

hipMemHandleTypeNone

@ hipMemHandleTypeNone

Does not allow any export mechanism.

Definition hip_runtime_api.h:968

hipMemHandleTypePosixFileDescriptor

@ hipMemHandleTypePosixFileDescriptor

Allows a file descriptor for exporting. Permitted only on POSIX systems.

Definition hip_runtime_api.h:969

hipGraphInstantiateNodeOperationNotSupported

@ hipGraphInstantiateNodeOperationNotSupported

Definition hip_runtime_api.h:1406

hipGraphInstantiateMultipleDevicesNotSupported

@ hipGraphInstantiateMultipleDevicesNotSupported

Definition hip_runtime_api.h:1408

hipGraphInstantiateError

@ hipGraphInstantiateError

Definition hip_runtime_api.h:1402

hipGraphInstantiateInvalidStructure

@ hipGraphInstantiateInvalidStructure

Definition hip_runtime_api.h:1404

hipGraphInstantiateSuccess

@ hipGraphInstantiateSuccess

Definition hip_runtime_api.h:1401

hipAccessPropertyNormal

@ hipAccessPropertyNormal

Definition hip_runtime_api.h:1289

hipAccessPropertyPersisting

@ hipAccessPropertyPersisting

Definition hip_runtime_api.h:1291

hipAccessPropertyStreaming

@ hipAccessPropertyStreaming

Definition hip_runtime_api.h:1290

hipMemRangeAttributeLastPrefetchLocation

@ hipMemRangeAttributeLastPrefetchLocation

prefetched

Definition hip_runtime_api.h:855

hipMemRangeAttributePreferredLocation

@ hipMemRangeAttributePreferredLocation

The preferred location of the range.

Definition hip_runtime_api.h:852

hipMemRangeAttributeAccessedBy

@ hipMemRangeAttributeAccessedBy

Definition hip_runtime_api.h:853

hipMemRangeAttributeReadMostly

@ hipMemRangeAttributeReadMostly

Definition hip_runtime_api.h:850

hipMemRangeAttributeCoherencyMode

@ hipMemRangeAttributeCoherencyMode

Definition hip_runtime_api.h:857

hipMemAdviseUnsetAccessedBy

@ hipMemAdviseUnsetAccessedBy

Definition hip_runtime_api.h:825

hipMemAdviseUnsetCoarseGrain

@ hipMemAdviseUnsetCoarseGrain

Restores cache coherency policy back to fine-grain.

Definition hip_runtime_api.h:832

hipMemAdviseSetCoarseGrain

@ hipMemAdviseSetCoarseGrain

Definition hip_runtime_api.h:827

hipMemAdviseUnsetPreferredLocation

@ hipMemAdviseUnsetPreferredLocation

Clear the preferred location for the data.

Definition hip_runtime_api.h:822

hipMemAdviseSetAccessedBy

@ hipMemAdviseSetAccessedBy

Definition hip_runtime_api.h:823

hipMemAdviseSetPreferredLocation

@ hipMemAdviseSetPreferredLocation

Definition hip_runtime_api.h:820

hipMemAdviseSetReadMostly

@ hipMemAdviseSetReadMostly

Definition hip_runtime_api.h:817

hipMemAdviseUnsetReadMostly

@ hipMemAdviseUnsetReadMostly

Undo the effect of hipMemAdviseSetReadMostly.

Definition hip_runtime_api.h:819

hipSharedMemBankSizeFourByte

@ hipSharedMemBankSizeFourByte

Definition hip_runtime_api.h:1038

hipSharedMemBankSizeEightByte

@ hipSharedMemBankSizeEightByte

Definition hip_runtime_api.h:1040

hipSharedMemBankSizeDefault

@ hipSharedMemBankSizeDefault

The compiler selects a device-specific value for the banking.

Definition hip_runtime_api.h:1037

hipComputeModeProhibited

@ hipComputeModeProhibited

Definition hip_runtime_api.h:552

hipComputeModeExclusive

@ hipComputeModeExclusive

Definition hip_runtime_api.h:551

hipComputeModeDefault

@ hipComputeModeDefault

Definition hip_runtime_api.h:550

hipComputeModeExclusiveProcess

@ hipComputeModeExclusiveProcess

Definition hip_runtime_api.h:553

hipStreamCaptureModeRelaxed

@ hipStreamCaptureModeRelaxed

Definition hip_runtime_api.h:1339

hipStreamCaptureModeThreadLocal

@ hipStreamCaptureModeThreadLocal

Definition hip_runtime_api.h:1338

hipStreamCaptureModeGlobal

@ hipStreamCaptureModeGlobal

Definition hip_runtime_api.h:1337

HIP_GET_PROC_ADDRESS_SYMBOL_NOT_FOUND

@ HIP_GET_PROC_ADDRESS_SYMBOL_NOT_FOUND

Definition hip_runtime_api.h:545

HIP_GET_PROC_ADDRESS_SUCCESS

@ HIP_GET_PROC_ADDRESS_SUCCESS

Definition hip_runtime_api.h:544

HIP_GET_PROC_ADDRESS_VERSION_NOT_SUFFICIENT

@ HIP_GET_PROC_ADDRESS_VERSION_NOT_SUFFICIENT

Definition hip_runtime_api.h:546

hipGraphNodeTypeGraph

@ hipGraphNodeTypeGraph

Node which executes an embedded graph.

Definition hip_runtime_api.h:1235

hipGraphNodeTypeMemset

@ hipGraphNodeTypeMemset

Memset node.

Definition hip_runtime_api.h:1233

hipGraphNodeTypeEventRecord

@ hipGraphNodeTypeEventRecord

External event record node.

Definition hip_runtime_api.h:1238

hipGraphNodeTypeExtSemaphoreSignal

@ hipGraphNodeTypeExtSemaphoreSignal

External Semaphore signal node.

Definition hip_runtime_api.h:1239

hipGraphNodeTypeMemcpy

@ hipGraphNodeTypeMemcpy

Memcpy node.

Definition hip_runtime_api.h:1232

hipGraphNodeTypeWaitEvent

@ hipGraphNodeTypeWaitEvent

External event wait node.

Definition hip_runtime_api.h:1237

hipGraphNodeTypeCount

@ hipGraphNodeTypeCount

Definition hip_runtime_api.h:1245

hipGraphNodeTypeKernel

@ hipGraphNodeTypeKernel

GPU kernel node.

Definition hip_runtime_api.h:1231

hipGraphNodeTypeHost

@ hipGraphNodeTypeHost

Host (executable) node.

Definition hip_runtime_api.h:1234

hipGraphNodeTypeMemAlloc

@ hipGraphNodeTypeMemAlloc

Memory alloc node.

Definition hip_runtime_api.h:1241

hipGraphNodeTypeMemFree

@ hipGraphNodeTypeMemFree

Memory free node.

Definition hip_runtime_api.h:1242

hipGraphNodeTypeMemcpyFromSymbol

@ hipGraphNodeTypeMemcpyFromSymbol

MemcpyFromSymbol node.

Definition hip_runtime_api.h:1243

hipGraphNodeTypeMemcpyToSymbol

@ hipGraphNodeTypeMemcpyToSymbol

MemcpyToSymbol node.

Definition hip_runtime_api.h:1244

hipGraphNodeTypeEmpty

@ hipGraphNodeTypeEmpty

Empty (no-op) node.

Definition hip_runtime_api.h:1236

hipGraphNodeTypeExtSemaphoreWait

@ hipGraphNodeTypeExtSemaphoreWait

External Semaphore wait node.

Definition hip_runtime_api.h:1240

hipExternalMemoryHandleTypeD3D11Resource

@ hipExternalMemoryHandleTypeD3D11Resource

Definition hip_runtime_api.h:1086

hipExternalMemoryHandleTypeD3D12Resource

@ hipExternalMemoryHandleTypeD3D12Resource

Definition hip_runtime_api.h:1085

hipExternalMemoryHandleTypeNvSciBuf

@ hipExternalMemoryHandleTypeNvSciBuf

Definition hip_runtime_api.h:1088

hipExternalMemoryHandleTypeOpaqueFd

@ hipExternalMemoryHandleTypeOpaqueFd

Definition hip_runtime_api.h:1081

hipExternalMemoryHandleTypeD3D12Heap

@ hipExternalMemoryHandleTypeD3D12Heap

Definition hip_runtime_api.h:1084

hipExternalMemoryHandleTypeOpaqueWin32Kmt

@ hipExternalMemoryHandleTypeOpaqueWin32Kmt

Definition hip_runtime_api.h:1083

hipExternalMemoryHandleTypeOpaqueWin32

@ hipExternalMemoryHandleTypeOpaqueWin32

Definition hip_runtime_api.h:1082

hipExternalMemoryHandleTypeD3D11ResourceKmt

@ hipExternalMemoryHandleTypeD3D11ResourceKmt

Definition hip_runtime_api.h:1087

hipFuncAttributePreferredSharedMemoryCarveout

@ hipFuncAttributePreferredSharedMemoryCarveout

Definition hip_runtime_api.h:1021

hipFuncAttributeMaxDynamicSharedMemorySize

@ hipFuncAttributeMaxDynamicSharedMemorySize

Definition hip_runtime_api.h:1020

hipFuncAttributeMax

@ hipFuncAttributeMax

Definition hip_runtime_api.h:1022

hipExternalSemaphoreHandleTypeNvSciSync

@ hipExternalSemaphoreHandleTypeNvSciSync

Definition hip_runtime_api.h:1124

hipExternalSemaphoreHandleTypeKeyedMutexKmt

@ hipExternalSemaphoreHandleTypeKeyedMutexKmt

Definition hip_runtime_api.h:1126

hipExternalSemaphoreHandleTypeOpaqueWin32Kmt

@ hipExternalSemaphoreHandleTypeOpaqueWin32Kmt

Definition hip_runtime_api.h:1121

hipExternalSemaphoreHandleTypeKeyedMutex

@ hipExternalSemaphoreHandleTypeKeyedMutex

Definition hip_runtime_api.h:1125

hipExternalSemaphoreHandleTypeD3D11Fence

@ hipExternalSemaphoreHandleTypeD3D11Fence

Definition hip_runtime_api.h:1123

hipExternalSemaphoreHandleTypeTimelineSemaphoreWin32

@ hipExternalSemaphoreHandleTypeTimelineSemaphoreWin32

Definition hip_runtime_api.h:1128

hipExternalSemaphoreHandleTypeOpaqueFd

@ hipExternalSemaphoreHandleTypeOpaqueFd

Definition hip_runtime_api.h:1119

hipExternalSemaphoreHandleTypeOpaqueWin32

@ hipExternalSemaphoreHandleTypeOpaqueWin32

Definition hip_runtime_api.h:1120

hipExternalSemaphoreHandleTypeTimelineSemaphoreFd

@ hipExternalSemaphoreHandleTypeTimelineSemaphoreFd

Definition hip_runtime_api.h:1127

hipExternalSemaphoreHandleTypeD3D12Fence

@ hipExternalSemaphoreHandleTypeD3D12Fence

Definition hip_runtime_api.h:1122

hipJitOptionCacheMode

@ hipJitOptionCacheMode

Definition hip_runtime_api.h:1011

hipJitOptionFastCompile

@ hipJitOptionFastCompile

Definition hip_runtime_api.h:1013

hipJitOptionInfoLogBuffer

@ hipJitOptionInfoLogBuffer

Definition hip_runtime_api.h:1000

hipJitOptionErrorLogBuffer

@ hipJitOptionErrorLogBuffer

Definition hip_runtime_api.h:1002

hipJitOptionTarget

@ hipJitOptionTarget

Definition hip_runtime_api.h:1006

hipJitOptionThreadsPerBlock

@ hipJitOptionThreadsPerBlock

Definition hip_runtime_api.h:998

hipJitOptionNumOptions

@ hipJitOptionNumOptions

Definition hip_runtime_api.h:1014

hipJitOptionGenerateLineInfo

@ hipJitOptionGenerateLineInfo

Definition hip_runtime_api.h:1010

hipJitOptionOptimizationLevel

@ hipJitOptionOptimizationLevel

Definition hip_runtime_api.h:1004

hipJitOptionErrorLogBufferSizeBytes

@ hipJitOptionErrorLogBufferSizeBytes

Definition hip_runtime_api.h:1003

hipJitOptionWallTime

@ hipJitOptionWallTime

Definition hip_runtime_api.h:999

hipJitOptionInfoLogBufferSizeBytes

@ hipJitOptionInfoLogBufferSizeBytes

Definition hip_runtime_api.h:1001

hipJitOptionTargetFromContext

@ hipJitOptionTargetFromContext

Definition hip_runtime_api.h:1005

hipJitOptionGenerateDebugInfo

@ hipJitOptionGenerateDebugInfo

Definition hip_runtime_api.h:1008

hipJitOptionLogVerbose

@ hipJitOptionLogVerbose

Definition hip_runtime_api.h:1009

hipJitOptionMaxRegisters

@ hipJitOptionMaxRegisters

Definition hip_runtime_api.h:997

hipJitOptionSm3xOpt

@ hipJitOptionSm3xOpt

Definition hip_runtime_api.h:1012

hipJitOptionFallbackStrategy

@ hipJitOptionFallbackStrategy

Definition hip_runtime_api.h:1007

hipDevP2PAttrAccessSupported

@ hipDevP2PAttrAccessSupported

Definition hip_runtime_api.h:612

hipDevP2PAttrHipArrayAccessSupported

@ hipDevP2PAttrHipArrayAccessSupported

Definition hip_runtime_api.h:614

hipDevP2PAttrNativeAtomicSupported

@ hipDevP2PAttrNativeAtomicSupported

Definition hip_runtime_api.h:613

hipDevP2PAttrPerformanceRank

@ hipDevP2PAttrPerformanceRank

Definition hip_runtime_api.h:611

hipGraphDebugDotFlagsKernelNodeAttributes

@ hipGraphDebugDotFlagsKernelNodeAttributes

Definition hip_runtime_api.h:1391

hipGraphDebugDotFlagsMemsetNodeParams

@ hipGraphDebugDotFlagsMemsetNodeParams

Definition hip_runtime_api.h:1383

hipGraphDebugDotFlagsKernelNodeParams

@ hipGraphDebugDotFlagsKernelNodeParams

Definition hip_runtime_api.h:1381

hipGraphDebugDotFlagsExtSemasWaitNodeParams

@ hipGraphDebugDotFlagsExtSemasWaitNodeParams

Definition hip_runtime_api.h:1389

hipGraphDebugDotFlagsHandles

@ hipGraphDebugDotFlagsHandles

Definition hip_runtime_api.h:1393

hipGraphDebugDotFlagsExtSemasSignalNodeParams

@ hipGraphDebugDotFlagsExtSemasSignalNodeParams

Definition hip_runtime_api.h:1387

hipGraphDebugDotFlagsHostNodeParams

@ hipGraphDebugDotFlagsHostNodeParams

Definition hip_runtime_api.h:1384

hipGraphDebugDotFlagsEventNodeParams

@ hipGraphDebugDotFlagsEventNodeParams

Definition hip_runtime_api.h:1385

hipGraphDebugDotFlagsVerbose

@ hipGraphDebugDotFlagsVerbose

Definition hip_runtime_api.h:1379

hipGraphDebugDotFlagsMemcpyNodeParams

@ hipGraphDebugDotFlagsMemcpyNodeParams

Definition hip_runtime_api.h:1382

hipGraphUserObjectMove

@ hipGraphUserObjectMove

Add new reference or retain.

Definition hip_runtime_api.h:1364

hipStreamAddCaptureDependencies

@ hipStreamAddCaptureDependencies

Add new nodes to the dependency set.

Definition hip_runtime_api.h:1349

hipStreamSetCaptureDependencies

@ hipStreamSetCaptureDependencies

Replace the dependency set with the new nodes.

Definition hip_runtime_api.h:1350

hipMemHandleTypeGeneric

@ hipMemHandleTypeGeneric

Generic handle type.

Definition hip_runtime_api.h:1480

hipFlushGPUDirectRDMAWritesOptionHost

@ hipFlushGPUDirectRDMAWritesOptionHost

Definition hip_runtime_api.h:557

hipFlushGPUDirectRDMAWritesOptionMemOps

@ hipFlushGPUDirectRDMAWritesOptionMemOps

Definition hip_runtime_api.h:558

hipFuncCachePreferNone

@ hipFuncCachePreferNone

no preference for shared memory or L1 (default)

Definition hip_runtime_api.h:1028

hipFuncCachePreferEqual

@ hipFuncCachePreferEqual

prefer equal size L1 cache and shared memory

Definition hip_runtime_api.h:1031

hipFuncCachePreferL1

@ hipFuncCachePreferL1

prefer larger L1 cache and smaller shared memory

Definition hip_runtime_api.h:1030

hipFuncCachePreferShared

@ hipFuncCachePreferShared

prefer larger shared memory and smaller L1 cache

Definition hip_runtime_api.h:1029

hipUserObjectNoDestructorSync

@ hipUserObjectNoDestructorSync

Destructor execution is not synchronized.

Definition hip_runtime_api.h:1360

hipGraphMemAttrReservedMemHigh

@ hipGraphMemAttrReservedMemHigh

High watermark of memory, in bytes, currently allocated for graphs.

Definition hip_runtime_api.h:1357

hipGraphMemAttrUsedMemCurrent

@ hipGraphMemAttrUsedMemCurrent

Amount of memory, in bytes, currently associated with graphs.

Definition hip_runtime_api.h:1354

hipGraphMemAttrUsedMemHigh

@ hipGraphMemAttrUsedMemHigh

High watermark of memory, in bytes, associated with graphs since the last time.

Definition hip_runtime_api.h:1355

hipGraphMemAttrReservedMemCurrent

@ hipGraphMemAttrReservedMemCurrent

Amount of memory, in bytes, currently allocated for graphs.

Definition hip_runtime_api.h:1356

hipMemPoolAttrUsedMemCurrent

@ hipMemPoolAttrUsedMemCurrent

Definition hip_runtime_api.h:912

hipMemPoolAttrReservedMemHigh

@ hipMemPoolAttrReservedMemHigh

Definition hip_runtime_api.h:907

hipMemPoolAttrReservedMemCurrent

@ hipMemPoolAttrReservedMemCurrent

Definition hip_runtime_api.h:901

hipMemPoolAttrReleaseThreshold

@ hipMemPoolAttrReleaseThreshold

Definition hip_runtime_api.h:896

hipMemPoolAttrUsedMemHigh

@ hipMemPoolAttrUsedMemHigh

Definition hip_runtime_api.h:918

hipMemPoolReuseAllowInternalDependencies

@ hipMemPoolReuseAllowInternalDependencies

Definition hip_runtime_api.h:887

hipMemPoolReuseFollowEventDependencies

@ hipMemPoolReuseFollowEventDependencies

Definition hip_runtime_api.h:874

hipMemPoolReuseAllowOpportunistic

@ hipMemPoolReuseAllowOpportunistic

Definition hip_runtime_api.h:880

hipMemOperationTypeMap

@ hipMemOperationTypeMap

Map operation.

Definition hip_runtime_api.h:1487

hipMemOperationTypeUnmap

@ hipMemOperationTypeUnmap

Unmap operation.

Definition hip_runtime_api.h:1488

hipGraphicsRegisterFlagsReadOnly

@ hipGraphicsRegisterFlagsReadOnly

HIP will not write to this registered resource.

Definition hip_runtime_api.h:1196

hipGraphicsRegisterFlagsTextureGather

@ hipGraphicsRegisterFlagsTextureGather

HIP will perform texture gather operations on this registered resource.

Definition hip_runtime_api.h:1200

hipGraphicsRegisterFlagsWriteDiscard

@ hipGraphicsRegisterFlagsWriteDiscard

HIP will only write and will not read from this registered resource.

Definition hip_runtime_api.h:1197

hipGraphicsRegisterFlagsNone

@ hipGraphicsRegisterFlagsNone

Definition hip_runtime_api.h:1195

hipGraphicsRegisterFlagsSurfaceLoadStore

@ hipGraphicsRegisterFlagsSurfaceLoadStore

HIP will bind this resource to a surface.

Definition hip_runtime_api.h:1199

hipMemRangeCoherencyModeFineGrain

@ hipMemRangeCoherencyModeFineGrain

Definition hip_runtime_api.h:838

hipMemRangeCoherencyModeIndeterminate

@ hipMemRangeCoherencyModeIndeterminate

Definition hip_runtime_api.h:842

hipMemRangeCoherencyModeCoarseGrain

@ hipMemRangeCoherencyModeCoarseGrain

Definition hip_runtime_api.h:840

hipMemAccessFlagsProtRead

@ hipMemAccessFlagsProtRead

Set the address range read accessible.

Definition hip_runtime_api.h:942

hipMemAccessFlagsProtNone

@ hipMemAccessFlagsProtNone

Default, make the address range not accessible.

Definition hip_runtime_api.h:941

hipMemAccessFlagsProtReadWrite

@ hipMemAccessFlagsProtReadWrite

Set the address range read-write accessible.

Definition hip_runtime_api.h:943

hipMemAllocationGranularityMinimum

@ hipMemAllocationGranularityMinimum

Minimum granularity.

Definition hip_runtime_api.h:1472

hipMemAllocationGranularityRecommended

@ hipMemAllocationGranularityRecommended

Recommended granularity for performance.

Definition hip_runtime_api.h:1473

hipGraphExecUpdateErrorNotSupported

@ hipGraphExecUpdateErrorNotSupported

The update failed because something about the node is not supported.

Definition hip_runtime_api.h:1331

hipGraphExecUpdateErrorNodeTypeChanged

@ hipGraphExecUpdateErrorNodeTypeChanged

The update failed because a node type changed.

Definition hip_runtime_api.h:1326

hipGraphExecUpdateErrorTopologyChanged

@ hipGraphExecUpdateErrorTopologyChanged

The update failed because the topology changed.

Definition hip_runtime_api.h:1325

hipGraphExecUpdateErrorUnsupportedFunctionChange

@ hipGraphExecUpdateErrorUnsupportedFunctionChange

Definition hip_runtime_api.h:1333

hipGraphExecUpdateError

@ hipGraphExecUpdateError

Definition hip_runtime_api.h:1323

hipGraphExecUpdateErrorFunctionChanged

@ hipGraphExecUpdateErrorFunctionChanged

The update failed because the function of a kernel node changed.

Definition hip_runtime_api.h:1327

hipGraphExecUpdateSuccess

@ hipGraphExecUpdateSuccess

The update succeeded.

Definition hip_runtime_api.h:1322

hipGraphExecUpdateErrorParametersChanged

@ hipGraphExecUpdateErrorParametersChanged

The update failed because the parameters changed in a way that is not supported.

Definition hip_runtime_api.h:1329

hipStreamCaptureStatusInvalidated

@ hipStreamCaptureStatusInvalidated

Definition hip_runtime_api.h:1344

hipStreamCaptureStatusNone

@ hipStreamCaptureStatusNone

Stream is not capturing.

Definition hip_runtime_api.h:1342

hipStreamCaptureStatusActive

@ hipStreamCaptureStatusActive

Stream is actively capturing.

Definition hip_runtime_api.h:1343

hipDeviceAttributeDirectManagedMemAccessFromHost

@ hipDeviceAttributeDirectManagedMemAccessFromHost

Definition hip_runtime_api.h:426

hipDeviceAttributeSurfaceAlignment

@ hipDeviceAttributeSurfaceAlignment

Alignment requirement for surfaces.

Definition hip_runtime_api.h:496

hipDeviceAttributeMaxGridDimX

@ hipDeviceAttributeMaxGridDimX

Max grid size in width.

Definition hip_runtime_api.h:443

hipDeviceAttributeMaxSurfaceCubemapLayered

@ hipDeviceAttributeMaxSurfaceCubemapLayered

Cuda only. Maximum dimension of Cubemap layered surface.

Definition hip_runtime_api.h:452

hipDeviceAttributeMaxSurface3D

@ hipDeviceAttributeMaxSurface3D

Maximum dimension (width, height, depth) of 3D surface.

Definition hip_runtime_api.h:450

hipDeviceAttributeMaxPitch

@ hipDeviceAttributeMaxPitch

Maximum pitch in bytes allowed by memory copies.

Definition hip_runtime_api.h:473

hipDeviceAttributeTccDriver

@ hipDeviceAttributeTccDriver

Cuda only. Whether device is a Tesla device using TCC driver.

Definition hip_runtime_api.h:497

hipDeviceAttributeHostNativeAtomicSupported

@ hipDeviceAttributeHostNativeAtomicSupported

Link between the device and the host supports native atomic operations.

Definition hip_runtime_api.h:429

hipDeviceAttributePageableMemoryAccessUsesHostPageTables

@ hipDeviceAttributePageableMemoryAccessUsesHostPageTables

Device accesses pageable memory via the host's page tables.

Definition hip_runtime_api.h:482

hipDeviceAttributeUnused5

@ hipDeviceAttributeUnused5

Previously hipDeviceAttributeGcnArchName.

Definition hip_runtime_api.h:517

hipDeviceAttributeMaxBlockDimY

@ hipDeviceAttributeMaxBlockDimY

Max block size in height.

Definition hip_runtime_api.h:441

hipDeviceAttributeMaxSurfaceCubemap

@ hipDeviceAttributeMaxSurfaceCubemap

Cuda only. Maximum dimensions of Cubemap surface.

Definition hip_runtime_api.h:451

hipDeviceAttributePageableMemoryAccess

@ hipDeviceAttributePageableMemoryAccess

Definition hip_runtime_api.h:480

hipDeviceAttributeClockRate

@ hipDeviceAttributeClockRate

Peak clock frequency in kilohertz.

Definition hip_runtime_api.h:417

hipDeviceAttributeCudaCompatibleEnd

@ hipDeviceAttributeCudaCompatibleEnd

Definition hip_runtime_api.h:510

hipDeviceAttributeMaxTexture1DMipmap

@ hipDeviceAttributeMaxTexture1DMipmap

Maximum size of 1D mipmapped texture.

Definition hip_runtime_api.h:457

hipDeviceAttributeComputeCapabilityMajor

@ hipDeviceAttributeComputeCapabilityMajor

Major compute capability version number.

Definition hip_runtime_api.h:437

hipDeviceAttributeGlobalL1CacheSupported

@ hipDeviceAttributeGlobalL1CacheSupported

Device supports caching globals in L1.

Definition hip_runtime_api.h:428

hipDeviceAttributeCooperativeMultiDeviceUnmatchedSharedMem

@ hipDeviceAttributeCooperativeMultiDeviceUnmatchedSharedMem

Definition hip_runtime_api.h:526

hipDeviceAttributeAccessPolicyMaxWindowSize

@ hipDeviceAttributeAccessPolicyMaxWindowSize

Cuda only. The maximum size of the window policy in bytes.

Definition hip_runtime_api.h:412

hipDeviceAttributeMaxTexture3DHeight

@ hipDeviceAttributeMaxTexture3DHeight

Maximum dimension height of 3D texture.

Definition hip_runtime_api.h:465

hipDeviceAttributeComputeCapabilityMinor

@ hipDeviceAttributeComputeCapabilityMinor

Minor compute capability version number.

Definition hip_runtime_api.h:476

hipDeviceAttributeMaxTextureCubemap

@ hipDeviceAttributeMaxTextureCubemap

Maximum dimensions of Cubemap texture.

Definition hip_runtime_api.h:468

hipDeviceAttributeDeviceOverlap

@ hipDeviceAttributeDeviceOverlap

Definition hip_runtime_api.h:424

hipDeviceAttributeMaxTexture2DLinear

@ hipDeviceAttributeMaxTexture2DLinear

Maximum dimensions (width, height, pitch) of 2D textures bound to pitched memory.

Definition hip_runtime_api.h:462

hipDeviceAttributeMaxSurface2D

@ hipDeviceAttributeMaxSurface2D

Maximum dimension (width, height) of 2D surface.

Definition hip_runtime_api.h:448

hipDeviceAttributeMaxSurface1DLayered

@ hipDeviceAttributeMaxSurface1DLayered

Cuda only. Maximum dimensions of 1D layered surface.

Definition hip_runtime_api.h:447

hipDeviceAttributeHdpRegFlushCntl

@ hipDeviceAttributeHdpRegFlushCntl

Address of the HDP_REG_COHERENCY_FLUSH_CNTL register.

Definition hip_runtime_api.h:519

hipDeviceAttributeComputeMode

@ hipDeviceAttributeComputeMode

Compute mode that device is currently in.

Definition hip_runtime_api.h:418

hipDeviceAttributeCooperativeMultiDeviceUnmatchedFunc

@ hipDeviceAttributeCooperativeMultiDeviceUnmatchedFunc

Definition hip_runtime_api.h:520

hipDeviceAttributeAsicRevision

@ hipDeviceAttributeAsicRevision

Revision of the GPU in this device.

Definition hip_runtime_api.h:529

hipDeviceAttributeUnused4

@ hipDeviceAttributeUnused4

Previously hipDeviceAttributeGcnArch.

Definition hip_runtime_api.h:516

hipDeviceAttributeCooperativeMultiDeviceLaunch

@ hipDeviceAttributeCooperativeMultiDeviceLaunch

Support cooperative launch on multiple devices.

Definition hip_runtime_api.h:423

hipDeviceAttributeMaxTexture2DHeight

@ hipDeviceAttributeMaxTexture2DHeight

Maximum dimension hight of 2D texture.

Definition hip_runtime_api.h:459

hipDeviceAttributePersistingL2CacheMaxSize

@ hipDeviceAttributePersistingL2CacheMaxSize

Maximum l2 persisting lines capacity in bytes.

Definition hip_runtime_api.h:486

hipDeviceAttributeEccEnabled

@ hipDeviceAttributeEccEnabled

Whether ECC support is enabled.

Definition hip_runtime_api.h:411

hipDeviceAttributeCanUseHostPointerForRegisteredMem

@ hipDeviceAttributeCanUseHostPointerForRegisteredMem

Definition hip_runtime_api.h:415

hipDeviceAttributePciBusId

@ hipDeviceAttributePciBusId

PCI Bus ID.

Definition hip_runtime_api.h:483

hipDeviceAttributeL2CacheSize

@ hipDeviceAttributeL2CacheSize

Size of L2 cache in bytes. 0 if the device doesn't have L2 cache.

Definition hip_runtime_api.h:433

hipDeviceAttributeKernelExecTimeout

@ hipDeviceAttributeKernelExecTimeout

Run time limit for kernels executed on the device.

Definition hip_runtime_api.h:432

hipDeviceAttributeMaxThreadsDim

@ hipDeviceAttributeMaxThreadsDim

Maximum dimension of a block.

Definition hip_runtime_api.h:470

hipDeviceAttributeSingleToDoublePrecisionPerfRatio

@ hipDeviceAttributeSingleToDoublePrecisionPerfRatio

Cuda only. Performance ratio of single precision to double precision.

Definition hip_runtime_api.h:494

hipDeviceAttributeMaxGridDimY

@ hipDeviceAttributeMaxGridDimY

Max grid size in height.

Definition hip_runtime_api.h:444

hipDeviceAttributeMultiprocessorCount

@ hipDeviceAttributeMultiprocessorCount

Number of multiprocessors on the device.

Definition hip_runtime_api.h:478

hipDeviceAttributeAmdSpecificBegin

@ hipDeviceAttributeAmdSpecificBegin

Definition hip_runtime_api.h:511

hipDeviceAttributeMaxRegistersPerMultiprocessor

@ hipDeviceAttributeMaxRegistersPerMultiprocessor

32-bit registers available per block.

Definition hip_runtime_api.h:489

hipDeviceAttributeIsMultiGpuBoard

@ hipDeviceAttributeIsMultiGpuBoard

Multiple GPU devices.

Definition hip_runtime_api.h:431

hipDeviceAttributeSharedMemPerBlockOptin

@ hipDeviceAttributeSharedMemPerBlockOptin

Maximum shared memory per block usable by special opt in.

Definition hip_runtime_api.h:492

hipDeviceAttributeMaxSurface2DLayered

@ hipDeviceAttributeMaxSurface2DLayered

Cuda only. Maximum dimensions of 2D layered surface.

Definition hip_runtime_api.h:449

hipDeviceAttributeAmdSpecificEnd

@ hipDeviceAttributeAmdSpecificEnd

Definition hip_runtime_api.h:538

hipDeviceAttributeMemoryClockRate

@ hipDeviceAttributeMemoryClockRate

Peak memory clock frequency in kilohertz.

Definition hip_runtime_api.h:475

hipDeviceAttributeMaxGridDimZ

@ hipDeviceAttributeMaxGridDimZ

Max grid size in depth.

Definition hip_runtime_api.h:445

hipDeviceAttributeHdpMemFlushCntl

@ hipDeviceAttributeHdpMemFlushCntl

Address of the HDP_MEM_COHERENCY_FLUSH_CNTL register.

Definition hip_runtime_api.h:518

hipDeviceAttributeUnused2

@ hipDeviceAttributeUnused2

Previously hipDeviceAttributeUuid.

Definition hip_runtime_api.h:503

hipDeviceAttributeFineGrainSupport

@ hipDeviceAttributeFineGrainSupport

'1' if Device supports fine grain, '0' otherwise

Definition hip_runtime_api.h:535

hipDeviceAttributeCooperativeLaunch

@ hipDeviceAttributeCooperativeLaunch

Support cooperative launch.

Definition hip_runtime_api.h:422

hipDeviceAttributeUnifiedAddressing

@ hipDeviceAttributeUnifiedAddressing

Cuda only. An unified address space shared with the host.

Definition hip_runtime_api.h:502

hipDeviceAttributeAsyncEngineCount

@ hipDeviceAttributeAsyncEngineCount

Asynchronous engines number.

Definition hip_runtime_api.h:413

hipDeviceAttributeMultiGpuBoardGroupID

@ hipDeviceAttributeMultiGpuBoardGroupID

Unique ID of device group on the same multi-GPU board.

Definition hip_runtime_api.h:477

hipDeviceAttributeStreamPrioritiesSupported

@ hipDeviceAttributeStreamPrioritiesSupported

Whether to support stream priorities.

Definition hip_runtime_api.h:495

hipDeviceAttributeMaxSharedMemoryPerBlock

@ hipDeviceAttributeMaxSharedMemoryPerBlock

Maximum shared memory available per block in bytes.

Definition hip_runtime_api.h:491

hipDeviceAttributeLocalL1CacheSupported

@ hipDeviceAttributeLocalL1CacheSupported

caching locals in L1 is supported

Definition hip_runtime_api.h:434

hipDeviceAttributeCanUseStreamWaitValue

@ hipDeviceAttributeCanUseStreamWaitValue

Definition hip_runtime_api.h:530

hipDeviceAttributeMaxRegistersPerBlock

@ hipDeviceAttributeMaxRegistersPerBlock

Definition hip_runtime_api.h:487

hipDeviceAttributeMaxThreadsPerBlock

@ hipDeviceAttributeMaxThreadsPerBlock

Maximum number of threads per block.

Definition hip_runtime_api.h:471

hipDeviceAttributeMemoryBusWidth

@ hipDeviceAttributeMemoryBusWidth

Global memory bus width in bits.

Definition hip_runtime_api.h:474

hipDeviceAttributeMemoryPoolSupportedHandleTypes

@ hipDeviceAttributeMemoryPoolSupportedHandleTypes

Supported handle mask for HIP Stream Ordered Memory Allocator.

Definition hip_runtime_api.h:508

hipDeviceAttributeComputePreemptionSupported

@ hipDeviceAttributeComputePreemptionSupported

Device supports Compute Preemption.

Definition hip_runtime_api.h:419

hipDeviceAttributeMaxSurface1D

@ hipDeviceAttributeMaxSurface1D

Maximum size of 1D surface.

Definition hip_runtime_api.h:446

hipDeviceAttributeUnused1

@ hipDeviceAttributeUnused1

Previously hipDeviceAttributeName.

Definition hip_runtime_api.h:479

hipDeviceAttributeMaxTexture3DAlt

@ hipDeviceAttributeMaxTexture3DAlt

Maximum dimensions of alternate 3D texture.

Definition hip_runtime_api.h:467

hipDeviceAttributeMaxTexture1DLinear

@ hipDeviceAttributeMaxTexture1DLinear

Definition hip_runtime_api.h:455

hipDeviceAttributeMaxTexture2DGather

@ hipDeviceAttributeMaxTexture2DGather

Maximum dimensions of 2D texture if gather operations performed.

Definition hip_runtime_api.h:460

hipDeviceAttributeWallClockRate

@ hipDeviceAttributeWallClockRate

Constant frequency of wall clock in kilohertz.

Definition hip_runtime_api.h:536

hipDeviceAttributePciDeviceId

@ hipDeviceAttributePciDeviceId

PCI Device ID.

Definition hip_runtime_api.h:484

hipDeviceAttributeCanMapHostMemory

@ hipDeviceAttributeCanMapHostMemory

Whether host memory can be mapped into device address space.

Definition hip_runtime_api.h:414

hipDeviceAttributeMaxTexture1DWidth

@ hipDeviceAttributeMaxTexture1DWidth

Maximum size of 1D texture.

Definition hip_runtime_api.h:453

hipDeviceAttributeConcurrentManagedAccess

@ hipDeviceAttributeConcurrentManagedAccess

Device can coherently access managed memory concurrently with the CPU.

Definition hip_runtime_api.h:421

hipDeviceAttributeVendorSpecificBegin

@ hipDeviceAttributeVendorSpecificBegin

Definition hip_runtime_api.h:539

hipDeviceAttributeManagedMemory

@ hipDeviceAttributeManagedMemory

Device supports allocating managed memory on this system.

Definition hip_runtime_api.h:438

hipDeviceAttributeIntegrated

@ hipDeviceAttributeIntegrated

Device is integrated GPU.

Definition hip_runtime_api.h:430

hipDeviceAttributeMaxTexture2DLayered

@ hipDeviceAttributeMaxTexture2DLayered

Maximum dimensions of 2D layered texture.

Definition hip_runtime_api.h:461

hipDeviceAttributeCooperativeMultiDeviceUnmatchedGridDim

@ hipDeviceAttributeCooperativeMultiDeviceUnmatchedGridDim

Definition hip_runtime_api.h:522

hipDeviceAttributeMaxTexture3DDepth

@ hipDeviceAttributeMaxTexture3DDepth

Maximum dimension depth of 3D texture.

Definition hip_runtime_api.h:466

hipDeviceAttributeImageSupport

@ hipDeviceAttributeImageSupport

'1' if Device supports image, '0' otherwise.

Definition hip_runtime_api.h:532

hipDeviceAttributeTotalGlobalMem

@ hipDeviceAttributeTotalGlobalMem

Global memory available on devicice.

Definition hip_runtime_api.h:501

hipDeviceAttributeMaxBlocksPerMultiProcessor

@ hipDeviceAttributeMaxBlocksPerMultiProcessor

Max block size per multiprocessor.

Definition hip_runtime_api.h:439

hipDeviceAttributeIsLargeBar

@ hipDeviceAttributeIsLargeBar

Whether it is LargeBar.

Definition hip_runtime_api.h:528

hipDeviceAttributeMaxTexture2DWidth

@ hipDeviceAttributeMaxTexture2DWidth

Maximum dimension width of 2D texture.

Definition hip_runtime_api.h:458

hipDeviceAttributeMaxBlockDimX

@ hipDeviceAttributeMaxBlockDimX

Max block size in width.

Definition hip_runtime_api.h:440

hipDeviceAttributeMaxTexture3DWidth

@ hipDeviceAttributeMaxTexture3DWidth

Maximum dimension width of 3D texture.

Definition hip_runtime_api.h:464

hipDeviceAttributeUnused3

@ hipDeviceAttributeUnused3

Previously hipDeviceAttributeArch.

Definition hip_runtime_api.h:514

hipDeviceAttributeTotalConstantMemory

@ hipDeviceAttributeTotalConstantMemory

Constant memory size in bytes.

Definition hip_runtime_api.h:500

hipDeviceAttributeTextureAlignment

@ hipDeviceAttributeTextureAlignment

Alignment requirement for textures.

Definition hip_runtime_api.h:498

hipDeviceAttributeMaxTexture1DLayered

@ hipDeviceAttributeMaxTexture1DLayered

Maximum dimensions of 1D layered texture.

Definition hip_runtime_api.h:454

hipDeviceAttributeMaxSharedMemoryPerMultiprocessor

@ hipDeviceAttributeMaxSharedMemoryPerMultiprocessor

Maximum Shared Memory PerMultiprocessor.

Definition hip_runtime_api.h:515

hipDeviceAttributeReservedSharedMemPerBlock

@ hipDeviceAttributeReservedSharedMemPerBlock

Shared memory reserved by CUDA driver per block.

Definition hip_runtime_api.h:490

hipDeviceAttributeCudaCompatibleBegin

@ hipDeviceAttributeCudaCompatibleBegin

Definition hip_runtime_api.h:409

hipDeviceAttributeConcurrentKernels

@ hipDeviceAttributeConcurrentKernels

Device can possibly execute multiple kernels concurrently.

Definition hip_runtime_api.h:420

hipDeviceAttributeLuid

@ hipDeviceAttributeLuid

8-byte locally unique identifier in 8 bytes. Undefined on TCC and non-Windows platforms

Definition hip_runtime_api.h:435

hipDeviceAttributePciDomainID

@ hipDeviceAttributePciDomainID

PCI Domain ID.

Definition hip_runtime_api.h:485

hipDeviceAttributeMaxThreadsPerMultiProcessor

@ hipDeviceAttributeMaxThreadsPerMultiProcessor

Maximum resident threads per multiprocessor.

Definition hip_runtime_api.h:472

hipDeviceAttributeTexturePitchAlignment

@ hipDeviceAttributeTexturePitchAlignment

Pitch alignment requirement for 2D texture references bound to pitched memory;.

Definition hip_runtime_api.h:499

hipDeviceAttributePhysicalMultiProcessorCount

@ hipDeviceAttributePhysicalMultiProcessorCount

Definition hip_runtime_api.h:533

hipDeviceAttributeHostRegisterSupported

@ hipDeviceAttributeHostRegisterSupported

Can device support host memory registration via hipHostRegister.

Definition hip_runtime_api.h:507

hipDeviceAttributeSharedMemPerMultiprocessor

@ hipDeviceAttributeSharedMemPerMultiprocessor

Shared memory available per multiprocessor.

Definition hip_runtime_api.h:493

hipDeviceAttributeLuidDeviceNodeMask

@ hipDeviceAttributeLuidDeviceNodeMask

Luid device node mask. Undefined on TCC and non-Windows platforms.

Definition hip_runtime_api.h:436

hipDeviceAttributeMaxTextureCubemapLayered

@ hipDeviceAttributeMaxTextureCubemapLayered

Maximum dimensions of Cubemap layered texture.

Definition hip_runtime_api.h:469

hipDeviceAttributeCooperativeMultiDeviceUnmatchedBlockDim

@ hipDeviceAttributeCooperativeMultiDeviceUnmatchedBlockDim

Definition hip_runtime_api.h:524

hipDeviceAttributeVirtualMemoryManagementSupported

@ hipDeviceAttributeVirtualMemoryManagementSupported

Device supports HIP virtual memory management.

Definition hip_runtime_api.h:506

hipDeviceAttributeMemoryPoolsSupported

@ hipDeviceAttributeMemoryPoolsSupported

Device supports HIP Stream Ordered Memory Allocator.

Definition hip_runtime_api.h:505

hipDeviceAttributeClockInstructionRate

@ hipDeviceAttributeClockInstructionRate

Frequency in khz of the timer used by the device-side "clock*".

Definition hip_runtime_api.h:513

hipDeviceAttributeMaxTexture2DMipmap

@ hipDeviceAttributeMaxTexture2DMipmap

Maximum dimensions of 2D mipmapped texture.

Definition hip_runtime_api.h:463

hipDeviceAttributeMaxBlockDimZ

@ hipDeviceAttributeMaxBlockDimZ

Max block size in depth.

Definition hip_runtime_api.h:442

hipDeviceAttributeWarpSize

@ hipDeviceAttributeWarpSize

Warp size in threads.

Definition hip_runtime_api.h:504

hipGPUDirectRDMAWritesOrderingOwner

@ hipGPUDirectRDMAWritesOrderingOwner

Definition hip_runtime_api.h:563

hipGPUDirectRDMAWritesOrderingNone

@ hipGPUDirectRDMAWritesOrderingNone

Definition hip_runtime_api.h:562

hipGPUDirectRDMAWritesOrderingAllDevices

@ hipGPUDirectRDMAWritesOrderingAllDevices

Definition hip_runtime_api.h:564

hipMemAllocationTypeMax

@ hipMemAllocationTypeMax

Definition hip_runtime_api.h:961

hipMemAllocationTypePinned

@ hipMemAllocationTypePinned

Definition hip_runtime_api.h:960

hipMemAllocationTypeInvalid

@ hipMemAllocationTypeInvalid

Definition hip_runtime_api.h:956

hipMemoryTypeDevice

@ hipMemoryTypeDevice

Definition hip_runtime_api.h:247

hipMemoryTypeHost

@ hipMemoryTypeHost

Memory is physically located on host.

Definition hip_runtime_api.h:246

hipMemoryTypeUnregistered

@ hipMemoryTypeUnregistered

Unregistered memory.

Definition hip_runtime_api.h:245

hipMemoryTypeArray

@ hipMemoryTypeArray

Definition hip_runtime_api.h:252

hipMemoryTypeManaged

@ hipMemoryTypeManaged

Definition hip_runtime_api.h:249

hipMemoryTypeUnified

@ hipMemoryTypeUnified

unified address space

Definition hip_runtime_api.h:254

hipGraphInstantiateFlagAutoFreeOnLaunch

@ hipGraphInstantiateFlagAutoFreeOnLaunch

Automatically free memory allocated in a graph before relaunching.

Definition hip_runtime_api.h:1368

hipGraphInstantiateFlagUseNodePriority

@ hipGraphInstantiateFlagUseNodePriority

Run the graph using the per-node priority attributes rather than the priority of the stream it is lau...

Definition hip_runtime_api.h:1374

hipGraphInstantiateFlagUpload

@ hipGraphInstantiateFlagUpload

Automatically upload the graph after instantiaton.

Definition hip_runtime_api.h:1370

hipGraphInstantiateFlagDeviceLaunch

@ hipGraphInstantiateFlagDeviceLaunch

Instantiate the graph to be launchable from the device.

Definition hip_runtime_api.h:1372

hipLaunchAttributePriority

@ hipLaunchAttributePriority

Definition hip_runtime_api.h:1286

hipKernelNodeAttributeCooperative

@ hipKernelNodeAttributeCooperative

Definition hip_runtime_api.h:1285

hipKernelNodeAttributeAccessPolicyWindow

@ hipKernelNodeAttributeAccessPolicyWindow

Definition hip_runtime_api.h:1284

hipMemLocationTypeInvalid

@ hipMemLocationTypeInvalid

Definition hip_runtime_api.h:924

hipMemLocationTypeDevice

@ hipMemLocationTypeDevice

Device location, thus it's HIP device ID.

Definition hip_runtime_api.h:925

hipArraySparseSubresourceTypeSparseLevel

@ hipArraySparseSubresourceTypeSparseLevel

Sparse level.

Definition hip_runtime_api.h:1495

hipArraySparseSubresourceTypeMiptail

@ hipArraySparseSubresourceTypeMiptail

Miptail.

Definition hip_runtime_api.h:1496

hipGraphKernelNodeSetParams

hipError_t hipGraphKernelNodeSetParams(hipGraphNode_t node, const hipKernelNodeParams *pNodeParams)

Sets a kernel node's parameters.

hipGraphMemFreeNodeGetParams

hipError_t hipGraphMemFreeNodeGetParams(hipGraphNode_t node, void *dev_ptr)

Returns parameters for memory free node.

hipGraphNodeGetDependencies

hipError_t hipGraphNodeGetDependencies(hipGraphNode_t node, hipGraphNode_t *pDependencies, size_t *pNumDependencies)

Returns a node's dependencies.

hipGraphCreate

hipError_t hipGraphCreate(hipGraph_t *pGraph, unsigned int flags)

Creates a graph.

hipGraphAddMemcpyNode1D

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.

hipDrvGraphMemcpyNodeGetParams

hipError_t hipDrvGraphMemcpyNodeGetParams(hipGraphNode_t hNode, HIP_MEMCPY3D *nodeParams)

Gets a memcpy node's parameters.

hipDeviceSetGraphMemAttribute

hipError_t hipDeviceSetGraphMemAttribute(int device, hipGraphMemAttributeType attr, void *value)

Set the mem attribute for graphs.

hipGraphMemcpyNodeSetParams

hipError_t hipGraphMemcpyNodeSetParams(hipGraphNode_t node, const hipMemcpy3DParms *pNodeParams)

Sets a memcpy node's parameters.

hipUserObjectCreate

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.

hipGraphExecUpdate

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.

hipGraphNodeFindInClone

hipError_t hipGraphNodeFindInClone(hipGraphNode_t *pNode, hipGraphNode_t originalNode, hipGraph_t clonedGraph)

Finds a cloned version of a node.

hipGraphAddEventWaitNode

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.

hipGraphMemcpyNodeSetParamsToSymbol

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.

hipStreamIsCapturing

hipError_t hipStreamIsCapturing(hipStream_t stream, hipStreamCaptureStatus *pCaptureStatus)

Get stream's capture state.

hipGraphNodeGetEnabled

hipError_t hipGraphNodeGetEnabled(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, unsigned int *isEnabled)

Query whether a node in the given graphExec is enabled.

hipGraphAddChildGraphNode

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.

hipGraphExternalSemaphoresSignalNodeSetParams

hipError_t hipGraphExternalSemaphoresSignalNodeSetParams(hipGraphNode_t hNode, const hipExternalSemaphoreSignalNodeParams *nodeParams)

Updates node parameters in the external semaphore signal node.

hipGraphDestroyNode

hipError_t hipGraphDestroyNode(hipGraphNode_t node)

Remove a node from the graph.

hipGraphMemcpyNodeSetParamsFromSymbol

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.

hipGraphReleaseUserObject

hipError_t hipGraphReleaseUserObject(hipGraph_t graph, hipUserObject_t object, unsigned int count)

Release user object from graphs.

hipDrvGraphAddMemcpyNode

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.

hipGraphRemoveDependencies

hipError_t hipGraphRemoveDependencies(hipGraph_t graph, const hipGraphNode_t *from, const hipGraphNode_t *to, size_t numDependencies)

Removes dependency edges from a graph.

hipGraphMemcpyNodeSetParams1D

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.

hipGraphExecMemcpyNodeSetParams1D

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.

hipGraphExecDestroy

hipError_t hipGraphExecDestroy(hipGraphExec_t graphExec)

Destroys an executable graph.

hipGraphAddExternalSemaphoresSignalNode

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.

hipGraphExecExternalSemaphoresWaitNodeSetParams

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.

hipGraphExecHostNodeSetParams

hipError_t hipGraphExecHostNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node, const hipHostNodeParams *pNodeParams)

Sets the parameters for a host node in the given graphExec.

hipGraphExecChildGraphNodeSetParams

hipError_t hipGraphExecChildGraphNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node, hipGraph_t childGraph)

Updates node parameters in the child graph node in the given graphExec.

hipStreamGetCaptureInfo

hipError_t hipStreamGetCaptureInfo(hipStream_t stream, hipStreamCaptureStatus *pCaptureStatus, unsigned long long *pId)

Get capture status of a stream.

hipGraphAddDependencies

hipError_t hipGraphAddDependencies(hipGraph_t graph, const hipGraphNode_t *from, const hipGraphNode_t *to, size_t numDependencies)

Adds dependency edges to a graph.

hipDrvGraphExecMemsetNodeSetParams

hipError_t hipDrvGraphExecMemsetNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, const HIP_MEMSET_NODE_PARAMS *memsetParams, hipCtx_t ctx)

Sets the parameters for a memset node in the given graphExec.

hipDrvGraphAddMemFreeNode

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.

hipGraphExecKernelNodeSetParams

hipError_t hipGraphExecKernelNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node, const hipKernelNodeParams *pNodeParams)

Sets the parameters for a kernel node in the given graphExec.

hipGraphNodeGetDependentNodes

hipError_t hipGraphNodeGetDependentNodes(hipGraphNode_t node, hipGraphNode_t *pDependentNodes, size_t *pNumDependentNodes)

Returns a node's dependent nodes.

hipDeviceGetGraphMemAttribute

hipError_t hipDeviceGetGraphMemAttribute(int device, hipGraphMemAttributeType attr, void *value)

Get the mem attribute for graphs.

hipGraphHostNodeGetParams

hipError_t hipGraphHostNodeGetParams(hipGraphNode_t node, hipHostNodeParams *pNodeParams)

Returns a host node's parameters.

hipGraphInstantiateWithFlags

hipError_t hipGraphInstantiateWithFlags(hipGraphExec_t *pGraphExec, hipGraph_t graph, unsigned long long flags)

Creates an executable graph from a graph.

hipGraphExternalSemaphoresSignalNodeGetParams

hipError_t hipGraphExternalSemaphoresSignalNodeGetParams(hipGraphNode_t hNode, hipExternalSemaphoreSignalNodeParams *params_out)

Returns external semaphore signal node params.

hipGraphUpload

hipError_t hipGraphUpload(hipGraphExec_t graphExec, hipStream_t stream)

uploads an executable graph in a stream

hipGraphExecExternalSemaphoresSignalNodeSetParams

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.

hipGraphExecMemcpyNodeSetParamsToSymbol

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.

hipUserObjectRelease

hipError_t hipUserObjectRelease(hipUserObject_t object, unsigned int count)

Release number of references to resource.

hipGraphKernelNodeGetParams

hipError_t hipGraphKernelNodeGetParams(hipGraphNode_t node, hipKernelNodeParams *pNodeParams)

Gets kernel node's parameters.

hipGraphAddMemcpyNodeFromSymbol

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.

hipGraphKernelNodeCopyAttributes

hipError_t hipGraphKernelNodeCopyAttributes(hipGraphNode_t hSrc, hipGraphNode_t hDst)

Copies attributes from source node to destination node.

hipGraphAddMemFreeNode

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.

hipDrvGraphMemcpyNodeSetParams

hipError_t hipDrvGraphMemcpyNodeSetParams(hipGraphNode_t hNode, const HIP_MEMCPY3D *nodeParams)

Sets a memcpy node's parameters.

hipGraphMemcpyNodeGetParams

hipError_t hipGraphMemcpyNodeGetParams(hipGraphNode_t node, hipMemcpy3DParms *pNodeParams)

Gets a memcpy node's parameters.

hipGraphNodeSetParams

hipError_t hipGraphNodeSetParams(hipGraphNode_t node, hipGraphNodeParams *nodeParams)

Updates parameters of a created node.

hipGraphAddEventRecordNode

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.

hipDrvGraphExecMemcpyNodeSetParams

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.

hipStreamBeginCapture

hipError_t hipStreamBeginCapture(hipStream_t stream, hipStreamCaptureMode mode)

Begins graph capture on a stream.

hipStreamEndCapture

hipError_t hipStreamEndCapture(hipStream_t stream, hipGraph_t *pGraph)

Ends capture on a stream, returning the captured graph.

hipGraphExecGetFlags

hipError_t hipGraphExecGetFlags(hipGraphExec_t graphExec, unsigned long long *flags)

Return the flags on executable graph.

hipUserObjectRetain

hipError_t hipUserObjectRetain(hipUserObject_t object, unsigned int count)

Retain number of references to resource.

hipGraphNodeGetType

hipError_t hipGraphNodeGetType(hipGraphNode_t node, hipGraphNodeType *pType)

Returns a node's type.

hipGraphNodeSetEnabled

hipError_t hipGraphNodeSetEnabled(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, unsigned int isEnabled)

Enables or disables the specified node in the given graphExec.

hipGraphExecMemcpyNodeSetParams

hipError_t hipGraphExecMemcpyNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node, hipMemcpy3DParms *pNodeParams)

Sets the parameters for a memcpy node in the given graphExec.

hipGraphExecNodeSetParams

hipError_t hipGraphExecNodeSetParams(hipGraphExec_t graphExec, hipGraphNode_t node, hipGraphNodeParams *nodeParams)

Updates parameters of a created node on executable graph.

hipGraphHostNodeSetParams

hipError_t hipGraphHostNodeSetParams(hipGraphNode_t node, const hipHostNodeParams *pNodeParams)

Sets a host node's parameters.

hipGraphMemAllocNodeGetParams

hipError_t hipGraphMemAllocNodeGetParams(hipGraphNode_t node, hipMemAllocNodeParams *pNodeParams)

Returns parameters for memory allocation node.

hipGraphInstantiateWithParams

hipError_t hipGraphInstantiateWithParams(hipGraphExec_t *pGraphExec, hipGraph_t graph, hipGraphInstantiateParams *instantiateParams)

Creates an executable graph from a graph.

hipGraphExecEventRecordNodeSetEvent

hipError_t hipGraphExecEventRecordNodeSetEvent(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, hipEvent_t event)

Sets the event for an event record node in the given graphExec.

hipGraphExternalSemaphoresWaitNodeSetParams

hipError_t hipGraphExternalSemaphoresWaitNodeSetParams(hipGraphNode_t hNode, const hipExternalSemaphoreWaitNodeParams *nodeParams)

Updates node parameters in the external semaphore wait node.

hipGraphMemsetNodeGetParams

hipError_t hipGraphMemsetNodeGetParams(hipGraphNode_t node, hipMemsetParams *pNodeParams)

Gets a memset node's parameters.

hipGraphChildGraphNodeGetGraph

hipError_t hipGraphChildGraphNodeGetGraph(hipGraphNode_t node, hipGraph_t *pGraph)

Gets a handle to the embedded graph of a child graph node.

hipGraphKernelNodeGetAttribute

hipError_t hipGraphKernelNodeGetAttribute(hipGraphNode_t hNode, hipKernelNodeAttrID attr, hipKernelNodeAttrValue *value)

Gets a node attribute.

hipThreadExchangeStreamCaptureMode

hipError_t hipThreadExchangeStreamCaptureMode(hipStreamCaptureMode *mode)

Swaps the stream capture mode of a thread.

hipGraphLaunch

hipError_t hipGraphLaunch(hipGraphExec_t graphExec, hipStream_t stream)

launches an executable graph in a stream

hipGraphDebugDotPrint

hipError_t hipGraphDebugDotPrint(hipGraph_t graph, const char *path, unsigned int flags)

Write a DOT file describing graph structure.

hipGraphExecMemsetNodeSetParams

hipError_t hipGraphExecMemsetNodeSetParams(hipGraphExec_t hGraphExec, hipGraphNode_t node, const hipMemsetParams *pNodeParams)

Sets the parameters for a memset node in the given graphExec.

hipGraphGetEdges

hipError_t hipGraphGetEdges(hipGraph_t graph, hipGraphNode_t *from, hipGraphNode_t *to, size_t *numEdges)

Returns a graph's dependency edges.

hipGraphAddKernelNode

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.

hipGraphExecEventWaitNodeSetEvent

hipError_t hipGraphExecEventWaitNodeSetEvent(hipGraphExec_t hGraphExec, hipGraphNode_t hNode, hipEvent_t event)

Sets the event for an event record node in the given graphExec.

hipStreamGetCaptureInfo_v2

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.

hipGraphAddExternalSemaphoresWaitNode

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.

hipGraphEventWaitNodeSetEvent

hipError_t hipGraphEventWaitNodeSetEvent(hipGraphNode_t node, hipEvent_t event)

Sets an event wait node's event.

hipGraphEventRecordNodeSetEvent

hipError_t hipGraphEventRecordNodeSetEvent(hipGraphNode_t node, hipEvent_t event)

Sets an event record node's event.

hipGraphEventWaitNodeGetEvent

hipError_t hipGraphEventWaitNodeGetEvent(hipGraphNode_t node, hipEvent_t *event_out)

Returns the event associated with an event wait node.

hipGraphKernelNodeSetAttribute

hipError_t hipGraphKernelNodeSetAttribute(hipGraphNode_t hNode, hipKernelNodeAttrID attr, const hipKernelNodeAttrValue *value)

Sets a node attribute.

hipGraphMemsetNodeSetParams

hipError_t hipGraphMemsetNodeSetParams(hipGraphNode_t node, const hipMemsetParams *pNodeParams)

Sets a memset node's parameters.

hipGraphEventRecordNodeGetEvent

hipError_t hipGraphEventRecordNodeGetEvent(hipGraphNode_t node, hipEvent_t *event_out)

Returns the event associated with an event record node.

hipGraphAddEmptyNode

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.

hipGraphAddMemcpyNodeToSymbol

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.

hipGraphDestroy

hipError_t hipGraphDestroy(hipGraph_t graph)

Destroys a graph.

hipGraphRetainUserObject

hipError_t hipGraphRetainUserObject(hipGraph_t graph, hipUserObject_t object, unsigned int count, unsigned int flags)

Retain user object for graphs.

hipGraphExecMemcpyNodeSetParamsFromSymbol

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.

hipGraphAddMemAllocNode

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.

hipGraphAddHostNode

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.

hipGraphAddNode

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.

hipGraphGetNodes

hipError_t hipGraphGetNodes(hipGraph_t graph, hipGraphNode_t *nodes, size_t *numNodes)

Returns graph nodes.

hipGraphAddMemsetNode

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.

hipStreamUpdateCaptureDependencies

hipError_t hipStreamUpdateCaptureDependencies(hipStream_t stream, hipGraphNode_t *dependencies, size_t numDependencies, unsigned int flags)

Update the set of dependencies in a capturing stream.

hipGraphInstantiate

hipError_t hipGraphInstantiate(hipGraphExec_t *pGraphExec, hipGraph_t graph, hipGraphNode_t *pErrorNode, char *pLogBuffer, size_t bufferSize)

Creates an executable graph from a graph.

hipDeviceGraphMemTrim

hipError_t hipDeviceGraphMemTrim(int device)

Free unused memory on specific device used for graph back to OS.

hipGraphExternalSemaphoresWaitNodeGetParams

hipError_t hipGraphExternalSemaphoresWaitNodeGetParams(hipGraphNode_t hNode, hipExternalSemaphoreWaitNodeParams *params_out)

Returns external semaphore wait node params.

hipGraphClone

hipError_t hipGraphClone(hipGraph_t *pGraphClone, hipGraph_t originalGraph)

Clones a graph.

hipDrvGraphAddMemsetNode

hipError_t hipDrvGraphAddMemsetNode(hipGraphNode_t *phGraphNode, hipGraph_t hGraph, const hipGraphNode_t *dependencies, size_t numDependencies, const HIP_MEMSET_NODE_PARAMS *memsetParams, hipCtx_t ctx)

Creates a memset node and adds it to a graph.

hipGraphGetRootNodes

hipError_t hipGraphGetRootNodes(hipGraph_t graph, hipGraphNode_t *pRootNodes, size_t *pNumRootNodes)

Returns graph's root nodes.

hipGraphAddMemcpyNode

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.

hipHostAlloc

hipError_t hipHostAlloc(void **ptr, size_t size, unsigned int flags)

Allocate device accessible page locked host memory [Deprecated].

hipMemsetD8Async

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...

hipFreeHost

hipError_t hipFreeHost(void *ptr)

Free memory allocated by the hcc hip host memory allocation API [Deprecated].

hipMemset2DAsync

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.

hipHostFree

hipError_t hipHostFree(void *ptr)

Free memory allocated by the hcc hip host memory allocation API This API performs an implicit hipDevi...

hipMemGetInfo

hipError_t hipMemGetInfo(size_t *free, size_t *total)

Query memory info.

hipExtMallocWithFlags

hipError_t hipExtMallocWithFlags(void **ptr, size_t sizeBytes, unsigned int flags)

Allocate memory on the default accelerator.

hipMemcpy3D

hipError_t hipMemcpy3D(const struct hipMemcpy3DParms *p)

Copies data between host and device.

hipMalloc3DArray

hipError_t hipMalloc3DArray(hipArray_t *array, const struct hipChannelFormatDesc *desc, struct hipExtent extent, unsigned int flags)

Allocate an array on the device.

hipArrayCreate

hipError_t hipArrayCreate(hipArray_t *pHandle, const HIP_ARRAY_DESCRIPTOR *pAllocateArray)

Create an array memory pointer on the device.

hipMemset3D

hipError_t hipMemset3D(hipPitchedPtr pitchedDevPtr, int value, hipExtent extent)

Fills synchronously the memory area pointed to by pitchedDevPtr with the constant value.

hipModuleGetGlobal

hipError_t hipModuleGetGlobal(hipDeviceptr_t *dptr, size_t *bytes, hipModule_t hmod, const char *name)

Returns a global pointer from a module. Returns in *dptr and *bytes the pointer and size of the globa...

hipMemsetD16

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...

hipMalloc

hipError_t hipMalloc(void **ptr, size_t size)

Allocate memory on the default accelerator.

hipHostUnregister

hipError_t hipHostUnregister(void *hostPtr)

Un-register host pointer.

hipHostGetFlags

hipError_t hipHostGetFlags(unsigned int *flagsPtr, void *hostPtr)

Return flags associated with host pointer.

hipMemcpyFromSymbolAsync

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.

hipMemsetD32

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...

hipMemset3DAsync

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.

hipMemcpyFromSymbol

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.

hipDrvMemcpy3DAsync

hipError_t hipDrvMemcpy3DAsync(const HIP_MEMCPY3D *pCopy, hipStream_t stream)

Copies data between host and device asynchronously.

hipMallocHost

hipError_t hipMallocHost(void **ptr, size_t size)

Allocate pinned host memory [Deprecated].

hipArray3DGetDescriptor

hipError_t hipArray3DGetDescriptor(HIP_ARRAY3D_DESCRIPTOR *pArrayDescriptor, hipArray_t array)

Gets a 3D array descriptor.

hipMemcpy2DAsync

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.

hipArrayGetDescriptor

hipError_t hipArrayGetDescriptor(HIP_ARRAY_DESCRIPTOR *pArrayDescriptor, hipArray_t array)

Gets a 1D or 2D array descriptor.

hipFree

hipError_t hipFree(void *ptr)

Free memory allocated by the hcc hip memory allocation API. This API performs an implicit hipDeviceSy...

hipMemsetD16Async

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...

hipGetProcAddress

hipError_t hipGetProcAddress(const char *symbol, void **pfn, int hipVersion, uint64_t flags, hipDriverProcAddressQueryResult *symbolStatus)

Gets the symbol's function address.

hipPointerGetAttributes

hipError_t hipPointerGetAttributes(hipPointerAttribute_t *attributes, const void *ptr)

Return attributes for the specified pointer.

hipMallocPitch

hipError_t hipMallocPitch(void **ptr, size_t *pitch, size_t width, size_t height)

hipMemcpyDtoD

hipError_t hipMemcpyDtoD(hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes)

Copy data from Device to Device.

hipMemcpyToArray

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.

hipMallocArray

hipError_t hipMallocArray(hipArray_t *array, const hipChannelFormatDesc *desc, size_t width, size_t height, unsigned int flags)

Allocate an array on the device.

hipMemcpy2D

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.

hipMemcpyFromArray

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.

hipHostGetDevicePointer

hipError_t hipHostGetDevicePointer(void **devPtr, void *hstPtr, unsigned int flags)

Get Device pointer from Host Pointer allocated through hipHostMalloc.

hipMemcpy2DFromArrayAsync

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.

hipMemcpy2DFromArray

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.

hipMemcpy3DAsync

hipError_t hipMemcpy3DAsync(const struct hipMemcpy3DParms *p, hipStream_t stream)

Copies data between host and device asynchronously.

hipArray3DCreate

hipError_t hipArray3DCreate(hipArray_t *array, const HIP_ARRAY3D_DESCRIPTOR *pAllocateArray)

Create a 3D array memory pointer on the device.

hipArrayGetInfo

hipError_t hipArrayGetInfo(hipChannelFormatDesc *desc, hipExtent *extent, unsigned int *flags, hipArray_t array)

Gets info about the specified array.

hipDrvMemcpy3D

hipError_t hipDrvMemcpy3D(const HIP_MEMCPY3D *pCopy)

Copies data between host and device.

hipMemcpyHtoD

hipError_t hipMemcpyHtoD(hipDeviceptr_t dst, void *src, size_t sizeBytes)

Copy data from Host to Device.

hipMemcpyParam2D

hipError_t hipMemcpyParam2D(const hip_Memcpy2D *pCopy)

Copies memory for 2D arrays.

hipMemcpyHtoA

hipError_t hipMemcpyHtoA(hipArray_t dstArray, size_t dstOffset, const void *srcHost, size_t count)

Copies data between host and device.

hipMemcpyToSymbolAsync

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.

hipHostMalloc

hipError_t hipHostMalloc(void **ptr, size_t size, unsigned int flags)

Allocates device accessible page locked (pinned) host memory.

hipMemcpy2DToArrayAsync

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.

hipHostRegister

hipError_t hipHostRegister(void *hostPtr, size_t sizeBytes, unsigned int flags)

Register host memory so it can be accessed from the current device.

hipMemcpyAtoH

hipError_t hipMemcpyAtoH(void *dst, hipArray_t srcArray, size_t srcOffset, size_t count)

Copies data between host and device.

hipMemcpyToSymbol

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...

hipMemcpy

hipError_t hipMemcpy(void *dst, const void *src, size_t sizeBytes, hipMemcpyKind kind)

Copy data from src to dst.

hipMemset

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...

hipMemcpy2DToArray

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.

hipMemcpyParam2DAsync

hipError_t hipMemcpyParam2DAsync(const hip_Memcpy2D *pCopy, hipStream_t stream)

Copies memory for 2D arrays.

hipDrvPointerGetAttributes

hipError_t hipDrvPointerGetAttributes(unsigned int numAttributes, hipPointer_attribute *attributes, void **data, hipDeviceptr_t ptr)

Returns information about the specified pointer.[BETA].

hipMalloc3D

hipError_t hipMalloc3D(hipPitchedPtr *pitchedDevPtr, hipExtent extent)

Create a 3D memory pointer on the device.

hipPointerSetAttribute

hipError_t hipPointerSetAttribute(const void *value, hipPointer_attribute attribute, hipDeviceptr_t ptr)

Sets information on the specified pointer.[BETA].

hipMemcpyDtoDAsync

hipError_t hipMemcpyDtoDAsync(hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream)

Copy data from Device to Device asynchronously.

hipMemAllocPitch

hipError_t hipMemAllocPitch(hipDeviceptr_t *dptr, size_t *pitch, size_t widthInBytes, size_t height, unsigned int elementSizeBytes)

hipMemsetD8

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...

hipMemcpyAsync

hipError_t hipMemcpyAsync(void *dst, const void *src, size_t sizeBytes, hipMemcpyKind kind, hipStream_t stream)

Copy data from src to dst asynchronously.

hipMemcpyDtoHAsync

hipError_t hipMemcpyDtoHAsync(void *dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream)

Copy data from Device to Host asynchronously.

hipFreeArray

hipError_t hipFreeArray(hipArray_t array)

Frees an array on the device.

hipMemsetD32Async

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...

hipMemset2D

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.

hipMemcpyHtoDAsync

hipError_t hipMemcpyHtoDAsync(hipDeviceptr_t dst, void *src, size_t sizeBytes, hipStream_t stream)

Copy data from Host to Device asynchronously.

hipGetSymbolSize

hipError_t hipGetSymbolSize(size_t *size, const void *symbol)

Gets the size of the given symbol on the device.

hipMemcpyDtoH

hipError_t hipMemcpyDtoH(void *dst, hipDeviceptr_t src, size_t sizeBytes)

Copy data from Device to Host.

hipMemsetAsync

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...

hipMemcpyWithStream

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...

hipGetSymbolAddress

hipError_t hipGetSymbolAddress(void **devPtr, const void *symbol)

Gets device pointer associated with symbol on the device.

hipMemAllocHost

hipError_t hipMemAllocHost(void **ptr, size_t size)

Allocate pinned host memory [Deprecated].

hipPointerGetAttribute

hipError_t hipPointerGetAttribute(void *data, hipPointer_attribute attribute, hipDeviceptr_t ptr)

Returns information about the specified pointer.[BETA].

hipMemPtrGetInfo

hipError_t hipMemPtrGetInfo(void *ptr, size_t *size)

Get allocated memory size via memory pointer.

hipArrayDestroy

hipError_t hipArrayDestroy(hipArray_t array)

Destroy an array memory pointer on the device.

hipMemPrefetchAsync

hipError_t hipMemPrefetchAsync(const void *dev_ptr, size_t count, int device, hipStream_t stream)

Prefetches memory to the specified destination device using HIP.

hipMemRangeGetAttributes

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.

hipMemAdvise

hipError_t hipMemAdvise(const void *dev_ptr, size_t count, hipMemoryAdvise advice, int device)

Advise about the usage of a given memory range to HIP.

hipMemRangeGetAttribute

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.

hipMallocManaged

hipError_t hipMallocManaged(void **dev_ptr, size_t size, unsigned int flags)

Allocates memory that will be automatically managed by HIP.

hipStreamAttachMemAsync

hipError_t hipStreamAttachMemAsync(hipStream_t stream, void *dev_ptr, size_t length, unsigned int flags)

Attach memory to a stream asynchronously in HIP.

hipModuleLaunchCooperativeKernelMultiDevice

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...

hipFuncGetAttributes

hipError_t hipFuncGetAttributes(struct hipFuncAttributes *attr, const void *func)

Find out attributes for a given function.

hipModuleGetTexRef

hipError_t hipModuleGetTexRef(textureReference **texRef, hipModule_t hmod, const char *name)

returns the handle of the texture reference with the name from the module.

hipExtLaunchMultiKernelMultiDevice

hipError_t hipExtLaunchMultiKernelMultiDevice(hipLaunchParams *launchParamsList, int numDevices, unsigned int flags)

Launches kernels on multiple devices and guarantees all specified kernels are dispatched on respectiv...

hipModuleLaunchKernel

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...

hipModuleLoad

hipError_t hipModuleLoad(hipModule_t *module, const char *fname)

Loads code object from file into a module the currrent context.

hipModuleLoadDataEx

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....

hipFuncGetAttribute

hipError_t hipFuncGetAttribute(int *value, hipFunction_attribute attrib, hipFunction_t hfunc)

Find out a specific attribute for a given function.

hipLaunchCooperativeKernelMultiDevice

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...

hipModuleLaunchCooperativeKernel

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...

hipModuleGetFunction

hipError_t hipModuleGetFunction(hipFunction_t *function, hipModule_t module, const char *kname)

Function with kname will be extracted if present in module.

hipLaunchCooperativeKernel

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...

hipModuleLoadData

hipError_t hipModuleLoadData(hipModule_t *module, const void *image)

builds module from code object which resides in host memory. Image is pointer to that location.

hipModuleUnload

hipError_t hipModuleUnload(hipModule_t module)

Frees the module.

hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags

hipError_t hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int *numBlocks, const void *f, int blockSize, size_t dynSharedMemPerBlk, unsigned int flags)

Returns occupancy for a device function.

hipModuleOccupancyMaxPotentialBlockSize

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

hipOccupancyMaxActiveBlocksPerMultiprocessor

hipError_t hipOccupancyMaxActiveBlocksPerMultiprocessor(int *numBlocks, const void *f, int blockSize, size_t dynSharedMemPerBlk)

Returns occupancy for a device function.

hipOccupancyMaxPotentialBlockSize

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

hipModuleOccupancyMaxActiveBlocksPerMultiprocessor

hipError_t hipModuleOccupancyMaxActiveBlocksPerMultiprocessor(int *numBlocks, hipFunction_t f, int blockSize, size_t dynSharedMemPerBlk)

Returns occupancy for a device function.

hipModuleOccupancyMaxActiveBlocksPerMultiprocessorWithFlags

hipError_t hipModuleOccupancyMaxActiveBlocksPerMultiprocessorWithFlags(int *numBlocks, hipFunction_t f, int blockSize, size_t dynSharedMemPerBlk, unsigned int flags)

Returns occupancy for a device function.

hipModuleOccupancyMaxPotentialBlockSizeWithFlags

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

hipDeviceCanAccessPeer

hipError_t hipDeviceCanAccessPeer(int *canAccessPeer, int deviceId, int peerDeviceId)

Determine if a device can access a peer's memory.

hipDeviceEnablePeerAccess

hipError_t hipDeviceEnablePeerAccess(int peerDeviceId, unsigned int flags)

Enable direct access from current device's virtual address space to memory allocations physically loc...

hipDeviceDisablePeerAccess

hipError_t hipDeviceDisablePeerAccess(int peerDeviceId)

Disable direct access from current device's virtual address space to memory allocations physically lo...

hipMemGetAddressRange

hipError_t hipMemGetAddressRange(hipDeviceptr_t *pbase, size_t *psize, hipDeviceptr_t dptr)

Get information on memory allocations.

hipProfilerStart

hipError_t hipProfilerStart()

Start recording of profiling information When using this API, start the profiler with profiling disab...

hipProfilerStop

hipError_t hipProfilerStop()

Stop recording of profiling information. When using this API, start the profiler with profiling disab...

hipDeviceGetStreamPriorityRange

hipError_t hipDeviceGetStreamPriorityRange(int *leastPriority, int *greatestPriority)

Returns numerical values that correspond to the least and greatest stream priority.

hipStreamDestroy

hipError_t hipStreamDestroy(hipStream_t stream)

Destroys the specified stream.

hipStreamGetFlags

hipError_t hipStreamGetFlags(hipStream_t stream, unsigned int *flags)

Return flags associated with this stream.

hipStreamAddCallback

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...

hipStreamCallback_t

void(* hipStreamCallback_t)(hipStream_t stream, hipError_t status, void *userData)

Definition hip_runtime_api.h:2525

hipStreamGetDevice

hipError_t hipStreamGetDevice(hipStream_t stream, hipDevice_t *device)

Get the device assocaited with the stream.

hipStreamQuery

hipError_t hipStreamQuery(hipStream_t stream)

Return hipSuccess if all of the operations in the specified stream have completed,...

hipStreamSynchronize

hipError_t hipStreamSynchronize(hipStream_t stream)

Wait for all commands in stream to complete.

hipStreamWaitEvent

hipError_t hipStreamWaitEvent(hipStream_t stream, hipEvent_t event, unsigned int flags)

Make the specified compute stream wait for an event.

hipStreamCreateWithPriority

hipError_t hipStreamCreateWithPriority(hipStream_t *stream, unsigned int flags, int priority)

Create an asynchronous stream with the specified priority.

hipExtStreamCreateWithCUMask

hipError_t hipExtStreamCreateWithCUMask(hipStream_t *stream, uint32_t cuMaskSize, const uint32_t *cuMask)

Create an asynchronous stream with the specified CU mask.

hipStreamGetPriority

hipError_t hipStreamGetPriority(hipStream_t stream, int *priority)

Query the priority of a stream.

hipExtStreamGetCUMask

hipError_t hipExtStreamGetCUMask(hipStream_t stream, uint32_t cuMaskSize, uint32_t *cuMask)

Get CU mask associated with an asynchronous stream.

hipStreamCreateWithFlags

hipError_t hipStreamCreateWithFlags(hipStream_t *stream, unsigned int flags)

Create an asynchronous stream.

hipStreamCreate

hipError_t hipStreamCreate(hipStream_t *stream)

Create an asynchronous stream.

hipStreamWriteValue64

hipError_t hipStreamWriteValue64(hipStream_t stream, void *ptr, uint64_t value, unsigned int flags)

Enqueues a write command to the stream.[BETA].

hipStreamWriteValue32

hipError_t hipStreamWriteValue32(hipStream_t stream, void *ptr, uint32_t value, unsigned int flags)

Enqueues a write command to the stream.[BETA].

hipStreamWaitValue64

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].

hipStreamWaitValue32

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].

hipMemPoolImportPointer

hipError_t hipMemPoolImportPointer(void **dev_ptr, hipMemPool_t mem_pool, hipMemPoolPtrExportData *export_data)

Import a memory pool allocation from another process.

hipMemPoolImportFromShareableHandle

hipError_t hipMemPoolImportFromShareableHandle(hipMemPool_t *mem_pool, void *shared_handle, hipMemAllocationHandleType handle_type, unsigned int flags)

Imports a memory pool from a shared handle.

hipMallocFromPoolAsync

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.

hipFreeAsync

hipError_t hipFreeAsync(void *dev_ptr, hipStream_t stream)

Frees memory with stream ordered semantics.

hipMemPoolTrimTo

hipError_t hipMemPoolTrimTo(hipMemPool_t mem_pool, size_t min_bytes_to_hold)

Releases freed memory back to the OS.

hipMemPoolCreate

hipError_t hipMemPoolCreate(hipMemPool_t *mem_pool, const hipMemPoolProps *pool_props)

Creates a memory pool.

hipMemPoolSetAccess

hipError_t hipMemPoolSetAccess(hipMemPool_t mem_pool, const hipMemAccessDesc *desc_list, size_t count)

Controls visibility of the specified pool between devices.

hipMemPoolDestroy

hipError_t hipMemPoolDestroy(hipMemPool_t mem_pool)

Destroys the specified memory pool.

hipMemPoolSetAttribute

hipError_t hipMemPoolSetAttribute(hipMemPool_t mem_pool, hipMemPoolAttr attr, void *value)

Sets attributes of a memory pool.

hipMemPoolGetAttribute

hipError_t hipMemPoolGetAttribute(hipMemPool_t mem_pool, hipMemPoolAttr attr, void *value)

Gets attributes of a memory pool.

hipMemPoolExportToShareableHandle

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.

hipMemPoolExportPointer

hipError_t hipMemPoolExportPointer(hipMemPoolPtrExportData *export_data, void *dev_ptr)

Export data to share a memory pool allocation between processes.

hipMallocAsync

hipError_t hipMallocAsync(void **dev_ptr, size_t size, hipStream_t stream)

Allocates memory with stream ordered semantics.

hipMemPoolGetAccess

hipError_t hipMemPoolGetAccess(hipMemAccessFlags *flags, hipMemPool_t mem_pool, hipMemLocation *location)

Returns the accessibility of a pool from a device.

hipDestroySurfaceObject

hipError_t hipDestroySurfaceObject(hipSurfaceObject_t surfaceObject)

Destroy a surface object.

hipCreateSurfaceObject

hipError_t hipCreateSurfaceObject(hipSurfaceObject_t *pSurfObject, const hipResourceDesc *pResDesc)

Create a surface object.

hipTexRefGetFilterMode

hipError_t hipTexRefGetFilterMode(enum hipTextureFilterMode *pfm, const textureReference *texRef)

Gets filter mode for a texture reference.

hipBindTextureToMipmappedArray

hipError_t hipBindTextureToMipmappedArray(const textureReference *tex, hipMipmappedArray_const_t mipmappedArray, const hipChannelFormatDesc *desc)

Binds a mipmapped array to a texture.

hipTexRefGetMipmapLevelClamp

hipError_t hipTexRefGetMipmapLevelClamp(float *pminMipmapLevelClamp, float *pmaxMipmapLevelClamp, const textureReference *texRef)

Gets the minimum and maximum mipmap level clamps for a texture reference.

hipTexRefGetAddressMode

hipError_t hipTexRefGetAddressMode(enum hipTextureAddressMode *pam, const textureReference *texRef, int dim)

Gets the address mode for a texture reference.

hipTexRefGetFlags

hipError_t hipTexRefGetFlags(unsigned int *pFlags, const textureReference *texRef)

Gets flags for a texture reference.

hipTexRefSetAddress

hipError_t hipTexRefSetAddress(size_t *ByteOffset, textureReference *texRef, hipDeviceptr_t dptr, size_t bytes)

Sets an bound address for a texture reference.

hipTexRefSetFilterMode

hipError_t hipTexRefSetFilterMode(textureReference *texRef, enum hipTextureFilterMode fm)

Set filter mode for a texture reference.

hipTexRefSetMipmappedArray

hipError_t hipTexRefSetMipmappedArray(textureReference *texRef, struct hipMipmappedArray *mipmappedArray, unsigned int Flags)

Binds mipmapped array to a texture reference.

hipTexRefGetMipmapFilterMode

hipError_t hipTexRefGetMipmapFilterMode(enum hipTextureFilterMode *pfm, const textureReference *texRef)

Gets the mipmap filter mode for a texture reference.

hipGetTextureAlignmentOffset

hipError_t hipGetTextureAlignmentOffset(size_t *offset, const textureReference *texref)

Get the offset of the alignment in a texture.

hipBindTexture2D

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.

hipTexRefGetMaxAnisotropy

hipError_t hipTexRefGetMaxAnisotropy(int *pmaxAnsio, const textureReference *texRef)

Gets the maximum anisotropy for a texture reference.

hipBindTexture

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.

hipUnbindTexture

hipError_t hipUnbindTexture(const textureReference *tex)

Unbinds a texture.

hipTexRefSetFormat

hipError_t hipTexRefSetFormat(textureReference *texRef, hipArray_Format fmt, int NumPackedComponents)

Set format for a texture reference.

hipTexRefGetAddress

hipError_t hipTexRefGetAddress(hipDeviceptr_t *dev_ptr, const textureReference *texRef)

Gets the the address for a texture reference.

hipTexRefSetFlags

hipError_t hipTexRefSetFlags(textureReference *texRef, unsigned int Flags)

Set flags for a texture reference.

hipTexRefSetAddressMode

hipError_t hipTexRefSetAddressMode(textureReference *texRef, int dim, enum hipTextureAddressMode am)

Sets address mode for a texture reference.

hipTexRefGetMipMappedArray

hipError_t hipTexRefGetMipMappedArray(hipMipmappedArray_t *pArray, const textureReference *texRef)

Gets the mipmapped array bound to a texture reference.

hipTexRefSetMaxAnisotropy

hipError_t hipTexRefSetMaxAnisotropy(textureReference *texRef, unsigned int maxAniso)

Sets the maximum anisotropy for a texture reference.

hipTexRefSetMipmapLevelClamp

hipError_t hipTexRefSetMipmapLevelClamp(textureReference *texRef, float minMipMapLevelClamp, float maxMipMapLevelClamp)

Sets mipmap level clamp for a texture reference.

hipTexRefSetBorderColor

hipError_t hipTexRefSetBorderColor(textureReference *texRef, float *pBorderColor)

Sets border color for a texture reference.

hipTexRefSetArray

hipError_t hipTexRefSetArray(textureReference *tex, hipArray_const_t array, unsigned int flags)

Binds an array as a texture reference.

hipTexRefSetMipmapLevelBias

hipError_t hipTexRefSetMipmapLevelBias(textureReference *texRef, float bias)

Sets mipmap level bias for a texture reference.

hipTexRefGetMipmapLevelBias

hipError_t hipTexRefGetMipmapLevelBias(float *pbias, const textureReference *texRef)

Gets the mipmap level bias for a texture reference.

hipBindTextureToArray

hipError_t hipBindTextureToArray(const textureReference *tex, hipArray_const_t array, const hipChannelFormatDesc *desc)

Binds a memory area to a texture.

hipGetTextureReference

hipError_t hipGetTextureReference(const textureReference **texref, const void *symbol)

Gets the texture reference related with the symbol.

hipTexRefSetAddress2D

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.

hipTexRefSetMipmapFilterMode

hipError_t hipTexRefSetMipmapFilterMode(textureReference *texRef, enum hipTextureFilterMode fm)

Sets mipmap filter mode for a texture reference.

hipTexRefGetFormat

hipError_t hipTexRefGetFormat(hipArray_Format *pFormat, int *pNumChannels, const textureReference *texRef)

Gets texture format for a texture reference.

hipFreeMipmappedArray

hipError_t hipFreeMipmappedArray(hipMipmappedArray_t mipmappedArray)

Frees a mipmapped array on the device.

hipGetMipmappedArrayLevel

hipError_t hipGetMipmappedArrayLevel(hipArray_t *levelArray, hipMipmappedArray_const_t mipmappedArray, unsigned int level)

Gets a mipmap level of a HIP mipmapped array.

hipMipmappedArrayGetLevel

hipError_t hipMipmappedArrayGetLevel(hipArray_t *pLevelArray, hipMipmappedArray_t hMipMappedArray, unsigned int level)

Get a mipmapped array on a mipmapped level.

hipMipmappedArrayDestroy

hipError_t hipMipmappedArrayDestroy(hipMipmappedArray_t hMipmappedArray)

Destroy a mipmapped array.

hipTexObjectCreate

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.

hipGetTextureObjectResourceDesc

hipError_t hipGetTextureObjectResourceDesc(hipResourceDesc *pResDesc, hipTextureObject_t textureObject)

Gets resource descriptor for the texture object.

hipGetTextureObjectResourceViewDesc

hipError_t hipGetTextureObjectResourceViewDesc(struct hipResourceViewDesc *pResViewDesc, hipTextureObject_t textureObject)

Gets resource view descriptor for the texture object.

hipTexObjectGetTextureDesc

hipError_t hipTexObjectGetTextureDesc(HIP_TEXTURE_DESC *pTexDesc, hipTextureObject_t texObject)

Gets texture descriptor of a texture object.

hipCreateTextureObject

hipError_t hipCreateTextureObject(hipTextureObject_t *pTexObject, const hipResourceDesc *pResDesc, const hipTextureDesc *pTexDesc, const struct hipResourceViewDesc *pResViewDesc)

Creates a texture object.

hipTexObjectDestroy

hipError_t hipTexObjectDestroy(hipTextureObject_t texObject)

Destroys a texture object.

hipMipmappedArrayCreate

hipError_t hipMipmappedArrayCreate(hipMipmappedArray_t *pHandle, HIP_ARRAY3D_DESCRIPTOR *pMipmappedArrayDesc, unsigned int numMipmapLevels)

Create a mipmapped array.

hipGetChannelDesc

hipError_t hipGetChannelDesc(hipChannelFormatDesc *desc, hipArray_const_t array)

Gets the channel descriptor in an array.

hipTexObjectGetResourceDesc

hipError_t hipTexObjectGetResourceDesc(HIP_RESOURCE_DESC *pResDesc, hipTextureObject_t texObject)

Gets resource descriptor of a texture object.

hipTexObjectGetResourceViewDesc

hipError_t hipTexObjectGetResourceViewDesc(HIP_RESOURCE_VIEW_DESC *pResViewDesc, hipTextureObject_t texObject)

Gets resource view descriptor of a texture object.

hipMallocMipmappedArray

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.

hipDestroyTextureObject

hipError_t hipDestroyTextureObject(hipTextureObject_t textureObject)

Destroys a texture object.

hipGetTextureObjectTextureDesc

hipError_t hipGetTextureObjectTextureDesc(hipTextureDesc *pTexDesc, hipTextureObject_t textureObject)

Gets texture descriptor for the texture object.

hipMemAddressFree

hipError_t hipMemAddressFree(void *devPtr, size_t size)

Frees an address range reservation made via hipMemAddressReserve.

hipMemExportToShareableHandle

hipError_t hipMemExportToShareableHandle(void *shareableHandle, hipMemGenericAllocationHandle_t handle, hipMemAllocationHandleType handleType, unsigned long long flags)

Exports an allocation to a requested shareable handle type.

hipMemGetAccess

hipError_t hipMemGetAccess(unsigned long long *flags, const hipMemLocation *location, void *ptr)

Get the access flags set for the given location and ptr.

hipMemSetAccess

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.

hipMemRelease

hipError_t hipMemRelease(hipMemGenericAllocationHandle_t handle)

Release a memory handle representing a memory allocation which was previously allocated through hipMe...

hipMemUnmap

hipError_t hipMemUnmap(void *ptr, size_t size)

Unmap memory allocation of a given address range.

hipMemGetAllocationGranularity

hipError_t hipMemGetAllocationGranularity(size_t *granularity, const hipMemAllocationProp *prop, hipMemAllocationGranularity_flags option)

Calculates either the minimal or recommended granularity.

hipMemRetainAllocationHandle

hipError_t hipMemRetainAllocationHandle(hipMemGenericAllocationHandle_t *handle, void *addr)

Returns the allocation handle of the backing memory allocation given the address.

hipMemCreate

hipError_t hipMemCreate(hipMemGenericAllocationHandle_t *handle, size_t size, const hipMemAllocationProp *prop, unsigned long long flags)

Creates a memory allocation described by the properties and size.

hipMemMap

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.

hipMemAddressReserve

hipError_t hipMemAddressReserve(void **ptr, size_t size, size_t alignment, void *addr, unsigned long long flags)

Reserves an address range.

hipMemGetAllocationPropertiesFromHandle

hipError_t hipMemGetAllocationPropertiesFromHandle(hipMemAllocationProp *prop, hipMemGenericAllocationHandle_t handle)

Retrieve the property structure of the given handle.

hipMemMapArrayAsync

hipError_t hipMemMapArrayAsync(hipArrayMapInfo *mapInfoList, unsigned int count, hipStream_t stream)

Maps or unmaps subregions of sparse HIP arrays and sparse HIP mipmapped arrays.

hipMemImportFromShareableHandle

hipError_t hipMemImportFromShareableHandle(hipMemGenericAllocationHandle_t *handle, void *osHandle, hipMemAllocationHandleType shHandleType)

Imports an allocation from a requested shareable handle type.

hip_common.h

hipErrorIllegalAddress

hipErrorIllegalAddress

Definition hip_runtime_api.h:346

hipErrorMemoryAllocation

hipErrorMemoryAllocation

Memory allocation error.

Definition hip_runtime_api.h:292

hipErrorNotFound

hipErrorNotFound

Not found.

Definition hip_runtime_api.h:341

hipErrorProfilerDisabled

hipErrorProfilerDisabled

Definition hip_runtime_api.h:297

hipErrorInvalidDevicePointer

hipErrorInvalidDevicePointer

Invalid Device Pointer.

Definition hip_runtime_api.h:304

hipErrorRuntimeMemory

hipErrorRuntimeMemory

Definition hip_runtime_api.h:395

hipErrorInvalidImage

hipErrorInvalidImage

Invalid image.

Definition hip_runtime_api.h:312

hipErrorPeerAccessUnsupported

hipErrorPeerAccessUnsupported

Definition hip_runtime_api.h:329

hipErrorArrayIsMapped

hipErrorArrayIsMapped

Definition hip_runtime_api.h:319

hipErrorStreamCaptureIsolation

hipErrorStreamCaptureIsolation

Definition hip_runtime_api.h:376

hipErrorInvalidKernelFile

hipErrorInvalidKernelFile

In CUDA DRV, it is CUDA_ERROR_INVALID_PTX.

Definition hip_runtime_api.h:330

hipErrorNotMapped

hipErrorNotMapped

Definition hip_runtime_api.h:323

hipErrorGraphExecUpdateFailure

hipErrorGraphExecUpdateFailure

Definition hip_runtime_api.h:389

hipErrorNotInitialized

hipErrorNotInitialized

Invalid not initialized.

Definition hip_runtime_api.h:293

hipErrorInvalidResourceHandle

hipErrorInvalidResourceHandle

Resource handle (hipEvent_t or hipStream_t) invalid.

Definition hip_runtime_api.h:339

hipErrorSharedObjectInitFailed

hipErrorSharedObjectInitFailed

Failed to initialize shared object.

Definition hip_runtime_api.h:335

hipErrorInvalidPitchValue

hipErrorInvalidPitchValue

Invalid pitch value.

Definition hip_runtime_api.h:302

hipErrorNoBinaryForGpu

hipErrorNoBinaryForGpu

Definition hip_runtime_api.h:321

hipErrorInvalidContext

hipErrorInvalidContext

Produced when input context is invalid.

Definition hip_runtime_api.h:313

hipErrorStreamCaptureUnsupported

hipErrorStreamCaptureUnsupported

Definition hip_runtime_api.h:367

hipErrorPeerAccessNotEnabled

hipErrorPeerAccessNotEnabled

Peer access was never enabled from the current device.

Definition hip_runtime_api.h:351

hipErrorOperatingSystem

hipErrorOperatingSystem

Not the correct operating system.

Definition hip_runtime_api.h:336

hipErrorStreamCaptureUnjoined

hipErrorStreamCaptureUnjoined

Definition hip_runtime_api.h:374

hipErrorInitializationError

hipErrorInitializationError

Definition hip_runtime_api.h:295

hipErrorNotMappedAsPointer

hipErrorNotMappedAsPointer

Definition hip_runtime_api.h:325

hipErrorPriorLaunchFailure

hipErrorPriorLaunchFailure

Definition hip_runtime_api.h:308

hipErrorContextIsDestroyed

hipErrorContextIsDestroyed

The context is already destroyed.

Definition hip_runtime_api.h:354

hipErrorInvalidValue

hipErrorInvalidValue

Definition hip_runtime_api.h:288

hipErrorLaunchTimeOut

hipErrorLaunchTimeOut

Timeout for the launch.

Definition hip_runtime_api.h:348

hipErrorUnmapFailed

hipErrorUnmapFailed

Definition hip_runtime_api.h:318

hipErrorSetOnActiveProcess

hipErrorSetOnActiveProcess

The process is active.

Definition hip_runtime_api.h:353

hipErrorFileNotFound

hipErrorFileNotFound

the file is not found.

Definition hip_runtime_api.h:333

hipErrorLaunchFailure

hipErrorLaunchFailure

An exception occurred on the device while executing a kernel.

Definition hip_runtime_api.h:360

hipErrorInvalidDevice

hipErrorInvalidDevice

DeviceID must be in range from 0 to compute-devices.

Definition hip_runtime_api.h:311

hipErrorUnsupportedLimit

hipErrorUnsupportedLimit

Unsupported limit.

Definition hip_runtime_api.h:327

hipErrorMapBufferObjectFailed

hipErrorMapBufferObjectFailed

Produced when the IPC memory attach failed from ROCr.

Definition hip_runtime_api.h:317

hipErrorHostMemoryAlreadyRegistered

hipErrorHostMemoryAlreadyRegistered

Produced when trying to lock a page-locked memory.

Definition hip_runtime_api.h:356

hipErrorMissingConfiguration

hipErrorMissingConfiguration

Definition hip_runtime_api.h:307

hipErrorSharedObjectSymbolNotFound

hipErrorSharedObjectSymbolNotFound

Definition hip_runtime_api.h:334

hipErrorECCNotCorrectable

hipErrorECCNotCorrectable

Definition hip_runtime_api.h:326

hipErrorStreamCaptureWrongThread

hipErrorStreamCaptureWrongThread

Definition hip_runtime_api.h:385

hipErrorAssert

hipErrorAssert

Produced when the kernel calls assert.

Definition hip_runtime_api.h:355

hipErrorContextAlreadyInUse

hipErrorContextAlreadyInUse

The context is already in use.

Definition hip_runtime_api.h:328

hipErrorNotReady

hipErrorNotReady

Definition hip_runtime_api.h:342

hipErrorInvalidSource

hipErrorInvalidSource

Invalid source.

Definition hip_runtime_api.h:332

hipErrorLaunchOutOfResources

hipErrorLaunchOutOfResources

Out of resources error.

Definition hip_runtime_api.h:347

hipErrorInvalidDeviceFunction

hipErrorInvalidDeviceFunction

Invalid device function.

Definition hip_runtime_api.h:309

hipErrorCooperativeLaunchTooLarge

hipErrorCooperativeLaunchTooLarge

Definition hip_runtime_api.h:362

hipErrorAlreadyMapped

hipErrorAlreadyMapped

Definition hip_runtime_api.h:320

hipErrorProfilerNotInitialized

hipErrorProfilerNotInitialized

Definition hip_runtime_api.h:298

hipErrorProfilerAlreadyStarted

hipErrorProfilerAlreadyStarted

Definition hip_runtime_api.h:299

hipErrorNoDevice

hipErrorNoDevice

Call to hipGetDeviceCount returned 0 devices.

Definition hip_runtime_api.h:310

HIP_ERROR_LAUNCH_OUT_OF_RESOURCES

@ HIP_ERROR_LAUNCH_OUT_OF_RESOURCES

Definition hip_runtime_api.h:41

HIP_ERROR_INVALID_VALUE

@ HIP_ERROR_INVALID_VALUE

Definition hip_runtime_api.h:39

HIP_SUCCESS

@ HIP_SUCCESS

Definition hip_runtime_api.h:38

HIP_ERROR_NOT_INITIALIZED

@ HIP_ERROR_NOT_INITIALIZED

Definition hip_runtime_api.h:40

hipErrorMapFailed

hipErrorMapFailed

Definition hip_runtime_api.h:315

hipErrorStreamCaptureInvalidated

hipErrorStreamCaptureInvalidated

Definition hip_runtime_api.h:369

hipErrorProfilerAlreadyStopped

hipErrorProfilerAlreadyStopped

Definition hip_runtime_api.h:300

hipErrorDeinitialized

hipErrorDeinitialized

Deinitialized.

Definition hip_runtime_api.h:296

hipErrorPeerAccessAlreadyEnabled

hipErrorPeerAccessAlreadyEnabled

Peer access was already enabled from the current device.

Definition hip_runtime_api.h:349

hipErrorNotMappedAsArray

hipErrorNotMappedAsArray

Definition hip_runtime_api.h:324

hipErrorNotSupported

hipErrorNotSupported

Produced when the hip API is not supported/implemented.

Definition hip_runtime_api.h:366

hipErrorInvalidConfiguration

hipErrorInvalidConfiguration

Invalide configuration.

Definition hip_runtime_api.h:301

hipErrorStreamCaptureImplicit

hipErrorStreamCaptureImplicit

Definition hip_runtime_api.h:380

hipErrorStreamCaptureMerge

hipErrorStreamCaptureMerge

Definition hip_runtime_api.h:371

hipErrorInvalidGraphicsContext

hipErrorInvalidGraphicsContext

Definition hip_runtime_api.h:331

hipErrorIllegalState

hipErrorIllegalState

Resource required is not in a valid state to perform operation.

Definition hip_runtime_api.h:340

hipErrorOutOfMemory

hipErrorOutOfMemory

out of memory range.

Definition hip_runtime_api.h:290

hipErrorInvalidSymbol

hipErrorInvalidSymbol

Invalid symbol.

Definition hip_runtime_api.h:303

hipSuccess

hipSuccess

Successful completion.

Definition hip_runtime_api.h:287

hipErrorUnknown

hipErrorUnknown

Unknown error.

Definition hip_runtime_api.h:393

hipErrorInvalidHandle

hipErrorInvalidHandle

Invalide handle.

Definition hip_runtime_api.h:337

hipErrorStreamCaptureUnmatched

hipErrorStreamCaptureUnmatched

The capture was not initiated in this stream.

Definition hip_runtime_api.h:373

hipErrorCapturedEvent

hipErrorCapturedEvent

Definition hip_runtime_api.h:383

hipErrorAlreadyAcquired

hipErrorAlreadyAcquired

Definition hip_runtime_api.h:322

hipErrorInsufficientDriver

hipErrorInsufficientDriver

Definition hip_runtime_api.h:306

hipErrorHostMemoryNotRegistered

hipErrorHostMemoryNotRegistered

Produced when trying to unlock a non-page-locked memory.

Definition hip_runtime_api.h:358

hipErrorRuntimeOther

hipErrorRuntimeOther

Definition hip_runtime_api.h:397

hipErrorContextAlreadyCurrent

hipErrorContextAlreadyCurrent

Definition hip_runtime_api.h:314

hipErrorInvalidMemcpyDirection

hipErrorInvalidMemcpyDirection

Invalid memory copy direction.

Definition hip_runtime_api.h:305

HIP_ARRAY3D_DESCRIPTOR

Definition driver_types.h:76

HIP_ARRAY_DESCRIPTOR

Definition driver_types.h:70

HIP_MEMCPY3D

Definition driver_types.h:369

HIP_MEMSET_NODE_PARAMS

Definition hip_runtime_api.h:1309

HIP_MEMSET_NODE_PARAMS::height

size_t height

Number of rows.

Definition hip_runtime_api.h:1315

HIP_MEMSET_NODE_PARAMS::pitch

size_t pitch

Destination device pointer pitch. Unused if height equals 1.

Definition hip_runtime_api.h:1311

HIP_MEMSET_NODE_PARAMS::dst

hipDeviceptr_t dst

Destination pointer on device.

Definition hip_runtime_api.h:1310

HIP_MEMSET_NODE_PARAMS::value

unsigned int value

Value of memset to be set.

Definition hip_runtime_api.h:1312

HIP_MEMSET_NODE_PARAMS::elementSize

unsigned int elementSize

Element in bytes. Must be 1, 2, or 4.

Definition hip_runtime_api.h:1313

HIP_MEMSET_NODE_PARAMS::width

size_t width

Width of a row.

Definition hip_runtime_api.h:1314

HIP_RESOURCE_DESC

Definition driver_types.h:271

HIP_RESOURCE_VIEW_DESC

Definition driver_types.h:317

HIP_TEXTURE_DESC

Definition driver_types.h:154

dim3

Definition hip_runtime_api.h:1046

dim3::y

uint32_t y

y

Definition hip_runtime_api.h:1048

dim3::z

uint32_t z

z

Definition hip_runtime_api.h:1049

dim3::x

uint32_t x

x

Definition hip_runtime_api.h:1047

hip_Memcpy2D

Definition driver_types.h:85

hipAccessPolicyWindow

Definition hip_runtime_api.h:1293

hipAccessPolicyWindow::hitProp

hipAccessProperty hitProp

Definition hip_runtime_api.h:1295

hipAccessPolicyWindow::missProp

hipAccessProperty missProp

Definition hip_runtime_api.h:1297

hipAccessPolicyWindow::hitRatio

float hitRatio

Definition hip_runtime_api.h:1296

hipAccessPolicyWindow::base_ptr

void * base_ptr

Definition hip_runtime_api.h:1294

hipAccessPolicyWindow::num_bytes

size_t num_bytes

Definition hip_runtime_api.h:1298

hipArrayMapInfo

Definition hip_runtime_api.h:1502

hipArrayMapInfo::level

unsigned int level

For mipmapped arrays must be a valid mipmap level. For arrays must be zero.

Definition hip_runtime_api.h:1511

hipArrayMapInfo::sparseLevel

struct hipArrayMapInfo::@26::@28 sparseLevel

hipArrayMapInfo::flags

unsigned int flags

flags for future use, must be zero now.

Definition hip_runtime_api.h:1533

hipArrayMapInfo::resource

union hipArrayMapInfo::@25 resource

hipArrayMapInfo::subresourceType

hipArraySparseSubresourceType subresourceType

Sparse subresource type.

Definition hip_runtime_api.h:1508

hipArrayMapInfo::extentDepth

unsigned int extentDepth

Depth in elements.

Definition hip_runtime_api.h:1518

hipArrayMapInfo::offsetX

unsigned int offsetX

X offset in elements.

Definition hip_runtime_api.h:1513

hipArrayMapInfo::array

hipArray_t array

Definition hip_runtime_api.h:1506

hipArrayMapInfo::resourceType

hipResourceType resourceType

Resource type.

Definition hip_runtime_api.h:1503

hipArrayMapInfo::memOperationType

hipMemOperationType memOperationType

Memory operation type.

Definition hip_runtime_api.h:1526

hipArrayMapInfo::reserved

unsigned int reserved[2]

Reserved for future use, must be zero now.

Definition hip_runtime_api.h:1534

hipArrayMapInfo::extentWidth

unsigned int extentWidth

Width in elements.

Definition hip_runtime_api.h:1516

hipArrayMapInfo::subresource

union hipArrayMapInfo::@26 subresource

hipArrayMapInfo::extentHeight

unsigned int extentHeight

Height in elements.

Definition hip_runtime_api.h:1517

hipArrayMapInfo::offsetY

unsigned int offsetY

Y offset in elements.

Definition hip_runtime_api.h:1514

hipArrayMapInfo::memHandleType

hipMemHandleType memHandleType

Memory handle type.

Definition hip_runtime_api.h:1527

hipArrayMapInfo::miptail

struct hipArrayMapInfo::@26::@29 miptail

hipArrayMapInfo::memHandle

hipMemGenericAllocationHandle_t memHandle

Definition hip_runtime_api.h:1529

hipArrayMapInfo::mipmap

hipMipmappedArray mipmap

Definition hip_runtime_api.h:1505

hipArrayMapInfo::layer

unsigned int layer

For layered arrays must be a valid layer index. Otherwise, must be zero.

Definition hip_runtime_api.h:1512

hipArrayMapInfo::deviceBitMask

unsigned int deviceBitMask

Device ordinal bit mask.

Definition hip_runtime_api.h:1532

hipArrayMapInfo::size

unsigned long long size

Extent in bytes.

Definition hip_runtime_api.h:1523

hipArrayMapInfo::offset

unsigned long long offset

Offset within mip tail.

Definition hip_runtime_api.h:1522

hipArrayMapInfo::offsetZ

unsigned int offsetZ

Z offset in elements.

Definition hip_runtime_api.h:1515

hipChannelFormatDesc

Definition driver_types.h:46

hipChildGraphNodeParams

Definition hip_runtime_api.h:1549

hipChildGraphNodeParams::graph

hipGraph_t graph

Definition hip_runtime_api.h:1550

hipDeviceArch_t

Definition hip_runtime_api.h:53

hipDeviceArch_t::hasSharedInt64Atomics

unsigned hasSharedInt64Atomics

64-bit integer atomics for shared memory.

Definition hip_runtime_api.h:63

hipDeviceArch_t::hasSharedInt32Atomics

unsigned hasSharedInt32Atomics

32-bit integer atomics for shared memory.

Definition hip_runtime_api.h:57

hipDeviceArch_t::hasFloatAtomicAdd

unsigned hasFloatAtomicAdd

32-bit float atomic add in global and shared memory.

Definition hip_runtime_api.h:59

hipDeviceArch_t::hasDoubles

unsigned hasDoubles

Double-precision floating point.

Definition hip_runtime_api.h:66

hipDeviceArch_t::hasWarpVote

unsigned hasWarpVote

Warp vote instructions (__any, __all).

Definition hip_runtime_api.h:69

hipDeviceArch_t::hasWarpShuffle

unsigned hasWarpShuffle

Warp shuffle operations. (__shfl_*).

Definition hip_runtime_api.h:71

hipDeviceArch_t::hasGlobalInt32Atomics

unsigned hasGlobalInt32Atomics

32-bit integer atomics for global memory.

Definition hip_runtime_api.h:55

hipDeviceArch_t::hasGlobalFloatAtomicExch

unsigned hasGlobalFloatAtomicExch

32-bit float atomic exch for global memory.

Definition hip_runtime_api.h:56

hipDeviceArch_t::hasDynamicParallelism

unsigned hasDynamicParallelism

Dynamic parallelism.

Definition hip_runtime_api.h:81

hipDeviceArch_t::hasSurfaceFuncs

unsigned hasSurfaceFuncs

Surface functions.

Definition hip_runtime_api.h:79

hipDeviceArch_t::has3dGrid

unsigned has3dGrid

Grid and group dims are 3D (rather than 2D).

Definition hip_runtime_api.h:80

hipDeviceArch_t::hasFunnelShift

unsigned hasFunnelShift

Funnel two words into one with shift&mask caps.

Definition hip_runtime_api.h:72

hipDeviceArch_t::hasThreadFenceSystem

unsigned hasThreadFenceSystem

__threadfence_system.

Definition hip_runtime_api.h:75

hipDeviceArch_t::hasGlobalInt64Atomics

unsigned hasGlobalInt64Atomics

64-bit integer atomics for global memory.

Definition hip_runtime_api.h:62

hipDeviceArch_t::hasSyncThreadsExt

unsigned hasSyncThreadsExt

__syncthreads_count, syncthreads_and, syncthreads_or.

Definition hip_runtime_api.h:76

hipDeviceArch_t::hasWarpBallot

unsigned hasWarpBallot

Warp ballot instructions (__ballot).

Definition hip_runtime_api.h:70

hipDeviceArch_t::hasSharedFloatAtomicExch

unsigned hasSharedFloatAtomicExch

32-bit float atomic exch for shared memory.

Definition hip_runtime_api.h:58

hipDeviceProp_t

Definition hip_runtime_api.h:99

hipDeviceProp_t::ECCEnabled

int ECCEnabled

Device has ECC support enabled.

Definition hip_runtime_api.h:152

hipDeviceProp_t::ipcEventSupported

int ipcEventSupported

Device supports IPC events.

Definition hip_runtime_api.h:207

hipDeviceProp_t::computePreemptionSupported

int computePreemptionSupported

Is compute preemption supported on the device.

Definition hip_runtime_api.h:178

hipDeviceProp_t::maxTexture1DLinear

int maxTexture1DLinear

Maximum size for 1D textures bound to linear memory.

Definition hip_runtime_api.h:131

hipDeviceProp_t::timelineSemaphoreInteropSupported

int timelineSemaphoreInteropSupported

Indicates external timeline semaphore support.

Definition hip_runtime_api.h:197

hipDeviceProp_t::pciBusID

int pciBusID

PCI Bus ID.

Definition hip_runtime_api.h:153

hipDeviceProp_t::maxTexture1D

int maxTexture1D

Maximum number of elements in 1D images.

Definition hip_runtime_api.h:129

hipDeviceProp_t::memoryBusWidth

int memoryBusWidth

Global memory bus width in bits.

Definition hip_runtime_api.h:160

hipDeviceProp_t::maxTexture2DMipmap

int maxTexture2DMipmap[2]

Maximum number of elements in 2D array mipmap of images.

Definition hip_runtime_api.h:133

hipDeviceProp_t::clockRate

int clockRate

Max clock frequency of the multiProcessors in khz.

Definition hip_runtime_api.h:113

hipDeviceProp_t::maxThreadsPerMultiProcessor

int maxThreadsPerMultiProcessor

Maximum resident threads per multi-processor.

Definition hip_runtime_api.h:163

hipDeviceProp_t::l2CacheSize

int l2CacheSize

L2 cache size.

Definition hip_runtime_api.h:161

hipDeviceProp_t::deferredMappingHipArraySupported

int deferredMappingHipArraySupported

Definition hip_runtime_api.h:205

hipDeviceProp_t::asyncEngineCount

int asyncEngineCount

Number of async engines.

Definition hip_runtime_api.h:157

hipDeviceProp_t::accessPolicyMaxWindowSize

int accessPolicyMaxWindowSize

Max value of access policy window.

Definition hip_runtime_api.h:191

hipDeviceProp_t::totalConstMem

size_t totalConstMem

Size of shared memory region (in bytes).

Definition hip_runtime_api.h:114

hipDeviceProp_t::memoryPoolsSupported

int memoryPoolsSupported

Indicates if device supports hipMallocAsync and hipMemPool APIs.

Definition hip_runtime_api.h:198

hipDeviceProp_t::unifiedFunctionPointers

int unifiedFunctionPointers

Indicates device supports unified function pointers.

Definition hip_runtime_api.h:209

hipDeviceProp_t::maxTexture2DGather

int maxTexture2DGather[2]

Maximum 2D tex dimensions if gather has to be performed.

Definition hip_runtime_api.h:135

hipDeviceProp_t::memPitch

size_t memPitch

Definition hip_runtime_api.h:108

hipDeviceProp_t::gpuDirectRDMAWritesOrdering

int gpuDirectRDMAWritesOrdering

value of hipGPUDirectRDMAWritesOrdering

Definition hip_runtime_api.h:202

hipDeviceProp_t::uuid

hipUUID uuid

UUID of a device.

Definition hip_runtime_api.h:101

hipDeviceProp_t::sharedMemPerBlock

size_t sharedMemPerBlock

Size of shared memory region (in bytes).

Definition hip_runtime_api.h:105

hipDeviceProp_t::gpuDirectRDMAFlushWritesOptions

unsigned int gpuDirectRDMAFlushWritesOptions

Definition hip_runtime_api.h:200

hipDeviceProp_t::surfaceAlignment

size_t surfaceAlignment

Alignment requirement for surface.

Definition hip_runtime_api.h:150

hipDeviceProp_t::reserved

int reserved[63]

CUDA Reserved.

Definition hip_runtime_api.h:210

hipDeviceProp_t::maxTexture2DLayered

int maxTexture2DLayered[3]

Maximum number of elements in 2D array images.

Definition hip_runtime_api.h:141

hipDeviceProp_t::streamPrioritiesSupported

int streamPrioritiesSupported

Device supports stream priority.

Definition hip_runtime_api.h:164

hipDeviceProp_t::cooperativeMultiDeviceLaunch

int cooperativeMultiDeviceLaunch

Definition hip_runtime_api.h:182

hipDeviceProp_t::hostRegisterSupported

int hostRegisterSupported

Device supports hipHostRegister.

Definition hip_runtime_api.h:193

hipDeviceProp_t::pageableMemoryAccess

int pageableMemoryAccess

Definition hip_runtime_api.h:174

hipDeviceProp_t::name

char name[256]

Device name.

Definition hip_runtime_api.h:100

hipDeviceProp_t::textureAlignment

size_t textureAlignment

Alignment requirement for textures.

Definition hip_runtime_api.h:121

hipDeviceProp_t::globalL1CacheSupported

int globalL1CacheSupported

Indicates globals are cached in L1.

Definition hip_runtime_api.h:165

hipDeviceProp_t::hostNativeAtomicSupported

int hostNativeAtomicSupported

Link between host and device supports native atomics.

Definition hip_runtime_api.h:172

hipDeviceProp_t::maxSurfaceCubemapLayered

int maxSurfaceCubemapLayered[2]

Maximum cubemap layered surface size.

Definition hip_runtime_api.h:149

hipDeviceProp_t::maxTextureCubemapLayered

int maxTextureCubemapLayered[2]

Maximum cubemaps layered texture dims.

Definition hip_runtime_api.h:142

hipDeviceProp_t::sharedMemPerBlockOptin

size_t sharedMemPerBlockOptin

Per device m ax shared mem per block usable by special opt in.

Definition hip_runtime_api.h:185

hipDeviceProp_t::sharedMemPerMultiprocessor

size_t sharedMemPerMultiprocessor

Amount of shared memory available per multiprocessor.

Definition hip_runtime_api.h:167

hipDeviceProp_t::singleToDoublePrecisionPerfRatio

int singleToDoublePrecisionPerfRatio

Deprecated. CUDA only.

Definition hip_runtime_api.h:173

hipDeviceProp_t::maxSurface2D

int maxSurface2D[2]

Maximum 2D surface size.

Definition hip_runtime_api.h:144

hipDeviceProp_t::memoryClockRate

int memoryClockRate

Max global memory clock frequency in khz.

Definition hip_runtime_api.h:159

hipDeviceProp_t::maxTexture2DLinear

int maxTexture2DLinear[3]

Maximum 2D tex dimensions if tex are bound to pitched memory.

Definition hip_runtime_api.h:134

hipDeviceProp_t::sparseHipArraySupported

int sparseHipArraySupported

Indicates if device supports sparse hip arrays.

Definition hip_runtime_api.h:194

hipDeviceProp_t::clockInstructionRate

int clockInstructionRate

Definition hip_runtime_api.h:217

hipDeviceProp_t::localL1CacheSupported

int localL1CacheSupported

Locals are cahced in L1.

Definition hip_runtime_api.h:166

hipDeviceProp_t::regsPerMultiprocessor

int regsPerMultiprocessor

registers available per multiprocessor

Definition hip_runtime_api.h:168

hipDeviceProp_t::regsPerBlock

int regsPerBlock

Registers per block.

Definition hip_runtime_api.h:106

hipDeviceProp_t::maxTexture2D

int maxTexture2D[2]

Maximum dimensions (width, height) of 2D images, in image elements.

Definition hip_runtime_api.h:132

hipDeviceProp_t::cooperativeLaunch

int cooperativeLaunch

HIP device supports cooperative launch.

Definition hip_runtime_api.h:181

hipDeviceProp_t::maxTexture3D

int maxTexture3D[3]

elements

Definition hip_runtime_api.h:136

hipDeviceProp_t::directManagedMemAccessFromHost

int directManagedMemAccessFromHost

Definition hip_runtime_api.h:188

hipDeviceProp_t::cooperativeMultiDeviceUnmatchedFunc

int cooperativeMultiDeviceUnmatchedFunc

Definition hip_runtime_api.h:222

hipDeviceProp_t::deviceOverlap

int deviceOverlap

Deprecated. Use asyncEngineCount instead.

Definition hip_runtime_api.h:123

hipDeviceProp_t::pageableMemoryAccessUsesHostPageTables

int pageableMemoryAccessUsesHostPageTables

Definition hip_runtime_api.h:186

hipDeviceProp_t::hdpRegFlushCntl

unsigned int * hdpRegFlushCntl

Addres of HDP_REG_COHERENCY_FLUSH_CNTL register.

Definition hip_runtime_api.h:221

hipDeviceProp_t::maxThreadsDim

int maxThreadsDim[3]

Max number of threads in each dimension (XYZ) of a block.

Definition hip_runtime_api.h:111

hipDeviceProp_t::unifiedAddressing

int unifiedAddressing

Does device and host share unified address space.

Definition hip_runtime_api.h:158

hipDeviceProp_t::multiGpuBoardGroupID

int multiGpuBoardGroupID

Unique identifier for a group of devices on same multiboard GPU.

Definition hip_runtime_api.h:171

hipDeviceProp_t::isMultiGpuBoard

int isMultiGpuBoard

1 if device is on a multi-GPU board, 0 if not.

Definition hip_runtime_api.h:170

hipDeviceProp_t::canUseHostPointerForRegisteredMem

int canUseHostPointerForRegisteredMem

Definition hip_runtime_api.h:179

hipDeviceProp_t::maxTexture1DLayered

int maxTexture1DLayered[2]

Maximum number of elements in 1D array images.

Definition hip_runtime_api.h:140

hipDeviceProp_t::pciDomainID

int pciDomainID

PCI Domain ID.

Definition hip_runtime_api.h:155

hipDeviceProp_t::maxSharedMemoryPerMultiProcessor

size_t maxSharedMemoryPerMultiProcessor

Maximum Shared Memory Per CU. HIP Only.

Definition hip_runtime_api.h:216

hipDeviceProp_t::maxTextureCubemap

int maxTextureCubemap

Maximum cubemap texture dims.

Definition hip_runtime_api.h:139

hipDeviceProp_t::hipReserved

int hipReserved[32]

Reserved for adding new entries for HIP/CUDA.

Definition hip_runtime_api.h:212

hipDeviceProp_t::cooperativeMultiDeviceUnmatchedGridDim

int cooperativeMultiDeviceUnmatchedGridDim

Definition hip_runtime_api.h:225

hipDeviceProp_t::gpuDirectRDMASupported

int gpuDirectRDMASupported

Indicates device support of RDMA APIs.

Definition hip_runtime_api.h:199

hipDeviceProp_t::minor

int minor

Definition hip_runtime_api.h:118

hipDeviceProp_t::gcnArchName

char gcnArchName[256]

AMD GCN Arch Name. HIP Only.

Definition hip_runtime_api.h:215

hipDeviceProp_t::luid

char luid[8]

8-byte unique identifier. Only valid on windows

Definition hip_runtime_api.h:102

hipDeviceProp_t::kernelExecTimeoutEnabled

int kernelExecTimeoutEnabled

Run time limit for kernels executed on the device.

Definition hip_runtime_api.h:125

hipDeviceProp_t::memoryPoolSupportedHandleTypes

unsigned int memoryPoolSupportedHandleTypes

Bitmask of handle types support with mempool based IPC.

Definition hip_runtime_api.h:204

hipDeviceProp_t::hdpMemFlushCntl

unsigned int * hdpMemFlushCntl

Addres of HDP_MEM_COHERENCY_FLUSH_CNTL register.

Definition hip_runtime_api.h:220

hipDeviceProp_t::concurrentManagedAccess

int concurrentManagedAccess

Definition hip_runtime_api.h:176

hipDeviceProp_t::integrated

int integrated

APU vs dGPU.

Definition hip_runtime_api.h:126

hipDeviceProp_t::canMapHostMemory

int canMapHostMemory

Check whether HIP can map host memory.

Definition hip_runtime_api.h:127

hipDeviceProp_t::reservedSharedMemPerBlock

size_t reservedSharedMemPerBlock

Shared memory reserved by driver per block.

Definition hip_runtime_api.h:192

hipDeviceProp_t::maxSurfaceCubemap

int maxSurfaceCubemap

Maximum cubemap surface size.

Definition hip_runtime_api.h:148

hipDeviceProp_t::maxSurface3D

int maxSurface3D[3]

Maximum 3D surface size.

Definition hip_runtime_api.h:145

hipDeviceProp_t::asicRevision

int asicRevision

Revision of the GPU in this device.

Definition hip_runtime_api.h:235

hipDeviceProp_t::totalGlobalMem

size_t totalGlobalMem

Size of global memory region (in bytes).

Definition hip_runtime_api.h:104

hipDeviceProp_t::cooperativeMultiDeviceUnmatchedBlockDim

int cooperativeMultiDeviceUnmatchedBlockDim

Definition hip_runtime_api.h:228

hipDeviceProp_t::maxSurface1DLayered

int maxSurface1DLayered[2]

Maximum 1D layered surface size.

Definition hip_runtime_api.h:146

hipDeviceProp_t::persistingL2CacheMaxSize

int persistingL2CacheMaxSize

Device's max L2 persisting lines in bytes.

Definition hip_runtime_api.h:162

hipDeviceProp_t::maxSurface1D

int maxSurface1D

Maximum 1D surface size.

Definition hip_runtime_api.h:143

hipDeviceProp_t::concurrentKernels

int concurrentKernels

Device can possibly execute multiple kernels concurrently.

Definition hip_runtime_api.h:151

hipDeviceProp_t::isLargeBar

int isLargeBar

1: if it is a large PCI bar device, else 0

Definition hip_runtime_api.h:234

hipDeviceProp_t::clusterLaunch

int clusterLaunch

Device supports cluster launch.

Definition hip_runtime_api.h:208

hipDeviceProp_t::maxTexture1DMipmap

int maxTexture1DMipmap

Maximum 1D mipmap texture size.

Definition hip_runtime_api.h:130

hipDeviceProp_t::multiProcessorCount

int multiProcessorCount

Number of multi-processors (compute units).

Definition hip_runtime_api.h:124

hipDeviceProp_t::maxTexture3DAlt

int maxTexture3DAlt[3]

Maximum alternate 3D texture dims.

Definition hip_runtime_api.h:138

hipDeviceProp_t::maxGridSize

int maxGridSize[3]

Max grid dimensions (XYZ).

Definition hip_runtime_api.h:112

hipDeviceProp_t::pciDeviceID

int pciDeviceID

PCI Device ID.

Definition hip_runtime_api.h:154

hipDeviceProp_t::maxBlocksPerMultiProcessor

int maxBlocksPerMultiProcessor

Max number of blocks on CU.

Definition hip_runtime_api.h:190

hipDeviceProp_t::computeMode

int computeMode

Compute mode.

Definition hip_runtime_api.h:128

hipDeviceProp_t::maxSurface2DLayered

int maxSurface2DLayered[3]

Maximum 2D layared surface size.

Definition hip_runtime_api.h:147

hipDeviceProp_t::major

int major

Definition hip_runtime_api.h:115

hipDeviceProp_t::warpSize

int warpSize

Warp size.

Definition hip_runtime_api.h:107

hipDeviceProp_t::tccDriver

int tccDriver

1:If device is Tesla device using TCC driver, else 0

Definition hip_runtime_api.h:156

hipDeviceProp_t::luidDeviceNodeMask

unsigned int luidDeviceNodeMask

LUID node mask.

Definition hip_runtime_api.h:103

hipDeviceProp_t::hostRegisterReadOnlySupported

int hostRegisterReadOnlySupported

Definition hip_runtime_api.h:195

hipDeviceProp_t::cooperativeMultiDeviceUnmatchedSharedMem

int cooperativeMultiDeviceUnmatchedSharedMem

Definition hip_runtime_api.h:231

hipDeviceProp_t::maxThreadsPerBlock

int maxThreadsPerBlock

Max work items per work group or workgroup max size.

Definition hip_runtime_api.h:110

hipDeviceProp_t::arch

hipDeviceArch_t arch

Architectural feature flags. New for HIP.

Definition hip_runtime_api.h:219

hipDeviceProp_t::managedMemory

int managedMemory

Device supports allocating managed memory on this system.

Definition hip_runtime_api.h:169

hipDeviceProp_t::texturePitchAlignment

size_t texturePitchAlignment

Pitch alignment requirement for texture references bound to.

Definition hip_runtime_api.h:122

hipEventRecordNodeParams

Definition hip_runtime_api.h:1564

hipEventRecordNodeParams::event

hipEvent_t event

The event to be recorded when node executes.

Definition hip_runtime_api.h:1565

hipEventWaitNodeParams

Definition hip_runtime_api.h:1557

hipEventWaitNodeParams::event

hipEvent_t event

Event to wait on.

Definition hip_runtime_api.h:1558

hipExtent

Definition driver_types.h:348

hipExternalMemoryBufferDesc

Definition hip_runtime_api.h:1104

hipExternalMemoryBufferDesc::flags

unsigned int flags

Definition hip_runtime_api.h:1107

hipExternalMemoryBufferDesc::offset

unsigned long long offset

Definition hip_runtime_api.h:1105

hipExternalMemoryBufferDesc::size

unsigned long long size

Definition hip_runtime_api.h:1106

hipExternalMemoryHandleDesc

Definition hip_runtime_api.h:1090

hipExternalMemoryHandleDesc::flags

unsigned int flags

Definition hip_runtime_api.h:1101

hipExternalMemoryHandleDesc::name

const void * name

Definition hip_runtime_api.h:1096

hipExternalMemoryHandleDesc::fd

int fd

Definition hip_runtime_api.h:1093

hipExternalMemoryHandleDesc::size

unsigned long long size

Definition hip_runtime_api.h:1100

hipExternalMemoryHandleDesc::type

hipExternalMemoryHandleType type

Definition hip_runtime_api.h:1091

hipExternalMemoryHandleDesc::nvSciBufObject

const void * nvSciBufObject

Definition hip_runtime_api.h:1098

hipExternalMemoryHandleDesc::handle

void * handle

Definition hip_runtime_api.h:1095

hipExternalMemoryMipmappedArrayDesc

Definition hip_runtime_api.h:1110

hipExternalMemoryMipmappedArrayDesc::extent

hipExtent extent

Definition hip_runtime_api.h:1113

hipExternalMemoryMipmappedArrayDesc::numLevels

unsigned int numLevels

Definition hip_runtime_api.h:1115

hipExternalMemoryMipmappedArrayDesc::flags

unsigned int flags

Definition hip_runtime_api.h:1114

hipExternalMemoryMipmappedArrayDesc::offset

unsigned long long offset

Definition hip_runtime_api.h:1111

hipExternalMemoryMipmappedArrayDesc::formatDesc

hipChannelFormatDesc formatDesc

Definition hip_runtime_api.h:1112

hipExternalSemaphoreHandleDesc

Definition hip_runtime_api.h:1130

hipExternalSemaphoreHandleDesc::flags

unsigned int flags

Definition hip_runtime_api.h:1140

hipExternalSemaphoreHandleDesc::name

const void * name

Definition hip_runtime_api.h:1136

hipExternalSemaphoreHandleDesc::NvSciSyncObj

const void * NvSciSyncObj

Definition hip_runtime_api.h:1138

hipExternalSemaphoreHandleDesc::type

hipExternalSemaphoreHandleType type

Definition hip_runtime_api.h:1131

hipExternalSemaphoreHandleDesc::handle

void * handle

Definition hip_runtime_api.h:1135

hipExternalSemaphoreHandleDesc::fd

int fd

Definition hip_runtime_api.h:1133

hipExternalSemaphoreSignalNodeParams

Definition hip_runtime_api.h:1442

hipExternalSemaphoreSignalNodeParams::paramsArray

const hipExternalSemaphoreSignalParams * paramsArray

Total number of handles and parameters contained in extSemArray and paramsArray.

Definition hip_runtime_api.h:1446

hipExternalSemaphoreSignalNodeParams::extSemArray

hipExternalSemaphore_t * extSemArray

< Array containing external semaphore handles.

Definition hip_runtime_api.h:1444

hipExternalSemaphoreSignalNodeParams::numExtSems

unsigned int numExtSems

Definition hip_runtime_api.h:1448

hipExternalSemaphoreSignalParams

Definition hip_runtime_api.h:1144

hipExternalSemaphoreSignalParams::reserved

unsigned long long reserved

Definition hip_runtime_api.h:1151

hipExternalSemaphoreSignalParams::value

unsigned long long value

Definition hip_runtime_api.h:1147

hipExternalSemaphoreSignalParams::fence

void * fence

Definition hip_runtime_api.h:1150

hipExternalSemaphoreSignalParams::flags

unsigned int flags

Definition hip_runtime_api.h:1158

hipExternalSemaphoreSignalParams::key

unsigned long long key

Definition hip_runtime_api.h:1154

hipExternalSemaphoreWaitNodeParams

Definition hip_runtime_api.h:1454

hipExternalSemaphoreWaitNodeParams::numExtSems

unsigned int numExtSems

Definition hip_runtime_api.h:1460

hipExternalSemaphoreWaitNodeParams::paramsArray

const hipExternalSemaphoreWaitParams * paramsArray

Total number of handles and parameters contained in extSemArray and paramsArray.

Definition hip_runtime_api.h:1458

hipExternalSemaphoreWaitNodeParams::extSemArray

hipExternalSemaphore_t * extSemArray

< Array containing external semaphore handles.

Definition hip_runtime_api.h:1456

hipExternalSemaphoreWaitParams

Definition hip_runtime_api.h:1164

hipExternalSemaphoreWaitParams::value

unsigned long long value

Definition hip_runtime_api.h:1167

hipExternalSemaphoreWaitParams::fence

void * fence

Definition hip_runtime_api.h:1170

hipExternalSemaphoreWaitParams::timeoutMs

unsigned int timeoutMs

Definition hip_runtime_api.h:1175

hipExternalSemaphoreWaitParams::key

unsigned long long key

Definition hip_runtime_api.h:1174

hipExternalSemaphoreWaitParams::flags

unsigned int flags

Definition hip_runtime_api.h:1179

hipExternalSemaphoreWaitParams::reserved

unsigned long long reserved

Definition hip_runtime_api.h:1171

hipFuncAttributes

Definition hip_runtime_api.h:632

hipFuncAttributes::cacheModeCA

int cacheModeCA

Definition hip_runtime_api.h:634

hipFuncAttributes::binaryVersion

int binaryVersion

Definition hip_runtime_api.h:633

hipFuncAttributes::constSizeBytes

size_t constSizeBytes

Definition hip_runtime_api.h:635

hipFuncAttributes::preferredShmemCarveout

int preferredShmemCarveout

Definition hip_runtime_api.h:640

hipFuncAttributes::sharedSizeBytes

size_t sharedSizeBytes

Definition hip_runtime_api.h:642

hipFuncAttributes::maxDynamicSharedSizeBytes

int maxDynamicSharedSizeBytes

Definition hip_runtime_api.h:637

hipFuncAttributes::ptxVersion

int ptxVersion

Definition hip_runtime_api.h:641

hipFuncAttributes::numRegs

int numRegs

Definition hip_runtime_api.h:639

hipFuncAttributes::localSizeBytes

size_t localSizeBytes

Definition hip_runtime_api.h:636

hipFuncAttributes::maxThreadsPerBlock

int maxThreadsPerBlock

Definition hip_runtime_api.h:638

hipFunctionLaunchParams

Definition hip_runtime_api.h:1068

hipFunctionLaunchParams::gridDimX

unsigned int gridDimX

Width(X) of grid in blocks.

Definition hip_runtime_api.h:1070

hipFunctionLaunchParams::blockDimX

unsigned int blockDimX

X dimension of each thread block.

Definition hip_runtime_api.h:1073

hipFunctionLaunchParams::function

hipFunction_t function

Kernel to launch.

Definition hip_runtime_api.h:1069

hipFunctionLaunchParams::hStream

hipStream_t hStream

Stream identifier.

Definition hip_runtime_api.h:1077

hipFunctionLaunchParams::blockDimY

unsigned int blockDimY

Y dimension of each thread block.

Definition hip_runtime_api.h:1074

hipFunctionLaunchParams::gridDimY

unsigned int gridDimY

Height(Y) of grid in blocks.

Definition hip_runtime_api.h:1071

hipFunctionLaunchParams::gridDimZ

unsigned int gridDimZ

Depth(Z) of grid in blocks.

Definition hip_runtime_api.h:1072

hipFunctionLaunchParams::sharedMemBytes

unsigned int sharedMemBytes

Shared memory.

Definition hip_runtime_api.h:1076

hipFunctionLaunchParams::blockDimZ

unsigned int blockDimZ

Z dimension of each thread block.

Definition hip_runtime_api.h:1075

hipFunctionLaunchParams::kernelParams

void ** kernelParams

Kernel parameters.

Definition hip_runtime_api.h:1078

hipGraphInstantiateParams

Definition hip_runtime_api.h:1415

hipGraphInstantiateParams::result_out

hipGraphInstantiateResult result_out

Definition hip_runtime_api.h:1418

hipGraphInstantiateParams::uploadStream

hipStream_t uploadStream

Definition hip_runtime_api.h:1420

hipGraphInstantiateParams::errNode_out

hipGraphNode_t errNode_out

Definition hip_runtime_api.h:1416

hipGraphInstantiateParams::flags

unsigned long long flags

Definition hip_runtime_api.h:1417

hipGraphNodeParams

Definition hip_runtime_api.h:1578

hipGraphNodeParams::type

hipGraphNodeType type

Definition hip_runtime_api.h:1579

hipGraphNodeParams::reserved0

int reserved0[3]

Definition hip_runtime_api.h:1580

hipGraphNodeParams::alloc

hipMemAllocNodeParams alloc

Definition hip_runtime_api.h:1592

hipGraphNodeParams::reserved1

long long reserved1[29]

Definition hip_runtime_api.h:1582

hipGraphNodeParams::eventRecord

hipEventRecordNodeParams eventRecord

Definition hip_runtime_api.h:1589

hipGraphNodeParams::extSemSignal

hipExternalSemaphoreSignalNodeParams extSemSignal

Definition hip_runtime_api.h:1590

hipGraphNodeParams::free

hipMemFreeNodeParams free

Definition hip_runtime_api.h:1593

hipGraphNodeParams::graph

hipChildGraphNodeParams graph

Definition hip_runtime_api.h:1587

hipGraphNodeParams::extSemWait

hipExternalSemaphoreWaitNodeParams extSemWait

Definition hip_runtime_api.h:1591

hipGraphNodeParams::memset

hipMemsetParams memset

Definition hip_runtime_api.h:1585

hipGraphNodeParams::host

hipHostNodeParams host

Definition hip_runtime_api.h:1586

hipGraphNodeParams::reserved2

long long reserved2

Definition hip_runtime_api.h:1596

hipGraphNodeParams::kernel

hipKernelNodeParams kernel

Definition hip_runtime_api.h:1583

hipGraphNodeParams::eventWait

hipEventWaitNodeParams eventWait

Definition hip_runtime_api.h:1588

hipGraphNodeParams::memcpy

hipMemcpyNodeParams memcpy

Definition hip_runtime_api.h:1584

hipHostNodeParams

Definition hip_runtime_api.h:1249

hipHostNodeParams::fn

hipHostFn_t fn

Definition hip_runtime_api.h:1250

hipHostNodeParams::userData

void * userData

Definition hip_runtime_api.h:1251

hipIpcEventHandle_t

Definition hip_runtime_api.h:622

hipIpcMemHandle_t

Definition hip_runtime_api.h:619

hipKernelNodeParams

Definition hip_runtime_api.h:1253

hipKernelNodeParams::gridDim

dim3 gridDim

Definition hip_runtime_api.h:1257

hipKernelNodeParams::sharedMemBytes

unsigned int sharedMemBytes

Definition hip_runtime_api.h:1259

hipKernelNodeParams::blockDim

dim3 blockDim

Definition hip_runtime_api.h:1254

hipKernelNodeParams::kernelParams

void ** kernelParams

Definition hip_runtime_api.h:1258

hipKernelNodeParams::extra

void ** extra

Definition hip_runtime_api.h:1255

hipKernelNodeParams::func

void * func

Definition hip_runtime_api.h:1256

hipLaunchParams

Definition hip_runtime_api.h:1057

hipLaunchParams::sharedMem

size_t sharedMem

Shared memory.

Definition hip_runtime_api.h:1062

hipLaunchParams::args

void ** args

Arguments.

Definition hip_runtime_api.h:1061

hipLaunchParams::blockDim

dim3 blockDim

Block dimentions.

Definition hip_runtime_api.h:1060

hipLaunchParams::gridDim

dim3 gridDim

Grid dimentions.

Definition hip_runtime_api.h:1059

hipLaunchParams::func

void * func

Device function symbol.

Definition hip_runtime_api.h:1058

hipLaunchParams::stream

hipStream_t stream

Stream identifier.

Definition hip_runtime_api.h:1063

hipMemAccessDesc

Definition hip_runtime_api.h:948

hipMemAccessDesc::flags

hipMemAccessFlags flags

Accessibility flags to set.

Definition hip_runtime_api.h:950

hipMemAccessDesc::location

hipMemLocation location

Location on which the accessibility has to change.

Definition hip_runtime_api.h:949

hipMemAllocNodeParams

Definition hip_runtime_api.h:1270

hipMemAllocNodeParams::accessDescs

const hipMemAccessDesc * accessDescs

Definition hip_runtime_api.h:1273

hipMemAllocNodeParams::bytesize

size_t bytesize

The size of the requested allocation in bytes.

Definition hip_runtime_api.h:1276

hipMemAllocNodeParams::poolProps

hipMemPoolProps poolProps

Definition hip_runtime_api.h:1271

hipMemAllocNodeParams::accessDescCount

size_t accessDescCount

The number of access descriptors.

Definition hip_runtime_api.h:1275

hipMemAllocNodeParams::dptr

void * dptr

Returned device address of the allocation.

Definition hip_runtime_api.h:1277

hipMemAllocationProp

Definition hip_runtime_api.h:1427

hipMemAllocationProp::win32HandleMetaData

void * win32HandleMetaData

Metadata for Win32 handles.

Definition hip_runtime_api.h:1431

hipMemAllocationProp::type

hipMemAllocationType type

Memory allocation type.

Definition hip_runtime_api.h:1428

hipMemAllocationProp::gpuDirectRDMACapable

unsigned char gpuDirectRDMACapable

RDMA capable.

Definition hip_runtime_api.h:1434

hipMemAllocationProp::allocFlags

struct hipMemAllocationProp::@24 allocFlags

hipMemAllocationProp::usage

unsigned short usage

Usage.

Definition hip_runtime_api.h:1435

hipMemAllocationProp::requestedHandleType

hipMemAllocationHandleType requestedHandleType

Requested handle type.

Definition hip_runtime_api.h:1429

hipMemAllocationProp::location

hipMemLocation location

Memory location.

Definition hip_runtime_api.h:1430

hipMemAllocationProp::compressionType

unsigned char compressionType

Compression type.

Definition hip_runtime_api.h:1433

hipMemFreeNodeParams

Definition hip_runtime_api.h:1571

hipMemFreeNodeParams::dptr

void * dptr

the pointer to be freed

Definition hip_runtime_api.h:1572

hipMemLocation

Definition hip_runtime_api.h:932

hipMemLocation::id

int id

Identifier for the provided location type hipMemLocationType.

Definition hip_runtime_api.h:934

hipMemLocation::type

hipMemLocationType type

Specifies the location type, which describes the meaning of id.

Definition hip_runtime_api.h:933

hipMemPoolProps

Definition hip_runtime_api.h:976

hipMemPoolProps::location

hipMemLocation location

Location where allocations should reside.

Definition hip_runtime_api.h:979

hipMemPoolProps::handleTypes

hipMemAllocationHandleType handleTypes

Handle types that will be supported by allocations from the pool.

Definition hip_runtime_api.h:978

hipMemPoolProps::allocType

hipMemAllocationType allocType

Allocation type. Currently must be specified as hipMemAllocationTypePinned.

Definition hip_runtime_api.h:977

hipMemPoolProps::reserved

unsigned char reserved[64]

Reserved for future use, must be 0.

Definition hip_runtime_api.h:984

hipMemPoolProps::win32SecurityAttributes

void * win32SecurityAttributes

Definition hip_runtime_api.h:983

hipMemPoolPtrExportData

Definition hip_runtime_api.h:989

hipMemPoolPtrExportData::reserved

unsigned char reserved[64]

Definition hip_runtime_api.h:990

hipMemcpy3DParms

Definition driver_types.h:359

hipMemcpyNodeParams

Definition hip_runtime_api.h:1540

hipMemcpyNodeParams::reserved

int reserved[3]

Must be zero.

Definition hip_runtime_api.h:1542

hipMemcpyNodeParams::flags

int flags

Must be zero.

Definition hip_runtime_api.h:1541

hipMemcpyNodeParams::copyParams

hipMemcpy3DParms copyParams

Params set for the memory copy.

Definition hip_runtime_api.h:1543

hipMemsetParams

Definition hip_runtime_api.h:1261

hipMemsetParams::dst

void * dst

Definition hip_runtime_api.h:1262

hipMemsetParams::value

unsigned int value

Definition hip_runtime_api.h:1266

hipMemsetParams::elementSize

unsigned int elementSize

Definition hip_runtime_api.h:1263

hipMemsetParams::width

size_t width

Definition hip_runtime_api.h:1267

hipMemsetParams::pitch

size_t pitch

Definition hip_runtime_api.h:1265

hipMemsetParams::height

size_t height

Definition hip_runtime_api.h:1264

hipMipmappedArray

Definition driver_types.h:104

hipPitchedPtr

Definition driver_types.h:342

hipPointerAttribute_t

Definition hip_runtime_api.h:261

hipPointerAttribute_t::device

int device

Definition hip_runtime_api.h:263

hipPointerAttribute_t::hostPointer

void * hostPointer

Definition hip_runtime_api.h:265

hipPointerAttribute_t::type

enum hipMemoryType type

Definition hip_runtime_api.h:262

hipPointerAttribute_t::isManaged

int isManaged

Definition hip_runtime_api.h:266

hipPointerAttribute_t::devicePointer

void * devicePointer

Definition hip_runtime_api.h:264

hipPointerAttribute_t::allocationFlags

unsigned allocationFlags

Definition hip_runtime_api.h:267

hipResourceDesc

Definition driver_types.h:247

hipResourceViewDesc

Definition driver_types.h:303

hipTextureDesc

Definition texture_types.h:117

hipUUID

Definition hip_runtime_api.h:84

textureReference

Definition texture_types.h:96

surface_types.h

Defines surface types for HIP runtime.

hipSurfaceObject_t

struct __hip_surface * hipSurfaceObject_t

Definition surface_types.h:41

texture_types.h

hipTextureObject_t

struct __hip_texture * hipTextureObject_t

Definition texture_types.h:71

hipTextureAddressMode

hipTextureAddressMode

Definition texture_types.h:76

hipTextureFilterMode

hipTextureFilterMode

Definition texture_types.h:86

hipKernelNodeAttrValue

Definition hip_runtime_api.h:1300

hipKernelNodeAttrValue::cooperative

int cooperative

Definition hip_runtime_api.h:1302

hipKernelNodeAttrValue::accessPolicyWindow

hipAccessPolicyWindow accessPolicyWindow

Definition hip_runtime_api.h:1301

hipKernelNodeAttrValue::priority

int priority

Definition hip_runtime_api.h:1303