AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity

[HIPIFY] Cooperative groups support

Browse Source
This commit is contained in:
Evgeny Mankov
2019-08-12 19:20:13 +03:00
parent f8084a4c91
commit af557aaaf6
6 changed files with 70 additions and 69 deletions
Download Patch File Download Diff File Expand all files Collapse all files
hipamd/docs/markdown/CUDA_Driver_API_functions_supported_by_HIP.md
+5 -5
View File
@@ -166,8 +166,8 @@
| 92 |*`CU_DEVICE_ATTRIBUTE_CAN_USE_STREAM_MEM_OPS`* | | 9.0 |
| 93 |*`CU_DEVICE_ATTRIBUTE_CAN_USE_64_BIT_STREAM_MEM_OPS`* | | 9.0 |
| 94 |*`CU_DEVICE_ATTRIBUTE_CAN_USE_STREAM_WAIT_VALUE_NOR`* | | 9.0 |
| 95 |*`CU_DEVICE_ATTRIBUTE_COOPERATIVE_LAUNCH`* | | 9.0 |
| 96 |*`CU_DEVICE_ATTRIBUTE_COOPERATIVE_MULTI_DEVICE_LAUNCH`* | | 9.0 |
| 95 |*`CU_DEVICE_ATTRIBUTE_COOPERATIVE_LAUNCH`* |*`hipDeviceAttributeCooperativeLaunch`* | 9.0 |
| 96 |*`CU_DEVICE_ATTRIBUTE_COOPERATIVE_MULTI_DEVICE_LAUNCH`* |*`hipDeviceAttributeCooperativeMultiDeviceLaunch`* | 9.0 |
| 97 |*`CU_DEVICE_ATTRIBUTE_MAX_SHARED_MEMORY_PER_BLOCK_OPTIN`* | | 9.0 |
| 98 |*`CU_DEVICE_ATTRIBUTE_CAN_FLUSH_REMOTE_WRITES`* | | 9.2 |
| 99 |*`CU_DEVICE_ATTRIBUTE_HOST_REGISTER_SUPPORTED`* | | 9.2 |
@@ -1044,9 +1044,9 @@
| **CUDA** | **HIP** |**CUDA version\***|
|-----------------------------------------------------------|---------------------------------------------------------|------------------|
| `cuOccupancyMaxActiveBlocksPerMultiprocessor` | `hipOccupancyMaxActiveBlocksPerMultiprocessor` |
| `cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags` | |
| `cuOccupancyMaxPotentialBlockSize` | `hipOccupancyMaxPotentialBlockSize` |
| `cuOccupancyMaxActiveBlocksPerMultiprocessor` |`hipOccupancyMaxActiveBlocksPerMultiprocessor` |
| `cuOccupancyMaxActiveBlocksPerMultiprocessorWithFlags` |`hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags` |
| `cuOccupancyMaxPotentialBlockSize` |`hipOccupancyMaxPotentialBlockSize` |
| `cuOccupancyMaxPotentialBlockSizeWithFlags` | |
## **21. Texture Reference Management**
hipamd/docs/markdown/CUDA_Runtime_API_functions_supported_by_HIP.md
+56 -55
View File
@@ -99,27 +99,27 @@
## **7. Execution Control**
| **CUDA** | **HIP** |**CUDA version\***|
|-----------------------------------------------------------|-------------------------------|:----------------:|
| `cudaFuncGetAttributes` | |
| `cudaFuncSetAttribute` | | 9.0 |
| `cudaFuncSetCacheConfig` | `hipFuncSetCacheConfig` |
| `cudaFuncSetSharedMemConfig` | |
| `cudaGetParameterBuffer` | |
| `cudaGetParameterBufferV2` | |
| `cudaLaunchKernel` | `hipLaunchKernel` |
| `cudaSetDoubleForDevice` | |
| `cudaSetDoubleForHost` | |
| `cudaLaunchCooperativeKernel` | | 9.0 |
| `cudaLaunchCooperativeKernelMultiDevice` | | 9.0 |
| `cudaLaunchHostFunc` | | 10.0 |
| **CUDA** | **HIP** |**CUDA version\***|
|-----------------------------------------------------------|---------------------------------------|:----------------:|
| `cudaFuncGetAttributes` | |
| `cudaFuncSetAttribute` | | 9.0 |
| `cudaFuncSetCacheConfig` |`hipFuncSetCacheConfig` |
| `cudaFuncSetSharedMemConfig` | |
| `cudaGetParameterBuffer` | |
| `cudaGetParameterBufferV2` | |
| `cudaLaunchKernel` |`hipLaunchKernel` |
| `cudaSetDoubleForDevice` | |
| `cudaSetDoubleForHost` | |
| `cudaLaunchCooperativeKernel` |`hipLaunchCooperativeKernel` | 9.0 |
| `cudaLaunchCooperativeKernelMultiDevice` |`hipLaunchCooperativeKernelMultiDevice`| 9.0 |
| `cudaLaunchHostFunc` | | 10.0 |
## **8. Occupancy**
| **CUDA** | **HIP** |**CUDA version\***|
|-----------------------------------------------------------|-----------------------------------------------|:----------------:|
| `cudaOccupancyMaxActiveBlocksPerMultiprocessor` | `hipOccupancyMaxActiveBlocksPerMultiprocessor`|
| `cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags` | |
| **CUDA** | **HIP** |**CUDA version\***|
|-----------------------------------------------------------|-------------------------------------------------------|:----------------:|
| `cudaOccupancyMaxActiveBlocksPerMultiprocessor` |`hipOccupancyMaxActiveBlocksPerMultiprocessor` |
| `cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags` |`hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags`|
## **9. Execution Control [DEPRECATED since 7.0]**
@@ -413,41 +413,42 @@
| `cudaGraphRemoveDependencies` | | 10.0 |
## **30. C++ API Routines**
*(7.0 contains, 7.5 doesn’t)*
*(7.0 contains, 7.5 doesn't)*
| **CUDA** | **HIP** |**CUDA version\***|
|-----------------------------------------------------------|------------------------------------------------|:----------------:|
| `cudaBindSurfaceToArray` | |
| `cudaBindTexture` | `hipBindTexture` |
| `cudaBindTexture2D` | |
| `cudaBindTextureToArray` | |
| `cudaBindTextureToMipmappedArray` | |
| `cudaCreateChannelDesc` | `hipCreateChannelDesc` |
| `cudaEventCreate` | |
| `cudaFuncGetAttributes` | |
| `cudaFuncSetAttribute` | |
| `cudaFuncSetCacheConfig` | |
| `cudaGetSymbolAddress` | `hipGetSymbolAddress` |
| `cudaGetSymbolSize` | `hipGetSymbolSize` |
| `cudaGetTextureAlignmentOffset` | |
| `cudaLaunch` | |
| `cudaLaunchCooperativeKernel` | |
| `cudaLaunchKernel` | |
| `cudaMallocHost` | |
| `cudaMallocManaged` | |
| `cudaMemcpyFromSymbol` | |
| `cudaMemcpyFromSymbolAsync` | |
| `cudaMemcpyToSymbol` | |
| `cudaMemcpyToSymbolAsync` | |
| `cudaOccupancyMaxActiveBlocksPerMultiprocessor` | `hipOccupancyMaxActiveBlocksPerMultiprocessor` |
| `cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags` | |
| `cudaOccupancyMaxPotentialBlockSize` | `hipOccupancyMaxPotentialBlockSize` |
| `cudaOccupancyMaxPotentialBlockSizeWithFlags` | |
| `cudaOccupancyMaxPotentialBlockSizeVariableSMem` | |
| `cudaOccupancyMaxPotentialBlockSizeVariableSMemWithFlags` | |
| `cudaSetupArgument` | |
| `cudaStreamAttachMemAsync` | |
| `cudaUnbindTexture` | `hipUnbindTexture` |
| **CUDA** | **HIP** |**CUDA version\***|
|-----------------------------------------------------------|-------------------------------------------------------|:----------------:|
| `cudaBindSurfaceToArray` | |
| `cudaBindTexture` |`hipBindTexture` |
| `cudaBindTexture2D` | |
| `cudaBindTextureToArray` | |
| `cudaBindTextureToMipmappedArray` | |
| `cudaCreateChannelDesc` |`hipCreateChannelDesc` |
| `cudaEventCreate` | |
| `cudaFuncGetAttributes` | |
| `cudaFuncSetAttribute` | |
| `cudaFuncSetCacheConfig` | |
| `cudaGetSymbolAddress` |`hipGetSymbolAddress` |
| `cudaGetSymbolSize` |`hipGetSymbolSize` |
| `cudaGetTextureAlignmentOffset` | |
| `cudaLaunch` | |
| `cudaLaunchCooperativeKernel` |`hipLaunchCooperativeKernel` |
| `cudaLaunchCooperativeKernelMultiDevice` |`hipLaunchCooperativeKernelMultiDevice` |
| `cudaLaunchKernel` | |
| `cudaMallocHost` | |
| `cudaMallocManaged` | |
| `cudaMemcpyFromSymbol` | |
| `cudaMemcpyFromSymbolAsync` | |
| `cudaMemcpyToSymbol` | |
| `cudaMemcpyToSymbolAsync` | |
| `cudaOccupancyMaxActiveBlocksPerMultiprocessor` |`hipOccupancyMaxActiveBlocksPerMultiprocessor` |
| `cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags` |`hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags`|
| `cudaOccupancyMaxPotentialBlockSize` |`hipOccupancyMaxPotentialBlockSize` |
| `cudaOccupancyMaxPotentialBlockSizeWithFlags` | |
| `cudaOccupancyMaxPotentialBlockSizeVariableSMem` | |
| `cudaOccupancyMaxPotentialBlockSizeVariableSMemWithFlags` | |
| `cudaSetupArgument` | |
| `cudaStreamAttachMemAsync` | |
| `cudaUnbindTexture` |`hipUnbindTexture` |
## **32. Profiler Control**
@@ -593,8 +594,8 @@
| 92 |*`cudaDevAttrReserved92`* | 9.0 | |
| 93 |*`cudaDevAttrReserved93`* | 9.0 | |
| 94 |*`cudaDevAttrReserved94`* | 9.0 | |
| 95 |*`cudaDevAttrCooperativeLaunch`* | 9.0 | |
| 96 |*`cudaDevAttrCooperativeMultiDeviceLaunch`* | 9.0 | |
| 95 |*`cudaDevAttrCooperativeLaunch`* | 9.0 |*`hipDeviceAttributeCooperativeLaunch`* |
| 96 |*`cudaDevAttrCooperativeMultiDeviceLaunch`* | 9.0 |*`hipDeviceAttributeCooperativeMultiDeviceLaunch`* |
| 97 |*`cudaDevAttrMaxSharedMemoryPerBlockOptin`* | 9.0 | |
| 98 |*`cudaDevAttrCanFlushRemoteWrites`* | 9.2 | |
| 99 |*`cudaDevAttrHostRegisterSupported`* | 9.2 | |
@@ -1063,7 +1064,7 @@
| struct |`cudaExternalSemaphoreSignalParams` | 10.0 | |
| struct |`cudaExternalSemaphoreWaitParams` | 10.0 | |
| struct |`cudaHostNodeParams` | 10.0 | |
| struct |`cudaLaunchParams` | 9.0 | |
| struct |`cudaLaunchParams` | 9.0 |`hipLaunchParams` |
| struct |`cudaMemsetParams` | 10.0 | |
| struct |`CUeglStreamConnection_st` | 9.1 | |
| typedef |`cudaEglStreamConnection` | 9.1 | |