Skip to content

Commit

Permalink
Merge pull request ROCm#1554 from emankov/HIPIFY
Browse files Browse the repository at this point in the history
[HIPIFY] Sync with CUDA 12.5.0 - Step 7 - Runtime API documentation
  • Loading branch information
emankov authored Jun 24, 2024
2 parents a7364ab + 2673fa0 commit 8f85a4d
Show file tree
Hide file tree
Showing 3 changed files with 136 additions and 118 deletions.
88 changes: 49 additions & 39 deletions docs/tables/CUDA_Runtime_API_functions_supported_by_HIP.md
Original file line number Diff line number Diff line change
Expand Up @@ -15,14 +15,12 @@
|`cudaDeviceGetNvSciSyncAttributes`|10.2| | | | | | | | | |
|`cudaDeviceGetP2PAttribute`|8.0| | | |`hipDeviceGetP2PAttribute`|3.8.0| | | | |
|`cudaDeviceGetPCIBusId`| | | | |`hipDeviceGetPCIBusId`|1.6.0| | | | |
|`cudaDeviceGetSharedMemConfig`| |12.4| | |`hipDeviceGetSharedMemConfig`|1.6.0| | | | |
|`cudaDeviceGetStreamPriorityRange`| | | | |`hipDeviceGetStreamPriorityRange`|2.0.0| | | | |
|`cudaDeviceGetTexture1DLinearMaxWidth`|11.1| | | | | | | | | |
|`cudaDeviceReset`| | | | |`hipDeviceReset`|1.6.0| | | | |
|`cudaDeviceSetCacheConfig`| | | | |`hipDeviceSetCacheConfig`|1.6.0| | | | |
|`cudaDeviceSetLimit`| | | | |`hipDeviceSetLimit`|5.3.0| | | | |
|`cudaDeviceSetMemPool`|11.2| | | |`hipDeviceSetMemPool`|5.2.0| | | | |
|`cudaDeviceSetSharedMemConfig`| |12.4| | |`hipDeviceSetSharedMemConfig`|1.6.0| | | | |
|`cudaDeviceSynchronize`| | | | |`hipDeviceSynchronize`|1.6.0| | | | |
|`cudaGetDevice`| | | | |`hipGetDevice`|1.6.0| | | | |
|`cudaGetDeviceCount`| | | | |`hipGetDeviceCount`|1.6.0| | | | |
Expand All @@ -38,7 +36,14 @@
|`cudaSetDeviceFlags`| | | | |`hipSetDeviceFlags`|1.6.0| | | | |
|`cudaSetValidDevices`| | | | | | | | | | |

## **2. Thread Management [DEPRECATED]**
## **2. Device Management [DEPRECATED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaDeviceGetSharedMemConfig`| |12.4| | |`hipDeviceGetSharedMemConfig`|1.6.0| | | | |
|`cudaDeviceSetSharedMemConfig`| |12.4| | |`hipDeviceSetSharedMemConfig`|1.6.0| | | | |

## **3. Thread Management [DEPRECATED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -49,7 +54,7 @@
|`cudaThreadSetLimit`| |10.0| | | | | | | | |
|`cudaThreadSynchronize`| |10.0| | |`hipDeviceSynchronize`|1.6.0| | | | |

## **3. Error Handling**
## **4. Error Handling**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -58,7 +63,7 @@
|`cudaGetLastError`| | | | |`hipGetLastError`|1.6.0| | | | |
|`cudaPeekAtLastError`| | | | |`hipPeekAtLastError`|1.6.0| | | | |

## **4. Stream Management**
## **5. Stream Management**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand Down Expand Up @@ -88,7 +93,7 @@
|`cudaStreamWaitEvent`| | | | |`hipStreamWaitEvent`|1.6.0| | | | |
|`cudaThreadExchangeStreamCaptureMode`|10.1| | | |`hipThreadExchangeStreamCaptureMode`|5.2.0| | | | |

## **5. Event Management**
## **6. Event Management**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -101,7 +106,7 @@
|`cudaEventRecordWithFlags`|11.1| | | | | | | | | |
|`cudaEventSynchronize`| | | | |`hipEventSynchronize`|1.6.0| | | | |

## **6. External Resource Interoperability**
## **7. External Resource Interoperability**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -114,7 +119,7 @@
|`cudaSignalExternalSemaphoresAsync`|10.0| | | |`hipSignalExternalSemaphoresAsync`|4.4.0| | | | |
|`cudaWaitExternalSemaphoresAsync`|10.0| | | |`hipWaitExternalSemaphoresAsync`|4.4.0| | | | |

