Skip to content

Commit

Permalink
[HIPIFY][DNN] cuDNN 9.5.0 is the latest supported version
Browse files Browse the repository at this point in the history
+ Updated the regenerated `hipify-perl` and `DNN` `CUDA2HIP` documentation
  • Loading branch information
emankov committed Oct 9, 2024
1 parent d4cd537 commit f127308
Show file tree
Hide file tree
Showing 9 changed files with 60 additions and 21 deletions.
6 changes: 6 additions & 0 deletions bin/hipify-perl
Original file line number Diff line number Diff line change
Expand Up @@ -9770,8 +9770,10 @@ sub warnUnsupportedFunctions {
"cudnnBatchNormalizationForwardTrainingEx",
"cudnnBatchNormalizationBackwardEx",
"cudnnBatchNormOps_t",
"cudnnBackendUpdateCudaGraph",
"cudnnBackendTensorReordering_t",
"cudnnBackendSetAttribute",
"cudnnBackendPopulateCudaGraph",
"cudnnBackendNumericalNote_t",
"cudnnBackendNormMode_t",
"cudnnBackendNormFwdPhase_t",
Expand Down Expand Up @@ -11342,6 +11344,7 @@ sub warnUnsupportedFunctions {
"CUDNN_STATUS_NOT_SUPPORTED_INCOMPATIBLE_CUDART",
"CUDNN_STATUS_NOT_SUPPORTED_GRAPH_PATTERN",
"CUDNN_STATUS_NOT_SUPPORTED_DATA_TYPE",
"CUDNN_STATUS_NOT_SUPPORTED_CUDA_GRAPH_NATIVE_API",
"CUDNN_STATUS_NOT_SUPPORTED_BAD_LAUNCH_PARAM",
"CUDNN_STATUS_NOT_SUPPORTED_ARCH_MISMATCH",
"CUDNN_STATUS_INTERNAL_ERROR_UNEXPECTED_VALUE",
Expand All @@ -11365,6 +11368,7 @@ sub warnUnsupportedFunctions {
"CUDNN_STATUS_BAD_PARAM_NOT_FINALIZED",
"CUDNN_STATUS_BAD_PARAM_MISALIGNED_POINTER",
"CUDNN_STATUS_BAD_PARAM_DUPLICATED_ENTRIES",
"CUDNN_STATUS_BAD_PARAM_CUDA_GRAPH_MISMATCH",
"CUDNN_STATUS_BAD_PARAM_ATTRIBUTE_TYPE",
"CUDNN_SIGNAL_WAIT",
"CUDNN_SIGNAL_SET",
Expand Down Expand Up @@ -11644,6 +11648,7 @@ sub warnUnsupportedFunctions {
"CUDNN_BN_FINALIZE_STATISTICS_TRAINING",
"CUDNN_BN_FINALIZE_STATISTICS_INFERENCE",
"CUDNN_BEHAVIOR_NOTE_TYPE_COUNT",
"CUDNN_BEHAVIOR_NOTE_SUPPORTS_CUDA_GRAPH_NATIVE_API",
"CUDNN_BEHAVIOR_NOTE_RUNTIME_COMPILATION",
"CUDNN_BEHAVIOR_NOTE_REQUIRES_FILTER_INT8x32_REORDER",
"CUDNN_BEHAVIOR_NOTE_REQUIRES_BIAS_INT8x32_REORDER",
Expand Down Expand Up @@ -11873,6 +11878,7 @@ sub warnUnsupportedFunctions {
"CUDNN_ATTR_KNOB_INFO_MAXIMUM_VALUE",
"CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE",
"CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE",
"CUDNN_ATTR_KERNEL_CACHE_OPERATION_GRAPH",
"CUDNN_ATTR_KERNEL_CACHE_IS_ENGINECFG_KERNEL_CACHED",
"CUDNN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID",
"CUDNN_ATTR_INTERMEDIATE_INFO_SIZE",
Expand Down
22 changes: 11 additions & 11 deletions docs/hipify-clang.rst
Original file line number Diff line number Diff line change
Expand Up @@ -546,7 +546,7 @@ LLVM >= 10.0.0

.. code-block:: shell
-DCUDA_DNN_ROOT_DIR=D:/CUDA/cuDNN/9.4.0
-DCUDA_DNN_ROOT_DIR=D:/CUDA/cuDNN/9.5.0
5. [Optional] Install `CUB 1.9.8 <https://github.com/NVIDIA/cub/releases/tag/1.9.8>`_ for ``CUDA < 11.0`` only;
for ``CUDA >= 11.0``, the CUB shipped with CUDA will be used for testing.
Expand Down Expand Up @@ -638,8 +638,8 @@ On Linux, the following configurations are tested:

* Ubuntu 14: LLVM 4.0.0 - 7.1.0, CUDA 7.0 - 9.0, cuDNN 5.0.5 - 7.6.5
* Ubuntu 16-19: LLVM 8.0.0 - 14.0.6, CUDA 7.0 - 10.2, cuDNN 5.1.10 - 8.0.5
* Ubuntu 20-21: LLVM 9.0.0 - 19.1.1, CUDA 7.0 - 12.6.1, cuDNN 5.1.10 - 9.4.0
* Ubuntu 22-23: LLVM 13.0.0 - 19.1.1, CUDA 7.0 - 12.6.1, cuDNN 8.0.5 - 9.4.0
* Ubuntu 20-21: LLVM 9.0.0 - 19.1.1, CUDA 7.0 - 12.6.1, cuDNN 5.1.10 - 9.5.0
* Ubuntu 22-23: LLVM 13.0.0 - 19.1.1, CUDA 7.0 - 12.6.1, cuDNN 8.0.5 - 9.5.0

Minimum build system requirements for the above configurations:

Expand All @@ -659,7 +659,7 @@ Here's how to build ``hipify-clang`` with testing support on ``Ubuntu 23.10.01``
-DCMAKE_INSTALL_PREFIX=../dist \
-DCMAKE_PREFIX_PATH=/usr/llvm/19.1.1/dist \
-DCUDA_TOOLKIT_ROOT_DIR=/usr/local/cuda-12.6.1 \
-DCUDA_DNN_ROOT_DIR=/usr/local/cudnn-9.4.0 \
-DCUDA_DNN_ROOT_DIR=/usr/local/cudnn-9.5.0 \
-DLLVM_EXTERNAL_LIT=/usr/llvm/19.1.1/build/bin/llvm-lit \
../hipify
Expand Down Expand Up @@ -697,7 +697,7 @@ The corresponding successful output is:
-- Initial CUDA to configure:
-- - CUDA Toolkit path : /usr/local/cuda-12.6.1
-- - CUDA Samples path :
-- - cuDNN path : /usr/local/cudnn-9.4.0
-- - cuDNN path : /usr/local/cudnn-9.5.0
-- - CUB path :
-- Found CUDAToolkit: /usr/local/cuda-12.6.1/targets/x86_64-linux/include (found version "12.6.68")
-- Performing Test CMAKE_HAVE_LIBC_PTHREAD
Expand All @@ -706,7 +706,7 @@ The corresponding successful output is:
-- Found CUDA config:
-- - CUDA Toolkit path : /usr/local/cuda-12.6.1
-- - CUDA Samples path : OFF
-- - cuDNN path : /usr/local/cudnn-9.4.0
-- - cuDNN path : /usr/local/cudnn-9.5.0
-- - CUB path : /usr/local/cuda-12.6.1/include/cub
-- Configuring done (0.5s)
-- Generating done (0.0s)
Expand Down Expand Up @@ -819,13 +819,13 @@ Tested configurations:
- ``3.11.4``
* - ``17.0.1`` :sup:`6` - ``18.1.8`` :sup:`7`
- ``7.0 - 12.3.2``
- ``8.0.5 - 9.4.0``
- ``8.0.5 - 9.5.0``
- ``2019.16.11.40, 2022.17.11.4``
- ``3.30.4``
- ``3.12.7``
* - ``19.1.1``
- ``7.0 - 12.6.1``
- ``8.0.5 - 9.4.0``
- ``8.0.5 - 9.5.0``
- ``2019.16.11.40, 2022.17.11.4``
- ``3.30.4``
- ``3.12.7``
Expand Down Expand Up @@ -856,7 +856,7 @@ Building with testing support using ``Visual Studio 17 2022`` on ``Windows 11``:
-DCMAKE_PREFIX_PATH=D:/LLVM/19.1.1/dist \
-DCUDA_TOOLKIT_ROOT_DIR="C:/Program Files/NVIDIA GPU Computing Toolkit/CUDA/v12.6" \
-DCUDA_SDK_ROOT_DIR="C:/ProgramData/NVIDIA Corporation/CUDA Samples/v12.5" \
-DCUDA_DNN_ROOT_DIR=D:/CUDA/cuDNN/9.4.0 \
-DCUDA_DNN_ROOT_DIR=D:/CUDA/cuDNN/9.5.0 \
-DLLVM_EXTERNAL_LIT=D:/LLVM/19.1.1/build/Release/bin/llvm-lit.py \
../hipify
Expand Down Expand Up @@ -893,13 +893,13 @@ The corresponding successful output is:
-- Initial CUDA to configure:
-- - CUDA Toolkit path : C:/Program Files/NVIDIA GPU Computing Toolkit/CUDA/v12.6
-- - CUDA Samples path : C:/ProgramData/NVIDIA Corporation/CUDA Samples/v12.5
-- - cuDNN path : D:/CUDA/cuDNN/9.4.0
-- - cuDNN path : D:/CUDA/cuDNN/9.5.0
-- - CUB path :
-- Found CUDAToolkit: C:/Program Files/NVIDIA GPU Computing Toolkit/CUDA/v12.6/include (found version "12.6.68")
-- Found CUDA config:
-- - CUDA Toolkit path : C:/Program Files/NVIDIA GPU Computing Toolkit/CUDA/v12.6
-- - CUDA Samples path : C:/ProgramData/NVIDIA Corporation/CUDA Samples/v12.5
-- - cuDNN path : D:/CUDA/cuDNN/9.4.0
-- - cuDNN path : D:/CUDA/cuDNN/9.5.0
-- - CUB path : C:/Program Files/NVIDIA GPU Computing Toolkit/CUDA/v12.6/include/cub
-- Configuring done (2.1s)
-- Generating done (0.1s)
Expand Down
6 changes: 6 additions & 0 deletions docs/tables/CUDNN_API_supported_by_HIP.md
Original file line number Diff line number Diff line change
Expand Up @@ -55,6 +55,7 @@
|`CUDNN_ATTR_INTERMEDIATE_INFO_SIZE`|8.0.1| | | | | | | | | |
|`CUDNN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID`|8.0.2| | | | | | | | | |
|`CUDNN_ATTR_KERNEL_CACHE_IS_ENGINECFG_KERNEL_CACHED`|9.4.0| | | | | | | | | |
|`CUDNN_ATTR_KERNEL_CACHE_OPERATION_GRAPH`|9.5.0| | | | | | | | | |
|`CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE`|8.0.1| | | | | | | | | |
|`CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE`|8.0.1| | | | | | | | | |
|`CUDNN_ATTR_KNOB_INFO_MAXIMUM_VALUE`|8.0.1| | | | | | | | | |
Expand Down Expand Up @@ -287,6 +288,7 @@
|`CUDNN_BEHAVIOR_NOTE_REQUIRES_BIAS_INT8x32_REORDER`|8.3.0| | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_REQUIRES_FILTER_INT8x32_REORDER`|8.3.0| | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_RUNTIME_COMPILATION`|8.2.0| | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_SUPPORTS_CUDA_GRAPH_NATIVE_API`|9.5.0| | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_TYPE_COUNT`|8.2.0| | | | | | | | | |
|`CUDNN_BIDIRECTIONAL`|5.0.0| | | |`HIPDNN_BIDIRECTIONAL`| | | | | |
|`CUDNN_BN_FINALIZE_STATISTICS_INFERENCE`|8.1.0| | | | | | | | | |
Expand Down Expand Up @@ -655,6 +657,7 @@
|`CUDNN_STATUS_ARCH_MISMATCH`|1.0.0|9.0.0| | |`HIPDNN_STATUS_ARCH_MISMATCH`| | | | | |
|`CUDNN_STATUS_BAD_PARAM`|1.0.0| | | |`HIPDNN_STATUS_BAD_PARAM`| | | | | |
|`CUDNN_STATUS_BAD_PARAM_ATTRIBUTE_TYPE`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_CUDA_GRAPH_MISMATCH`|9.5.0| | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_DUPLICATED_ENTRIES`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_MISALIGNED_POINTER`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_NOT_FINALIZED`|9.0.0| | | | | | | | | |
Expand Down Expand Up @@ -685,6 +688,7 @@
|`CUDNN_STATUS_NOT_SUPPORTED`|1.0.0| | | |`HIPDNN_STATUS_NOT_SUPPORTED`| | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_ARCH_MISMATCH`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_BAD_LAUNCH_PARAM`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_CUDA_GRAPH_NATIVE_API`|9.5.0| | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_DATA_TYPE`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_GRAPH_PATTERN`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_INCOMPATIBLE_CUDART`|9.0.0| | | | | | | | | |
Expand Down Expand Up @@ -899,7 +903,9 @@
|`cudnnBackendFinalize`|8.0.1| | | | | | | | | |
|`cudnnBackendGetAttribute`|8.0.1| | | | | | | | | |
|`cudnnBackendInitialize`|8.0.1|9.3.0| | | | | | | | |
|`cudnnBackendPopulateCudaGraph`|9.5.0| | | | | | | | | |
|`cudnnBackendSetAttribute`|8.0.1| | | | | | | | | |
|`cudnnBackendUpdateCudaGraph`|9.5.0| | | | | | | | | |
|`cudnnBatchNormalizationBackward`|4.0.0|9.0.0| | |`hipdnnBatchNormalizationBackward`| | | | | |
|`cudnnBatchNormalizationBackwardEx`|7.4.1|9.0.0| | | | | | | | |
|`cudnnBatchNormalizationForwardInference`|4.0.0|9.0.0| | |`hipdnnBatchNormalizationForwardInference`| | | | | |
Expand Down
6 changes: 6 additions & 0 deletions docs/tables/CUDNN_API_supported_by_HIP_and_MIOPEN.md
Original file line number Diff line number Diff line change
Expand Up @@ -55,6 +55,7 @@
|`CUDNN_ATTR_INTERMEDIATE_INFO_SIZE`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_INTERMEDIATE_INFO_SIZE`|6.2.0| | | | |
|`CUDNN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID`|8.0.2| | | | | | | | | |`MIOPEN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID`|6.2.0| | | | |
|`CUDNN_ATTR_KERNEL_CACHE_IS_ENGINECFG_KERNEL_CACHED`|9.4.0| | | | | | | | | | | | | | | |
|`CUDNN_ATTR_KERNEL_CACHE_OPERATION_GRAPH`|9.5.0| | | | | | | | | | | | | | | |
|`CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_KNOB_CHOICE_KNOB_TYPE`|6.2.0| | | | |
|`CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_KNOB_CHOICE_KNOB_VALUE`|6.2.0| | | | |
|`CUDNN_ATTR_KNOB_INFO_MAXIMUM_VALUE`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_KNOB_INFO_MAXIMUM_VALUE`|6.2.0| | | | |
Expand Down Expand Up @@ -287,6 +288,7 @@
|`CUDNN_BEHAVIOR_NOTE_REQUIRES_BIAS_INT8x32_REORDER`|8.3.0| | | | | | | | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_REQUIRES_FILTER_INT8x32_REORDER`|8.3.0| | | | | | | | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_RUNTIME_COMPILATION`|8.2.0| | | | | | | | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_SUPPORTS_CUDA_GRAPH_NATIVE_API`|9.5.0| | | | | | | | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_TYPE_COUNT`|8.2.0| | | | | | | | | | | | | | | |
|`CUDNN_BIDIRECTIONAL`|5.0.0| | | |`HIPDNN_BIDIRECTIONAL`| | | | | |`miopenRNNbidirection`|2.1.0| | | | |
|`CUDNN_BN_FINALIZE_STATISTICS_INFERENCE`|8.1.0| | | | | | | | | | | | | | | |
Expand Down Expand Up @@ -655,6 +657,7 @@
|`CUDNN_STATUS_ARCH_MISMATCH`|1.0.0|9.0.0| | |`HIPDNN_STATUS_ARCH_MISMATCH`| | | | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM`|1.0.0| | | |`HIPDNN_STATUS_BAD_PARAM`| | | | | |`miopenStatusBadParm`|2.1.0| | | | |
|`CUDNN_STATUS_BAD_PARAM_ATTRIBUTE_TYPE`|9.0.0| | | | | | | | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_CUDA_GRAPH_MISMATCH`|9.5.0| | | | | | | | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_DUPLICATED_ENTRIES`|9.0.0| | | | | | | | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_MISALIGNED_POINTER`|9.0.0| | | | | | | | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_NOT_FINALIZED`|9.0.0| | | | | | | | | | | | | | | |
Expand Down Expand Up @@ -685,6 +688,7 @@
|`CUDNN_STATUS_NOT_SUPPORTED`|1.0.0| | | |`HIPDNN_STATUS_NOT_SUPPORTED`| | | | | |`miopenStatusUnsupportedOp`|2.1.0| | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_ARCH_MISMATCH`|9.0.0| | | | | | | | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_BAD_LAUNCH_PARAM`|9.0.0| | | | | | | | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_CUDA_GRAPH_NATIVE_API`|9.5.0| | | | | | | | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_DATA_TYPE`|9.0.0| | | | | | | | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_GRAPH_PATTERN`|9.0.0| | | | | | | | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_INCOMPATIBLE_CUDART`|9.0.0| | | | | | | | | | | | | | | |
Expand Down Expand Up @@ -899,7 +903,9 @@
|`cudnnBackendFinalize`|8.0.1| | | | | | | | | |`miopenBackendFinalize`|6.2.0| | | | |
|`cudnnBackendGetAttribute`|8.0.1| | | | | | | | | |`miopenBackendGetAttribute`|6.2.0| | | | |
|`cudnnBackendInitialize`|8.0.1|9.3.0| | | | | | | | | | | | | | |
|`cudnnBackendPopulateCudaGraph`|9.5.0| | | | | | | | | | | | | | | |
|`cudnnBackendSetAttribute`|8.0.1| | | | | | | | | |`miopenBackendSetAttribute`|6.2.0| | | | |
|`cudnnBackendUpdateCudaGraph`|9.5.0| | | | | | | | | | | | | | | |
|`cudnnBatchNormalizationBackward`|4.0.0|9.0.0| | |`hipdnnBatchNormalizationBackward`| | | | | |`miopenBatchNormalizationBackward`|2.1.0| | | | |
|`cudnnBatchNormalizationBackwardEx`|7.4.1|9.0.0| | | | | | | | | | | | | | |
|`cudnnBatchNormalizationForwardInference`|4.0.0|9.0.0| | |`hipdnnBatchNormalizationForwardInference`| | | | | |`miopenBatchNormalizationForwardInference`|2.1.0| | | | |
Expand Down
6 changes: 6 additions & 0 deletions docs/tables/CUDNN_API_supported_by_MIOPEN.md
Original file line number Diff line number Diff line change
Expand Up @@ -55,6 +55,7 @@
|`CUDNN_ATTR_INTERMEDIATE_INFO_SIZE`|8.0.1| | | |`MIOPEN_ATTR_INTERMEDIATE_INFO_SIZE`|6.2.0| | | | |
|`CUDNN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID`|8.0.2| | | |`MIOPEN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID`|6.2.0| | | | |
|`CUDNN_ATTR_KERNEL_CACHE_IS_ENGINECFG_KERNEL_CACHED`|9.4.0| | | | | | | | | |
|`CUDNN_ATTR_KERNEL_CACHE_OPERATION_GRAPH`|9.5.0| | | | | | | | | |
|`CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE`|8.0.1| | | |`MIOPEN_ATTR_KNOB_CHOICE_KNOB_TYPE`|6.2.0| | | | |
|`CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE`|8.0.1| | | |`MIOPEN_ATTR_KNOB_CHOICE_KNOB_VALUE`|6.2.0| | | | |
|`CUDNN_ATTR_KNOB_INFO_MAXIMUM_VALUE`|8.0.1| | | |`MIOPEN_ATTR_KNOB_INFO_MAXIMUM_VALUE`|6.2.0| | | | |
Expand Down Expand Up @@ -287,6 +288,7 @@
|`CUDNN_BEHAVIOR_NOTE_REQUIRES_BIAS_INT8x32_REORDER`|8.3.0| | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_REQUIRES_FILTER_INT8x32_REORDER`|8.3.0| | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_RUNTIME_COMPILATION`|8.2.0| | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_SUPPORTS_CUDA_GRAPH_NATIVE_API`|9.5.0| | | | | | | | | |
|`CUDNN_BEHAVIOR_NOTE_TYPE_COUNT`|8.2.0| | | | | | | | | |
|`CUDNN_BIDIRECTIONAL`|5.0.0| | | |`miopenRNNbidirection`|2.1.0| | | | |
|`CUDNN_BN_FINALIZE_STATISTICS_INFERENCE`|8.1.0| | | | | | | | | |
Expand Down Expand Up @@ -655,6 +657,7 @@
|`CUDNN_STATUS_ARCH_MISMATCH`|1.0.0|9.0.0| | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM`|1.0.0| | | |`miopenStatusBadParm`|2.1.0| | | | |
|`CUDNN_STATUS_BAD_PARAM_ATTRIBUTE_TYPE`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_CUDA_GRAPH_MISMATCH`|9.5.0| | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_DUPLICATED_ENTRIES`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_MISALIGNED_POINTER`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_BAD_PARAM_NOT_FINALIZED`|9.0.0| | | | | | | | | |
Expand Down Expand Up @@ -685,6 +688,7 @@
|`CUDNN_STATUS_NOT_SUPPORTED`|1.0.0| | | |`miopenStatusUnsupportedOp`|2.1.0| | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_ARCH_MISMATCH`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_BAD_LAUNCH_PARAM`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_CUDA_GRAPH_NATIVE_API`|9.5.0| | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_DATA_TYPE`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_GRAPH_PATTERN`|9.0.0| | | | | | | | | |
|`CUDNN_STATUS_NOT_SUPPORTED_INCOMPATIBLE_CUDART`|9.0.0| | | | | | | | | |
Expand Down Expand Up @@ -899,7 +903,9 @@
|`cudnnBackendFinalize`|8.0.1| | | |`miopenBackendFinalize`|6.2.0| | | | |
|`cudnnBackendGetAttribute`|8.0.1| | | |`miopenBackendGetAttribute`|6.2.0| | | | |
|`cudnnBackendInitialize`|8.0.1|9.3.0| | | | | | | | |
|`cudnnBackendPopulateCudaGraph`|9.5.0| | | | | | | | | |
|`cudnnBackendSetAttribute`|8.0.1| | | |`miopenBackendSetAttribute`|6.2.0| | | | |
|`cudnnBackendUpdateCudaGraph`|9.5.0| | | | | | | | | |
|`cudnnBatchNormalizationBackward`|4.0.0|9.0.0| | |`miopenBatchNormalizationBackward`|2.1.0| | | | |
|`cudnnBatchNormalizationBackwardEx`|7.4.1|9.0.0| | | | | | | | |
|`cudnnBatchNormalizationForwardInference`|4.0.0|9.0.0| | |`miopenBatchNormalizationForwardInference`|2.1.0| | | | |
Expand Down
4 changes: 4 additions & 0 deletions src/CUDA2HIP_DNN_API_functions.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -347,6 +347,8 @@ const std::map<llvm::StringRef, hipCounter> CUDA_DNN_FUNCTION_MAP {
{"cudnnBackendSetAttribute", {"hipdnnBackendSetAttribute", "miopenBackendSetAttribute", CONV_LIB_FUNC, API_DNN, 2, HIP_UNSUPPORTED}},
{"cudnnBackendGetAttribute", {"hipdnnBackendGetAttribute", "miopenBackendGetAttribute", CONV_LIB_FUNC, API_DNN, 2, HIP_UNSUPPORTED}},
{"cudnnBackendExecute", {"hipdnnBackendExecute", "miopenBackendExecute", CONV_LIB_FUNC, API_DNN, 2, HIP_UNSUPPORTED}},
{"cudnnBackendPopulateCudaGraph", {"hipdnnBackendPopulateCudaGraph", "", CONV_LIB_FUNC, API_DNN, 2, UNSUPPORTED}},
{"cudnnBackendUpdateCudaGraph", {"hipdnnBackendUpdateCudaGraph", "", CONV_LIB_FUNC, API_DNN, 2, UNSUPPORTED}},
};

const std::map<llvm::StringRef, cudaAPIversions> CUDA_DNN_FUNCTION_VER_MAP {
Expand Down Expand Up @@ -628,6 +630,8 @@ const std::map<llvm::StringRef, cudaAPIversions> CUDA_DNN_FUNCTION_VER_MAP {
{"cudnnGetLastErrorString", {CUDNN_900, CUDA_0, CUDA_0 }},
{"cudnnGraphVersionCheck", {CUDNN_900, CUDA_0, CUDA_0 }},
{"cudnnOpsVersionCheck", {CUDNN_900, CUDA_0, CUDA_0 }},
{"cudnnBackendPopulateCudaGraph", {CUDNN_950, CUDA_0, CUDA_0 }},
{"cudnnBackendUpdateCudaGraph", {CUDNN_950, CUDA_0, CUDA_0 }},
};

const std::map<llvm::StringRef, hipAPIversions> HIP_DNN_FUNCTION_VER_MAP {
Expand Down
Loading

0 comments on commit f127308

Please sign in to comment.