Skip to content

Commit

Permalink
[HIPIFY][ROCm#584][ROCm#1624][MIOpen] Support for backend graphAPI …
Browse files Browse the repository at this point in the history 
…direct translation from `cuDNN` to `MIOpen` - Part 11 - final

+ `cudnnDataType_t` -> `miopenDataType_t` (missing float8 types)
+ `cudnnPoolingMode_t` -> `miopenPoolingMode_t`
+ `cudnnActivationMode_t` -> `miopenActivationMode_t` (missing `miopenActivationLOGISTIC`)
+ `cudnnRNNPaddingMode_t` -> `miopenRNNPaddingMode_t`
+ `cudnnForwardMode_t` -> `miopenRNNFWDMode_t`
+ `cudnnPaddingMode_t` -> `miopenPaddingMode_t`
+ [fix] `cudnnRNNPaddingMode_t` versioning
+ Updated synthetic tests, the regenerated `hipify-perl`, and `DNN` `CUDA2HIP` documentation
  • Loading branch information
@emankov
emankov committed Oct 2, 2024
1 parent e1fe277 commit a769683
Show file tree
Hide file tree
Showing 6 changed files with 133 additions and 54 deletions.
19 changes: 19 additions & 0 deletions bin/hipify-perl
View file
Original file line number Diff line number Diff line change
Expand Up @@ -1255,6 +1255,7 @@ my %removed_funcs = (
"cudnnSaveAlgorithm" => "9.0.0",
"cudnnRestoreAlgorithm" => "9.0.0",
"cudnnRNNSetClip" => "9.0.0",
"cudnnRNNPaddingMode_t" => "9.0.0",
"cudnnRNNGetClip" => "9.0.0",
"cudnnRNNForwardTrainingEx" => "9.0.0",
"cudnnRNNForwardTraining" => "9.0.0",
Expand Down Expand Up @@ -1375,6 +1376,8 @@ my %removed_funcs = (
"CUSPARSE_ALG_MERGE_PATH" => "12.0",
"CUSPARSE_ALG1" => "11.0",
"CUSPARSE_ALG0" => "11.0",
"CUDNN_RNN_PADDED_IO_ENABLED" => "9.0.0",
"CUDNN_RNN_PADDED_IO_DISABLED" => "9.0.0",
"CUDNN_CONVOLUTION_FWD_SPECIFY_WORKSPACE_LIMIT" => "8.0.1",
"CUDNN_CONVOLUTION_FWD_PREFER_FASTEST" => "8.0.1",
"CUDNN_CONVOLUTION_FWD_NO_WORKSPACE" => "8.0.1",
Expand Down Expand Up @@ -2764,6 +2767,7 @@ sub rocSubstitutions {
subst("cudnnLRNMode_t", "miopenLRNMode_t", "type");
subst("cudnnNanPropagation_t", "miopenNanPropagation_t", "type");
subst("cudnnOpTensorOp_t", "miopenTensorOp_t", "type");
subst("cudnnPaddingMode_t", "miopenPaddingMode_t", "type");
subst("cudnnPointwiseMode_t", "miopenPointwiseMode_t", "type");
subst("cudnnPoolingDescriptor_t", "miopenPoolingDescriptor_t", "type");
subst("cudnnPoolingMode_t", "miopenPoolingMode_t", "type");
Expand All @@ -2772,6 +2776,7 @@ sub rocSubstitutions {
subst("cudnnRNNDescriptor_t", "miopenRNNDescriptor_t", "type");
subst("cudnnRNNInputMode_t", "miopenRNNInputMode_t", "type");
subst("cudnnRNNMode_t", "miopenRNNMode_t", "type");
subst("cudnnRNNPaddingMode_t", "miopenRNNPaddingMode_t", "type");
subst("cudnnReduceTensorDescriptor_t", "miopenReduceTensorDescriptor_t", "type");
subst("cudnnReduceTensorIndices_t", "miopenReduceTensorIndices_t", "type");
subst("cudnnReduceTensorOp_t", "miopenReduceTensorOp_t", "type");
Expand Down Expand Up @@ -2895,6 +2900,7 @@ sub rocSubstitutions {
subst("CUDNN_ACTIVATION_ELU", "miopenActivationELU", "numeric_literal");
subst("CUDNN_ACTIVATION_IDENTITY", "miopenActivationPASTHRU", "numeric_literal");
subst("CUDNN_ACTIVATION_RELU", "miopenActivationRELU", "numeric_literal");
subst("CUDNN_ACTIVATION_SIGMOID", "miopenActivationLOGISTIC", "numeric_literal");
subst("CUDNN_ACTIVATION_TANH", "miopenActivationTANH", "numeric_literal");
subst("CUDNN_ATTR_CONVOLUTION_COMP_TYPE", "MIOPEN_ATTR_CONVOLUTION_COMP_TYPE", "numeric_literal");
subst("CUDNN_ATTR_CONVOLUTION_CONV_MODE", "MIOPEN_ATTR_CONVOLUTION_CONV_MODE", "numeric_literal");
Expand Down Expand Up @@ -3145,6 +3151,7 @@ sub rocSubstitutions {
subst("CUDNN_CONVOLUTION", "miopenConvolution", "numeric_literal");
subst("CUDNN_CONVOLUTION_BWD_DATA_ALGO_0", "miopenConvolutionBwdDataAlgoGEMM", "numeric_literal");
subst("CUDNN_CONVOLUTION_BWD_DATA_ALGO_1", "miopenConvolutionBwdDataAlgoDirect", "numeric_literal");
subst("CUDNN_CONVOLUTION_BWD_DATA_ALGO_COUNT", "miopenTransposeBwdDataAlgoGEMM", "numeric_literal");
subst("CUDNN_CONVOLUTION_BWD_DATA_ALGO_FFT", "miopenConvolutionBwdDataAlgoFFT", "numeric_literal");
subst("CUDNN_CONVOLUTION_BWD_DATA_ALGO_WINOGRAD", "miopenConvolutionBwdDataAlgoWinograd", "numeric_literal");
subst("CUDNN_CONVOLUTION_FWD_ALGO_DIRECT", "miopenConvolutionFwdAlgoDirect", "numeric_literal");
Expand All @@ -3157,11 +3164,16 @@ sub rocSubstitutions {
subst("CUDNN_DATA_BFLOAT16", "miopenBFloat16", "numeric_literal");
subst("CUDNN_DATA_DOUBLE", "miopenDouble", "numeric_literal");
subst("CUDNN_DATA_FLOAT", "miopenFloat", "numeric_literal");
subst("CUDNN_DATA_FP8_E4M3", "miopenFloat8", "numeric_literal");
subst("CUDNN_DATA_FP8_E5M2", "miopenBFloat8", "numeric_literal");
subst("CUDNN_DATA_HALF", "miopenHalf", "numeric_literal");
subst("CUDNN_DATA_INT32", "miopenInt32", "numeric_literal");
subst("CUDNN_DATA_INT64", "miopenInt64", "numeric_literal");
subst("CUDNN_DATA_INT8", "miopenInt8", "numeric_literal");
subst("CUDNN_DATA_INT8x4", "miopenInt8x4", "numeric_literal");
subst("CUDNN_EDGE_VAL_PAD", "miopenPaddingValid", "numeric_literal");
subst("CUDNN_FWD_MODE_INFERENCE", "miopenRNNInference", "numeric_literal");
subst("CUDNN_FWD_MODE_TRAINING", "miopenRNNTraining", "numeric_literal");
subst("CUDNN_GRU", "miopenGRU", "numeric_literal");
subst("CUDNN_HEUR_MODES_COUNT", "MIOPEN_HEUR_MODES_COUNT", "numeric_literal");
subst("CUDNN_HEUR_MODE_A", "MIOPEN_HEUR_MODE_A", "numeric_literal");
Expand All @@ -3171,6 +3183,7 @@ sub rocSubstitutions {
subst("CUDNN_LINEAR_INPUT", "miopenRNNlinear", "numeric_literal");
subst("CUDNN_LRN_CROSS_CHANNEL_DIM1", "miopenLRNCrossChannel", "numeric_literal");
subst("CUDNN_LSTM", "miopenLSTM", "numeric_literal");
subst("CUDNN_NEG_INF_PAD", "miopenPaddingSame", "numeric_literal");
subst("CUDNN_NOT_PROPAGATE_NAN", "MIOPEN_NOT_PROPAGATE_NAN", "numeric_literal");
subst("CUDNN_OP_TENSOR_ADD", "miopenTensorOpAdd", "numeric_literal");
subst("CUDNN_OP_TENSOR_MAX", "miopenTensorOpMax", "numeric_literal");
Expand Down Expand Up @@ -3226,6 +3239,8 @@ sub rocSubstitutions {
subst("CUDNN_POINTWISE_TAN", "MIOPEN_POINTWISE_TAN", "numeric_literal");
subst("CUDNN_POINTWISE_TANH_BWD", "MIOPEN_POINTWISE_TANH_BWD", "numeric_literal");
subst("CUDNN_POINTWISE_TANH_FWD", "MIOPEN_POINTWISE_TANH_FWD", "numeric_literal");
subst("CUDNN_POOLING_AVERAGE_COUNT_EXCLUDE_PADDING", "miopenPoolingAverage", "numeric_literal");
subst("CUDNN_POOLING_AVERAGE_COUNT_INCLUDE_PADDING", "miopenPoolingAverageInclusive", "numeric_literal");
subst("CUDNN_POOLING_MAX", "miopenPoolingMax", "numeric_literal");
subst("CUDNN_PROPAGATE_NAN", "MIOPEN_PROPAGATE_NAN", "numeric_literal");
subst("CUDNN_REDUCE_TENSOR_ADD", "MIOPEN_REDUCE_TENSOR_ADD", "numeric_literal");
Expand All @@ -3244,6 +3259,8 @@ sub rocSubstitutions {
subst("CUDNN_RNN_ALGO_STANDARD", "miopenRNNdefault", "numeric_literal");
subst("CUDNN_RNN_DOUBLE_BIAS", "miopenRNNwithBias", "numeric_literal");
subst("CUDNN_RNN_NO_BIAS", "miopenRNNNoBias", "numeric_literal");
subst("CUDNN_RNN_PADDED_IO_DISABLED", "miopenRNNIONotPadded", "numeric_literal");
subst("CUDNN_RNN_PADDED_IO_ENABLED", "miopenRNNIOWithPadding", "numeric_literal");
subst("CUDNN_RNN_RELU", "miopenRNNRELU", "numeric_literal");
subst("CUDNN_RNN_SINGLE_INP_BIAS", "miopenRNNwithBias", "numeric_literal");
subst("CUDNN_RNN_SINGLE_REC_BIAS", "miopenRNNwithBias", "numeric_literal");
Expand Down Expand Up @@ -3295,6 +3312,7 @@ sub rocSubstitutions {
subst("CUDNN_TYPE_TENSOR_REORDERING_MODE", "MIOPEN_TYPE_TENSOR_REORDERING_MODE", "numeric_literal");
subst("CUDNN_TYPE_VOID_PTR", "MIOPEN_TYPE_VOID_PTR", "numeric_literal");
subst("CUDNN_UNIDIRECTIONAL", "miopenRNNunidirection", "numeric_literal");
subst("CUDNN_ZERO_PAD", "miopenPaddingDefault", "numeric_literal");
subst("CURAND_DIRECTION_VECTORS_32_JOEKUO6", "ROCRAND_DIRECTION_VECTORS_32_JOEKUO6", "numeric_literal");
subst("CURAND_DIRECTION_VECTORS_64_JOEKUO6", "ROCRAND_DIRECTION_VECTORS_64_JOEKUO6", "numeric_literal");
subst("CURAND_ORDERING_PSEUDO_BEST", "ROCRAND_ORDERING_PSEUDO_BEST", "numeric_literal");
Expand Down Expand Up @@ -3410,6 +3428,7 @@ sub rocSubstitutions {
subst("CUSPARSE_STATUS_NOT_SUPPORTED", "rocsparse_status_not_implemented", "numeric_literal");
subst("CUSPARSE_STATUS_SUCCESS", "rocsparse_status_success", "numeric_literal");
subst("CUSPARSE_STATUS_ZERO_PIVOT", "rocsparse_status_zero_pivot", "numeric_literal");
subst("cudnnForwardMode_t", "miopenRNNFWDMode_t", "numeric_literal");
subst("cusolver_int_t", "rocblas_int", "numeric_literal");
}

Expand Down
6 changes: 3 additions & 3 deletions docs/tables/CUDNN_API_supported_by_HIP.md
View file
Original file line number Diff line number Diff line change
Expand Up @@ -620,8 +620,8 @@
|`CUDNN_RNN_DATA_LAYOUT_SEQ_MAJOR_UNPACKED`|7.2.1| | | | | | | | | |
|`CUDNN_RNN_DOUBLE_BIAS`|7.5.0| | | |`HIPDNN_RNN_WITH_BIAS`| | | | | |
|`CUDNN_RNN_NO_BIAS`|7.5.0| | | |`HIPDNN_RNN_NO_BIAS`| | | | | |
|`CUDNN_RNN_PADDED_IO_DISABLED`|7.2.1| | | | | | | | | |
|`CUDNN_RNN_PADDED_IO_ENABLED`|7.2.1| | | | | | | | | |
|`CUDNN_RNN_PADDED_IO_DISABLED`|7.2.1|8.0.1| |9.0.0| | | | | | |
|`CUDNN_RNN_PADDED_IO_ENABLED`|7.2.1|8.0.1| |9.0.0| | | | | | |
|`CUDNN_RNN_RELU`|5.0.0| | | |`HIPDNN_RNN_RELU`| | | | | |
|`CUDNN_RNN_SINGLE_INP_BIAS`|7.5.0| | | |`HIPDNN_RNN_WITH_BIAS`| | | | | |
|`CUDNN_RNN_SINGLE_REC_BIAS`|7.5.0| | | |`HIPDNN_RNN_WITH_BIAS`| | | | | |
Expand Down Expand Up @@ -853,7 +853,7 @@
|`cudnnRNNDescriptor_t`|5.0.0| | | |`hipdnnRNNDescriptor_t`| | | | | |
|`cudnnRNNInputMode_t`|5.0.0| | | |`hipdnnRNNInputMode_t`| | | | | |
|`cudnnRNNMode_t`|5.0.0| | | |`hipdnnRNNMode_t`| | | | | |
|`cudnnRNNPaddingMode_t`|7.2.1| | | | | | | | | |
|`cudnnRNNPaddingMode_t`|7.2.1|8.0.1| |9.0.0| | | | | | |
|`cudnnRNNStruct`|5.0.0| | | | | | | | | |
|`cudnnReduceTensorDescriptor_t`|6.0.0|9.0.0| | |`hipdnnReduceTensorDescriptor_t`| | | | | |
|`cudnnReduceTensorIndices_t`|6.0.0|9.0.0| | |`hipdnnReduceTensorIndices_t`| | | | | |
Expand Down
32 changes: 16 additions & 16 deletions docs/tables/CUDNN_API_supported_by_HIP_and_MIOPEN.md
View file
Original file line number Diff line number Diff line change
Expand Up @@ -12,7 +12,7 @@
|`CUDNN_ACTIVATION_ELU`|6.0.0|9.0.0| | |`HIPDNN_ACTIVATION_ELU`| | | | | |`miopenActivationELU`|2.1.0| | | | |
|`CUDNN_ACTIVATION_IDENTITY`|7.1.3|9.0.0| | |`HIPDNN_ACTIVATION_PATHTRU`| | | | | |`miopenActivationPASTHRU`|2.1.0| | | | |
|`CUDNN_ACTIVATION_RELU`|1.0.0|9.0.0| | |`HIPDNN_ACTIVATION_RELU`| | | | | |`miopenActivationRELU`|2.1.0| | | | |
|`CUDNN_ACTIVATION_SIGMOID`|1.0.0|9.0.0| | |`HIPDNN_ACTIVATION_SIGMOID`| | | | | | | | | | | |
|`CUDNN_ACTIVATION_SIGMOID`|1.0.0|9.0.0| | |`HIPDNN_ACTIVATION_SIGMOID`| | | | | |`miopenActivationLOGISTIC`|2.1.0| | | | |
|`CUDNN_ACTIVATION_SWISH`|8.2.0|9.0.0| | |`HIPDNN_ACTIVATION_SWISH`| | | | | | | | | | | |
|`CUDNN_ACTIVATION_TANH`|1.0.0|9.0.0| | |`HIPDNN_ACTIVATION_TANH`| | | | | |`miopenActivationTANH`|2.1.0| | | | |
|`CUDNN_ATTN_DISABLE_PROJ_BIASES`|7.6.3| | | | | | | | | | | | | | | |
Expand Down Expand Up @@ -295,7 +295,7 @@
|`CUDNN_CONVOLUTION`|1.0.0|9.0.0| | |`HIPDNN_CONVOLUTION`| | | | | |`miopenConvolution`|2.1.0| | | | |
|`CUDNN_CONVOLUTION_BWD_DATA_ALGO_0`|3.0.0| | | |`HIPDNN_CONVOLUTION_BWD_DATA_ALGO_0`| | | | | |`miopenConvolutionBwdDataAlgoGEMM`|2.1.0| | | | |
|`CUDNN_CONVOLUTION_BWD_DATA_ALGO_1`|3.0.0| | | |`HIPDNN_CONVOLUTION_BWD_DATA_ALGO_1`| | | | | |`miopenConvolutionBwdDataAlgoDirect`|2.1.0| | | | |
|`CUDNN_CONVOLUTION_BWD_DATA_ALGO_COUNT`|6.0.0| | | |`HIPDNN_CONVOLUTION_BWD_DATA_ALGO_TRANSPOSE_GEMM`| | | | | | | | | | | |
|`CUDNN_CONVOLUTION_BWD_DATA_ALGO_COUNT`|6.0.0| | | |`HIPDNN_CONVOLUTION_BWD_DATA_ALGO_TRANSPOSE_GEMM`| | | | | |`miopenTransposeBwdDataAlgoGEMM`|2.1.0| | | | |
|`CUDNN_CONVOLUTION_BWD_DATA_ALGO_FFT`|3.0.0| | | |`HIPDNN_CONVOLUTION_BWD_DATA_ALGO_FFT`| | | | | |`miopenConvolutionBwdDataAlgoFFT`|2.1.0| | | | |
|`CUDNN_CONVOLUTION_BWD_DATA_ALGO_FFT_TILING`|4.0.0| | | |`HIPDNN_CONVOLUTION_BWD_DATA_ALGO_FFT_TILING`| | | | | | | | | | | |
|`CUDNN_CONVOLUTION_BWD_DATA_ALGO_WINOGRAD`|5.0.0| | | |`HIPDNN_CONVOLUTION_BWD_DATA_ALGO_WINOGRAD`| | | | | |`miopenConvolutionBwdDataAlgoWinograd`|2.1.0| | | | |
Expand Down Expand Up @@ -336,8 +336,8 @@
|`CUDNN_DATA_DOUBLE`|1.0.0| | | |`HIPDNN_DATA_DOUBLE`| | | | | |`miopenDouble`|4.5.0| | | | |
|`CUDNN_DATA_FAST_FLOAT_FOR_FP8`|8.7.0| | | | | | | | | | | | | | | |
|`CUDNN_DATA_FLOAT`|1.0.0| | | |`HIPDNN_DATA_FLOAT`| | | | | |`miopenFloat`|2.1.0| | | | |
|`CUDNN_DATA_FP8_E4M3`|8.6.0| | | | | | | | | | | | | | | |
|`CUDNN_DATA_FP8_E5M2`|8.6.0| | | | | | | | | | | | | | | |
|`CUDNN_DATA_FP8_E4M3`|8.6.0| | | | | | | | | |`miopenFloat8`|6.0.0| | | | |
|`CUDNN_DATA_FP8_E5M2`|8.6.0| | | | | | | | | |`miopenBFloat8`|6.0.0| | | | |
|`CUDNN_DATA_HALF`|3.0.0| | | |`HIPDNN_DATA_HALF`| | | | | |`miopenHalf`|2.1.0| | | | |
|`CUDNN_DATA_INT32`|6.0.0| | | |`HIPDNN_DATA_INT32`| | | | | |`miopenInt32`|2.1.0| | | | |
|`CUDNN_DATA_INT64`|8.1.0| | | | | | | | | |`miopenInt64`|6.2.0| | | | |
Expand All @@ -351,7 +351,7 @@
|`CUDNN_DETERMINISTIC`|6.0.0| | | | | | | | | | | | | | | |
|`CUDNN_DIM_MAX`|4.0.0| | | | | | | | | | | | | | | |
|`CUDNN_DIVNORM_PRECOMPUTED_MEANS`|3.0.0| | | | | | | | | | | | | | | |
|`CUDNN_EDGE_VAL_PAD`|8.3.0| | | | | | | | | | | | | | | |
|`CUDNN_EDGE_VAL_PAD`|8.3.0| | | | | | | | | |`miopenPaddingValid`|2.1.0| | | | |
|`CUDNN_ERRQUERY_BLOCKING`|7.0.5| | | | | | | | | | | | | | | |
|`CUDNN_ERRQUERY_NONBLOCKING`|7.0.5| | | | | | | | | | | | | | | |
|`CUDNN_ERRQUERY_RAWCODE`|7.0.5| | | | | | | | | | | | | | | |
Expand All @@ -363,8 +363,8 @@
|`CUDNN_FUSED_SCALE_BIAS_ACTIVATION_CONV_BNSTATS`|7.6.0| | | | | | | | | | | | | | | |
|`CUDNN_FUSED_SCALE_BIAS_ACTIVATION_WGRAD`|7.6.0| | | | | | | | | | | | | | | |
|`CUDNN_FUSED_SCALE_BIAS_ADD_ACTIVATION_GEN_BITMASK`|7.6.0| | | | | | | | | | | | | | | |
|`CUDNN_FWD_MODE_INFERENCE`|8.0.1| | | | | | | | | | | | | | | |
|`CUDNN_FWD_MODE_TRAINING`|8.0.1| | | | | | | | | | | | | | | |
|`CUDNN_FWD_MODE_INFERENCE`|8.0.1| | | | | | | | | |`miopenRNNInference`|6.0.0| | | | |
|`CUDNN_FWD_MODE_TRAINING`|8.0.1| | | | | | | | | |`miopenRNNTraining`|6.0.0| | | | |
|`CUDNN_GENSTATS_SUM_SQSUM`|8.0.1| | | | | | | | | | | | | | | |
|`CUDNN_GROUP_NORM`|8.5.0| | | | | | | | | | | | | | | |
|`CUDNN_GRU`|5.0.0| | | |`HIPDNN_GRU`| | | | | |`miopenGRU`|2.1.0| | | | |
Expand Down Expand Up @@ -435,7 +435,7 @@
|`CUDNN_MH_ATTN_Q_WEIGHTS`|7.5.0| | | | | | | | | | | | | | | |
|`CUDNN_MH_ATTN_V_BIASES`|7.6.3| | | | | | | | | | | | | | | |
|`CUDNN_MH_ATTN_V_WEIGHTS`|7.5.0| | | | | | | | | | | | | | | |
|`CUDNN_NEG_INF_PAD`|8.3.0| | | | | | | | | | | | | | | |
|`CUDNN_NEG_INF_PAD`|8.3.0| | | | | | | | | |`miopenPaddingSame`|2.1.0| | | | |
|`CUDNN_NON_DETERMINISTIC`|6.0.0| | | | | | | | | | | | | | | |
|`CUDNN_NORM_ALGO_PERSIST`|8.0.1|9.0.0| | | | | | | | | | | | | | |
|`CUDNN_NORM_ALGO_STANDARD`|8.0.1|9.0.0| | | | | | | | | | | | | | |
Expand Down Expand Up @@ -555,8 +555,8 @@
|`CUDNN_POINTWISE_TAN`|8.3.0| | | | | | | | | |`MIOPEN_POINTWISE_TAN`|6.2.0| | | | |
|`CUDNN_POINTWISE_TANH_BWD`|8.1.0| | | | | | | | | |`MIOPEN_POINTWISE_TANH_BWD`|6.2.0| | | | |
|`CUDNN_POINTWISE_TANH_FWD`|8.0.1| | | | | | | | | |`MIOPEN_POINTWISE_TANH_FWD`|6.2.0| | | | |
|`CUDNN_POOLING_AVERAGE_COUNT_EXCLUDE_PADDING`|2.0.0|9.0.0| | |`HIPDNN_POOLING_AVERAGE_COUNT_EXCLUDE_PADDING`| | | | | | | | | | | |
|`CUDNN_POOLING_AVERAGE_COUNT_INCLUDE_PADDING`|2.0.0|9.0.0| | |`HIPDNN_POOLING_AVERAGE_COUNT_INCLUDE_PADDING`| | | | | | | | | | | |
|`CUDNN_POOLING_AVERAGE_COUNT_EXCLUDE_PADDING`|2.0.0|9.0.0| | |`HIPDNN_POOLING_AVERAGE_COUNT_EXCLUDE_PADDING`| | | | | |`miopenPoolingAverage`|2.1.0| | | | |
|`CUDNN_POOLING_AVERAGE_COUNT_INCLUDE_PADDING`|2.0.0|9.0.0| | |`HIPDNN_POOLING_AVERAGE_COUNT_INCLUDE_PADDING`| | | | | |`miopenPoolingAverageInclusive`|2.1.0| | | | |
|`CUDNN_POOLING_MAX`|1.0.0|9.0.0| | |`HIPDNN_POOLING_MAX`| | | | | |`miopenPoolingMax`|2.1.0| | | | |
|`CUDNN_POOLING_MAX_DETERMINISTIC`|6.0.0|9.0.0| | |`HIPDNN_POOLING_MAX_DETERMINISTIC`| | | | | | | | | | | |
|`CUDNN_PROPAGATE_NAN`|4.0.0|9.0.0| | |`HIPDNN_PROPAGATE_NAN`| | | | | |`MIOPEN_PROPAGATE_NAN`|3.9.0| | | | |
Expand Down Expand Up @@ -620,8 +620,8 @@
|`CUDNN_RNN_DATA_LAYOUT_SEQ_MAJOR_UNPACKED`|7.2.1| | | | | | | | | | | | | | | |
|`CUDNN_RNN_DOUBLE_BIAS`|7.5.0| | | |`HIPDNN_RNN_WITH_BIAS`| | | | | |`miopenRNNwithBias`|2.1.0| | | | |
|`CUDNN_RNN_NO_BIAS`|7.5.0| | | |`HIPDNN_RNN_NO_BIAS`| | | | | |`miopenRNNNoBias`|2.1.0| | | | |
|`CUDNN_RNN_PADDED_IO_DISABLED`|7.2.1| | | | | | | | | | | | | | | |
|`CUDNN_RNN_PADDED_IO_ENABLED`|7.2.1| | | | | | | | | | | | | | | |
|`CUDNN_RNN_PADDED_IO_DISABLED`|7.2.1|8.0.1| |9.0.0| | | | | | |`miopenRNNIONotPadded`|6.0.0| | | | |
|`CUDNN_RNN_PADDED_IO_ENABLED`|7.2.1|8.0.1| |9.0.0| | | | | | |`miopenRNNIOWithPadding`|6.0.0| | | | |
|`CUDNN_RNN_RELU`|5.0.0| | | |`HIPDNN_RNN_RELU`| | | | | |`miopenRNNRELU`|2.1.0| | | | |
|`CUDNN_RNN_SINGLE_INP_BIAS`|7.5.0| | | |`HIPDNN_RNN_WITH_BIAS`| | | | | |`miopenRNNwithBias`|2.1.0| | | | |
|`CUDNN_RNN_SINGLE_REC_BIAS`|7.5.0| | | |`HIPDNN_RNN_WITH_BIAS`| | | | | |`miopenRNNwithBias`|2.1.0| | | | |
Expand Down Expand Up @@ -747,7 +747,7 @@
|`CUDNN_UNIDIRECTIONAL`|5.0.0| | | |`HIPDNN_UNIDIRECTIONAL`| | | | | |`miopenRNNunidirection`|2.1.0| | | | |
|`CUDNN_WGRAD_MODE_ADD`|7.5.0| | | | | | | | | | | | | | | |
|`CUDNN_WGRAD_MODE_SET`|7.5.0| | | | | | | | | | | | | | | |
|`CUDNN_ZERO_PAD`|8.3.0| | | | | | | | | | | | | | | |
|`CUDNN_ZERO_PAD`|8.3.0| | | | | | | | | |`miopenPaddingDefault`|2.1.0| | | | |
|`cudnnActivationDescriptor_t`|4.0.0|9.0.0| | |`hipdnnActivationDescriptor_t`| | | | | |`miopenActivationDescriptor_t`|2.1.0| | | | |
|`cudnnActivationMode_t`|1.0.0|9.0.0| | |`hipdnnActivationMode_t`| | | | | |`miopenActivationMode_t`|2.1.0| | | | |
|`cudnnActivationStruct`|4.0.0|9.0.0| | | | | | | | | | | | | | |
Expand Down Expand Up @@ -808,7 +808,7 @@
|`cudnnFilterDescriptor_t`|1.0.0| | | |`hipdnnFilterDescriptor_t`| | | | | |`miopenTensorDescriptor_t`|2.1.0| | | | |
|`cudnnFilterStruct`|1.0.0|9.0.0| | | | | | | | | | | | | | |
|`cudnnFoldingDirection_t`|7.5.0| | | | | | | | | | | | | | | |
|`cudnnForwardMode_t`|8.0.1| | | | | | | | | | | | | | | |
|`cudnnForwardMode_t`|8.0.1| | | | | | | | | |`miopenRNNFWDMode_t`|6.0.0| | | | |
|`cudnnFractionStruct`|8.5.0| | | | | | | | | | | | | | | |
|`cudnnFraction_t`|8.5.0| | | | | | | | | | | | | | | |
|`cudnnFusedOpsConstParamLabel_t`|7.6.0|9.0.0| | | | | | | | | | | | | | |
Expand Down Expand Up @@ -837,7 +837,7 @@
|`cudnnOpTensorDescriptor_t`|5.0.0|9.0.0| | |`hipdnnOpTensorDescriptor_t`| | | | | | | | | | | |
|`cudnnOpTensorOp_t`|5.0.0| | | |`hipdnnOpTensorOp_t`| | | | | |`miopenTensorOp_t`|2.1.0| | | | |
|`cudnnOpTensorStruct`|5.0.0|9.0.0| | | | | | | | | | | | | | |
|`cudnnPaddingMode_t`|8.3.0| | | | | | | | | | | | | | | |
|`cudnnPaddingMode_t`|8.3.0| | | | | | | | | |`miopenPaddingMode_t`|2.1.0| | | | |
|`cudnnPersistentRNNPlan`|6.0.0| | | | | | | | | | | | | | | |
|`cudnnPersistentRNNPlan_t`|6.0.0| | | |`hipdnnPersistentRNNPlan_t`| | | | | | | | | | | |
|`cudnnPointwiseMode_t`|8.0.1| | | | | | | | | |`miopenPointwiseMode_t`|6.2.0| | | | |
Expand All @@ -853,7 +853,7 @@
|`cudnnRNNDescriptor_t`|5.0.0| | | |`hipdnnRNNDescriptor_t`| | | | | |`miopenRNNDescriptor_t`|2.1.0| | | | |
|`cudnnRNNInputMode_t`|5.0.0| | | |`hipdnnRNNInputMode_t`| | | | | |`miopenRNNInputMode_t`|2.1.0| | | | |
|`cudnnRNNMode_t`|5.0.0| | | |`hipdnnRNNMode_t`| | | | | |`miopenRNNMode_t`|2.1.0| | | | |
|`cudnnRNNPaddingMode_t`|7.2.1| | | | | | | | | | | | | | | |
|`cudnnRNNPaddingMode_t`|7.2.1|8.0.1| |9.0.0| | | | | | |`miopenRNNPaddingMode_t`|6.0.0| | | | |
|`cudnnRNNStruct`|5.0.0| | | | | | | | | | | | | | | |
|`cudnnReduceTensorDescriptor_t`|6.0.0|9.0.0| | |`hipdnnReduceTensorDescriptor_t`| | | | | |`miopenReduceTensorDescriptor_t`|3.9.0| | | | |
|`cudnnReduceTensorIndices_t`|6.0.0|9.0.0| | |`hipdnnReduceTensorIndices_t`| | | | | |`miopenReduceTensorIndices_t`|3.9.0| | | | |
Expand Down
Loading

0 comments on commit a769683

Please sign in to comment.