## **7. Execution Control**
## **8. Execution Control**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -123,7 +128,6 @@
|`cudaFuncGetParamInfo`|12.4| | | | | | | | | |
|`cudaFuncSetAttribute`|9.0| | | |`hipFuncSetAttribute`|3.9.0| | | | |
|`cudaFuncSetCacheConfig`| | | | |`hipFuncSetCacheConfig`|1.6.0| | | | |
|`cudaFuncSetSharedMemConfig`| |12.4| | |`hipFuncSetSharedMemConfig`|3.9.0| | | | |
|`cudaGetParameterBuffer`| | | | | | | | | | |
|`cudaGetParameterBufferV2`| | | | | | | | | | |
|`cudaLaunchCooperativeKernel`|9.0| | | |`hipLaunchCooperativeKernel`|2.6.0| | | | |
Expand All @@ -134,7 +138,13 @@
|`cudaSetDoubleForDevice`| |10.0| | | | | | | | |
|`cudaSetDoubleForHost`| |10.0| | | | | | | | |

## **8. Occupancy**
## **9. Execution Control [DEPRECATED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaFuncSetSharedMemConfig`| |12.4| | |`hipFuncSetSharedMemConfig`|3.9.0| | | | |

## **10. Occupancy**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -148,7 +158,7 @@
|`cudaOccupancyMaxPotentialBlockSizeWithFlags`| | | | |`hipOccupancyMaxPotentialBlockSizeWithFlags`|3.5.0| | | | |
|`cudaOccupancyMaxPotentialClusterSize`|11.8| | | | | | | | | |

## **9. Memory Management**
## **11. Memory Management**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand Down Expand Up @@ -214,7 +224,7 @@
|`make_cudaPitchedPtr`| | | | |`make_hipPitchedPtr`|1.7.0| | | | |
|`make_cudaPos`| | | | |`make_hipPos`|1.7.0| | | | |

## **10. Memory Management [DEPRECATED]**
## **12. Memory Management [DEPRECATED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -224,7 +234,7 @@
|`cudaMemcpyToArray`| |10.1| | |`hipMemcpyToArray`|1.6.0|3.8.0| | | |
|`cudaMemcpyToArrayAsync`| |10.1| | | | | | | | |

## **11. Stream Ordered Memory Allocator**
## **13. Stream Ordered Memory Allocator**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -243,21 +253,21 @@
|`cudaMemPoolSetAttribute`|11.2| | | |`hipMemPoolSetAttribute`|5.2.0| | | | |
|`cudaMemPoolTrimTo`|11.2| | | |`hipMemPoolTrimTo`|5.2.0| | | | |

## **12. Unified Addressing**
## **14. Unified Addressing**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaPointerGetAttributes`| | | | |`hipPointerGetAttributes`|1.6.0| | | | |

## **13. Peer Device Memory Access**
## **15. Peer Device Memory Access**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaDeviceCanAccessPeer`| | | | |`hipDeviceCanAccessPeer`|1.9.0| | | | |
|`cudaDeviceDisablePeerAccess`| | | | |`hipDeviceDisablePeerAccess`|1.9.0| | | | |
|`cudaDeviceEnablePeerAccess`| | | | |`hipDeviceEnablePeerAccess`|1.9.0| | | | |

## **14. OpenGL Interoperability**
## **16. OpenGL Interoperability**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -266,7 +276,7 @@
|`cudaGraphicsGLRegisterImage`| | | | |`hipGraphicsGLRegisterImage`|5.1.0| | | | |
|`cudaWGLGetDevice`| | | | | | | | | | |

## **15. OpenGL Interoperability [DEPRECATED]**
## **17. OpenGL Interoperability [DEPRECATED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -279,7 +289,7 @@
|`cudaGLUnmapBufferObjectAsync`| |10.0| | | | | | | | |
|`cudaGLUnregisterBufferObject`| |10.0| | | | | | | | |

## **16. Direct3D 9 Interoperability**
## **18. Direct3D 9 Interoperability**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -289,7 +299,7 @@
|`cudaD3D9SetDirect3DDevice`| | | | | | | | | | |
|`cudaGraphicsD3D9RegisterResource`| | | | | | | | | | |

## **17. Direct3D 9 Interoperability [DEPRECATED]**
## **19. Direct3D 9 Interoperability [DEPRECATED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -304,15 +314,15 @@
|`cudaD3D9UnmapResources`| |10.0| | | | | | | | |
|`cudaD3D9UnregisterResource`| |10.0| | | | | | | | |

## **18. Direct3D 10 Interoperability**
## **20. Direct3D 10 Interoperability**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaD3D10GetDevice`| | | | | | | | | | |
|`cudaD3D10GetDevices`| | | | | | | | | | |
|`cudaGraphicsD3D10RegisterResource`| | | | | | | | | | |

## **19. Direct3D 10 Interoperability [DEPRECATED]**
## **21. Direct3D 10 Interoperability [DEPRECATED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -329,22 +339,22 @@
|`cudaD3D10UnmapResources`| |10.0| | | | | | | | |
|`cudaD3D10UnregisterResource`| |10.0| | | | | | | | |

## **20. Direct3D 11 Interoperability**
## **22. Direct3D 11 Interoperability**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaD3D11GetDevice`| | | | | | | | | | |
|`cudaD3D11GetDevices`| | | | | | | | | | |
|`cudaGraphicsD3D11RegisterResource`| | | | | | | | | | |

