diff --git a/bin/hipify-perl b/bin/hipify-perl index 4eb4cf41..095ad793 100644 --- a/bin/hipify-perl +++ b/bin/hipify-perl @@ -8445,6 +8445,11 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'CUDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_UPPER_BANDWIDTH' => 1, 'CUDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_XDESC' => 1, 'CUDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_YDESC' => 1, + 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DOUTPUT_DESC' => 1, + 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DWEIGHT_DESC' => 1, + 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_FIRST_TOKEN_OFFSET_DESC' => 1, + 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_MATH_PREC' => 1, + 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_TOKEN_DESC' => 1, 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_FIRST_TOKEN_OFFSET_DESC' => 1, 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_MATH_PREC' => 1, 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_MODE' => 1, @@ -8458,6 +8463,7 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'CUDNN_ATTR_OPERATION_PAGED_CACHE_LOAD_PAGE_TABLE_DESC' => 1, 'CUDNN_ATTR_OPERATION_PAGED_CACHE_LOAD_SEQUENCE_DESC' => 1, 'CUDNN_ATTR_OPERATION_PAGED_CACHE_LOAD_YDESC' => 1, + 'CUDNN_ATTR_OPERATION_RESHAPE_MODE' => 1, 'CUDNN_ATTR_OPERATION_SDPA_BWD_DKDESC' => 1, 'CUDNN_ATTR_OPERATION_SDPA_BWD_DODDESC' => 1, 'CUDNN_ATTR_OPERATION_SDPA_BWD_DQDESC' => 1, @@ -8497,13 +8503,22 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'CUDNN_ATTR_OPERATION_SDPA_FWD_SUBGRAPH_OUTPUT_UID' => 1, 'CUDNN_ATTR_OPERATION_SDPA_FWD_UNFUSE_FMA' => 1, 'CUDNN_ATTR_OPERATION_SDPA_FWD_VDESC' => 1, + 'CUDNN_ATTR_OPERATION_SLICE_LIMIT_INDICES' => 1, + 'CUDNN_ATTR_OPERATION_SLICE_START_INDICES' => 1, + 'CUDNN_ATTR_OPERATION_SLICE_STRIDES' => 1, + 'CUDNN_ATTR_OPERATION_SLICE_XDESC' => 1, + 'CUDNN_ATTR_OPERATION_SLICE_YDESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_MAX_DESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_SINK_DESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_STATS_DESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_SUM_EXP_DESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_XDESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_YDESC' => 1, + 'CUDNN_ATTR_OPERATION_TRANSPOSE_PERMUTATION' => 1, + 'CUDNN_ATTR_OPERATION_TRANSPOSE_XDESC' => 1, + 'CUDNN_ATTR_OPERATION_TRANSPOSE_YDESC' => 1, 'CUDNN_ATTR_REDUCTION_IS_DETERMINISTIC' => 1, + 'CUDNN_ATTR_TENSOR_CONSTANT_VALUE' => 1, 'CUDNN_ATTR_VARIANT_PACK_OVERRIDE_SHAPES' => 1, 'CUDNN_ATTR_VARIANT_PACK_OVERRIDE_STRIDES' => 1, 'CUDNN_ATTR_VARIANT_PACK_OVERRIDE_UNIQUE_IDS' => 1, @@ -8516,11 +8531,14 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'CUDNN_BACKEND_OPERATION_CONTRACT_BAND_MATRIX_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_DIAGONAL_BAND_MASK_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_EXPAND_BAND_MATRIX_DESCRIPTOR' => 1, + 'CUDNN_BACKEND_OPERATION_MOE_GROUPED_MATMUL_BWD_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_MOE_GROUPED_MATMUL_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_PAGED_CACHE_LOAD_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_SDPA_BWD_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_SDPA_FWD_DESCRIPTOR' => 1, + 'CUDNN_BACKEND_OPERATION_SLICE_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_SOFTMAX_DESCRIPTOR' => 1, + 'CUDNN_BACKEND_OPERATION_TRANSPOSE_DESCRIPTOR' => 1, 'CUDNN_BATCHNORM_OPS_BN' => 1, 'CUDNN_BATCHNORM_OPS_BN_ACTIVATION' => 1, 'CUDNN_BATCHNORM_OPS_BN_ADD_ACTIVATION' => 1, @@ -8535,6 +8553,8 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'CUDNN_BN_FINALIZE_STATISTICS_INFERENCE' => 1, 'CUDNN_BN_FINALIZE_STATISTICS_TRAINING' => 1, 'CUDNN_BN_MIN_EPSILON' => 1, + 'CUDNN_CAUSAL_CONV1D_ACTIVATION_IDENTITY' => 1, + 'CUDNN_CAUSAL_CONV1D_ACTIVATION_SILU' => 1, 'CUDNN_CONVOLUTION_BWD_DATA_ALGO_FFT_TILING' => 1, 'CUDNN_CONVOLUTION_BWD_DATA_ALGO_WINOGRAD_NONFUSED' => 1, 'CUDNN_CONVOLUTION_BWD_DATA_NO_WORKSPACE' => 1, @@ -8599,6 +8619,7 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'CUDNN_KNOB_TYPE_CTA_SPLIT_K_MODE' => 1, 'CUDNN_KNOB_TYPE_EDGE' => 1, 'CUDNN_KNOB_TYPE_IDX_MODE' => 1, + 'CUDNN_KNOB_TYPE_INPUT_TMA_ENABLE' => 1, 'CUDNN_KNOB_TYPE_KBLOCK' => 1, 'CUDNN_KNOB_TYPE_KERNEL_CFG' => 1, 'CUDNN_KNOB_TYPE_LDGA' => 1, @@ -8608,6 +8629,7 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'CUDNN_KNOB_TYPE_MULTIPLY' => 1, 'CUDNN_KNOB_TYPE_NUM_C_PER_BLOCK' => 1, 'CUDNN_KNOB_TYPE_OCCUPANCY' => 1, + 'CUDNN_KNOB_TYPE_OUTPUT_TMA_ENABLE' => 1, 'CUDNN_KNOB_TYPE_REDUCTION_MODE' => 1, 'CUDNN_KNOB_TYPE_SINGLEBUFFER' => 1, 'CUDNN_KNOB_TYPE_SLICED' => 1, @@ -8758,6 +8780,8 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'CUDNN_RESAMPLE_BILINEAR' => 1, 'CUDNN_RESAMPLE_MAXPOOL' => 1, 'CUDNN_RESAMPLE_NEAREST' => 1, + 'CUDNN_RESHAPE_LOGICAL' => 1, + 'CUDNN_RESHAPE_VIEW_ONLY' => 1, 'CUDNN_RMS_NORM' => 1, 'CUDNN_RNN_ALGO_COUNT' => 1, 'CUDNN_RNN_ALGO_PERSIST_DYNAMIC' => 1, @@ -8845,6 +8869,7 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'CUDNN_TENSOR_REORDERING_NONE' => 1, 'CUDNN_TRANSFORM_FOLD' => 1, 'CUDNN_TRANSFORM_UNFOLD' => 1, + 'CUDNN_TYPE_RESHAPE_MODE' => 1, 'CUDNN_WGRAD_MODE_ADD' => 1, 'CUDNN_WGRAD_MODE_SET' => 1, 'cudnnActivationStruct' => 1, @@ -8869,6 +8894,7 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'cudnnBackendNormMode_t' => 1, 'cudnnBackendNumericalNote_t' => 1, 'cudnnBackendPopulateCudaGraph' => 1, + 'cudnnBackendReshapeMode_t' => 1, 'cudnnBackendTensorReordering_t' => 1, 'cudnnBackendUpdateCudaGraph' => 1, 'cudnnBatchNormOps_t' => 1, @@ -8880,6 +8906,9 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'cudnnCTCLossStruct' => 1, 'cudnnCTCLoss_v8' => 1, 'cudnnCallback_t' => 1, + 'cudnnCausalConv1dActivation_t' => 1, + 'cudnnCausalConv1dBackward' => 1, + 'cudnnCausalConv1dForward' => 1, 'cudnnCnnInferVersionCheck' => 1, 'cudnnCnnTrainVersionCheck' => 1, 'cudnnConvolutionBackwardFilter' => 1, @@ -9119,6 +9148,7 @@ my %hash_MIOpenOnlyUnsupportedFunctions = ( 'cudnnSpatialTfSamplerForward' => 1, 'cudnnSpatialTransformerDescriptor_t' => 1, 'cudnnSpatialTransformerStruct' => 1, + 'cudnnSubquadraticOpsVersionCheck' => 1, 'cudnnTensorStruct' => 1, 'cudnnTensorTransformDescriptor_t' => 1, 'cudnnTensorTransformStruct' => 1, @@ -9292,6 +9322,11 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_ATTR_OPERATION_MATMUL_GEMM_M_OVERRIDE_DESC' => 1, 'CUDNN_ATTR_OPERATION_MATMUL_GEMM_N_OVERRIDE_DESC' => 1, 'CUDNN_ATTR_OPERATION_MATMUL_IRREGULARLY_STRIDED_BATCH_COUNT' => 1, + 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DOUTPUT_DESC' => 1, + 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DWEIGHT_DESC' => 1, + 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_FIRST_TOKEN_OFFSET_DESC' => 1, + 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_MATH_PREC' => 1, + 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_TOKEN_DESC' => 1, 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_FIRST_TOKEN_OFFSET_DESC' => 1, 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_MATH_PREC' => 1, 'CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_MODE' => 1, @@ -9357,6 +9392,7 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_ATTR_OPERATION_RESAMPLE_FWD_IDXDESC' => 1, 'CUDNN_ATTR_OPERATION_RESAMPLE_FWD_XDESC' => 1, 'CUDNN_ATTR_OPERATION_RESAMPLE_FWD_YDESC' => 1, + 'CUDNN_ATTR_OPERATION_RESHAPE_MODE' => 1, 'CUDNN_ATTR_OPERATION_RESHAPE_XDESC' => 1, 'CUDNN_ATTR_OPERATION_RESHAPE_YDESC' => 1, 'CUDNN_ATTR_OPERATION_RNG_DESC' => 1, @@ -9407,12 +9443,20 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_ATTR_OPERATION_SIGNAL_VALUE' => 1, 'CUDNN_ATTR_OPERATION_SIGNAL_XDESC' => 1, 'CUDNN_ATTR_OPERATION_SIGNAL_YDESC' => 1, + 'CUDNN_ATTR_OPERATION_SLICE_LIMIT_INDICES' => 1, + 'CUDNN_ATTR_OPERATION_SLICE_START_INDICES' => 1, + 'CUDNN_ATTR_OPERATION_SLICE_STRIDES' => 1, + 'CUDNN_ATTR_OPERATION_SLICE_XDESC' => 1, + 'CUDNN_ATTR_OPERATION_SLICE_YDESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_MAX_DESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_SINK_DESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_STATS_DESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_SUM_EXP_DESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_XDESC' => 1, 'CUDNN_ATTR_OPERATION_SOFTMAX_YDESC' => 1, + 'CUDNN_ATTR_OPERATION_TRANSPOSE_PERMUTATION' => 1, + 'CUDNN_ATTR_OPERATION_TRANSPOSE_XDESC' => 1, + 'CUDNN_ATTR_OPERATION_TRANSPOSE_YDESC' => 1, 'CUDNN_ATTR_POINTWISE_AXIS' => 1, 'CUDNN_ATTR_POINTWISE_ELU_ALPHA' => 1, 'CUDNN_ATTR_POINTWISE_MATH_PREC' => 1, @@ -9442,6 +9486,7 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_ATTR_RNG_UNIFORM_DIST_MAXIMUM' => 1, 'CUDNN_ATTR_RNG_UNIFORM_DIST_MINIMUM' => 1, 'CUDNN_ATTR_TENSOR_BYTE_ALIGNMENT' => 1, + 'CUDNN_ATTR_TENSOR_CONSTANT_VALUE' => 1, 'CUDNN_ATTR_TENSOR_DATA_TYPE' => 1, 'CUDNN_ATTR_TENSOR_DIMENSIONS' => 1, 'CUDNN_ATTR_TENSOR_IS_BY_VALUE' => 1, @@ -9485,6 +9530,7 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_BACKEND_OPERATION_EXPAND_BAND_MATRIX_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_GEN_STATS_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_MATMUL_DESCRIPTOR' => 1, + 'CUDNN_BACKEND_OPERATION_MOE_GROUPED_MATMUL_BWD_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_MOE_GROUPED_MATMUL_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_NORM_BACKWARD_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_NORM_FORWARD_DESCRIPTOR' => 1, @@ -9498,7 +9544,9 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_BACKEND_OPERATION_SDPA_BWD_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_SDPA_FWD_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_SIGNAL_DESCRIPTOR' => 1, + 'CUDNN_BACKEND_OPERATION_SLICE_DESCRIPTOR' => 1, 'CUDNN_BACKEND_OPERATION_SOFTMAX_DESCRIPTOR' => 1, + 'CUDNN_BACKEND_OPERATION_TRANSPOSE_DESCRIPTOR' => 1, 'CUDNN_BACKEND_POINTWISE_DESCRIPTOR' => 1, 'CUDNN_BACKEND_REDUCTION_DESCRIPTOR' => 1, 'CUDNN_BACKEND_RESAMPLE_DESCRIPTOR' => 1, @@ -9517,6 +9565,8 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_BEHAVIOR_NOTE_TYPE_COUNT' => 1, 'CUDNN_BN_FINALIZE_STATISTICS_INFERENCE' => 1, 'CUDNN_BN_FINALIZE_STATISTICS_TRAINING' => 1, + 'CUDNN_CAUSAL_CONV1D_ACTIVATION_IDENTITY' => 1, + 'CUDNN_CAUSAL_CONV1D_ACTIVATION_SILU' => 1, 'CUDNN_CTC_LOSS_ALGO_DETERMINISTIC' => 1, 'CUDNN_CTC_LOSS_ALGO_NON_DETERMINISTIC' => 1, 'CUDNN_CTC_SKIP_OOB_GRADIENTS' => 1, @@ -9571,6 +9621,7 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_KNOB_TYPE_CTA_SPLIT_K_MODE' => 1, 'CUDNN_KNOB_TYPE_EDGE' => 1, 'CUDNN_KNOB_TYPE_IDX_MODE' => 1, + 'CUDNN_KNOB_TYPE_INPUT_TMA_ENABLE' => 1, 'CUDNN_KNOB_TYPE_KBLOCK' => 1, 'CUDNN_KNOB_TYPE_KERNEL_CFG' => 1, 'CUDNN_KNOB_TYPE_LDGA' => 1, @@ -9580,6 +9631,7 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_KNOB_TYPE_MULTIPLY' => 1, 'CUDNN_KNOB_TYPE_NUM_C_PER_BLOCK' => 1, 'CUDNN_KNOB_TYPE_OCCUPANCY' => 1, + 'CUDNN_KNOB_TYPE_OUTPUT_TMA_ENABLE' => 1, 'CUDNN_KNOB_TYPE_REDUCTION_MODE' => 1, 'CUDNN_KNOB_TYPE_SINGLEBUFFER' => 1, 'CUDNN_KNOB_TYPE_SLICED' => 1, @@ -9778,6 +9830,8 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_RESAMPLE_BILINEAR' => 1, 'CUDNN_RESAMPLE_MAXPOOL' => 1, 'CUDNN_RESAMPLE_NEAREST' => 1, + 'CUDNN_RESHAPE_LOGICAL' => 1, + 'CUDNN_RESHAPE_VIEW_ONLY' => 1, 'CUDNN_RMS_NORM' => 1, 'CUDNN_RNG_DISTRIBUTION_BERNOULLI' => 1, 'CUDNN_RNG_DISTRIBUTION_NORMAL' => 1, @@ -9888,6 +9942,7 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'CUDNN_TYPE_POINTWISE_MODE' => 1, 'CUDNN_TYPE_REDUCTION_OPERATOR_TYPE' => 1, 'CUDNN_TYPE_RESAMPLE_MODE' => 1, + 'CUDNN_TYPE_RESHAPE_MODE' => 1, 'CUDNN_TYPE_RNG_DISTRIBUTION' => 1, 'CUDNN_TYPE_SIGNAL_MODE' => 1, 'CUDNN_TYPE_TENSOR_REORDERING_MODE' => 1, @@ -9926,6 +9981,7 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'cudnnBackendNormMode_t' => 1, 'cudnnBackendNumericalNote_t' => 1, 'cudnnBackendPopulateCudaGraph' => 1, + 'cudnnBackendReshapeMode_t' => 1, 'cudnnBackendSetAttribute' => 1, 'cudnnBackendTensorReordering_t' => 1, 'cudnnBackendUpdateCudaGraph' => 1, @@ -9941,6 +9997,9 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'cudnnCTCLossStruct' => 1, 'cudnnCTCLoss_v8' => 1, 'cudnnCallback_t' => 1, + 'cudnnCausalConv1dActivation_t' => 1, + 'cudnnCausalConv1dBackward' => 1, + 'cudnnCausalConv1dForward' => 1, 'cudnnCnnInferVersionCheck' => 1, 'cudnnCnnTrainVersionCheck' => 1, 'cudnnContext' => 1, @@ -10151,6 +10210,7 @@ my %hash_HipDNNOnlyUnsupportedFunctions = ( 'cudnnSpatialTfSamplerForward' => 1, 'cudnnSpatialTransformerDescriptor_t' => 1, 'cudnnSpatialTransformerStruct' => 1, + 'cudnnSubquadraticOpsVersionCheck' => 1, 'cudnnTensorStruct' => 1, 'cudnnTensorTransformDescriptor_t' => 1, 'cudnnTensorTransformStruct' => 1, diff --git a/docs/reference/tables/CUDNN_API_supported_by_MIOPEN.md b/docs/reference/tables/CUDNN_API_supported_by_MIOPEN.md index 2b18769e..dc30fc6c 100644 --- a/docs/reference/tables/CUDNN_API_supported_by_MIOPEN.md +++ b/docs/reference/tables/CUDNN_API_supported_by_MIOPEN.md @@ -189,6 +189,11 @@ |`CUDNN_ATTR_OPERATION_MATMUL_GEMM_M_OVERRIDE_DESC`|8.7.0| | | |`MIOPEN_ATTR_OPERATION_MATMUL_GEMM_M_OVERRIDE_DESC`|6.2.0| | | | | | |`CUDNN_ATTR_OPERATION_MATMUL_GEMM_N_OVERRIDE_DESC`|8.7.0| | | |`MIOPEN_ATTR_OPERATION_MATMUL_GEMM_N_OVERRIDE_DESC`|6.2.0| | | | | | |`CUDNN_ATTR_OPERATION_MATMUL_IRREGULARLY_STRIDED_BATCH_COUNT`|8.1.0|9.0.0| | |`MIOPEN_ATTR_OPERATION_MATMUL_IRREGULARLY_STRIDED_BATCH_COUNT`|6.2.0| | | | | | +|`CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DOUTPUT_DESC`|9.22.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DWEIGHT_DESC`|9.22.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_FIRST_TOKEN_OFFSET_DESC`|9.22.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_MATH_PREC`|9.22.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_TOKEN_DESC`|9.22.0| | | | | | | | | | | |`CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_FIRST_TOKEN_OFFSET_DESC`|9.15.0| | | | | | | | | | | |`CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_MATH_PREC`|9.15.0| | | | | | | | | | | |`CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_MODE`|9.15.0| | | | | | | | | | | @@ -254,6 +259,7 @@ |`CUDNN_ATTR_OPERATION_RESAMPLE_FWD_IDXDESC`|8.3.0| | | |`MIOPEN_ATTR_OPERATION_RESAMPLE_FWD_IDXDESC`|6.2.0| | | | | | |`CUDNN_ATTR_OPERATION_RESAMPLE_FWD_XDESC`|8.3.0| | | |`MIOPEN_ATTR_OPERATION_RESAMPLE_FWD_XDESC`|6.2.0| | | | | | |`CUDNN_ATTR_OPERATION_RESAMPLE_FWD_YDESC`|8.3.0| | | |`MIOPEN_ATTR_OPERATION_RESAMPLE_FWD_YDESC`|6.2.0| | | | | | +|`CUDNN_ATTR_OPERATION_RESHAPE_MODE`|9.22.0| | | | | | | | | | | |`CUDNN_ATTR_OPERATION_RESHAPE_XDESC`|8.7.0| | | |`MIOPEN_ATTR_OPERATION_RESHAPE_XDESC`|6.2.0| | | | | | |`CUDNN_ATTR_OPERATION_RESHAPE_YDESC`|8.7.0| | | |`MIOPEN_ATTR_OPERATION_RESHAPE_YDESC`|6.2.0| | | | | | |`CUDNN_ATTR_OPERATION_RNG_DESC`|8.7.0| | | |`MIOPEN_ATTR_OPERATION_RNG_DESC`|6.2.0| | | | | | @@ -304,12 +310,20 @@ |`CUDNN_ATTR_OPERATION_SIGNAL_VALUE`|8.5.0| | | |`MIOPEN_ATTR_OPERATION_SIGNAL_VALUE`|6.2.0| | | | | | |`CUDNN_ATTR_OPERATION_SIGNAL_XDESC`|8.5.0| | | |`MIOPEN_ATTR_OPERATION_SIGNAL_XDESC`|6.2.0| | | | | | |`CUDNN_ATTR_OPERATION_SIGNAL_YDESC`|8.5.0| | | |`MIOPEN_ATTR_OPERATION_SIGNAL_YDESC`|6.2.0| | | | | | +|`CUDNN_ATTR_OPERATION_SLICE_LIMIT_INDICES`|9.22.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_SLICE_START_INDICES`|9.22.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_SLICE_STRIDES`|9.22.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_SLICE_XDESC`|9.22.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_SLICE_YDESC`|9.22.0| | | | | | | | | | | |`CUDNN_ATTR_OPERATION_SOFTMAX_MAX_DESC`|9.20.0| | | | | | | | | | | |`CUDNN_ATTR_OPERATION_SOFTMAX_SINK_DESC`|9.20.0| | | | | | | | | | | |`CUDNN_ATTR_OPERATION_SOFTMAX_STATS_DESC`|9.20.0| | | | | | | | | | | |`CUDNN_ATTR_OPERATION_SOFTMAX_SUM_EXP_DESC`|9.20.0| | | | | | | | | | | |`CUDNN_ATTR_OPERATION_SOFTMAX_XDESC`|9.20.0| | | | | | | | | | | |`CUDNN_ATTR_OPERATION_SOFTMAX_YDESC`|9.20.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_TRANSPOSE_PERMUTATION`|9.22.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_TRANSPOSE_XDESC`|9.22.0| | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_TRANSPOSE_YDESC`|9.22.0| | | | | | | | | | | |`CUDNN_ATTR_POINTWISE_AXIS`|8.4.0| | | |`MIOPEN_ATTR_POINTWISE_AXIS`|6.2.0| | | | | | |`CUDNN_ATTR_POINTWISE_ELU_ALPHA`|8.1.0| | | |`MIOPEN_ATTR_POINTWISE_ELU_ALPHA`|6.2.0| | | | | | |`CUDNN_ATTR_POINTWISE_MATH_PREC`|8.0.1| | | |`MIOPEN_ATTR_POINTWISE_MATH_PREC`|6.2.0| | | | | | @@ -339,6 +353,7 @@ |`CUDNN_ATTR_RNG_UNIFORM_DIST_MAXIMUM`|8.7.0| | | |`MIOPEN_ATTR_RNG_UNIFORM_DIST_MAXIMUM`|6.2.0| | | | | | |`CUDNN_ATTR_RNG_UNIFORM_DIST_MINIMUM`|8.7.0| | | |`MIOPEN_ATTR_RNG_UNIFORM_DIST_MINIMUM`|6.2.0| | | | | | |`CUDNN_ATTR_TENSOR_BYTE_ALIGNMENT`|8.0.1| | | |`MIOPEN_ATTR_TENSOR_BYTE_ALIGNMENT`|6.2.0| | | | | | +|`CUDNN_ATTR_TENSOR_CONSTANT_VALUE`|9.22.0| | | | | | | | | | | |`CUDNN_ATTR_TENSOR_DATA_TYPE`|8.0.1| | | |`MIOPEN_ATTR_TENSOR_DATA_TYPE`|6.2.0| | | | | | |`CUDNN_ATTR_TENSOR_DIMENSIONS`|8.0.1| | | |`MIOPEN_ATTR_TENSOR_DIMENSIONS`|6.2.0| | | | | | |`CUDNN_ATTR_TENSOR_IS_BY_VALUE`|8.1.0| | | |`MIOPEN_ATTR_TENSOR_IS_BY_VALUE`|6.2.0| | | | | | @@ -382,6 +397,7 @@ |`CUDNN_BACKEND_OPERATION_EXPAND_BAND_MATRIX_DESCRIPTOR`|9.10.0| | | | | | | | | | | |`CUDNN_BACKEND_OPERATION_GEN_STATS_DESCRIPTOR`|8.0.1| | | |`MIOPEN_BACKEND_OPERATION_GEN_STATS_DESCRIPTOR`|6.2.0| | | | | | |`CUDNN_BACKEND_OPERATION_MATMUL_DESCRIPTOR`|8.1.0| | | |`MIOPEN_BACKEND_OPERATION_MATMUL_DESCRIPTOR`|6.2.0| | | | | | +|`CUDNN_BACKEND_OPERATION_MOE_GROUPED_MATMUL_BWD_DESCRIPTOR`|9.22.0| | | | | | | | | | | |`CUDNN_BACKEND_OPERATION_MOE_GROUPED_MATMUL_DESCRIPTOR`|9.15.0| | | | | | | | | | | |`CUDNN_BACKEND_OPERATION_NORM_BACKWARD_DESCRIPTOR`|8.5.0| | | |`MIOPEN_BACKEND_OPERATION_NORM_BACKWARD_DESCRIPTOR`|6.2.0| | | | | | |`CUDNN_BACKEND_OPERATION_NORM_FORWARD_DESCRIPTOR`|8.5.0| | | |`MIOPEN_BACKEND_OPERATION_NORM_FORWARD_DESCRIPTOR`|6.2.0| | | | | | @@ -395,7 +411,9 @@ |`CUDNN_BACKEND_OPERATION_SDPA_BWD_DESCRIPTOR`|9.17.0| | | | | | | | | | | |`CUDNN_BACKEND_OPERATION_SDPA_FWD_DESCRIPTOR`|9.13.0| | | | | | | | | | | |`CUDNN_BACKEND_OPERATION_SIGNAL_DESCRIPTOR`|8.5.0| | | |`MIOPEN_BACKEND_OPERATION_SIGNAL_DESCRIPTOR`|6.2.0| | | | | | +|`CUDNN_BACKEND_OPERATION_SLICE_DESCRIPTOR`|9.22.0| | | | | | | | | | | |`CUDNN_BACKEND_OPERATION_SOFTMAX_DESCRIPTOR`|9.20.0| | | | | | | | | | | +|`CUDNN_BACKEND_OPERATION_TRANSPOSE_DESCRIPTOR`|9.22.0| | | | | | | | | | | |`CUDNN_BACKEND_POINTWISE_DESCRIPTOR`|8.0.1| | | |`MIOPEN_BACKEND_POINTWISE_DESCRIPTOR`|6.2.0| | | | | | |`CUDNN_BACKEND_REDUCTION_DESCRIPTOR`|8.1.0| | | |`MIOPEN_BACKEND_REDUCTION_DESCRIPTOR`|6.2.0| | | | | | |`CUDNN_BACKEND_RESAMPLE_DESCRIPTOR`|8.3.0| | | |`MIOPEN_BACKEND_RESAMPLE_DESCRIPTOR`|6.2.0| | | | | | @@ -419,6 +437,8 @@ |`CUDNN_BN_FINALIZE_STATISTICS_INFERENCE`|8.1.0| | | | | | | | | | | |`CUDNN_BN_FINALIZE_STATISTICS_TRAINING`|8.1.0| | | | | | | | | | | |`CUDNN_BN_MIN_EPSILON`|4.0.0| | | | | | | | | | | +|`CUDNN_CAUSAL_CONV1D_ACTIVATION_IDENTITY`|9.22.0| | | | | | | | | | | +|`CUDNN_CAUSAL_CONV1D_ACTIVATION_SILU`|9.22.0| | | | | | | | | | | |`CUDNN_CONVOLUTION`|1.0.0|9.0.0| | |`miopenConvolution`|2.1.0| | | | | | |`CUDNN_CONVOLUTION_BWD_DATA_ALGO_0`|3.0.0| | | |`miopenConvolutionBwdDataAlgoGEMM`|2.1.0| | | | | | |`CUDNN_CONVOLUTION_BWD_DATA_ALGO_1`|3.0.0| | | |`miopenConvolutionBwdDataAlgoDirect`|2.1.0| | | | | | @@ -516,6 +536,7 @@ |`CUDNN_KNOB_TYPE_CTA_SPLIT_K_MODE`|8.0.1|9.0.0| | | | | | | | | | |`CUDNN_KNOB_TYPE_EDGE`|8.0.1| | | | | | | | | | | |`CUDNN_KNOB_TYPE_IDX_MODE`|8.0.1|9.0.0| | | | | | | | | | +|`CUDNN_KNOB_TYPE_INPUT_TMA_ENABLE`|9.22.0| | | | | | | | | | | |`CUDNN_KNOB_TYPE_KBLOCK`|8.0.1|9.0.0| | | | | | | | | | |`CUDNN_KNOB_TYPE_KERNEL_CFG`|8.1.0| | | | | | | | | | | |`CUDNN_KNOB_TYPE_LDGA`|8.0.1|9.0.0| | | | | | | | | | @@ -525,6 +546,7 @@ |`CUDNN_KNOB_TYPE_MULTIPLY`|8.0.1| | | | | | | | | | | |`CUDNN_KNOB_TYPE_NUM_C_PER_BLOCK`|8.9.0|9.0.0| | | | | | | | | | |`CUDNN_KNOB_TYPE_OCCUPANCY`|8.9.0| | | | | | | | | | | +|`CUDNN_KNOB_TYPE_OUTPUT_TMA_ENABLE`|9.22.0| | | | | | | | | | | |`CUDNN_KNOB_TYPE_REDUCTION_MODE`|8.0.1| | | | | | | | | | | |`CUDNN_KNOB_TYPE_SINGLEBUFFER`|8.0.1|9.0.0| | | | | | | | | | |`CUDNN_KNOB_TYPE_SLICED`|8.0.1|9.0.0| | | | | | | | | | @@ -748,6 +770,8 @@ |`CUDNN_RESAMPLE_BILINEAR`|8.3.0| | | | | | | | | | | |`CUDNN_RESAMPLE_MAXPOOL`|8.3.0| | | | | | | | | | | |`CUDNN_RESAMPLE_NEAREST`|8.3.0| | | | | | | | | | | +|`CUDNN_RESHAPE_LOGICAL`|9.22.0| | | | | | | | | | | +|`CUDNN_RESHAPE_VIEW_ONLY`|9.22.0| | | | | | | | | | | |`CUDNN_RMS_NORM`|8.9.6| | | | | | | | | | | |`CUDNN_RNG_DISTRIBUTION_BERNOULLI`|8.7.0| | | |`MIOPEN_RNG_DISTRIBUTION_BERNOULLI`|6.2.0| | | | | | |`CUDNN_RNG_DISTRIBUTION_NORMAL`|8.7.0| | | |`MIOPEN_RNG_DISTRIBUTION_NORMAL`|6.2.0| | | | | | @@ -890,6 +914,7 @@ |`CUDNN_TYPE_POINTWISE_MODE`|8.0.1| | | |`MIOPEN_TYPE_POINTWISE_MODE`|6.2.0| | | | | | |`CUDNN_TYPE_REDUCTION_OPERATOR_TYPE`|8.1.0| | | |`MIOPEN_TYPE_REDUCTION_OPERATOR_TYPE`|6.2.0| | | | | | |`CUDNN_TYPE_RESAMPLE_MODE`|8.3.0| | | |`MIOPEN_TYPE_RESAMPLE_MODE`|6.2.0| | | | | | +|`CUDNN_TYPE_RESHAPE_MODE`|9.22.0| | | | | | | | | | | |`CUDNN_TYPE_RNG_DISTRIBUTION`|8.7.0| | | |`MIOPEN_TYPE_RNG_DISTRIBUTION`|6.2.0| | | | | | |`CUDNN_TYPE_SIGNAL_MODE`|8.5.0| | | |`MIOPEN_TYPE_SIGNAL_MODE`|6.2.0| | | | | | |`CUDNN_TYPE_TENSOR_REORDERING_MODE`|8.3.0| | | |`MIOPEN_TYPE_TENSOR_REORDERING_MODE`|6.2.0| | | | | | @@ -921,6 +946,7 @@ |`cudnnBackendNormFwdPhase_t`|8.5.0| | | | | | | | | | | |`cudnnBackendNormMode_t`|8.5.0| | | | | | | | | | | |`cudnnBackendNumericalNote_t`|8.0.1| | | | | | | | | | | +|`cudnnBackendReshapeMode_t`|9.22.0| | | | | | | | | | | |`cudnnBackendTensorReordering_t`|8.3.0| | | | | | | | | | | |`cudnnBatchNormMode_t`|4.0.0|9.0.0| | |`miopenBatchNormMode_t`|2.1.0| | | | | | |`cudnnBatchNormOps_t`|7.4.1|9.0.0| | | | | | | | | | @@ -930,6 +956,7 @@ |`cudnnCTCLossDescriptor_t`|7.0.5| | | |`miopenCTCLossDescriptor_t`|2.6.0| | | | | | |`cudnnCTCLossStruct`|7.0.5| | | | | | | | | | | |`cudnnCallback_t`|7.1.3| | | | | | | | | | | +|`cudnnCausalConv1dActivation_t`|9.22.0| | | | | | | | | | | |`cudnnContext`|1.0.0| | | |`miopenHandle`|2.1.0| | | | | | |`cudnnConvolutionBwdDataAlgoPerfStruct`|8.2.0|9.0.0| | |`miopenConvAlgoPerf_t`|2.1.0| | | | | | |`cudnnConvolutionBwdDataAlgoPerf_t`|3.0.0|9.0.0| | |`miopenConvAlgoPerf_t`|2.1.0| | | | | | @@ -1061,6 +1088,8 @@ |`cudnnBuildRNNDynamic`|8.0.1| | | | | | | | | | | |`cudnnCTCLoss`|7.0.5| | | |`miopenCTCLoss`|2.6.0| | | | | | |`cudnnCTCLoss_v8`|8.0.1| | | | | | | | | | | +|`cudnnCausalConv1dBackward`|9.22.0| | | | | | | | | | | +|`cudnnCausalConv1dForward`|9.22.0| | | | | | | | | | | |`cudnnCnnInferVersionCheck`|8.0.2| | | | | | | | | | | |`cudnnCnnTrainVersionCheck`|8.0.2| | | | | | | | | | | |`cudnnConvolutionBackwardBias`|1.0.0|9.0.0| | |`miopenConvolutionBackwardBias`|2.1.0| | | | | | @@ -1315,6 +1344,7 @@ |`cudnnSpatialTfGridGeneratorForward`|5.0.0| | | | | | | | | | | |`cudnnSpatialTfSamplerBackward`|5.0.0| | | | | | | | | | | |`cudnnSpatialTfSamplerForward`|5.0.0| | | | | | | | | | | +|`cudnnSubquadraticOpsVersionCheck`|9.22.0| | | | | | | | | | | |`cudnnTransformFilter`|7.6.0|9.0.0| | | | | | | | | | |`cudnnTransformTensor`|2.0.0|9.0.0| | |`miopenTransformTensor`|2.1.0| | | | | | |`cudnnTransformTensorEx`|7.5.0|9.0.0| | | | | | | | | | diff --git a/src/CUDA2HIP_DNN_API_functions.cpp b/src/CUDA2HIP_DNN_API_functions.cpp index 359522d9..1594a70f 100644 --- a/src/CUDA2HIP_DNN_API_functions.cpp +++ b/src/CUDA2HIP_DNN_API_functions.cpp @@ -351,6 +351,11 @@ const std::map CUDA_DNN_FUNCTION_MAP = [] { m["cudnnBackendPopulateCudaGraph"] = {"hipdnnBackendPopulateCudaGraph", "", CONV_LIB_FUNC, API_DNN, 2, UNSUPPORTED}; m["cudnnBackendUpdateCudaGraph"] = {"hipdnnBackendUpdateCudaGraph", "", CONV_LIB_FUNC, API_DNN, 2, UNSUPPORTED}; + // cuDNN Subquadratic Ops functions + m["cudnnSubquadraticOpsVersionCheck"] = {"hipdnnSubquadraticOpsVersionCheck", "", CONV_LIB_FUNC, API_DNN, 2, UNSUPPORTED}; + m["cudnnCausalConv1dForward"] = {"hipdnnCausalConv1dForward", "", CONV_LIB_FUNC, API_DNN, 2, UNSUPPORTED}; + m["cudnnCausalConv1dBackward"] = {"hipdnnCausalConv1dBackward", "", CONV_LIB_FUNC, API_DNN, 2, UNSUPPORTED}; + return m; }(); @@ -637,6 +642,9 @@ const std::map CUDA_DNN_FUNCTION_VER_MAP = [] m["cudnnOpsVersionCheck"] = {CUDNN_900, CUDA_0, CUDA_0 }; m["cudnnBackendPopulateCudaGraph"] = {CUDNN_950, CUDA_0, CUDA_0 }; m["cudnnBackendUpdateCudaGraph"] = {CUDNN_950, CUDA_0, CUDA_0 }; + m["cudnnSubquadraticOpsVersionCheck"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["cudnnCausalConv1dForward"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["cudnnCausalConv1dBackward"] = {CUDNN_9220,CUDA_0, CUDA_0 }; return m; }(); diff --git a/src/CUDA2HIP_DNN_API_types.cpp b/src/CUDA2HIP_DNN_API_types.cpp index 5e0e7bf2..2d8a600e 100644 --- a/src/CUDA2HIP_DNN_API_types.cpp +++ b/src/CUDA2HIP_DNN_API_types.cpp @@ -559,6 +559,7 @@ const std::map CUDA_DNN_TYPE_NAME_MAP = [] { m["CUDNN_ATTR_TENSOR_IS_VIRTUAL"] = {"HIPDNN_ATTR_TENSOR_IS_VIRTUAL", "MIOPEN_ATTR_TENSOR_IS_VIRTUAL", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; // 907 m["CUDNN_ATTR_TENSOR_IS_BY_VALUE"] = {"HIPDNN_ATTR_TENSOR_IS_BY_VALUE", "MIOPEN_ATTR_TENSOR_IS_BY_VALUE", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; // 908 m["CUDNN_ATTR_TENSOR_REORDERING_MODE"] = {"HIPDNN_ATTR_TENSOR_REORDERING_MODE", "MIOPEN_ATTR_TENSOR_REORDERING_MODE", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; // 909 + m["CUDNN_ATTR_TENSOR_CONSTANT_VALUE"] = {"HIPDNN_ATTR_TENSOR_CONSTANT_VALUE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 910 m["CUDNN_ATTR_TENSOR_RAGGED_OFFSET_DESC"] = {"HIPDNN_ATTR_TENSOR_RAGGED_OFFSET_DESC", "MIOPEN_ATTR_TENSOR_RAGGED_OFFSET_DESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; // 913 m["CUDNN_ATTR_VARIANT_PACK_UNIQUE_IDS"] = {"HIPDNN_ATTR_VARIANT_PACK_UNIQUE_IDS", "MIOPEN_ATTR_VARIANT_PACK_UNIQUE_IDS", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; // 1000 m["CUDNN_ATTR_VARIANT_PACK_DATA_POINTERS"] = {"HIPDNN_ATTR_VARIANT_PACK_DATA_POINTERS", "MIOPEN_ATTR_VARIANT_PACK_DATA_POINTERS", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; // 1001 @@ -673,6 +674,7 @@ const std::map CUDA_DNN_TYPE_NAME_MAP = [] { m["CUDNN_ATTR_OPERATION_NORM_BWD_PEER_STAT_DESCS"] = {"HIPDNN_ATTR_OPERATION_NORM_BWD_PEER_STAT_DESCS", "MIOPEN_ATTR_OPERATION_NORM_BWD_PEER_STAT_DESCS", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; // 2110 m["CUDNN_ATTR_OPERATION_RESHAPE_XDESC"] = {"HIPDNN_ATTR_OPERATION_RESHAPE_XDESC", "MIOPEN_ATTR_OPERATION_RESHAPE_XDESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; // 2200 m["CUDNN_ATTR_OPERATION_RESHAPE_YDESC"] = {"HIPDNN_ATTR_OPERATION_RESHAPE_YDESC", "MIOPEN_ATTR_OPERATION_RESHAPE_YDESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; // 2201 + m["CUDNN_ATTR_OPERATION_RESHAPE_MODE"] = {"HIPDNN_ATTR_OPERATION_RESHAPE_MODE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2202 m["CUDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_XDESC"] = {"HIPDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_XDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2250 m["CUDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_YDESC"] = {"HIPDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_YDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2251 m["CUDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_LOWER_BANDWIDTH"] = {"HIPDNN_ATTR_OPERATION_EXPAND_BAND_MATRIX_LOWER_BANDWIDTH", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2252 @@ -764,6 +766,11 @@ const std::map CUDA_DNN_TYPE_NAME_MAP = [] { m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_TOKEN_INDEX_DESC"] = {"HIPDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_TOKEN_INDEX_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2906 m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_TOKEN_KS_DESC"] = {"HIPDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_TOKEN_KS_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2907 m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_TOP_K"] = {"HIPDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_TOP_K", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2908 + m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_MATH_PREC"] = {"HIPDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_MATH_PREC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2951 + m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_TOKEN_DESC"] = {"HIPDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_TOKEN_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2952 + m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DWEIGHT_DESC"] = {"HIPDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DWEIGHT_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2953 + m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_FIRST_TOKEN_OFFSET_DESC"] = {"HIPDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_FIRST_TOKEN_OFFSET_DESC","", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2954 + m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DOUTPUT_DESC"] = {"HIPDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DOUTPUT_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 2955 m["CUDNN_ATTR_OPERATION_DIAGONAL_BAND_MASK_XDESC"] = {"HIPDNN_ATTR_OPERATION_DIAGONAL_BAND_MASK_XDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3000 m["CUDNN_ATTR_OPERATION_DIAGONAL_BAND_MASK_SEQ_LEN_KVDESC"] = {"HIPDNN_ATTR_OPERATION_DIAGONAL_BAND_MASK_SEQ_LEN_KVDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3001 m["CUDNN_ATTR_OPERATION_DIAGONAL_BAND_MASK_SEQ_LEN_QDESC"] = {"HIPDNN_ATTR_OPERATION_DIAGONAL_BAND_MASK_SEQ_LEN_QDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3002 @@ -778,6 +785,14 @@ const std::map CUDA_DNN_TYPE_NAME_MAP = [] { m["CUDNN_ATTR_OPERATION_SOFTMAX_MAX_DESC"] = {"HIPDNN_ATTR_OPERATION_SOFTMAX_MAX_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3103 m["CUDNN_ATTR_OPERATION_SOFTMAX_SUM_EXP_DESC"] = {"HIPDNN_ATTR_OPERATION_SOFTMAX_SUM_EXP_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3104 m["CUDNN_ATTR_OPERATION_SOFTMAX_SINK_DESC"] = {"HIPDNN_ATTR_OPERATION_SOFTMAX_SINK_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3105 + m["CUDNN_ATTR_OPERATION_TRANSPOSE_XDESC"] = {"HIPDNN_ATTR_OPERATION_TRANSPOSE_XDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3200 + m["CUDNN_ATTR_OPERATION_TRANSPOSE_YDESC"] = {"HIPDNN_ATTR_OPERATION_TRANSPOSE_YDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3201 + m["CUDNN_ATTR_OPERATION_TRANSPOSE_PERMUTATION"] = {"HIPDNN_ATTR_OPERATION_TRANSPOSE_PERMUTATION", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3202 + m["CUDNN_ATTR_OPERATION_SLICE_XDESC"] = {"HIPDNN_ATTR_OPERATION_SLICE_XDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3300 + m["CUDNN_ATTR_OPERATION_SLICE_YDESC"] = {"HIPDNN_ATTR_OPERATION_SLICE_YDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3301 + m["CUDNN_ATTR_OPERATION_SLICE_START_INDICES"] = {"HIPDNN_ATTR_OPERATION_SLICE_START_INDICES", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3302 + m["CUDNN_ATTR_OPERATION_SLICE_LIMIT_INDICES"] = {"HIPDNN_ATTR_OPERATION_SLICE_LIMIT_INDICES", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3303 + m["CUDNN_ATTR_OPERATION_SLICE_STRIDES"] = {"HIPDNN_ATTR_OPERATION_SLICE_STRIDES", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // 3304 m["cudnnBackendAttributeType_t"] = {"hipdnnBackendAttributeType_t", "miopenBackendAttributeType_t", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}; m["CUDNN_TYPE_HANDLE"] = {"HIPDNN_TYPE_HANDLE", "MIOPEN_TYPE_HANDLE", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; m["CUDNN_TYPE_DATA_TYPE"] = {"HIPDNN_TYPE_DATA_TYPE", "MIOPEN_TYPE_DATA_TYPE", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; @@ -810,6 +825,7 @@ const std::map CUDA_DNN_TYPE_NAME_MAP = [] { m["CUDNN_TYPE_NORM_FWD_PHASE"] = {"HIPDNN_TYPE_NORM_FWD_PHASE", "MIOPEN_TYPE_NORM_FWD_PHASE", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; m["CUDNN_TYPE_RNG_DISTRIBUTION"] = {"HIPDNN_TYPE_RNG_DISTRIBUTION", "MIOPEN_TYPE_RNG_DISTRIBUTION", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; m["CUDNN_TYPE_MOE_GROUPED_MATMUL_MODE"] = {"HIPDNN_TYPE_MOE_GROUPED_MATMUL_MODE", "MIOPEN_TYPE_RNG_DISTRIBUTION", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; + m["CUDNN_TYPE_RESHAPE_MODE"] = {"HIPDNN_TYPE_RESHAPE_MODE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["cudnnBackendDescriptorType_t"] = {"hipdnnBackendDescriptorType_t", "miopenBackendDescriptorType_t", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}; m["CUDNN_BACKEND_POINTWISE_DESCRIPTOR"] = {"HIPDNN_BACKEND_POINTWISE_DESCRIPTOR", "MIOPEN_BACKEND_POINTWISE_DESCRIPTOR", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; m["CUDNN_BACKEND_CONVOLUTION_DESCRIPTOR"] = {"HIPDNN_BACKEND_CONVOLUTION_DESCRIPTOR", "MIOPEN_BACKEND_CONVOLUTION_DESCRIPTOR", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; @@ -857,6 +873,9 @@ const std::map CUDA_DNN_TYPE_NAME_MAP = [] { m["CUDNN_BACKEND_OPERATION_SDPA_BWD_DESCRIPTOR"] = {"HIPDNN_BACKEND_OPERATION_SDPA_BWD_DESCRIPTOR", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["CUDNN_BACKEND_OPERATION_DIAGONAL_BAND_MASK_DESCRIPTOR"] = {"HIPDNN_BACKEND_OPERATION_DIAGONAL_BAND_MASK_DESCRIPTOR", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["CUDNN_BACKEND_OPERATION_SOFTMAX_DESCRIPTOR"] = {"HIPDNN_BACKEND_OPERATION_SOFTMAX_DESCRIPTOR", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; + m["CUDNN_BACKEND_OPERATION_TRANSPOSE_DESCRIPTOR"] = {"HIPDNN_BACKEND_OPERATION_TRANSPOSE_DESCRIPTOR", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; + m["CUDNN_BACKEND_OPERATION_SLICE_DESCRIPTOR"] = {"HIPDNN_BACKEND_OPERATION_SLICE_DESCRIPTOR", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; + m["CUDNN_BACKEND_OPERATION_MOE_GROUPED_MATMUL_BWD_DESCRIPTOR"] = {"HIPDNN_BACKEND_OPERATION_MOE_GROUPED_MATMUL_BWD_DESCRIPTOR", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["cudnnBackendNumericalNote_t"] = {"hipdnnBackendNumericalNote_t", "", CONV_TYPE, API_DNN, 1, UNSUPPORTED}; m["CUDNN_NUMERICAL_NOTE_TENSOR_CORE"] = {"HIPDNN_NUMERICAL_NOTE_TENSOR_CORE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["CUDNN_NUMERICAL_NOTE_DOWN_CONVERT_INPUTS"] = {"HIPDNN_NUMERICAL_NOTE_DOWN_CONVERT_INPUTS", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; @@ -920,6 +939,8 @@ const std::map CUDA_DNN_TYPE_NAME_MAP = [] { m["CUDNN_KNOB_TYPE_TILE_N"] = {"HIPDNN_KNOB_TYPE_TILE_N", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["CUDNN_KNOB_TYPE_WARP_SPEC_CFG"] = {"HIPDNN_KNOB_TYPE_WARP_SPEC_CFG", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["CUDNN_KNOB_TYPE_SWAP_AB"] = {"HIPDNN_KNOB_TYPE_SWAP_AB", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; + m["CUDNN_KNOB_TYPE_INPUT_TMA_ENABLE"] = {"HIPDNN_KNOB_TYPE_INPUT_TMA_ENABLE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; + m["CUDNN_KNOB_TYPE_OUTPUT_TMA_ENABLE"] = {"HIPDNN_KNOB_TYPE_OUTPUT_TMA_ENABLE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["CUDNN_KNOB_TYPE_COUNTS"] = {"HIPDNN_KNOB_TYPE_COUNTS", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["cudnnBackendHeurMode_t"] = {"hipdnnBackendHeurMode_t", "miopenBackendHeurMode_t", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}; m["CUDNN_HEUR_MODE_INSTANT"] = {"HIPDNN_HEUR_MODE_INSTANT", "MIOPEN_HEUR_MODE_INSTANT", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}; @@ -987,6 +1008,12 @@ const std::map CUDA_DNN_TYPE_NAME_MAP = [] { m["CUDNN_MOE_GROUPED_MATMUL_MODE_NONE"] = {"HIPDNN_MOE_GROUPED_MATMUL_MODE_NONE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["CUDNN_MOE_GROUPED_MATMUL_MODE_GATHER"] = {"HIPDNN_MOE_GROUPED_MATMUL_MODE_GATHER", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; m["CUDNN_MOE_GROUPED_MATMUL_MODE_SCATTER"] = {"HIPDNN_MOE_GROUPED_MATMUL_MODE_SCATTER", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; + m["cudnnBackendReshapeMode_t"] = {"hipdnnBackendReshapeMode_t", "", CONV_TYPE, API_DNN, 1, UNSUPPORTED}; + m["CUDNN_RESHAPE_VIEW_ONLY"] = {"HIPDNN_RESHAPE_VIEW_ONLY", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; + m["CUDNN_RESHAPE_LOGICAL"] = {"HIPDNN_RESHAPE_LOGICAL", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; + m["cudnnCausalConv1dActivation_t"] = {"hipdnnCausalConv1dActivation_t", "", CONV_TYPE, API_DNN, 1, UNSUPPORTED}; + m["CUDNN_CAUSAL_CONV1D_ACTIVATION_IDENTITY"] = {"HIPDNN_CAUSAL_CONV1D_ACTIVATION_IDENTITY", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; + m["CUDNN_CAUSAL_CONV1D_ACTIVATION_SILU"] = {"HIPDNN_CAUSAL_CONV1D_ACTIVATION_SILU", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}; // cuDNN types m["cudnnContext"] = {"hipdnnContext", "miopenHandle", CONV_TYPE, API_DNN, 1, HIP_UNSUPPORTED}; @@ -2078,6 +2105,33 @@ const std::map CUDA_DNN_TYPE_NAME_VER_MAP = [] m["CUDNN_ATTR_OPERATION_SDPA_BWD_SUBGRAPH"] = {CUDNN_9210,CUDA_0, CUDA_0 }; m["CUDNN_ATTR_OPERATION_SDPA_BWD_SUBGRAPH_INPUT_UID"] = {CUDNN_9210,CUDA_0, CUDA_0 }; m["CUDNN_ATTR_OPERATION_SDPA_BWD_SUBGRAPH_OUTPUT_UID"] = {CUDNN_9210,CUDA_0, CUDA_0 }; + m["cudnnBackendReshapeMode_t"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_RESHAPE_VIEW_ONLY"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_RESHAPE_LOGICAL"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_TYPE_RESHAPE_MODE"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_RESHAPE_MODE"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_TENSOR_CONSTANT_VALUE"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_MATH_PREC"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_TOKEN_DESC"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DWEIGHT_DESC"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_FIRST_TOKEN_OFFSET_DESC"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_MOE_GROUPED_MATMUL_BWD_DOUTPUT_DESC"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_TRANSPOSE_XDESC"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_TRANSPOSE_YDESC"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_TRANSPOSE_PERMUTATION"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_SLICE_XDESC"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_SLICE_YDESC"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_SLICE_START_INDICES"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_SLICE_LIMIT_INDICES"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_ATTR_OPERATION_SLICE_STRIDES"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_BACKEND_OPERATION_TRANSPOSE_DESCRIPTOR"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_BACKEND_OPERATION_SLICE_DESCRIPTOR"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_BACKEND_OPERATION_MOE_GROUPED_MATMUL_BWD_DESCRIPTOR"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_KNOB_TYPE_INPUT_TMA_ENABLE"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_KNOB_TYPE_OUTPUT_TMA_ENABLE"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["cudnnCausalConv1dActivation_t"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_CAUSAL_CONV1D_ACTIVATION_IDENTITY"] = {CUDNN_9220,CUDA_0, CUDA_0 }; + m["CUDNN_CAUSAL_CONV1D_ACTIVATION_SILU"] = {CUDNN_9220,CUDA_0, CUDA_0 }; return m; }();