AI/rocm-systems
2
0
フォーク 0
コード イシュー プルリクエスト Actions パッケージ プロジェクト リリース Wiki アクティビティ

[HIPIFY] CUDA Runtime API functions total revise (up to CUDA 10.0)

ソースを参照 
+ for all CUDA versions starting from 7.0
+ add missing functions
+ sync with HIP
+ update CUDA_Runtime_API_functions_supported_by_HIP.md
+ update affected tests
+ fix typos
+ formatting, annotating
このコミットが含まれているのは:
Evgeny Mankov
2019-01-24 14:05:36 +03:00
親 bd658aa9ea
コミット 4ff355357f
6個のファイルの変更、676行の追加、388行の削除
Patchファイルをダウンロード Diffファイルをダウンロード すべてのファイルを展開 すべてのファイルを折り畳む
docs/markdown/CUDA_Driver_API_functions_supported_by_HIP.md
+3 -3
ファイルの表示
@@ -770,7 +770,7 @@
| **CUDA** | **HIP** |
|-----------------------------------------------------------|-------------------------------|
| `cuDeviceComputeCapability` | `hipDeviceComputeCapability` |
| `cuDeviceGetProperties` | `hipGetDeviceProperties` |
| `cuDeviceGetProperties` | |
## **7. Primary Context Management**
@@ -800,7 +800,7 @@
| `cuCtxPushCurrent` | `hipCtxPushCurrent` |
| `cuCtxSetCacheConfig` | `hipCtxSetCacheConfig` |
| `cuCtxSetCurrent` | `hipCtxSetCurrent` |
| `cuCtxSetLimit` | |
| `cuCtxSetLimit` | `hipDeviceSetLimit` |
| `cuCtxSetSharedMemConfig` | `hipCtxSetSharedMemConfig` |
| `cuCtxSynchronize` | `hipCtxSynchronize` |
@@ -861,7 +861,7 @@
| `cuMemcpyAsync` | |
| `cuMemcpyAtoA` | |
| `cuMemcpyAtoD` | |
| `cuMemcpyAtoH` | |
| `cuMemcpyAtoH` | `hipMemcpyAtoH` |
| `cuMemcpyAtoHAsync` | |
| `cuMemcpyDtoA` | |
| `cuMemcpyDtoD` | `hipMemcpyDtoD` |
docs/markdown/CUDA_Runtime_API_functions_supported_by_HIP.md
+56 -19
ファイルの表示
@@ -29,6 +29,7 @@
| `cudaSetDevice` | `hipSetDevice` |
| `cudaSetDeviceFlags` | `hipSetDeviceFlags` |
| `cudaSetValidDevices` | |
| `cudaDeviceGetP2PAttribute` | |
## **2. Thread Management [DEPRECATED]**
@@ -99,6 +100,7 @@
| **CUDA** | **HIP** |
|-----------------------------------------------------------|-------------------------------|
| `cudaFuncGetAttributes` | |
| `cudaFuncSetAttribute` | |
| `cudaFuncSetCacheConfig` | `hipFuncSetCacheConfig` |
| `cudaFuncSetSharedMemConfig` | |
| `cudaGetParameterBuffer` | |
@@ -106,6 +108,9 @@
| `cudaLaunchKernel` | `hipLaunchKernel` |
| `cudaSetDoubleForDevice` | |
| `cudaSetDoubleForHost` | |
| `cudaLaunchCooperativeKernel` | |
| `cudaLaunchCooperativeKernelMultiDevice` | |
| `cudaLaunchHostFunc` | |
## **8. Occupancy**
@@ -148,6 +153,7 @@
| `cudaMallocMipmappedArray` | |
| `cudaMallocPitch` | |
| `cudaMemGetInfo` | `hipMemGetInfo` |
| `cudaMemPrefetchAsync` | |
| `cudaMemcpy` | `hipMemcpy` |
| `cudaMemcpy2D` | `hipMemcpy2D` |
| `cudaMemcpy2DArrayToArray` | |
@@ -162,10 +168,10 @@
| `cudaMemcpy3DPeerAsync` | |
| `cudaMemcpyArrayToArray` | |
| `cudaMemcpyAsync` | `hipMemcpyAsync` |
| `cudaMemcpyFromArray` | `MemcpyFromArray` |
| `cudaMemcpyFromArray` | `hipMemcpyFromArray` |
| `cudaMemcpyFromArrayAsync` | |
| `cudaMemcpyFromSymbol` | `hipMemcpyFromSymbol` |
| `cudaMemcpyFromSymbolAsync` | |
| `cudaMemcpyFromSymbolAsync` | `hipMemcpyFromSymbolAsync` |
| `cudaMemcpyPeer` | `hipMemcpyPeer` |
| `cudaMemcpyPeerAsync` | `hipMemcpyPeerAsync` |
| `cudaMemcpyToArray` | `hipMemcpyToArray` |
@@ -299,11 +305,13 @@
| `cudaEGLStreamConsumerAcquireFrame` | |
| `cudaEGLStreamConsumerConnect` | |
| `cudaEGLStreamConsumerConnectWithFlags` | |
| `cudaEGLStreamConsumerDisconnect` | |
| `cudaEGLStreamConsumerReleaseFrame` | |
| `cudaEGLStreamProducerConnect` | |
| `cudaEGLStreamProducerDisconnect` | |
| `cudaEGLStreamProducerPresentFrame` | |
| `cudaEGLStreamProducerReturnFrame` | |
| `cudaEventCreateFromEGLSync` | |
| `cudaGraphicsEGLRegisterImage` | |
| `cudaGraphicsResourceGetMappedEglFrame` | |
@@ -321,17 +329,17 @@
## **24. Texture Reference Management**
| **CUDA** | **HIP** |
|-----------------------------------------------------------|-------------------------------|
| `cudaBindTexture` | `hipBindTexture` |
| `cudaBindTexture2D` | `hipBindTexture2D` |
| `cudaBindTextureToArray` | `hipBindTextureToArray` |
| `cudaBindTextureToMipmappedArray` | |
| `cudaCreateChannelDesc` | `hipCreateChannelDesc` |
| `cudaGetChannelDesc` | `hipGetChannelDesc` |
| `cudaGetTextureAlignmentOffset` | |
| `cudaGetTextureReference` | |
| `cudaUnbindTexture` | `hipUnbindTexture` |
| **CUDA** | **HIP** |
|-----------------------------------------------------------|----------------------------------|
| `cudaBindTexture` | `hipBindTexture` |
| `cudaBindTexture2D` | `hipBindTexture2D` |
| `cudaBindTextureToArray` | `hipBindTextureToArray` |
| `cudaBindTextureToMipmappedArray` | `hipBindTextureToMipmappedArray` |
| `cudaCreateChannelDesc` | `hipCreateChannelDesc` |
| `cudaGetChannelDesc` | `hipGetChannelDesc` |
| `cudaGetTextureAlignmentOffset` | `hipGetTextureAlignmentOffset` |
| `cudaGetTextureReference` | `hipGetTextureReference` |
| `cudaUnbindTexture` | `hipUnbindTexture` |
## **25. Surface Reference Management**
@@ -369,6 +377,37 @@
| **CUDA** | **HIP** |
|-----------------------------------------------------------|-------------------------------|
| `cudaGraphAddChildGraphNode` | |
| `cudaGraphAddDependencies` | |
| `cudaGraphAddEmptyNode` | |
| `cudaGraphAddHostNode` | |
| `cudaGraphAddKernelNode` | |
| `cudaGraphAddMemcpyNode` | |
| `cudaGraphAddMemsetNode` | |
| `cudaGraphChildGraphNodeGetGraph` | |
| `cudaGraphClone` | |
| `cudaGraphCreate` | |
| `cudaGraphDestroy` | |
| `cudaGraphDestroyNode` | |
| `cudaGraphExecDestroy` | |
| `cudaGraphGetEdges` | |
| `cudaGraphGetNodes` | |
| `cudaGraphGetRootNodes` | |
| `cudaGraphHostNodeGetParams` | |
| `cudaGraphHostNodeSetParams` | |
| `cudaGraphInstantiate` | |
| `cudaGraphKernelNodeGetParams` | |
| `cudaGraphKernelNodeSetParams` | |
| `cudaGraphLaunch` | |
| `cudaGraphMemcpyNodeGetParams` | |
| `cudaGraphMemcpyNodeSetParams` | |
| `cudaGraphMemsetNodeGetParams` | |
| `cudaGraphMemsetNodeSetParams` | |
| `cudaGraphNodeFindInClone` | |
| `cudaGraphNodeGetDependencies` | |
| `cudaGraphNodeGetDependentNodes` | |
| `cudaGraphNodeGetType` | |
| `cudaGraphRemoveDependencies` | |
## **30. C++ API Routines**
*(7.0 contains, 7.5 doesn’t)*
@@ -381,12 +420,15 @@
| `cudaBindTextureToArray` | |
| `cudaBindTextureToMipmappedArray` | |
| `cudaCreateChannelDesc` | `hipCreateChannelDesc` |
| `cudaEventCreate` | |
| `cudaFuncGetAttributes` | |
| `cudaFuncSetAttribute` | |
| `cudaFuncSetCacheConfig` | |
| `cudaGetSymbolAddress` | `hipGetSymbolAddress` |
| `cudaGetSymbolSize` | `hipGetSymbolSize` |
| `cudaGetTextureAlignmentOffset` | |
| `cudaLaunch` | |
| `cudaLaunchCooperativeKernel` | |
| `cudaLaunchKernel` | |
| `cudaMallocHost` | |
| `cudaMallocManaged` | |
@@ -397,9 +439,9 @@
| `cudaOccupancyMaxActiveBlocksPerMultiprocessor` | `hipOccupancyMaxActiveBlocksPerMultiprocessor` |
| `cudaOccupancyMaxActiveBlocksPerMultiprocessorWithFlags` | |
| `cudaOccupancyMaxPotentialBlockSize` | `hipOccupancyMaxPotentialBlockSize` |
| `cudaOccupancyMaxPotentialBlockSizeWithFlags` | |
| `cudaOccupancyMaxPotentialBlockSizeVariableSMem` | |
| `cudaOccupancyMaxPotentialBlockSizeVariableSMemWithFlags` | |
| `cudaOccupancyMaxPotentialBlockSizeWithFlags` | |
| `cudaSetupArgument` | |
| `cudaStreamAttachMemAsync` | |
| `cudaUnbindTexture` | `hipUnbindTexture` |
@@ -876,11 +918,6 @@
| 1 |*`cudaAddressModeClamp`* |*`hipAddressModeClamp`* |
| 2 |*`cudaAddressModeMirror`* |*`hipAddressModeMirror`* |
| 3 |*`cudaAddressModeBorder`* |*`hipAddressModeBorder`* |
| enum |***`cudaTextureAddressMode`*** |***`hipTextureAddressMode`*** |
| 0 |*`cudaAddressModeWrap`* |*`hipAddressModeWrap`* |
| 1 |*`cudaAddressModeClamp`* |*`hipAddressModeClamp`* |
| 2 |*`cudaAddressModeMirror`* |*`hipAddressModeMirror`* |
| 3 |*`cudaAddressModeBorder`* |*`hipAddressModeBorder`* |
| enum |***`cudaTextureFilterMode`*** |***`hipTextureFilterMode`*** |
| 0 |*`cudaFilterModePoint`* |*`hipFilterModePoint`* |
| 1 |*`cudaFilterModeLinear`* |*`hipFilterModeLinear`* |