## **21. Direct3D 11 Interoperability [DEPRECATED]**
## **23. Direct3D 11 Interoperability [DEPRECATED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaD3D11GetDirect3DDevice`| |10.0| | | | | | | | |
|`cudaD3D11SetDirect3DDevice`| |10.0| | | | | | | | |

## **22. VDPAU Interoperability**
## **24. VDPAU Interoperability**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -353,7 +363,7 @@
|`cudaVDPAUGetDevice`| | | | | | | | | | |
|`cudaVDPAUSetVDPAUDevice`| | | | | | | | | | |

## **23. EGL Interoperability**
## **25. EGL Interoperability**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -370,7 +380,7 @@
|`cudaGraphicsEGLRegisterImage`|9.1| | | | | | | | | |
|`cudaGraphicsResourceGetMappedEglFrame`|9.1| | | | | | | | | |

## **24. Graphics Interoperability**
## **26. Graphics Interoperability**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -382,7 +392,7 @@
|`cudaGraphicsUnmapResources`| | | | |`hipGraphicsUnmapResources`|4.5.0| | | | |
|`cudaGraphicsUnregisterResource`| | | | |`hipGraphicsUnregisterResource`|4.5.0| | | | |

## **25. Texture Object Management**
## **27. Texture Object Management**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -396,22 +406,22 @@
|`cudaGetTextureObjectTextureDesc`| | | | |`hipGetTextureObjectTextureDesc`|1.7.0| | | | |
|`cudaGetTextureObjectTextureDesc_v2`|11.8| | |12.0| | | | | | |

## **26. Surface Object Management**
## **28. Surface Object Management**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaCreateSurfaceObject`| | | | |`hipCreateSurfaceObject`|1.9.0| | | | |
|`cudaDestroySurfaceObject`| | | | |`hipDestroySurfaceObject`|1.9.0| | | | |
|`cudaGetSurfaceObjectResourceDesc`| | | | | | | | | | |

## **27. Version Management**
## **29. Version Management**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaDriverGetVersion`| | | | |`hipDriverGetVersion`|1.6.0| | | | |
|`cudaRuntimeGetVersion`| | | | |`hipRuntimeGetVersion`|1.6.0| | | | |

## **28. Graph Management**
## **30. Graph Management**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand Down Expand Up @@ -510,33 +520,33 @@
|`cudaUserObjectRelease`|11.3| | | |`hipUserObjectRelease`|5.3.0| | | | |
|`cudaUserObjectRetain`|11.3| | | |`hipUserObjectRetain`|5.3.0| | | | |

## **29. Driver Entry Point Access**
## **31. Driver Entry Point Access**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaGetDriverEntryPoint`|11.3| |12.0| |`hipGetProcAddress`|6.2.0| | | |6.2.0|
|`cudaGetDriverEntryPointByVersion`|12.5| | | | | | | | | |

## **30. C++ API Routines**
## **32. C++ API Routines**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaGetKernel`|12.1| | | | | | | | | |

## **31. Interactions with the CUDA Driver API**
## **33. Interactions with the CUDA Driver API**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaGetFuncBySymbol`|11.0| | | |`hipGetFuncBySymbol`|6.2.0| | | |6.2.0|

## **32. Profiler Control**
## **34. Profiler Control**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaProfilerStart`| | | | |`hipProfilerStart`|1.6.0|3.0.0| | | |
|`cudaProfilerStop`| | | | |`hipProfilerStop`|1.6.0|3.0.0| | | |

## **33. Data types used by CUDA Runtime**
## **35. Data types used by CUDA Runtime**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand Down Expand Up @@ -1490,15 +1500,15 @@
|`texture`| | | |12.0|`texture`| | | | | |
|`textureReference`| | | | |`textureReference`|1.6.0| | | | |

## **34. Execution Control [REMOVED]**
## **36. Execution Control [REMOVED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaConfigureCall`| | | |10.1|`hipConfigureCall`|1.9.0| | | | |
|`cudaLaunch`| | | |10.1|`hipLaunchByPtr`|1.9.0| | | | |
|`cudaSetupArgument`| | | |10.1|`hipSetupArgument`|1.9.0| | | | |

## **35. Texture Reference Management [REMOVED]**
## **37. Texture Reference Management [REMOVED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand All @@ -1510,14 +1520,14 @@
|`cudaGetTextureReference`| |11.0| |12.0|`hipGetTextureReference`|1.7.0|5.3.0| | | |
|`cudaUnbindTexture`| |11.0| |12.0|`hipUnbindTexture`|1.6.0|3.8.0| | | |

## **36. Surface Reference Management [REMOVED]**
## **38. Surface Reference Management [REMOVED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
|`cudaBindSurfaceToArray`| |11.0| |12.0| | | | | | |
|`cudaGetSurfaceReference`| |11.0| |12.0| | | | | | |

## **37. Profiler Control [REMOVED]**
## **39. Profiler Control [REMOVED]**

|**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|
|:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
Expand Down
Loading

0 comments on commit 8f85a4d

Please sign in to comment.