diff --git a/src/CUDA2HIP_DNN_API_types.cpp b/src/CUDA2HIP_DNN_API_types.cpp index 22f5d559..f2c6ed2b 100644 --- a/src/CUDA2HIP_DNN_API_types.cpp +++ b/src/CUDA2HIP_DNN_API_types.cpp @@ -76,7 +76,7 @@ const std::map CUDA_DNN_TYPE_NAME_MAP { {"CUDNN_STATUS_RUNTIME_FP_OVERFLOW", {"HIPDNN_STATUS_RUNTIME_FP_OVERFLOW", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 13 {"CUDNN_STATUS_VERSION_MISMATCH", {"HIPDNN_STATUS_VERSION_MISMATCH", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 14 {"cudnnRuntimeTag_t", {"hipdnnRuntimeTag_t", "", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}}, - {"cudnnConvolutionMode_t", {"hipdnnConvolutionMode_t", "", CONV_TYPE, API_DNN, 1}}, + {"cudnnConvolutionMode_t", {"hipdnnConvolutionMode_t", "miopenConvolutionMode_t", CONV_TYPE, API_DNN, 1}}, {"CUDNN_CONVOLUTION", {"HIPDNN_CONVOLUTION", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 {"CUDNN_CROSS_CORRELATION", {"HIPDNN_CROSS_CORRELATION", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 {"cudnnTensorFormat_t", {"hipdnnTensorFormat_t", "", CONV_TYPE, API_DNN, 1}}, @@ -132,8 +132,8 @@ const std::map CUDA_DNN_TYPE_NAME_MAP { {"cudnnCTCLossAlgo_t", {"hipdnnCTCLossAlgo_t", "", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}}, {"CUDNN_CTC_LOSS_ALGO_DETERMINISTIC", {"HIPDNN_CTC_LOSS_ALGO_DETERMINISTIC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 0 {"CUDNN_CTC_LOSS_ALGO_NON_DETERMINISTIC", {"HIPDNN_CTC_LOSS_ALGO_NON_DETERMINISTIC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 1 - {"cudnnLRNMode_t", {"hipdnnLRNMode_t", "", CONV_TYPE, API_DNN, 1}}, - {"CUDNN_LRN_CROSS_CHANNEL_DIM1", {"HIPDNN_LRN_CROSS_CHANNEL", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 vs 1 + {"cudnnLRNMode_t", {"hipdnnLRNMode_t", "miopenLRNMode_t", CONV_TYPE, API_DNN, 1}}, + {"CUDNN_LRN_CROSS_CHANNEL_DIM1", {"HIPDNN_LRN_CROSS_CHANNEL", "miopenLRNCrossChannel", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 vs 1 {"cudnnRNNInputMode_t", {"hipdnnRNNInputMode_t", "", CONV_TYPE, API_DNN, 1}}, {"CUDNN_LINEAR_INPUT", {"HIPDNN_LINEAR_INPUT", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 {"CUDNN_SKIP_INPUT", {"HIPDNN_SKIP_INPUT", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 @@ -185,23 +185,23 @@ const std::map CUDA_DNN_TYPE_NAME_MAP { {"CUDNN_RNN_SINGLE_INP_BIAS", {"HIPDNN_RNN_WITH_BIAS", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 {"CUDNN_RNN_DOUBLE_BIAS", {"HIPDNN_RNN_WITH_BIAS", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 {"CUDNN_RNN_SINGLE_REC_BIAS", {"HIPDNN_RNN_WITH_BIAS", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 - {"cudnnOpTensorOp_t", {"hipdnnOpTensorOp_t", "", CONV_TYPE, API_DNN, 1}}, - {"CUDNN_OP_TENSOR_ADD", {"HIPDNN_OP_TENSOR_ADD", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 - {"CUDNN_OP_TENSOR_MUL", {"HIPDNN_OP_TENSOR_MUL", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 - {"CUDNN_OP_TENSOR_MIN", {"HIPDNN_OP_TENSOR_MIN", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 - {"CUDNN_OP_TENSOR_MAX", {"HIPDNN_OP_TENSOR_MAX", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 3 - {"CUDNN_OP_TENSOR_SQRT", {"HIPDNN_OP_TENSOR_SQRT", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 4 - {"CUDNN_OP_TENSOR_NOT", {"HIPDNN_OP_TENSOR_NOT", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 5 - {"cudnnReduceTensorOp_t", {"hipdnnReduceTensorOp_t", "", CONV_TYPE, API_DNN, 1}}, - {"CUDNN_REDUCE_TENSOR_ADD", {"HIPDNN_REDUCE_TENSOR_ADD", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 - {"CUDNN_REDUCE_TENSOR_MUL", {"HIPDNN_REDUCE_TENSOR_MUL", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 - {"CUDNN_REDUCE_TENSOR_MIN", {"HIPDNN_REDUCE_TENSOR_MIN", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 - {"CUDNN_REDUCE_TENSOR_MAX", {"HIPDNN_REDUCE_TENSOR_MAX", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 3 - {"CUDNN_REDUCE_TENSOR_AMAX", {"HIPDNN_REDUCE_TENSOR_AMAX", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 4 - {"CUDNN_REDUCE_TENSOR_AVG", {"HIPDNN_REDUCE_TENSOR_AVG", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 5 - {"CUDNN_REDUCE_TENSOR_NORM1", {"HIPDNN_REDUCE_TENSOR_NORM1", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 6 - {"CUDNN_REDUCE_TENSOR_NORM2", {"HIPDNN_REDUCE_TENSOR_NORM2", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 7 - {"CUDNN_REDUCE_TENSOR_MUL_NO_ZEROS", {"HIPDNN_REDUCE_TENSOR_MUL_NO_ZEROS", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 8 + {"cudnnOpTensorOp_t", {"hipdnnOpTensorOp_t", "miopenTensorOp_t", CONV_TYPE, API_DNN, 1}}, + {"CUDNN_OP_TENSOR_ADD", {"HIPDNN_OP_TENSOR_ADD", "miopenTensorOpAdd", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 + {"CUDNN_OP_TENSOR_MUL", {"HIPDNN_OP_TENSOR_MUL", "miopenTensorOpMul", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 + {"CUDNN_OP_TENSOR_MIN", {"HIPDNN_OP_TENSOR_MIN", "miopenTensorOpMin", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 + {"CUDNN_OP_TENSOR_MAX", {"HIPDNN_OP_TENSOR_MAX", "miopenTensorOpMax", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 3 + {"CUDNN_OP_TENSOR_SQRT", {"HIPDNN_OP_TENSOR_SQRT", "", CONV_NUMERIC_LITERAL, API_DNN, 1, ROC_UNSUPPORTED}}, // 4 + {"CUDNN_OP_TENSOR_NOT", {"HIPDNN_OP_TENSOR_NOT", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 5 + {"cudnnReduceTensorOp_t", {"hipdnnReduceTensorOp_t", "miopenReduceTensorOp_t", CONV_TYPE, API_DNN, 1}}, + {"CUDNN_REDUCE_TENSOR_ADD", {"HIPDNN_REDUCE_TENSOR_ADD", "MIOPEN_REDUCE_TENSOR_ADD", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 + {"CUDNN_REDUCE_TENSOR_MUL", {"HIPDNN_REDUCE_TENSOR_MUL", "MIOPEN_REDUCE_TENSOR_MUL", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 + {"CUDNN_REDUCE_TENSOR_MIN", {"HIPDNN_REDUCE_TENSOR_MIN", "MIOPEN_REDUCE_TENSOR_MIN", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 + {"CUDNN_REDUCE_TENSOR_MAX", {"HIPDNN_REDUCE_TENSOR_MAX", "MIOPEN_REDUCE_TENSOR_MAX", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 3 + {"CUDNN_REDUCE_TENSOR_AMAX", {"HIPDNN_REDUCE_TENSOR_AMAX", "MIOPEN_REDUCE_TENSOR_AMAX", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 4 + {"CUDNN_REDUCE_TENSOR_AVG", {"HIPDNN_REDUCE_TENSOR_AVG", "MIOPEN_REDUCE_TENSOR_AVG", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 5 + {"CUDNN_REDUCE_TENSOR_NORM1", {"HIPDNN_REDUCE_TENSOR_NORM1", "MIOPEN_REDUCE_TENSOR_NORM1", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 6 + {"CUDNN_REDUCE_TENSOR_NORM2", {"HIPDNN_REDUCE_TENSOR_NORM2", "MIOPEN_REDUCE_TENSOR_NORM2", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 7 + {"CUDNN_REDUCE_TENSOR_MUL_NO_ZEROS", {"HIPDNN_REDUCE_TENSOR_MUL_NO_ZEROS", "", CONV_NUMERIC_LITERAL, API_DNN, 1, ROC_UNSUPPORTED}}, // 8 {"cudnnReduceTensorIndices_t", {"hipdnnReduceTensorIndices_t", "", CONV_TYPE, API_DNN, 1}}, {"CUDNN_REDUCE_TENSOR_NO_INDICES", {"HIPDNN_REDUCE_TENSOR_NO_INDICES", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 {"CUDNN_REDUCE_TENSOR_FLATTENED_INDICES", {"HIPDNN_REDUCE_TENSOR_FLATTENED_INDICES", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 @@ -214,30 +214,30 @@ const std::map CUDA_DNN_TYPE_NAME_MAP { {"CUDNN_64BIT_INDICES", {"HIPDNN_64BIT_INDICES", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 {"CUDNN_16BIT_INDICES", {"HIPDNN_16BIT_INDICES", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 {"CUDNN_8BIT_INDICES", {"HIPDNN_8BIT_INDICES", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 3 - {"cudnnSoftmaxAlgorithm_t", {"hipdnnSoftmaxAlgorithm_t", "", CONV_TYPE, API_DNN, 1}}, - {"CUDNN_SOFTMAX_FAST", {"HIPDNN_SOFTMAX_FAST", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 - {"CUDNN_SOFTMAX_ACCURATE", {"HIPDNN_SOFTMAX_ACCURATE", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 - {"CUDNN_SOFTMAX_LOG", {"HIPDNN_SOFTMAX_LOG", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 - {"cudnnSoftmaxMode_t", {"hipdnnSoftmaxMode_t", "", CONV_TYPE, API_DNN, 1}}, - {"CUDNN_SOFTMAX_MODE_INSTANCE", {"HIPDNN_SOFTMAX_MODE_INSTANCE", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 - {"CUDNN_SOFTMAX_MODE_CHANNEL", {"HIPDNN_SOFTMAX_MODE_CHANNEL", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 - {"cudnnPoolingMode_t", {"hipdnnPoolingMode_t", "", CONV_TYPE, API_DNN, 1}}, - {"CUDNN_POOLING_MAX", {"HIPDNN_POOLING_MAX", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 + {"cudnnSoftmaxAlgorithm_t", {"hipdnnSoftmaxAlgorithm_t", "miopenSoftmaxAlgorithm_t", CONV_TYPE, API_DNN, 1}}, + {"CUDNN_SOFTMAX_FAST", {"HIPDNN_SOFTMAX_FAST", "MIOPEN_SOFTMAX_FAST", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 + {"CUDNN_SOFTMAX_ACCURATE", {"HIPDNN_SOFTMAX_ACCURATE", "MIOPEN_SOFTMAX_ACCURATE", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 + {"CUDNN_SOFTMAX_LOG", {"HIPDNN_SOFTMAX_LOG", "MIOPEN_SOFTMAX_LOG", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 + {"cudnnSoftmaxMode_t", {"hipdnnSoftmaxMode_t", "miopenSoftmaxMode_t", CONV_TYPE, API_DNN, 1}}, + {"CUDNN_SOFTMAX_MODE_INSTANCE", {"HIPDNN_SOFTMAX_MODE_INSTANCE", "MIOPEN_SOFTMAX_MODE_INSTANCE", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 + {"CUDNN_SOFTMAX_MODE_CHANNEL", {"HIPDNN_SOFTMAX_MODE_CHANNEL", "MIOPEN_SOFTMAX_MODE_CHANNEL", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 + {"cudnnPoolingMode_t", {"hipdnnPoolingMode_t", "miopenPoolingMode_t", CONV_TYPE, API_DNN, 1}}, + {"CUDNN_POOLING_MAX", {"HIPDNN_POOLING_MAX", "miopenPoolingMax", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 {"CUDNN_POOLING_AVERAGE_COUNT_INCLUDE_PADDING", {"HIPDNN_POOLING_AVERAGE_COUNT_INCLUDE_PADDING", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 {"CUDNN_POOLING_AVERAGE_COUNT_EXCLUDE_PADDING", {"HIPDNN_POOLING_AVERAGE_COUNT_EXCLUDE_PADDING", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 {"CUDNN_POOLING_MAX_DETERMINISTIC", {"HIPDNN_POOLING_MAX_DETERMINISTIC", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 3 - {"cudnnActivationMode_t", {"hipdnnActivationMode_t", "", CONV_TYPE, API_DNN, 1}}, + {"cudnnActivationMode_t", {"hipdnnActivationMode_t", "miopenActivationMode_t", CONV_TYPE, API_DNN, 1}}, {"CUDNN_ACTIVATION_SIGMOID", {"HIPDNN_ACTIVATION_SIGMOID", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 - {"CUDNN_ACTIVATION_RELU", {"HIPDNN_ACTIVATION_RELU", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 - {"CUDNN_ACTIVATION_TANH", {"HIPDNN_ACTIVATION_TANH", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 - {"CUDNN_ACTIVATION_CLIPPED_RELU", {"HIPDNN_ACTIVATION_CLIPPED_RELU", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 3 - {"CUDNN_ACTIVATION_ELU", {"HIPDNN_ACTIVATION_ELU", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 4 - {"CUDNN_ACTIVATION_IDENTITY", {"HIPDNN_ACTIVATION_PATHTRU", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 5 + {"CUDNN_ACTIVATION_RELU", {"HIPDNN_ACTIVATION_RELU", "miopenActivationRELU", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 + {"CUDNN_ACTIVATION_TANH", {"HIPDNN_ACTIVATION_TANH", "miopenActivationTANH", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 + {"CUDNN_ACTIVATION_CLIPPED_RELU", {"HIPDNN_ACTIVATION_CLIPPED_RELU", "miopenActivationCLIPPEDRELU", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 3 + {"CUDNN_ACTIVATION_ELU", {"HIPDNN_ACTIVATION_ELU", "miopenActivationELU", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 4 + {"CUDNN_ACTIVATION_IDENTITY", {"HIPDNN_ACTIVATION_PATHTRU", "miopenActivationPASTHRU", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 5 {"CUDNN_ACTIVATION_SWISH", {"HIPDNN_ACTIVATION_SWISH", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 6 - {"cudnnBatchNormMode_t", {"hipdnnBatchNormMode_t", "", CONV_TYPE, API_DNN, 1}}, - {"CUDNN_BATCHNORM_PER_ACTIVATION", {"HIPDNN_BATCHNORM_PER_ACTIVATION", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 - {"CUDNN_BATCHNORM_SPATIAL", {"HIPDNN_BATCHNORM_SPATIAL", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 - {"CUDNN_BATCHNORM_SPATIAL_PERSISTENT", {"HIPDNN_BATCHNORM_SPATIAL_PERSISTENT", "", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 2 + {"cudnnBatchNormMode_t", {"hipdnnBatchNormMode_t", "miopenBatchNormMode_t", CONV_TYPE, API_DNN, 1}}, + {"CUDNN_BATCHNORM_PER_ACTIVATION", {"HIPDNN_BATCHNORM_PER_ACTIVATION", "miopenBNPerActivation", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 0 + {"CUDNN_BATCHNORM_SPATIAL", {"HIPDNN_BATCHNORM_SPATIAL", "miopenBNSpatial", CONV_NUMERIC_LITERAL, API_DNN, 1}}, // 1 + {"CUDNN_BATCHNORM_SPATIAL_PERSISTENT", {"HIPDNN_BATCHNORM_SPATIAL_PERSISTENT", "", CONV_NUMERIC_LITERAL, API_DNN, 1, ROC_UNSUPPORTED}}, // 2 {"cudnnSamplerType_t", {"hipdnnSamplerType_t", "", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}}, {"CUDNN_SAMPLER_BILINEAR", {"HIPDNN_SAMPLER_BILINEAR", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 0 {"cudnnBatchNormOps_t", {"hipdnnBatchNormOps_t", "", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}}, @@ -331,10 +331,10 @@ const std::map CUDA_DNN_TYPE_NAME_MAP { {"CUDNN_PARAM_DZDATA_PLACEHOLDER", {"HIPDNN_PARAM_DZDATA_PLACEHOLDER", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 36 {"CUDNN_PARAM_BN_DSCALE_PLACEHOLDER", {"HIPDNN_PARAM_BN_DSCALE_PLACEHOLDER", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 37 {"CUDNN_PARAM_BN_DBIAS_PLACEHOLDER", {"HIPDNN_PARAM_BN_DBIAS_PLACEHOLDER", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 38 - {"cudnnFusedOpsPointerPlaceHolder_t", {"hipdnnActivationMode_t", "", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}}, - {"CUDNN_PTR_NULL", {"HIPDNN_ACTIVATION_SIGMOID", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 0 - {"CUDNN_PTR_ELEM_ALIGNED", {"HIPDNN_ACTIVATION_RELU", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 1 - {"CUDNN_PTR_16B_ALIGNED", {"HIPDNN_ACTIVATION_TANH", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 2 + {"cudnnFusedOpsPointerPlaceHolder_t", {"hipdnnFusedOpsPointerPlaceHolder_t", "", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}}, + {"CUDNN_PTR_NULL", {"HIPDNN_PTR_NULL", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 0 + {"CUDNN_PTR_ELEM_ALIGNED", {"HIPDNN_PTR_ELEM_ALIGNED", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 1 + {"CUDNN_PTR_16B_ALIGNED", {"HIPDNN_PTR_16B_ALIGNED", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 2 {"cudnnFusedOpsVariantParamLabel_t", {"hipdnnFusedOpsVariantParamLabel_t", "", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}}, {"CUDNN_PTR_XDATA", {"HIPDNN_PTR_XDATA", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 0 {"CUDNN_PTR_BN_EQSCALE", {"HIPDNN_PTR_BN_EQSCALE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 1 diff --git a/tests/unit_tests/synthetic/libraries/cudnn2miopen.cu b/tests/unit_tests/synthetic/libraries/cudnn2miopen.cu index c15aae9a..4434036a 100644 --- a/tests/unit_tests/synthetic/libraries/cudnn2miopen.cu +++ b/tests/unit_tests/synthetic/libraries/cudnn2miopen.cu @@ -106,5 +106,77 @@ int main() { cudnnDataType_t DATA_INT8x4 = CUDNN_DATA_INT8x4; cudnnDataType_t DATA_BFLOAT16 = CUDNN_DATA_BFLOAT16; + // CHECK: miopenTensorOp_t tensorOp; + // CHECK-NEXT: miopenTensorOp_t OP_TENSOR_ADD = miopenTensorOpAdd; + // CHECK-NEXT: miopenTensorOp_t OP_TENSOR_MUL = miopenTensorOpMul; + // CHECK-NEXT: miopenTensorOp_t OP_TENSOR_MIN = miopenTensorOpMin; + // CHECK-NEXT: miopenTensorOp_t OP_TENSOR_MAX = miopenTensorOpMax; + cudnnOpTensorOp_t tensorOp; + cudnnOpTensorOp_t OP_TENSOR_ADD = CUDNN_OP_TENSOR_ADD; + cudnnOpTensorOp_t OP_TENSOR_MUL = CUDNN_OP_TENSOR_MUL; + cudnnOpTensorOp_t OP_TENSOR_MIN = CUDNN_OP_TENSOR_MIN; + cudnnOpTensorOp_t OP_TENSOR_MAX = CUDNN_OP_TENSOR_MAX; + + // CHECK: miopenConvolutionMode_t convolutionMode; + cudnnConvolutionMode_t convolutionMode; + + // CHECK: miopenPoolingMode_t poolingMode; + // CHECK-NEXT: miopenPoolingMode_t POOLING_MAX = miopenPoolingMax; + cudnnPoolingMode_t poolingMode; + cudnnPoolingMode_t POOLING_MAX = CUDNN_POOLING_MAX; + + // CHECK: miopenLRNMode_t LRNMode; + // CHECK-NEXT: miopenLRNMode_t LRN_CROSS_CHANNEL_DIM1 = miopenLRNCrossChannel; + cudnnLRNMode_t LRNMode; + cudnnLRNMode_t LRN_CROSS_CHANNEL_DIM1 = CUDNN_LRN_CROSS_CHANNEL_DIM1; + + // CHECK: miopenBatchNormMode_t batchNormMode; + // CHECK-NEXT: miopenBatchNormMode_t BATCHNORM_PER_ACTIVATION = miopenBNPerActivation; + // CHECK-NEXT: miopenBatchNormMode_t BATCHNORM_SPATIAL = miopenBNSpatial; + cudnnBatchNormMode_t batchNormMode; + cudnnBatchNormMode_t BATCHNORM_PER_ACTIVATION = CUDNN_BATCHNORM_PER_ACTIVATION; + cudnnBatchNormMode_t BATCHNORM_SPATIAL = CUDNN_BATCHNORM_SPATIAL; + + // CHECK: miopenActivationMode_t activationMode; + // CHECK-NEXT: miopenActivationMode_t ACTIVATION_RELU = miopenActivationRELU; + // CHECK-NEXT: miopenActivationMode_t ACTIVATION_TANH = miopenActivationTANH; + // CHECK-NEXT: miopenActivationMode_t ACTIVATION_CLIPPED_RELU = miopenActivationCLIPPEDRELU; + // CHECK-NEXT: miopenActivationMode_t ACTIVATION_ELU = miopenActivationELU; + // CHECK-NEXT: miopenActivationMode_t ACTIVATION_IDENTITY = miopenActivationPASTHRU; + cudnnActivationMode_t activationMode; + cudnnActivationMode_t ACTIVATION_RELU = CUDNN_ACTIVATION_RELU; + cudnnActivationMode_t ACTIVATION_TANH = CUDNN_ACTIVATION_TANH; + cudnnActivationMode_t ACTIVATION_CLIPPED_RELU = CUDNN_ACTIVATION_CLIPPED_RELU; + cudnnActivationMode_t ACTIVATION_ELU = CUDNN_ACTIVATION_ELU; + cudnnActivationMode_t ACTIVATION_IDENTITY = CUDNN_ACTIVATION_IDENTITY; + + // CHECK: miopenSoftmaxAlgorithm_t softmaxAlgorithm; + // CHECK-NEXT: miopenSoftmaxAlgorithm_t SOFTMAX_FAST = MIOPEN_SOFTMAX_FAST; + // CHECK-NEXT: miopenSoftmaxAlgorithm_t SOFTMAX_ACCURATE = MIOPEN_SOFTMAX_ACCURATE; + // CHECK-NEXT: miopenSoftmaxAlgorithm_t SOFTMAX_LOG = MIOPEN_SOFTMAX_LOG; + cudnnSoftmaxAlgorithm_t softmaxAlgorithm; + cudnnSoftmaxAlgorithm_t SOFTMAX_FAST = CUDNN_SOFTMAX_FAST; + cudnnSoftmaxAlgorithm_t SOFTMAX_ACCURATE = CUDNN_SOFTMAX_ACCURATE; + cudnnSoftmaxAlgorithm_t SOFTMAX_LOG = CUDNN_SOFTMAX_LOG; + + // CHECK: miopenReduceTensorOp_t reduceTensorOp; + // CHECK-NEXT: miopenReduceTensorOp_t REDUCE_TENSOR_ADD = MIOPEN_REDUCE_TENSOR_ADD; + // CHECK-NEXT: miopenReduceTensorOp_t REDUCE_TENSOR_MUL = MIOPEN_REDUCE_TENSOR_MUL; + // CHECK-NEXT: miopenReduceTensorOp_t REDUCE_TENSOR_MIN = MIOPEN_REDUCE_TENSOR_MIN; + // CHECK-NEXT: miopenReduceTensorOp_t REDUCE_TENSOR_MAX = MIOPEN_REDUCE_TENSOR_MAX; + // CHECK-NEXT: miopenReduceTensorOp_t REDUCE_TENSOR_AMAX = MIOPEN_REDUCE_TENSOR_AMAX; + // CHECK-NEXT: miopenReduceTensorOp_t REDUCE_TENSOR_AVG = MIOPEN_REDUCE_TENSOR_AVG; + // CHECK-NEXT: miopenReduceTensorOp_t REDUCE_TENSOR_NORM1 = MIOPEN_REDUCE_TENSOR_NORM1; + // CHECK-NEXT: miopenReduceTensorOp_t REDUCE_TENSOR_NORM2 = MIOPEN_REDUCE_TENSOR_NORM2; + cudnnReduceTensorOp_t reduceTensorOp; + cudnnReduceTensorOp_t REDUCE_TENSOR_ADD = CUDNN_REDUCE_TENSOR_ADD; + cudnnReduceTensorOp_t REDUCE_TENSOR_MUL = CUDNN_REDUCE_TENSOR_MUL; + cudnnReduceTensorOp_t REDUCE_TENSOR_MIN = CUDNN_REDUCE_TENSOR_MIN; + cudnnReduceTensorOp_t REDUCE_TENSOR_MAX = CUDNN_REDUCE_TENSOR_MAX; + cudnnReduceTensorOp_t REDUCE_TENSOR_AMAX = CUDNN_REDUCE_TENSOR_AMAX; + cudnnReduceTensorOp_t REDUCE_TENSOR_AVG = CUDNN_REDUCE_TENSOR_AVG; + cudnnReduceTensorOp_t REDUCE_TENSOR_NORM1 = CUDNN_REDUCE_TENSOR_NORM1; + cudnnReduceTensorOp_t REDUCE_TENSOR_NORM2 = CUDNN_REDUCE_TENSOR_NORM2; + return 0; }