From 6c074cedc2ed51e3554fc688b447801d4da550a4 Mon Sep 17 00:00:00 2001 From: Evgeny Mankov Date: Wed, 4 Sep 2024 13:53:28 +0100 Subject: [PATCH] [HIPIFY][#584][#1624][MIOpen] Support for backend `graphAPI` direct translation from `cuDNN` to `MIOpen` - Part 4 + `cudnnBackendAttributeName_t` -> `miopenBackendAttributeName_t` - continuation + Updated synthetic tests, the regenerated `hipify-perl`, and `DNN` `CUDA2HIP` documentation --- bin/hipify-perl | 29 ++++ .../CUDNN_API_supported_by_HIP_and_MIOPEN.md | 58 +++---- docs/tables/CUDNN_API_supported_by_MIOPEN.md | 58 +++---- src/CUDA2HIP_DNN_API_types.cpp | 58 +++---- .../synthetic/libraries/cudnn2miopen.cu | 152 +++++++++++++++++- 5 files changed, 260 insertions(+), 95 deletions(-) diff --git a/bin/hipify-perl b/bin/hipify-perl index 94f9d65b..b701e876 100755 --- a/bin/hipify-perl +++ b/bin/hipify-perl @@ -3338,6 +3338,35 @@ sub rocSubstitutions { subst("CUDNN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS", "MIOPEN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS", "numeric_literal"); subst("CUDNN_ATTR_INTERMEDIATE_INFO_SIZE", "MIOPEN_ATTR_INTERMEDIATE_INFO_SIZE", "numeric_literal"); subst("CUDNN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID", "MIOPEN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID", "numeric_literal"); + subst("CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE", "MIOPEN_ATTR_KNOB_CHOICE_KNOB_TYPE", "numeric_literal"); + subst("CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE", "MIOPEN_ATTR_KNOB_CHOICE_KNOB_VALUE", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_W", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_W", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_X", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_X", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_POINTWISE_ALPHA1", "MIOPEN_ATTR_OPERATION_POINTWISE_ALPHA1", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_POINTWISE_ALPHA2", "MIOPEN_ATTR_OPERATION_POINTWISE_ALPHA2", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_POINTWISE_BDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_BDESC", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_POINTWISE_DXDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_DXDESC", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_POINTWISE_DYDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_DYDESC", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR", "MIOPEN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_POINTWISE_TDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_TDESC", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_POINTWISE_XDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_XDESC", "numeric_literal"); + subst("CUDNN_ATTR_OPERATION_POINTWISE_YDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_YDESC", "numeric_literal"); subst("CUDNN_ATTR_POINTWISE_AXIS", "MIOPEN_ATTR_POINTWISE_AXIS", "numeric_literal"); subst("CUDNN_ATTR_POINTWISE_ELU_ALPHA", "MIOPEN_ATTR_POINTWISE_ELU_ALPHA", "numeric_literal"); subst("CUDNN_ATTR_POINTWISE_MATH_PREC", "MIOPEN_ATTR_POINTWISE_MATH_PREC", "numeric_literal"); diff --git a/docs/tables/CUDNN_API_supported_by_HIP_and_MIOPEN.md b/docs/tables/CUDNN_API_supported_by_HIP_and_MIOPEN.md index 49c54c25..6545e50d 100644 --- a/docs/tables/CUDNN_API_supported_by_HIP_and_MIOPEN.md +++ b/docs/tables/CUDNN_API_supported_by_HIP_and_MIOPEN.md @@ -53,8 +53,8 @@ |`CUDNN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS`|8.0.2| | | | | | | | | |`MIOPEN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS`| | | | | | |`CUDNN_ATTR_INTERMEDIATE_INFO_SIZE`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_INTERMEDIATE_INFO_SIZE`| | | | | | |`CUDNN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID`|8.0.2| | | | | | | | | |`MIOPEN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID`| | | | | | -|`CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE`|8.0.1| | | | | | | | | | | | | | | | +|`CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_KNOB_CHOICE_KNOB_TYPE`| | | | | | +|`CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_KNOB_CHOICE_KNOB_VALUE`| | | | | | |`CUDNN_ATTR_KNOB_INFO_MAXIMUM_VALUE`|8.0.1| | | | | | | | | | | | | | | | |`CUDNN_ATTR_KNOB_INFO_MINIMUM_VALUE`|8.0.1| | | | | | | | | | | | | | | | |`CUDNN_ATTR_KNOB_INFO_STRIDE`|8.0.1| | | | | | | | | | | | | | | | @@ -98,24 +98,24 @@ |`CUDNN_ATTR_OPERATION_CONCAT_INPLACE_INDEX`|8.5.0| | | | | | | | | | | | | | | | |`CUDNN_ATTR_OPERATION_CONCAT_INPUT_DESCS`|8.5.0| | | | | | | | | | | | | | | | |`CUDNN_ATTR_OPERATION_CONCAT_OUTPUT_DESC`|8.5.0| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_W`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_X`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y`|8.0.1| | | | | | | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_W`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_W`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_X`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_X`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y`| | | | | | |`CUDNN_ATTR_OPERATION_GENSTATS_MATH_PREC`|8.0.1| | | | | | | | | | | | | | | | |`CUDNN_ATTR_OPERATION_GENSTATS_MODE`|8.0.1| | | | | | | | | | | | | | | | |`CUDNN_ATTR_OPERATION_GENSTATS_SQSUMDESC`|8.0.1| | | | | | | | | | | | | | | | @@ -155,15 +155,15 @@ |`CUDNN_ATTR_OPERATION_NORM_FWD_SCALE_DESC`|8.5.0| | | | | | | | | | | | | | | | |`CUDNN_ATTR_OPERATION_NORM_FWD_XDESC`|8.5.0| | | | | | | | | | | | | | | | |`CUDNN_ATTR_OPERATION_NORM_FWD_YDESC`|8.5.0| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_ALPHA1`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_ALPHA2`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_BDESC`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_DXDESC`|8.1.0| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_DYDESC`|8.1.0| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_TDESC`|8.3.0| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_XDESC`|8.0.1| | | | | | | | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_YDESC`|8.0.1| | | | | | | | | | | | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_ALPHA1`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_POINTWISE_ALPHA1`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_ALPHA2`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_POINTWISE_ALPHA2`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_BDESC`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_POINTWISE_BDESC`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_DXDESC`|8.1.0| | | | | | | | | |`MIOPEN_ATTR_OPERATION_POINTWISE_DXDESC`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_DYDESC`|8.1.0| | | | | | | | | |`MIOPEN_ATTR_OPERATION_POINTWISE_DYDESC`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_TDESC`|8.3.0| | | | | | | | | |`MIOPEN_ATTR_OPERATION_POINTWISE_TDESC`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_XDESC`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_POINTWISE_XDESC`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_YDESC`|8.0.1| | | | | | | | | |`MIOPEN_ATTR_OPERATION_POINTWISE_YDESC`| | | | | | |`CUDNN_ATTR_OPERATION_REDUCTION_DESC`|8.1.0| | | | | | | | | | | | | | | | |`CUDNN_ATTR_OPERATION_REDUCTION_XDESC`|8.1.0| | | | | | | | | | | | | | | | |`CUDNN_ATTR_OPERATION_REDUCTION_YDESC`|8.1.0| | | | | | | | | | | | | | | | diff --git a/docs/tables/CUDNN_API_supported_by_MIOPEN.md b/docs/tables/CUDNN_API_supported_by_MIOPEN.md index 38d3ab45..0d4814ba 100644 --- a/docs/tables/CUDNN_API_supported_by_MIOPEN.md +++ b/docs/tables/CUDNN_API_supported_by_MIOPEN.md @@ -53,8 +53,8 @@ |`CUDNN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS`|8.0.2| | | |`MIOPEN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS`| | | | | | |`CUDNN_ATTR_INTERMEDIATE_INFO_SIZE`|8.0.1| | | |`MIOPEN_ATTR_INTERMEDIATE_INFO_SIZE`| | | | | | |`CUDNN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID`|8.0.2| | | |`MIOPEN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID`| | | | | | -|`CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE`|8.0.1| | | | | | | | | | +|`CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE`|8.0.1| | | |`MIOPEN_ATTR_KNOB_CHOICE_KNOB_TYPE`| | | | | | +|`CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE`|8.0.1| | | |`MIOPEN_ATTR_KNOB_CHOICE_KNOB_VALUE`| | | | | | |`CUDNN_ATTR_KNOB_INFO_MAXIMUM_VALUE`|8.0.1| | | | | | | | | | |`CUDNN_ATTR_KNOB_INFO_MINIMUM_VALUE`|8.0.1| | | | | | | | | | |`CUDNN_ATTR_KNOB_INFO_STRIDE`|8.0.1| | | | | | | | | | @@ -98,24 +98,24 @@ |`CUDNN_ATTR_OPERATION_CONCAT_INPLACE_INDEX`|8.5.0| | | | | | | | | | |`CUDNN_ATTR_OPERATION_CONCAT_INPUT_DESCS`|8.5.0| | | | | | | | | | |`CUDNN_ATTR_OPERATION_CONCAT_OUTPUT_DESC`|8.5.0| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_W`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_X`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y`|8.0.1| | | | | | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_W`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_W`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_X`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_X`| | | | | | +|`CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y`| | | | | | |`CUDNN_ATTR_OPERATION_GENSTATS_MATH_PREC`|8.0.1| | | | | | | | | | |`CUDNN_ATTR_OPERATION_GENSTATS_MODE`|8.0.1| | | | | | | | | | |`CUDNN_ATTR_OPERATION_GENSTATS_SQSUMDESC`|8.0.1| | | | | | | | | | @@ -155,15 +155,15 @@ |`CUDNN_ATTR_OPERATION_NORM_FWD_SCALE_DESC`|8.5.0| | | | | | | | | | |`CUDNN_ATTR_OPERATION_NORM_FWD_XDESC`|8.5.0| | | | | | | | | | |`CUDNN_ATTR_OPERATION_NORM_FWD_YDESC`|8.5.0| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_ALPHA1`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_ALPHA2`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_BDESC`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_DXDESC`|8.1.0| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_DYDESC`|8.1.0| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_TDESC`|8.3.0| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_XDESC`|8.0.1| | | | | | | | | | -|`CUDNN_ATTR_OPERATION_POINTWISE_YDESC`|8.0.1| | | | | | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_ALPHA1`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_POINTWISE_ALPHA1`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_ALPHA2`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_POINTWISE_ALPHA2`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_BDESC`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_POINTWISE_BDESC`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_DXDESC`|8.1.0| | | |`MIOPEN_ATTR_OPERATION_POINTWISE_DXDESC`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_DYDESC`|8.1.0| | | |`MIOPEN_ATTR_OPERATION_POINTWISE_DYDESC`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_TDESC`|8.3.0| | | |`MIOPEN_ATTR_OPERATION_POINTWISE_TDESC`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_XDESC`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_POINTWISE_XDESC`| | | | | | +|`CUDNN_ATTR_OPERATION_POINTWISE_YDESC`|8.0.1| | | |`MIOPEN_ATTR_OPERATION_POINTWISE_YDESC`| | | | | | |`CUDNN_ATTR_OPERATION_REDUCTION_DESC`|8.1.0| | | | | | | | | | |`CUDNN_ATTR_OPERATION_REDUCTION_XDESC`|8.1.0| | | | | | | | | | |`CUDNN_ATTR_OPERATION_REDUCTION_YDESC`|8.1.0| | | | | | | | | | diff --git a/src/CUDA2HIP_DNN_API_types.cpp b/src/CUDA2HIP_DNN_API_types.cpp index acc76548..d2db1356 100644 --- a/src/CUDA2HIP_DNN_API_types.cpp +++ b/src/CUDA2HIP_DNN_API_types.cpp @@ -476,35 +476,35 @@ const std::map CUDA_DNN_TYPE_NAME_MAP { {"CUDNN_ATTR_INTERMEDIATE_INFO_SIZE", {"HIPDNN_ATTR_INTERMEDIATE_INFO_SIZE", "MIOPEN_ATTR_INTERMEDIATE_INFO_SIZE", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 501 {"CUDNN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS", {"HIPDNN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS", "MIOPEN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 502 {"CUDNN_ATTR_INTERMEDIATE_INFO_DEPENDENT_ATTRIBUTES", {"HIPDNN_ATTR_INTERMEDIATE_INFO_DEPENDENT_ATTRIBUTES", "MIOPEN_ATTR_INTERMEDIATE_INFO_DEPENDENT_ATTRIBUTES", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 503 - {"CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE", {"HIPDNN_ATTR_KNOB_CHOICE_KNOB_TYPE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 600 - {"CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE", {"HIPDNN_ATTR_KNOB_CHOICE_KNOB_VALUE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 601 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 700 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 701 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 702 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_W", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_W", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 703 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_X", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_X", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 704 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 705 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 706 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 707 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 708 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 709 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 710 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 711 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 712 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 713 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 714 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 715 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 716 - {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 717 - {"CUDNN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR", {"HIPDNN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 750 - {"CUDNN_ATTR_OPERATION_POINTWISE_XDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_XDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 751 - {"CUDNN_ATTR_OPERATION_POINTWISE_BDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_BDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 752 - {"CUDNN_ATTR_OPERATION_POINTWISE_YDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_YDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 753 - {"CUDNN_ATTR_OPERATION_POINTWISE_ALPHA1", {"HIPDNN_ATTR_OPERATION_POINTWISE_ALPHA1", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 754 - {"CUDNN_ATTR_OPERATION_POINTWISE_ALPHA2", {"HIPDNN_ATTR_OPERATION_POINTWISE_ALPHA2", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 755 - {"CUDNN_ATTR_OPERATION_POINTWISE_DXDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_DXDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 756 - {"CUDNN_ATTR_OPERATION_POINTWISE_DYDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_DYDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 757 - {"CUDNN_ATTR_OPERATION_POINTWISE_TDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_TDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 758 + {"CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE", {"HIPDNN_ATTR_KNOB_CHOICE_KNOB_TYPE", "MIOPEN_ATTR_KNOB_CHOICE_KNOB_TYPE", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 600 + {"CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE", {"HIPDNN_ATTR_KNOB_CHOICE_KNOB_VALUE", "MIOPEN_ATTR_KNOB_CHOICE_KNOB_VALUE", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 601 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 700 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 701 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 702 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_W", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_W", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_W", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 703 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_X", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_X", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_X", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 704 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y", "MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 705 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 706 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 707 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 708 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 709 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 710 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 711 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 712 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 713 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 714 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 715 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 716 + {"CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY", {"HIPDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY", "MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 717 + {"CUDNN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR", {"HIPDNN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR", "MIOPEN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 750 + {"CUDNN_ATTR_OPERATION_POINTWISE_XDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_XDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_XDESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 751 + {"CUDNN_ATTR_OPERATION_POINTWISE_BDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_BDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_BDESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 752 + {"CUDNN_ATTR_OPERATION_POINTWISE_YDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_YDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_YDESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 753 + {"CUDNN_ATTR_OPERATION_POINTWISE_ALPHA1", {"HIPDNN_ATTR_OPERATION_POINTWISE_ALPHA1", "MIOPEN_ATTR_OPERATION_POINTWISE_ALPHA1", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 754 + {"CUDNN_ATTR_OPERATION_POINTWISE_ALPHA2", {"HIPDNN_ATTR_OPERATION_POINTWISE_ALPHA2", "MIOPEN_ATTR_OPERATION_POINTWISE_ALPHA2", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 755 + {"CUDNN_ATTR_OPERATION_POINTWISE_DXDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_DXDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_DXDESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 756 + {"CUDNN_ATTR_OPERATION_POINTWISE_DYDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_DYDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_DYDESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 757 + {"CUDNN_ATTR_OPERATION_POINTWISE_TDESC", {"HIPDNN_ATTR_OPERATION_POINTWISE_TDESC", "MIOPEN_ATTR_OPERATION_POINTWISE_TDESC", CONV_NUMERIC_LITERAL, API_DNN, 1, HIP_UNSUPPORTED}}, // 758 {"CUDNN_ATTR_OPERATION_GENSTATS_MODE", {"HIPDNN_ATTR_OPERATION_GENSTATS_MODE", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 770 {"CUDNN_ATTR_OPERATION_GENSTATS_MATH_PREC", {"HIPDNN_ATTR_OPERATION_GENSTATS_MATH_PREC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 771 {"CUDNN_ATTR_OPERATION_GENSTATS_XDESC", {"HIPDNN_ATTR_OPERATION_GENSTATS_XDESC", "", CONV_NUMERIC_LITERAL, API_DNN, 1, UNSUPPORTED}}, // 772 diff --git a/tests/unit_tests/synthetic/libraries/cudnn2miopen.cu b/tests/unit_tests/synthetic/libraries/cudnn2miopen.cu index 2ad9481d..cf91a082 100644 --- a/tests/unit_tests/synthetic/libraries/cudnn2miopen.cu +++ b/tests/unit_tests/synthetic/libraries/cudnn2miopen.cu @@ -822,7 +822,7 @@ int main() { // CHECK: status = miopenReduceTensor(handle, ReduceTensorDescriptor, indices, indicesSizeInBytes, workSpace, workSpaceSizeInBytes, alpha, aD, A, beta, cD, C); status = cudnnReduceTensor(handle, ReduceTensorDescriptor, indices, indicesSizeInBytes, workSpace, workSpaceSizeInBytes, alpha, aD, A, beta, cD, C); -#if CUDNN_VERSION >= 80001 +#if CUDNN_VERSION >= 8001 // CHECK: miopenBackendDescriptorType_t backendDescriptorType_t; // CHECK-NEXT: miopenBackendDescriptorType_t BACKEND_POINTWISE_DESCRIPTOR = MIOPEN_BACKEND_POINTWISE_DESCRIPTOR; // CHECK-NEXT: miopenBackendDescriptorType_t BACKEND_CONVOLUTION_DESCRIPTOR = MIOPEN_BACKEND_CONVOLUTION_DESCRIPTOR; @@ -896,14 +896,124 @@ int main() { cudnnBackendAttributeType_t TYPE_POINTWISE_MODE = CUDNN_TYPE_POINTWISE_MODE; cudnnBackendAttributeType_t TYPE_BACKEND_DESCRIPTOR = CUDNN_TYPE_BACKEND_DESCRIPTOR; cudnnBackendAttributeType_t TYPE_GENSTATS_MODE = CUDNN_TYPE_GENSTATS_MODE; + + // CHECK: miopenBackendAttributeName_t backendAttributeName_t; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_POINTWISE_MODE = MIOPEN_ATTR_POINTWISE_MODE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_POINTWISE_MATH_PREC = MIOPEN_ATTR_POINTWISE_MATH_PREC; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_POINTWISE_NAN_PROPAGATION = MIOPEN_ATTR_POINTWISE_NAN_PROPAGATION; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_POINTWISE_RELU_LOWER_CLIP = MIOPEN_ATTR_POINTWISE_RELU_LOWER_CLIP; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_POINTWISE_RELU_UPPER_CLIP = MIOPEN_ATTR_POINTWISE_RELU_UPPER_CLIP; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_CONVOLUTION_COMP_TYPE = MIOPEN_ATTR_CONVOLUTION_COMP_TYPE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_CONVOLUTION_DILATIONS = MIOPEN_ATTR_CONVOLUTION_DILATIONS; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_CONVOLUTION_FILTER_STRIDES = MIOPEN_ATTR_CONVOLUTION_FILTER_STRIDES; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_CONVOLUTION_POST_PADDINGS = MIOPEN_ATTR_CONVOLUTION_POST_PADDINGS; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_CONVOLUTION_PRE_PADDINGS = MIOPEN_ATTR_CONVOLUTION_PRE_PADDINGS; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_CONVOLUTION_SPATIAL_DIMS = MIOPEN_ATTR_CONVOLUTION_SPATIAL_DIMS; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_ENGINEHEUR_MODE = MIOPEN_ATTR_ENGINEHEUR_MODE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_ENGINEHEUR_OPERATION_GRAPH = MIOPEN_ATTR_ENGINEHEUR_OPERATION_GRAPH; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_ENGINEHEUR_RESULTS = MIOPEN_ATTR_ENGINEHEUR_RESULTS; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_ENGINECFG_ENGINE = MIOPEN_ATTR_ENGINECFG_ENGINE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_ENGINECFG_INTERMEDIATE_INFO = MIOPEN_ATTR_ENGINECFG_INTERMEDIATE_INFO; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_ENGINECFG_KNOB_CHOICES = MIOPEN_ATTR_ENGINECFG_KNOB_CHOICES; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_EXECUTION_PLAN_HANDLE = MIOPEN_ATTR_EXECUTION_PLAN_HANDLE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_EXECUTION_PLAN_ENGINE_CONFIG = MIOPEN_ATTR_EXECUTION_PLAN_ENGINE_CONFIG; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_EXECUTION_PLAN_WORKSPACE_SIZE = MIOPEN_ATTR_EXECUTION_PLAN_WORKSPACE_SIZE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_INTERMEDIATE_INFO_SIZE = MIOPEN_ATTR_INTERMEDIATE_INFO_SIZE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_KNOB_CHOICE_KNOB_TYPE = MIOPEN_ATTR_KNOB_CHOICE_KNOB_TYPE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_KNOB_CHOICE_KNOB_VALUE = MIOPEN_ATTR_KNOB_CHOICE_KNOB_VALUE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA = MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_BETA = MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC = MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_W = MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_W; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_X = MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_X; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_Y = MIOPEN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_W = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY = MIOPEN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR = MIOPEN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_POINTWISE_XDESC = MIOPEN_ATTR_OPERATION_POINTWISE_XDESC; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_POINTWISE_BDESC = MIOPEN_ATTR_OPERATION_POINTWISE_BDESC; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_POINTWISE_YDESC = MIOPEN_ATTR_OPERATION_POINTWISE_YDESC; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_POINTWISE_ALPHA1 = MIOPEN_ATTR_OPERATION_POINTWISE_ALPHA1; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_POINTWISE_ALPHA2 = MIOPEN_ATTR_OPERATION_POINTWISE_ALPHA2; + cudnnBackendAttributeName_t backendAttributeName_t; + cudnnBackendAttributeName_t ATTR_POINTWISE_MODE = CUDNN_ATTR_POINTWISE_MODE; + cudnnBackendAttributeName_t ATTR_POINTWISE_MATH_PREC = CUDNN_ATTR_POINTWISE_MATH_PREC; + cudnnBackendAttributeName_t ATTR_POINTWISE_NAN_PROPAGATION = CUDNN_ATTR_POINTWISE_NAN_PROPAGATION; + cudnnBackendAttributeName_t ATTR_POINTWISE_RELU_LOWER_CLIP = CUDNN_ATTR_POINTWISE_RELU_LOWER_CLIP; + cudnnBackendAttributeName_t ATTR_POINTWISE_RELU_UPPER_CLIP = CUDNN_ATTR_POINTWISE_RELU_UPPER_CLIP; + cudnnBackendAttributeName_t ATTR_CONVOLUTION_COMP_TYPE = CUDNN_ATTR_CONVOLUTION_COMP_TYPE; + cudnnBackendAttributeName_t ATTR_CONVOLUTION_DILATIONS = CUDNN_ATTR_CONVOLUTION_DILATIONS; + cudnnBackendAttributeName_t ATTR_CONVOLUTION_FILTER_STRIDES = CUDNN_ATTR_CONVOLUTION_FILTER_STRIDES; + cudnnBackendAttributeName_t ATTR_CONVOLUTION_POST_PADDINGS = CUDNN_ATTR_CONVOLUTION_POST_PADDINGS; + cudnnBackendAttributeName_t ATTR_CONVOLUTION_PRE_PADDINGS = CUDNN_ATTR_CONVOLUTION_PRE_PADDINGS; + cudnnBackendAttributeName_t ATTR_CONVOLUTION_SPATIAL_DIMS = CUDNN_ATTR_CONVOLUTION_SPATIAL_DIMS; + cudnnBackendAttributeName_t ATTR_ENGINEHEUR_MODE = CUDNN_ATTR_ENGINEHEUR_MODE; + cudnnBackendAttributeName_t ATTR_ENGINEHEUR_OPERATION_GRAPH = CUDNN_ATTR_ENGINEHEUR_OPERATION_GRAPH; + cudnnBackendAttributeName_t ATTR_ENGINEHEUR_RESULTS = CUDNN_ATTR_ENGINEHEUR_RESULTS; + cudnnBackendAttributeName_t ATTR_ENGINECFG_ENGINE = CUDNN_ATTR_ENGINECFG_ENGINE; + cudnnBackendAttributeName_t ATTR_ENGINECFG_INTERMEDIATE_INFO = CUDNN_ATTR_ENGINECFG_INTERMEDIATE_INFO; + cudnnBackendAttributeName_t ATTR_ENGINECFG_KNOB_CHOICES = CUDNN_ATTR_ENGINECFG_KNOB_CHOICES; + cudnnBackendAttributeName_t ATTR_EXECUTION_PLAN_HANDLE = CUDNN_ATTR_EXECUTION_PLAN_HANDLE; + cudnnBackendAttributeName_t ATTR_EXECUTION_PLAN_ENGINE_CONFIG = CUDNN_ATTR_EXECUTION_PLAN_ENGINE_CONFIG; + cudnnBackendAttributeName_t ATTR_EXECUTION_PLAN_WORKSPACE_SIZE = CUDNN_ATTR_EXECUTION_PLAN_WORKSPACE_SIZE; + cudnnBackendAttributeName_t ATTR_INTERMEDIATE_INFO_SIZE = CUDNN_ATTR_INTERMEDIATE_INFO_SIZE; + cudnnBackendAttributeName_t ATTR_KNOB_CHOICE_KNOB_TYPE = CUDNN_ATTR_KNOB_CHOICE_KNOB_TYPE; + cudnnBackendAttributeName_t ATTR_KNOB_CHOICE_KNOB_VALUE = CUDNN_ATTR_KNOB_CHOICE_KNOB_VALUE; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA = CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_ALPHA; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_BETA = CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_BETA; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC = CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_CONV_DESC; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_W = CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_W; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_X = CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_X; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_FORWARD_Y = CUDNN_ATTR_OPERATION_CONVOLUTION_FORWARD_Y; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_ALPHA; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_BETA; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_CONV_DESC; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_W = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_W; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DX; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_DATA_DY; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_ALPHA; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_BETA; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_CONV_DESC; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DW; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_X; + cudnnBackendAttributeName_t ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY = CUDNN_ATTR_OPERATION_CONVOLUTION_BWD_FILTER_DY; + cudnnBackendAttributeName_t ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR = CUDNN_ATTR_OPERATION_POINTWISE_PW_DESCRIPTOR; + cudnnBackendAttributeName_t ATTR_OPERATION_POINTWISE_XDESC = CUDNN_ATTR_OPERATION_POINTWISE_XDESC; + cudnnBackendAttributeName_t ATTR_OPERATION_POINTWISE_BDESC = CUDNN_ATTR_OPERATION_POINTWISE_BDESC; + cudnnBackendAttributeName_t ATTR_OPERATION_POINTWISE_YDESC = CUDNN_ATTR_OPERATION_POINTWISE_YDESC; + cudnnBackendAttributeName_t ATTR_OPERATION_POINTWISE_ALPHA1 = CUDNN_ATTR_OPERATION_POINTWISE_ALPHA1; + cudnnBackendAttributeName_t ATTR_OPERATION_POINTWISE_ALPHA2 = CUDNN_ATTR_OPERATION_POINTWISE_ALPHA2; #endif -#if CUDNN_VERSION >= 80002 +#if CUDNN_VERSION >= 8002 // CHECK: miopenBackendAttributeType_t TYPE_LAYOUT_TYPE = MIOPEN_TYPE_LAYOUT_TYPE; cudnnBackendAttributeType_t TYPE_LAYOUT_TYPE = CUDNN_TYPE_LAYOUT_TYPE; + + // CHECK: miopenBackendAttributeName_t ATTR_CONVOLUTION_CONV_MODE = MIOPEN_ATTR_CONVOLUTION_CONV_MODE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_EXECUTION_PLAN_COMPUTED_INTERMEDIATE_UIDS = MIOPEN_ATTR_EXECUTION_PLAN_COMPUTED_INTERMEDIATE_UIDS; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_EXECUTION_PLAN_RUN_ONLY_INTERMEDIATE_UIDS = MIOPEN_ATTR_EXECUTION_PLAN_RUN_ONLY_INTERMEDIATE_UIDS; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_INTERMEDIATE_INFO_UNIQUE_ID = MIOPEN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS = MIOPEN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_INTERMEDIATE_INFO_DEPENDENT_ATTRIBUTES = MIOPEN_ATTR_INTERMEDIATE_INFO_DEPENDENT_ATTRIBUTES; + cudnnBackendAttributeName_t ATTR_CONVOLUTION_CONV_MODE = CUDNN_ATTR_CONVOLUTION_CONV_MODE; + cudnnBackendAttributeName_t ATTR_EXECUTION_PLAN_COMPUTED_INTERMEDIATE_UIDS = CUDNN_ATTR_EXECUTION_PLAN_COMPUTED_INTERMEDIATE_UIDS; + cudnnBackendAttributeName_t ATTR_EXECUTION_PLAN_RUN_ONLY_INTERMEDIATE_UIDS = CUDNN_ATTR_EXECUTION_PLAN_RUN_ONLY_INTERMEDIATE_UIDS; + cudnnBackendAttributeName_t ATTR_INTERMEDIATE_INFO_UNIQUE_ID = CUDNN_ATTR_INTERMEDIATE_INFO_UNIQUE_ID; + cudnnBackendAttributeName_t ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS = CUDNN_ATTR_INTERMEDIATE_INFO_DEPENDENT_DATA_UIDS; + cudnnBackendAttributeName_t ATTR_INTERMEDIATE_INFO_DEPENDENT_ATTRIBUTES = CUDNN_ATTR_INTERMEDIATE_INFO_DEPENDENT_ATTRIBUTES; #endif -#if CUDNN_VERSION >= 80100 +#if CUDNN_VERSION >= 8100 // CHECK: miopenBackendDescriptorType_t BACKEND_MATMUL_DESCRIPTOR = MIOPEN_BACKEND_MATMUL_DESCRIPTOR; // CHECK-NEXT: miopenBackendDescriptorType_t BACKEND_OPERATION_MATMUL_DESCRIPTOR = MIOPEN_BACKEND_OPERATION_MATMUL_DESCRIPTOR; // CHECK-NEXT: miopenBackendDescriptorType_t BACKEND_REDUCTION_DESCRIPTOR = MIOPEN_BACKEND_REDUCTION_DESCRIPTOR; @@ -917,14 +1027,27 @@ int main() { // CHECK-NEXT: miopenBackendAttributeType_t TYPE_REDUCTION_OPERATOR_TYPE = MIOPEN_TYPE_REDUCTION_OPERATOR_TYPE; cudnnBackendAttributeType_t TYPE_BN_FINALIZE_STATS_MODE = CUDNN_TYPE_BN_FINALIZE_STATS_MODE; cudnnBackendAttributeType_t TYPE_REDUCTION_OPERATOR_TYPE = CUDNN_TYPE_REDUCTION_OPERATOR_TYPE; + + // CHECK: miopenBackendAttributeName_t ATTR_POINTWISE_RELU_LOWER_CLIP_SLOPE = MIOPEN_ATTR_POINTWISE_RELU_LOWER_CLIP_SLOPE; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_POINTWISE_ELU_ALPHA = MIOPEN_ATTR_POINTWISE_ELU_ALPHA; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_POINTWISE_SOFTPLUS_BETA = MIOPEN_ATTR_POINTWISE_SOFTPLUS_BETA; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_POINTWISE_SWISH_BETA = MIOPEN_ATTR_POINTWISE_SWISH_BETA; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_POINTWISE_DXDESC = MIOPEN_ATTR_OPERATION_POINTWISE_DXDESC; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_OPERATION_POINTWISE_DYDESC = MIOPEN_ATTR_OPERATION_POINTWISE_DYDESC; + cudnnBackendAttributeName_t ATTR_POINTWISE_RELU_LOWER_CLIP_SLOPE = CUDNN_ATTR_POINTWISE_RELU_LOWER_CLIP_SLOPE; + cudnnBackendAttributeName_t ATTR_POINTWISE_ELU_ALPHA = CUDNN_ATTR_POINTWISE_ELU_ALPHA; + cudnnBackendAttributeName_t ATTR_POINTWISE_SOFTPLUS_BETA = CUDNN_ATTR_POINTWISE_SOFTPLUS_BETA; + cudnnBackendAttributeName_t ATTR_POINTWISE_SWISH_BETA = CUDNN_ATTR_POINTWISE_SWISH_BETA; + cudnnBackendAttributeName_t ATTR_OPERATION_POINTWISE_DXDESC = CUDNN_ATTR_OPERATION_POINTWISE_DXDESC; + cudnnBackendAttributeName_t ATTR_OPERATION_POINTWISE_DYDESC = CUDNN_ATTR_OPERATION_POINTWISE_DYDESC; #endif -#if CUDNN_VERSION >= 80200 +#if CUDNN_VERSION >= 8200 // CHECK: miopenBackendAttributeType_t TYPE_BEHAVIOR_NOTE = MIOPEN_TYPE_BEHAVIOR_NOTE; cudnnBackendAttributeType_t TYPE_BEHAVIOR_NOTE = CUDNN_TYPE_BEHAVIOR_NOTE; #endif -#if CUDNN_VERSION >= 80300 +#if CUDNN_VERSION >= 8300 // CHECK: miopenBackendDescriptorType_t BACKEND_RESAMPLE_DESCRIPTOR = MIOPEN_BACKEND_RESAMPLE_DESCRIPTOR; // CHECK-NEXT: miopenBackendDescriptorType_t BACKEND_OPERATION_RESAMPLE_FWD_DESCRIPTOR = MIOPEN_BACKEND_OPERATION_RESAMPLE_FWD_DESCRIPTOR; // CHECK-NEXT: miopenBackendDescriptorType_t BACKEND_OPERATION_RESAMPLE_BWD_DESCRIPTOR = MIOPEN_BACKEND_OPERATION_RESAMPLE_BWD_DESCRIPTOR; @@ -940,14 +1063,22 @@ int main() { cudnnBackendAttributeType_t TYPE_RESAMPLE_MODE = CUDNN_TYPE_RESAMPLE_MODE; cudnnBackendAttributeType_t TYPE_PADDING_MODE = CUDNN_TYPE_PADDING_MODE; cudnnBackendAttributeType_t TYPE_INT32 = CUDNN_TYPE_INT32; + + // CHECK: miopenBackendAttributeName_t ATTR_OPERATION_POINTWISE_TDESC = MIOPEN_ATTR_OPERATION_POINTWISE_TDESC; + cudnnBackendAttributeName_t ATTR_OPERATION_POINTWISE_TDESC = CUDNN_ATTR_OPERATION_POINTWISE_TDESC; #endif -#if CUDNN_VERSION >= 80400 +#if CUDNN_VERSION >= 8400 // CHECK: miopenBackendAttributeType_t TYPE_CHAR = MIOPEN_TYPE_CHAR; cudnnBackendAttributeType_t TYPE_CHAR = CUDNN_TYPE_CHAR; + + // CHECK: miopenBackendAttributeName_t ATTR_POINTWISE_AXIS = MIOPEN_ATTR_POINTWISE_AXIS; + // CHECK-NEXT: miopenBackendAttributeName_t ATTR_EXECUTION_PLAN_JSON_REPRESENTATION = MIOPEN_ATTR_EXECUTION_PLAN_JSON_REPRESENTATION; + cudnnBackendAttributeName_t ATTR_POINTWISE_AXIS = CUDNN_ATTR_POINTWISE_AXIS; + cudnnBackendAttributeName_t ATTR_EXECUTION_PLAN_JSON_REPRESENTATION = CUDNN_ATTR_EXECUTION_PLAN_JSON_REPRESENTATION; #endif -#if CUDNN_VERSION >= 80500 +#if CUDNN_VERSION >= 8500 // CHECK: miopenBackendDescriptorType_t BACKEND_OPERATION_CONCAT_DESCRIPTOR = MIOPEN_BACKEND_OPERATION_CONCAT_DESCRIPTOR; // CHECK-NEXT: miopenBackendDescriptorType_t BACKEND_OPERATION_SIGNAL_DESCRIPTOR = MIOPEN_BACKEND_OPERATION_SIGNAL_DESCRIPTOR; // CHECK-NEXT: miopenBackendDescriptorType_t BACKEND_OPERATION_NORM_FORWARD_DESCRIPTOR = MIOPEN_BACKEND_OPERATION_NORM_FORWARD_DESCRIPTOR; @@ -967,7 +1098,7 @@ int main() { cudnnBackendAttributeType_t TYPE_NORM_FWD_PHASE = CUDNN_TYPE_NORM_FWD_PHASE; #endif -#if CUDNN_VERSION >= 80700 +#if CUDNN_VERSION >= 8700 // CHECK: miopenBackendDescriptorType_t BACKEND_RNG_DESCRIPTOR = MIOPEN_BACKEND_RNG_DESCRIPTOR; // CHECK-NEXT: miopenBackendDescriptorType_t BACKEND_OPERATION_RNG_DESCRIPTOR = MIOPEN_BACKEND_OPERATION_RNG_DESCRIPTOR; cudnnBackendDescriptorType_t BACKEND_RNG_DESCRIPTOR = CUDNN_BACKEND_RNG_DESCRIPTOR; @@ -977,5 +1108,10 @@ int main() { cudnnBackendAttributeType_t TYPE_RNG_DISTRIBUTION = CUDNN_TYPE_RNG_DISTRIBUTION; #endif +#if CUDNN_VERSION >= 8905 + // CHECK: miopenBackendAttributeName_t ATTR_ENGINEHEUR_SM_COUNT_TARGET = MIOPEN_ATTR_ENGINEHEUR_SM_COUNT_TARGET; + cudnnBackendAttributeName_t ATTR_ENGINEHEUR_SM_COUNT_TARGET = CUDNN_ATTR_ENGINEHEUR_SM_COUNT_TARGET; +#endif + return 0; }