diff --git a/bin/hipify-perl b/bin/hipify-perl index c3a3c5d1..525532eb 100755 --- a/bin/hipify-perl +++ b/bin/hipify-perl @@ -11168,6 +11168,7 @@ my %hash_HipOnlyUnsupportedFunctions = ( 'CUBLASLT_ALGO_CAP_NUMERICAL_IMPL_FLAGS' => 1, 'CUBLASLT_ALGO_CAP_OUT_OF_PLACE_RESULT_SUPPORT' => 1, 'CUBLASLT_ALGO_CAP_POINTER_ARRAY_BATCH_SUPPORT' => 1, + 'CUBLASLT_ALGO_CAP_POINTER_ARRAY_GROUPED_SUPPORT' => 1, 'CUBLASLT_ALGO_CAP_POINTER_MODE_MASK' => 1, 'CUBLASLT_ALGO_CAP_REDUCTION_SCHEME_MASK' => 1, 'CUBLASLT_ALGO_CAP_SPLITK_SUPPORT' => 1, @@ -11184,6 +11185,7 @@ my %hash_HipOnlyUnsupportedFunctions = ( 'CUBLASLT_ALGO_CONFIG_SPLITK_NUM' => 1, 'CUBLASLT_ALGO_CONFIG_STAGES_ID' => 1, 'CUBLASLT_ALGO_CONFIG_TILE_ID' => 1, + 'CUBLASLT_BATCH_MODE_GROUPED' => 1, 'CUBLASLT_BATCH_MODE_POINTER_ARRAY' => 1, 'CUBLASLT_BATCH_MODE_STRIDED' => 1, 'CUBLASLT_CLUSTER_SHAPE_10x1x1' => 1, @@ -11246,11 +11248,20 @@ my %hash_HipOnlyUnsupportedFunctions = ( 'CUBLASLT_EMULATION_DESC_STRATEGY' => 1, 'CUBLASLT_EPILOGUE_DRELU' => 1, 'CUBLASLT_EPILOGUE_DRELU_BGRAD' => 1, + 'CUBLASLT_GROUPED_MATRIX_LAYOUT_COLS_ARRAY' => 1, + 'CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY' => 1, + 'CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY_INTEGER_WIDTH' => 1, + 'CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_ARRAY' => 1, + 'CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_COLS_ARRAY_INTEGER_WIDTH' => 1, + 'CUBLASLT_INTEGER_WIDTH_32' => 1, + 'CUBLASLT_INTEGER_WIDTH_64' => 1, + 'CUBLASLT_MATMUL_DESC_ALPHA_BATCH_STRIDE' => 1, 'CUBLASLT_MATMUL_DESC_ALPHA_VECTOR_BATCH_STRIDE' => 1, 'CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_IN_COUNTERS_POINTER' => 1, 'CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_NUM_CHUNKS_D_COLS' => 1, 'CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_NUM_CHUNKS_D_ROWS' => 1, 'CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_OUT_COUNTERS_POINTER' => 1, + 'CUBLASLT_MATMUL_DESC_BETA_BATCH_STRIDE' => 1, 'CUBLASLT_MATMUL_DESC_BIAS_BATCH_STRIDE' => 1, 'CUBLASLT_MATMUL_DESC_COMPUTE_TYPE' => 1, 'CUBLASLT_MATMUL_DESC_C_SCALE_MODE' => 1, @@ -11271,6 +11282,10 @@ my %hash_HipOnlyUnsupportedFunctions = ( 'CUBLASLT_MATMUL_INNER_SHAPE_MMA1688' => 1, 'CUBLASLT_MATMUL_INNER_SHAPE_MMA884' => 1, 'CUBLASLT_MATMUL_INNER_SHAPE_UNDEFINED' => 1, + 'CUBLASLT_MATMUL_MATRIX_SCALE_PER_BATCH_SCALAR_32F' => 1, + 'CUBLASLT_MATMUL_PREF_GROUPED_AVERAGE_REDUCTION_DIM' => 1, + 'CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_COLS' => 1, + 'CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_ROWS' => 1, 'CUBLASLT_MATMUL_PREF_IMPL_MASK' => 1, 'CUBLASLT_MATMUL_PREF_MAX_WAVES_COUNT' => 1, 'CUBLASLT_MATMUL_PREF_MIN_ALIGNMENT_A_BYTES' => 1, @@ -13414,6 +13429,7 @@ my %hash_HipOnlyUnsupportedFunctions = ( 'cublasLtGetVersion' => 1, 'cublasLtHeuristicsCacheGetCapacity' => 1, 'cublasLtHeuristicsCacheSetCapacity' => 1, + 'cublasLtIntegerWidth_t' => 1, 'cublasLtLoggerCallback_t' => 1, 'cublasLtLoggerForceDisable' => 1, 'cublasLtLoggerOpenFile' => 1, @@ -14758,6 +14774,7 @@ my %hash_RocOnlyUnsupportedFunctions = ( 'CUBLASLT_ALGO_CAP_NUMERICAL_IMPL_FLAGS' => 1, 'CUBLASLT_ALGO_CAP_OUT_OF_PLACE_RESULT_SUPPORT' => 1, 'CUBLASLT_ALGO_CAP_POINTER_ARRAY_BATCH_SUPPORT' => 1, + 'CUBLASLT_ALGO_CAP_POINTER_ARRAY_GROUPED_SUPPORT' => 1, 'CUBLASLT_ALGO_CAP_POINTER_MODE_MASK' => 1, 'CUBLASLT_ALGO_CAP_REDUCTION_SCHEME_MASK' => 1, 'CUBLASLT_ALGO_CAP_SPLITK_SUPPORT' => 1, @@ -14774,6 +14791,7 @@ my %hash_RocOnlyUnsupportedFunctions = ( 'CUBLASLT_ALGO_CONFIG_SPLITK_NUM' => 1, 'CUBLASLT_ALGO_CONFIG_STAGES_ID' => 1, 'CUBLASLT_ALGO_CONFIG_TILE_ID' => 1, + 'CUBLASLT_BATCH_MODE_GROUPED' => 1, 'CUBLASLT_BATCH_MODE_POINTER_ARRAY' => 1, 'CUBLASLT_BATCH_MODE_STRIDED' => 1, 'CUBLASLT_CLUSTER_SHAPE_10x1x1' => 1, @@ -14850,6 +14868,14 @@ my %hash_RocOnlyUnsupportedFunctions = ( 'CUBLASLT_EPILOGUE_RELU_AUX' => 1, 'CUBLASLT_EPILOGUE_RELU_AUX_BIAS' => 1, 'CUBLASLT_EPILOGUE_RELU_BIAS' => 1, + 'CUBLASLT_GROUPED_MATRIX_LAYOUT_COLS_ARRAY' => 1, + 'CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY' => 1, + 'CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY_INTEGER_WIDTH' => 1, + 'CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_ARRAY' => 1, + 'CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_COLS_ARRAY_INTEGER_WIDTH' => 1, + 'CUBLASLT_INTEGER_WIDTH_32' => 1, + 'CUBLASLT_INTEGER_WIDTH_64' => 1, + 'CUBLASLT_MATMUL_DESC_ALPHA_BATCH_STRIDE' => 1, 'CUBLASLT_MATMUL_DESC_ALPHA_VECTOR_BATCH_STRIDE' => 1, 'CUBLASLT_MATMUL_DESC_AMAX_D_POINTER' => 1, 'CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_IN_COUNTERS_POINTER' => 1, @@ -14858,6 +14884,7 @@ my %hash_RocOnlyUnsupportedFunctions = ( 'CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_OUT_COUNTERS_POINTER' => 1, 'CUBLASLT_MATMUL_DESC_A_SCALE_MODE' => 1, 'CUBLASLT_MATMUL_DESC_A_SCALE_POINTER' => 1, + 'CUBLASLT_MATMUL_DESC_BETA_BATCH_STRIDE' => 1, 'CUBLASLT_MATMUL_DESC_BIAS_BATCH_STRIDE' => 1, 'CUBLASLT_MATMUL_DESC_BIAS_DATA_TYPE' => 1, 'CUBLASLT_MATMUL_DESC_BIAS_POINTER' => 1, @@ -14896,10 +14923,14 @@ my %hash_RocOnlyUnsupportedFunctions = ( 'CUBLASLT_MATMUL_MATRIX_SCALE_BLK128x128_32F' => 1, 'CUBLASLT_MATMUL_MATRIX_SCALE_END' => 1, 'CUBLASLT_MATMUL_MATRIX_SCALE_OUTER_VEC_32F' => 1, + 'CUBLASLT_MATMUL_MATRIX_SCALE_PER_BATCH_SCALAR_32F' => 1, 'CUBLASLT_MATMUL_MATRIX_SCALE_SCALAR_32F' => 1, 'CUBLASLT_MATMUL_MATRIX_SCALE_VEC128_32F' => 1, 'CUBLASLT_MATMUL_MATRIX_SCALE_VEC16_UE4M3' => 1, 'CUBLASLT_MATMUL_MATRIX_SCALE_VEC32_UE8M0' => 1, + 'CUBLASLT_MATMUL_PREF_GROUPED_AVERAGE_REDUCTION_DIM' => 1, + 'CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_COLS' => 1, + 'CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_ROWS' => 1, 'CUBLASLT_MATMUL_PREF_IMPL_MASK' => 1, 'CUBLASLT_MATMUL_PREF_MAX_WAVES_COUNT' => 1, 'CUBLASLT_MATMUL_PREF_MAX_WORKSPACE_BYTES' => 1, @@ -15916,6 +15947,7 @@ my %hash_RocOnlyUnsupportedFunctions = ( 'cublasLtGetVersion' => 1, 'cublasLtHeuristicsCacheGetCapacity' => 1, 'cublasLtHeuristicsCacheSetCapacity' => 1, + 'cublasLtIntegerWidth_t' => 1, 'cublasLtLoggerCallback_t' => 1, 'cublasLtLoggerForceDisable' => 1, 'cublasLtLoggerOpenFile' => 1, diff --git a/docs/reference/tables/CUBLAS_API_supported_by_HIP.md b/docs/reference/tables/CUBLAS_API_supported_by_HIP.md index 447a282c..7db6492c 100644 --- a/docs/reference/tables/CUBLAS_API_supported_by_HIP.md +++ b/docs/reference/tables/CUBLAS_API_supported_by_HIP.md @@ -184,6 +184,7 @@ |`CUBLASLT_ALGO_CAP_NUMERICAL_IMPL_FLAGS`|11.0| | | | | | | | | | | |`CUBLASLT_ALGO_CAP_OUT_OF_PLACE_RESULT_SUPPORT`|10.1| | | | | | | | | | | |`CUBLASLT_ALGO_CAP_POINTER_ARRAY_BATCH_SUPPORT`|12.9| | | | | | | | | | | +|`CUBLASLT_ALGO_CAP_POINTER_ARRAY_GROUPED_SUPPORT`|13.1| | | | | | | | | | | |`CUBLASLT_ALGO_CAP_POINTER_MODE_MASK`|10.1| | | | | | | | | | | |`CUBLASLT_ALGO_CAP_REDUCTION_SCHEME_MASK`|10.1| | | | | | | | | | | |`CUBLASLT_ALGO_CAP_SPLITK_SUPPORT`|10.1| | | | | | | | | | | @@ -200,6 +201,7 @@ |`CUBLASLT_ALGO_CONFIG_SPLITK_NUM`|10.1| | | | | | | | | | | |`CUBLASLT_ALGO_CONFIG_STAGES_ID`|11.0| | | | | | | | | | | |`CUBLASLT_ALGO_CONFIG_TILE_ID`|10.1| | | | | | | | | | | +|`CUBLASLT_BATCH_MODE_GROUPED`|13.1| | | | | | | | | | | |`CUBLASLT_BATCH_MODE_POINTER_ARRAY`|12.9| | | | | | | | | | | |`CUBLASLT_BATCH_MODE_STRIDED`|12.9| | | | | | | | | | | |`CUBLASLT_CLUSTER_SHAPE_10x1x1`|11.8| | | | | | | | | | | @@ -276,6 +278,14 @@ |`CUBLASLT_EPILOGUE_RELU_AUX`|11.3| | | |`HIPBLASLT_EPILOGUE_RELU_AUX`|7.1.0| | | | | | |`CUBLASLT_EPILOGUE_RELU_AUX_BIAS`|11.3| | | |`HIPBLASLT_EPILOGUE_RELU_AUX_BIAS`|7.1.0| | | | | | |`CUBLASLT_EPILOGUE_RELU_BIAS`|10.1| | | |`HIPBLASLT_EPILOGUE_RELU_BIAS`|5.5.0| | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_COLS_ARRAY`|13.1| | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY`|13.1| | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY_INTEGER_WIDTH`|13.1| | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_ARRAY`|13.1| | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_COLS_ARRAY_INTEGER_WIDTH`|13.1| | | | | | | | | | | +|`CUBLASLT_INTEGER_WIDTH_32`|13.1| | | | | | | | | | | +|`CUBLASLT_INTEGER_WIDTH_64`|13.1| | | | | | | | | | | +|`CUBLASLT_MATMUL_DESC_ALPHA_BATCH_STRIDE`|13.1| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_ALPHA_VECTOR_BATCH_STRIDE`|11.4| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_AMAX_D_POINTER`|11.8| | | |`HIPBLASLT_MATMUL_DESC_AMAX_D_POINTER`|6.2.0| | | | | | |`CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_IN_COUNTERS_POINTER`|12.2| | |13.0| | | | | | | | @@ -284,6 +294,7 @@ |`CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_OUT_COUNTERS_POINTER`|12.2| | |13.0| | | | | | | | |`CUBLASLT_MATMUL_DESC_A_SCALE_MODE`|12.8| | | |`HIPBLASLT_MATMUL_DESC_A_SCALE_MODE`|7.0.0| | | | | | |`CUBLASLT_MATMUL_DESC_A_SCALE_POINTER`|11.8| | | |`HIPBLASLT_MATMUL_DESC_A_SCALE_POINTER`|6.0.0| | | | | | +|`CUBLASLT_MATMUL_DESC_BETA_BATCH_STRIDE`|13.1| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_BIAS_BATCH_STRIDE`|11.3| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_BIAS_DATA_TYPE`|11.8| | | |`HIPBLASLT_MATMUL_DESC_BIAS_DATA_TYPE`|5.5.0| | | | | | |`CUBLASLT_MATMUL_DESC_BIAS_POINTER`|10.1| | | |`HIPBLASLT_MATMUL_DESC_BIAS_POINTER`|5.5.0| | | | | | @@ -322,10 +333,14 @@ |`CUBLASLT_MATMUL_MATRIX_SCALE_BLK128x128_32F`|12.9| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_BLK128x128_32F`|7.0.0| | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_END`|12.8| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_END`|7.0.0| | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_OUTER_VEC_32F`|12.9| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_OUTER_VEC_32F`|7.0.0| | | | | | +|`CUBLASLT_MATMUL_MATRIX_SCALE_PER_BATCH_SCALAR_32F`|13.1| | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_SCALAR_32F`|12.8| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_SCALAR_32F`|7.0.0| | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_VEC128_32F`|12.9| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_VEC128_32F`|7.0.0| | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_VEC16_UE4M3`|12.8| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_VEC16_UE4M3`|7.0.0| | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_VEC32_UE8M0`|12.8| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_VEC32_UE8M0`|7.0.0| | | | | | +|`CUBLASLT_MATMUL_PREF_GROUPED_AVERAGE_REDUCTION_DIM`|13.1| | | | | | | | | | | +|`CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_COLS`|13.1| | | | | | | | | | | +|`CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_ROWS`|13.1| | | | | | | | | | | |`CUBLASLT_MATMUL_PREF_IMPL_MASK`|11.0| | | | | | | | | | | |`CUBLASLT_MATMUL_PREF_MAX_WAVES_COUNT`|10.1| | | | | | | | | | | |`CUBLASLT_MATMUL_PREF_MAX_WORKSPACE_BYTES`|10.1| | | |`HIPBLASLT_MATMUL_PREF_MAX_WORKSPACE_BYTES`|5.5.0| | | | | | @@ -1080,6 +1095,7 @@ |`cublasLtEmulationDesc_t`|13.0| | | | | | | | | | | |`cublasLtEpilogue_t`|10.1| | | |`hipblasLtEpilogue_t`|5.5.0| | | | | | |`cublasLtHandle_t`|10.1| | | |`hipblasLtHandle_t`|5.5.0| | | | | | +|`cublasLtIntegerWidth_t`|13.1| | | | | | | | | | | |`cublasLtLoggerCallback_t`|11.0| | | | | | | | | | | |`cublasLtMatmulAlgoCapAttributes_t`|10.1| | | | | | | | | | | |`cublasLtMatmulAlgoConfigAttributes_t`|10.1| | | | | | | | | | | @@ -1091,13 +1107,13 @@ |`cublasLtMatmulInnerShape_t`|11.8| | | | | | | | | | | |`cublasLtMatmulMatrixScale_t`|12.8| | | |`hipblasLtMatmulMatrixScale_t`|7.0.0| | | | | | |`cublasLtMatmulPreferenceAttributes_t`|10.1| | | |`hipblasLtMatmulPreferenceAttributes_t`|5.5.0| | | | | | -|`cublasLtMatmulPreferenceOpaque_t`|11.0| | | |`hipblasLtMatmulPreferenceOpaque_t`|5.5.0| | | | | | +|`cublasLtMatmulPreferenceOpaque_t`|11.0| |13.1| |`hipblasLtMatmulPreferenceOpaque_t`|5.5.0| | | | | | |`cublasLtMatmulPreference_t`|10.1| | | |`hipblasLtMatmulPreference_t`|5.5.0| | | | | | |`cublasLtMatmulSearch_t`|10.1| | | | | | | | | | | |`cublasLtMatmulStages_t`|11.0| | | | | | | | | | | |`cublasLtMatmulTile_t`|10.1| | | | | | | | | | | |`cublasLtMatrixLayoutAttribute_t`|10.1| | | |`hipblasLtMatrixLayoutAttribute_t`|5.5.0| | | | | | -|`cublasLtMatrixLayoutOpaque_t`|11.0| | | |`hipblasLtMatrixLayoutOpaque_t`| | | | | | | +|`cublasLtMatrixLayoutOpaque_t`|11.0| |13.1| |`hipblasLtMatrixLayoutOpaque_t`| | | | | | | |`cublasLtMatrixLayoutStruct`|10.1| | |10.2|`hipblasLtMatrixLayoutOpaque_t`| | | | | | | |`cublasLtMatrixLayout_t`|10.1| | | |`hipblasLtMatrixLayout_t`| | | | | | | |`cublasLtMatrixTransformDescAttributes_t`|10.1| | | |`hipblasLtMatrixTransformDescAttributes_t`|6.0.0| | | | | | diff --git a/docs/reference/tables/CUBLAS_API_supported_by_HIP_and_ROC.md b/docs/reference/tables/CUBLAS_API_supported_by_HIP_and_ROC.md index 576050cc..37ef8dc0 100644 --- a/docs/reference/tables/CUBLAS_API_supported_by_HIP_and_ROC.md +++ b/docs/reference/tables/CUBLAS_API_supported_by_HIP_and_ROC.md @@ -184,6 +184,7 @@ |`CUBLASLT_ALGO_CAP_NUMERICAL_IMPL_FLAGS`|11.0| | | | | | | | | | | | | | | | | |`CUBLASLT_ALGO_CAP_OUT_OF_PLACE_RESULT_SUPPORT`|10.1| | | | | | | | | | | | | | | | | |`CUBLASLT_ALGO_CAP_POINTER_ARRAY_BATCH_SUPPORT`|12.9| | | | | | | | | | | | | | | | | +|`CUBLASLT_ALGO_CAP_POINTER_ARRAY_GROUPED_SUPPORT`|13.1| | | | | | | | | | | | | | | | | |`CUBLASLT_ALGO_CAP_POINTER_MODE_MASK`|10.1| | | | | | | | | | | | | | | | | |`CUBLASLT_ALGO_CAP_REDUCTION_SCHEME_MASK`|10.1| | | | | | | | | | | | | | | | | |`CUBLASLT_ALGO_CAP_SPLITK_SUPPORT`|10.1| | | | | | | | | | | | | | | | | @@ -200,6 +201,7 @@ |`CUBLASLT_ALGO_CONFIG_SPLITK_NUM`|10.1| | | | | | | | | | | | | | | | | |`CUBLASLT_ALGO_CONFIG_STAGES_ID`|11.0| | | | | | | | | | | | | | | | | |`CUBLASLT_ALGO_CONFIG_TILE_ID`|10.1| | | | | | | | | | | | | | | | | +|`CUBLASLT_BATCH_MODE_GROUPED`|13.1| | | | | | | | | | | | | | | | | |`CUBLASLT_BATCH_MODE_POINTER_ARRAY`|12.9| | | | | | | | | | | | | | | | | |`CUBLASLT_BATCH_MODE_STRIDED`|12.9| | | | | | | | | | | | | | | | | |`CUBLASLT_CLUSTER_SHAPE_10x1x1`|11.8| | | | | | | | | | | | | | | | | @@ -276,6 +278,14 @@ |`CUBLASLT_EPILOGUE_RELU_AUX`|11.3| | | |`HIPBLASLT_EPILOGUE_RELU_AUX`|7.1.0| | | | | | | | | | | | |`CUBLASLT_EPILOGUE_RELU_AUX_BIAS`|11.3| | | |`HIPBLASLT_EPILOGUE_RELU_AUX_BIAS`|7.1.0| | | | | | | | | | | | |`CUBLASLT_EPILOGUE_RELU_BIAS`|10.1| | | |`HIPBLASLT_EPILOGUE_RELU_BIAS`|5.5.0| | | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_COLS_ARRAY`|13.1| | | | | | | | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY`|13.1| | | | | | | | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY_INTEGER_WIDTH`|13.1| | | | | | | | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_ARRAY`|13.1| | | | | | | | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_COLS_ARRAY_INTEGER_WIDTH`|13.1| | | | | | | | | | | | | | | | | +|`CUBLASLT_INTEGER_WIDTH_32`|13.1| | | | | | | | | | | | | | | | | +|`CUBLASLT_INTEGER_WIDTH_64`|13.1| | | | | | | | | | | | | | | | | +|`CUBLASLT_MATMUL_DESC_ALPHA_BATCH_STRIDE`|13.1| | | | | | | | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_ALPHA_VECTOR_BATCH_STRIDE`|11.4| | | | | | | | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_AMAX_D_POINTER`|11.8| | | |`HIPBLASLT_MATMUL_DESC_AMAX_D_POINTER`|6.2.0| | | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_IN_COUNTERS_POINTER`|12.2| | |13.0| | | | | | | | | | | | | | @@ -284,6 +294,7 @@ |`CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_OUT_COUNTERS_POINTER`|12.2| | |13.0| | | | | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_A_SCALE_MODE`|12.8| | | |`HIPBLASLT_MATMUL_DESC_A_SCALE_MODE`|7.0.0| | | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_A_SCALE_POINTER`|11.8| | | |`HIPBLASLT_MATMUL_DESC_A_SCALE_POINTER`|6.0.0| | | | | | | | | | | | +|`CUBLASLT_MATMUL_DESC_BETA_BATCH_STRIDE`|13.1| | | | | | | | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_BIAS_BATCH_STRIDE`|11.3| | | | | | | | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_BIAS_DATA_TYPE`|11.8| | | |`HIPBLASLT_MATMUL_DESC_BIAS_DATA_TYPE`|5.5.0| | | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_BIAS_POINTER`|10.1| | | |`HIPBLASLT_MATMUL_DESC_BIAS_POINTER`|5.5.0| | | | | | | | | | | | @@ -322,10 +333,14 @@ |`CUBLASLT_MATMUL_MATRIX_SCALE_BLK128x128_32F`|12.9| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_BLK128x128_32F`|7.0.0| | | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_END`|12.8| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_END`|7.0.0| | | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_OUTER_VEC_32F`|12.9| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_OUTER_VEC_32F`|7.0.0| | | | | | | | | | | | +|`CUBLASLT_MATMUL_MATRIX_SCALE_PER_BATCH_SCALAR_32F`|13.1| | | | | | | | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_SCALAR_32F`|12.8| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_SCALAR_32F`|7.0.0| | | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_VEC128_32F`|12.9| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_VEC128_32F`|7.0.0| | | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_VEC16_UE4M3`|12.8| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_VEC16_UE4M3`|7.0.0| | | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_VEC32_UE8M0`|12.8| | | |`HIPBLASLT_MATMUL_MATRIX_SCALE_VEC32_UE8M0`|7.0.0| | | | | | | | | | | | +|`CUBLASLT_MATMUL_PREF_GROUPED_AVERAGE_REDUCTION_DIM`|13.1| | | | | | | | | | | | | | | | | +|`CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_COLS`|13.1| | | | | | | | | | | | | | | | | +|`CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_ROWS`|13.1| | | | | | | | | | | | | | | | | |`CUBLASLT_MATMUL_PREF_IMPL_MASK`|11.0| | | | | | | | | | | | | | | | | |`CUBLASLT_MATMUL_PREF_MAX_WAVES_COUNT`|10.1| | | | | | | | | | | | | | | | | |`CUBLASLT_MATMUL_PREF_MAX_WORKSPACE_BYTES`|10.1| | | |`HIPBLASLT_MATMUL_PREF_MAX_WORKSPACE_BYTES`|5.5.0| | | | | | | | | | | | @@ -1080,6 +1095,7 @@ |`cublasLtEmulationDesc_t`|13.0| | | | | | | | | | | | | | | | | |`cublasLtEpilogue_t`|10.1| | | |`hipblasLtEpilogue_t`|5.5.0| | | | | | | | | | | | |`cublasLtHandle_t`|10.1| | | |`hipblasLtHandle_t`|5.5.0| | | | | | | | | | | | +|`cublasLtIntegerWidth_t`|13.1| | | | | | | | | | | | | | | | | |`cublasLtLoggerCallback_t`|11.0| | | | | | | | | | | | | | | | | |`cublasLtMatmulAlgoCapAttributes_t`|10.1| | | | | | | | | | | | | | | | | |`cublasLtMatmulAlgoConfigAttributes_t`|10.1| | | | | | | | | | | | | | | | | @@ -1091,13 +1107,13 @@ |`cublasLtMatmulInnerShape_t`|11.8| | | | | | | | | | | | | | | | | |`cublasLtMatmulMatrixScale_t`|12.8| | | |`hipblasLtMatmulMatrixScale_t`|7.0.0| | | | | | | | | | | | |`cublasLtMatmulPreferenceAttributes_t`|10.1| | | |`hipblasLtMatmulPreferenceAttributes_t`|5.5.0| | | | | | | | | | | | -|`cublasLtMatmulPreferenceOpaque_t`|11.0| | | |`hipblasLtMatmulPreferenceOpaque_t`|5.5.0| | | | | | | | | | | | +|`cublasLtMatmulPreferenceOpaque_t`|11.0| |13.1| |`hipblasLtMatmulPreferenceOpaque_t`|5.5.0| | | | | | | | | | | | |`cublasLtMatmulPreference_t`|10.1| | | |`hipblasLtMatmulPreference_t`|5.5.0| | | | | | | | | | | | |`cublasLtMatmulSearch_t`|10.1| | | | | | | | | | | | | | | | | |`cublasLtMatmulStages_t`|11.0| | | | | | | | | | | | | | | | | |`cublasLtMatmulTile_t`|10.1| | | | | | | | | | | | | | | | | |`cublasLtMatrixLayoutAttribute_t`|10.1| | | |`hipblasLtMatrixLayoutAttribute_t`|5.5.0| | | | | | | | | | | | -|`cublasLtMatrixLayoutOpaque_t`|11.0| | | |`hipblasLtMatrixLayoutOpaque_t`| | | | | | | | | | | | | +|`cublasLtMatrixLayoutOpaque_t`|11.0| |13.1| |`hipblasLtMatrixLayoutOpaque_t`| | | | | | | | | | | | | |`cublasLtMatrixLayoutStruct`|10.1| | |10.2|`hipblasLtMatrixLayoutOpaque_t`| | | | | | | | | | | | | |`cublasLtMatrixLayout_t`|10.1| | | |`hipblasLtMatrixLayout_t`| | | | | | | | | | | | | |`cublasLtMatrixTransformDescAttributes_t`|10.1| | | |`hipblasLtMatrixTransformDescAttributes_t`|6.0.0| | | | | | | | | | | | diff --git a/docs/reference/tables/CUBLAS_API_supported_by_ROC.md b/docs/reference/tables/CUBLAS_API_supported_by_ROC.md index f72d9a0b..b31d1f1e 100644 --- a/docs/reference/tables/CUBLAS_API_supported_by_ROC.md +++ b/docs/reference/tables/CUBLAS_API_supported_by_ROC.md @@ -184,6 +184,7 @@ |`CUBLASLT_ALGO_CAP_NUMERICAL_IMPL_FLAGS`|11.0| | | | | | | | | | | |`CUBLASLT_ALGO_CAP_OUT_OF_PLACE_RESULT_SUPPORT`|10.1| | | | | | | | | | | |`CUBLASLT_ALGO_CAP_POINTER_ARRAY_BATCH_SUPPORT`|12.9| | | | | | | | | | | +|`CUBLASLT_ALGO_CAP_POINTER_ARRAY_GROUPED_SUPPORT`|13.1| | | | | | | | | | | |`CUBLASLT_ALGO_CAP_POINTER_MODE_MASK`|10.1| | | | | | | | | | | |`CUBLASLT_ALGO_CAP_REDUCTION_SCHEME_MASK`|10.1| | | | | | | | | | | |`CUBLASLT_ALGO_CAP_SPLITK_SUPPORT`|10.1| | | | | | | | | | | @@ -200,6 +201,7 @@ |`CUBLASLT_ALGO_CONFIG_SPLITK_NUM`|10.1| | | | | | | | | | | |`CUBLASLT_ALGO_CONFIG_STAGES_ID`|11.0| | | | | | | | | | | |`CUBLASLT_ALGO_CONFIG_TILE_ID`|10.1| | | | | | | | | | | +|`CUBLASLT_BATCH_MODE_GROUPED`|13.1| | | | | | | | | | | |`CUBLASLT_BATCH_MODE_POINTER_ARRAY`|12.9| | | | | | | | | | | |`CUBLASLT_BATCH_MODE_STRIDED`|12.9| | | | | | | | | | | |`CUBLASLT_CLUSTER_SHAPE_10x1x1`|11.8| | | | | | | | | | | @@ -276,6 +278,14 @@ |`CUBLASLT_EPILOGUE_RELU_AUX`|11.3| | | | | | | | | | | |`CUBLASLT_EPILOGUE_RELU_AUX_BIAS`|11.3| | | | | | | | | | | |`CUBLASLT_EPILOGUE_RELU_BIAS`|10.1| | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_COLS_ARRAY`|13.1| | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY`|13.1| | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY_INTEGER_WIDTH`|13.1| | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_ARRAY`|13.1| | | | | | | | | | | +|`CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_COLS_ARRAY_INTEGER_WIDTH`|13.1| | | | | | | | | | | +|`CUBLASLT_INTEGER_WIDTH_32`|13.1| | | | | | | | | | | +|`CUBLASLT_INTEGER_WIDTH_64`|13.1| | | | | | | | | | | +|`CUBLASLT_MATMUL_DESC_ALPHA_BATCH_STRIDE`|13.1| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_ALPHA_VECTOR_BATCH_STRIDE`|11.4| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_AMAX_D_POINTER`|11.8| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_IN_COUNTERS_POINTER`|12.2| | |13.0| | | | | | | | @@ -284,6 +294,7 @@ |`CUBLASLT_MATMUL_DESC_ATOMIC_SYNC_OUT_COUNTERS_POINTER`|12.2| | |13.0| | | | | | | | |`CUBLASLT_MATMUL_DESC_A_SCALE_MODE`|12.8| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_A_SCALE_POINTER`|11.8| | | | | | | | | | | +|`CUBLASLT_MATMUL_DESC_BETA_BATCH_STRIDE`|13.1| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_BIAS_BATCH_STRIDE`|11.3| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_BIAS_DATA_TYPE`|11.8| | | | | | | | | | | |`CUBLASLT_MATMUL_DESC_BIAS_POINTER`|10.1| | | | | | | | | | | @@ -322,10 +333,14 @@ |`CUBLASLT_MATMUL_MATRIX_SCALE_BLK128x128_32F`|12.9| | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_END`|12.8| | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_OUTER_VEC_32F`|12.9| | | | | | | | | | | +|`CUBLASLT_MATMUL_MATRIX_SCALE_PER_BATCH_SCALAR_32F`|13.1| | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_SCALAR_32F`|12.8| | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_VEC128_32F`|12.9| | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_VEC16_UE4M3`|12.8| | | | | | | | | | | |`CUBLASLT_MATMUL_MATRIX_SCALE_VEC32_UE8M0`|12.8| | | | | | | | | | | +|`CUBLASLT_MATMUL_PREF_GROUPED_AVERAGE_REDUCTION_DIM`|13.1| | | | | | | | | | | +|`CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_COLS`|13.1| | | | | | | | | | | +|`CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_ROWS`|13.1| | | | | | | | | | | |`CUBLASLT_MATMUL_PREF_IMPL_MASK`|11.0| | | | | | | | | | | |`CUBLASLT_MATMUL_PREF_MAX_WAVES_COUNT`|10.1| | | | | | | | | | | |`CUBLASLT_MATMUL_PREF_MAX_WORKSPACE_BYTES`|10.1| | | | | | | | | | | @@ -1080,6 +1095,7 @@ |`cublasLtEmulationDesc_t`|13.0| | | | | | | | | | | |`cublasLtEpilogue_t`|10.1| | | | | | | | | | | |`cublasLtHandle_t`|10.1| | | | | | | | | | | +|`cublasLtIntegerWidth_t`|13.1| | | | | | | | | | | |`cublasLtLoggerCallback_t`|11.0| | | | | | | | | | | |`cublasLtMatmulAlgoCapAttributes_t`|10.1| | | | | | | | | | | |`cublasLtMatmulAlgoConfigAttributes_t`|10.1| | | | | | | | | | | @@ -1091,13 +1107,13 @@ |`cublasLtMatmulInnerShape_t`|11.8| | | | | | | | | | | |`cublasLtMatmulMatrixScale_t`|12.8| | | | | | | | | | | |`cublasLtMatmulPreferenceAttributes_t`|10.1| | | | | | | | | | | -|`cublasLtMatmulPreferenceOpaque_t`|11.0| | | | | | | | | | | +|`cublasLtMatmulPreferenceOpaque_t`|11.0| |13.1| | | | | | | | | |`cublasLtMatmulPreference_t`|10.1| | | | | | | | | | | |`cublasLtMatmulSearch_t`|10.1| | | | | | | | | | | |`cublasLtMatmulStages_t`|11.0| | | | | | | | | | | |`cublasLtMatmulTile_t`|10.1| | | | | | | | | | | |`cublasLtMatrixLayoutAttribute_t`|10.1| | | | | | | | | | | -|`cublasLtMatrixLayoutOpaque_t`|11.0| | | | | | | | | | | +|`cublasLtMatrixLayoutOpaque_t`|11.0| |13.1| | | | | | | | | |`cublasLtMatrixLayoutStruct`|10.1| | |10.2| | | | | | | | |`cublasLtMatrixLayout_t`|10.1| | | | | | | | | | | |`cublasLtMatrixTransformDescAttributes_t`|10.1| | | | | | | | | | | diff --git a/src/CUDA2HIP.h b/src/CUDA2HIP.h index 1dc87d59..4a17248d 100644 --- a/src/CUDA2HIP.h +++ b/src/CUDA2HIP.h @@ -147,6 +147,7 @@ extern const std::map HIP_BLAS_TYPE_NAME_VER_MA extern const std::map HIP_BLAS_FUNCTION_VER_MAP; extern const std::map HIP_BLAS_FUNCTION_CHANGED_VER_MAP; extern const std::map CUDA_BLAS_FUNCTION_CHANGED_VER_MAP; +extern const std::map CUDA_BLAS_TYPE_CHANGED_VER_MAP; extern const std::map HIP_RAND_TYPE_NAME_VER_MAP; extern const std::map HIP_RAND_FUNCTION_VER_MAP; extern const std::map HIP_DNN_TYPE_NAME_VER_MAP; diff --git a/src/CUDA2HIP_BLAS_API_types.cpp b/src/CUDA2HIP_BLAS_API_types.cpp index 92b84a82..bf23cda6 100644 --- a/src/CUDA2HIP_BLAS_API_types.cpp +++ b/src/CUDA2HIP_BLAS_API_types.cpp @@ -1005,6 +1005,11 @@ const std::map CUDA_BLAS_TYPE_NAME_MAP = [] { m["CUBLASLT_MATRIX_LAYOUT_STRIDED_BATCH_OFFSET"] = {"HIPBLASLT_MATRIX_LAYOUT_STRIDED_BATCH_OFFSET", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, ROC_UNSUPPORTED}; m["CUBLASLT_MATRIX_LAYOUT_PLANE_OFFSET"] = {"HIPBLASLT_MATRIX_LAYOUT_PLANE_OFFSET", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_MATRIX_LAYOUT_BATCH_MODE"] = {"HIPBLASLT_MATRIX_LAYOUT_BATCH_MODE", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_ARRAY"] = {"HIPBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_ARRAY", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_GROUPED_MATRIX_LAYOUT_COLS_ARRAY"] = {"HIPBLASLT_GROUPED_MATRIX_LAYOUT_COLS_ARRAY", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY"] = {"HIPBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_COLS_ARRAY_INTEGER_WIDTH"] = {"HIPBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_COLS_ARRAY_INTEGER_WIDTH", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY_INTEGER_WIDTH"] = {"HIPBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY_INTEGER_WIDTH", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["cublasLtMatmulDescAttributes_t"] = {"hipblasLtMatmulDescAttributes_t", "", CONV_TYPE, API_BLAS, SEC::BLAS_LT_DATA_TYPES, ROC_UNSUPPORTED}; m["CUBLASLT_MATMUL_DESC_COMPUTE_TYPE"] = {"HIPBLASLT_MATMUL_DESC_COMPUTE_TYPE", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_MATMUL_DESC_SCALE_TYPE"] = {"HIPBLASLT_MATMUL_DESC_SCALE_TYPE", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; @@ -1043,6 +1048,8 @@ const std::map CUDA_BLAS_TYPE_NAME_MAP = [] { m["CUBLASLT_MATMUL_DESC_D_OUT_SCALE_POINTER"] = {"HIPBLASLT_MATMUL_DESC_D_OUT_SCALE_POINTER", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_MATMUL_DESC_D_OUT_SCALE_MODE"] = {"HIPBLASLT_MATMUL_DESC_D_OUT_SCALE_MODE", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_MATMUL_DESC_EMULATION_DESCRIPTOR"] = {"HIPBLASLT_MATMUL_DESC_EMULATION_DESCRIPTOR", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_MATMUL_DESC_ALPHA_BATCH_STRIDE"] = {"HIPBLASLT_MATMUL_DESC_ALPHA_BATCH_STRIDE", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_MATMUL_DESC_BETA_BATCH_STRIDE"] = {"HIPBLASLT_MATMUL_DESC_BETA_BATCH_STRIDE", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["cublasLtMatrixTransformDescAttributes_t"] = {"hipblasLtMatrixTransformDescAttributes_t", "", CONV_TYPE, API_BLAS, SEC::BLAS_LT_DATA_TYPES, ROC_UNSUPPORTED}; m["CUBLASLT_MATRIX_TRANSFORM_DESC_SCALE_TYPE"] = {"HIPBLASLT_MATRIX_TRANSFORM_DESC_SCALE_TYPE", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, ROC_UNSUPPORTED}; m["CUBLASLT_MATRIX_TRANSFORM_DESC_POINTER_MODE"] = {"HIPBLASLT_MATRIX_TRANSFORM_DESC_POINTER_MODE", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, ROC_UNSUPPORTED}; @@ -1092,6 +1099,9 @@ const std::map CUDA_BLAS_TYPE_NAME_MAP = [] { m["CUBLASLT_MATMUL_PREF_MIN_ALIGNMENT_D_BYTES"] = {"HIPBLASLT_MATMUL_PREF_MIN_ALIGNMENT_D_BYTES", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_MATMUL_PREF_MAX_WAVES_COUNT"] = {"HIPBLASLT_MATMUL_PREF_MAX_WAVES_COUNT", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_MATMUL_PREF_IMPL_MASK"] = {"HIPBLASLT_MATMUL_PREF_IMPL_MASK", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_MATMUL_PREF_GROUPED_AVERAGE_REDUCTION_DIM"] = {"HIPBLASLT_MATMUL_PREF_GROUPED_AVERAGE_REDUCTION_DIM", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_ROWS"] = {"HIPBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_ROWS", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_COLS"] = {"HIPBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_COLS", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["cublasLtMatmulHeuristicResult_t"] = {"hipblasLtMatmulHeuristicResult_t", "", CONV_TYPE, API_BLAS, SEC::BLAS_LT_DATA_TYPES, ROC_UNSUPPORTED}; m["cublasLtMatmulAlgoCapAttributes_t"] = {"hipblasLtMatmulAlgoCapAttributes_t", "", CONV_TYPE, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_ALGO_CAP_SPLITK_SUPPORT"] = {"HIPBLASLT_ALGO_CAP_SPLITK_SUPPORT", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; @@ -1115,6 +1125,7 @@ const std::map CUDA_BLAS_TYPE_NAME_MAP = [] { m["CUBLASLT_ALGO_CAP_ATOMIC_SYNC"] = {"HIPBLASLT_ALGO_CAP_ATOMIC_SYNC", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED | CUDA_REMOVED}; m["CUBLASLT_ALGO_CAP_POINTER_ARRAY_BATCH_SUPPORT"] = {"HIPBLASLT_ALGO_CAP_POINTER_ARRAY_BATCH_SUPPORT", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_ALGO_CAP_FLOATING_POINT_EMULATION_SUPPORT"] = {"HIPBLASLT_ALGO_CAP_FLOATING_POINT_EMULATION_SUPPORT", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_ALGO_CAP_POINTER_ARRAY_GROUPED_SUPPORT"] = {"HIPBLASLT_ALGO_CAP_POINTER_ARRAY_GROUPED_SUPPORT", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["cublasLtMatmulAlgoConfigAttributes_t"] = {"hipblasLtMatmulAlgoConfigAttributes_t", "", CONV_TYPE, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_ALGO_CONFIG_ID"] = {"HIPBLASLT_ALGO_CONFIG_ID", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_ALGO_CONFIG_TILE_ID"] = {"HIPBLASLT_ALGO_CONFIG_TILE_ID", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; @@ -1133,10 +1144,12 @@ const std::map CUDA_BLAS_TYPE_NAME_MAP = [] { m["CUBLASLT_MATMUL_MATRIX_SCALE_OUTER_VEC_32F"] = {"HIPBLASLT_MATMUL_MATRIX_SCALE_OUTER_VEC_32F", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, ROC_UNSUPPORTED}; m["CUBLASLT_MATMUL_MATRIX_SCALE_VEC128_32F"] = {"HIPBLASLT_MATMUL_MATRIX_SCALE_VEC128_32F", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, ROC_UNSUPPORTED}; m["CUBLASLT_MATMUL_MATRIX_SCALE_BLK128x128_32F"] = {"HIPBLASLT_MATMUL_MATRIX_SCALE_BLK128x128_32F", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, ROC_UNSUPPORTED}; + m["CUBLASLT_MATMUL_MATRIX_SCALE_PER_BATCH_SCALAR_32F"] = {"HIPBLASLT_MATMUL_MATRIX_SCALE_PER_BATCH_SCALAR_32F", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_MATMUL_MATRIX_SCALE_END"] = {"HIPBLASLT_MATMUL_MATRIX_SCALE_END", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, ROC_UNSUPPORTED}; m["cublasLtBatchMode_t"] = {"hipblasLtBatchMode_t", "", CONV_TYPE, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_BATCH_MODE_STRIDED"] = {"HIPBLASLT_BATCH_MODE_STRIDED", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_BATCH_MODE_POINTER_ARRAY"] = {"HIPBLASLT_BATCH_MODE_POINTER_ARRAY", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_BATCH_MODE_GROUPED"] = {"HIPBLASLT_BATCH_MODE_GROUPED", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["cublasLtEmulationDesc_t"] = {"hipblasLtEmulationDesc_t", "", CONV_TYPE, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["cublasLtEmulationDescOpaque_t"] = {"hipblasLtEmulationDescOpaque_t", "", CONV_TYPE, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["cublasLtEmulationDescAttributes_t"] = {"hipblasLtEmulationDescAttributes_t", "", CONV_TYPE, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; @@ -1146,6 +1159,9 @@ const std::map CUDA_BLAS_TYPE_NAME_MAP = [] { m["CUBLASLT_EMULATION_DESC_FIXEDPOINT_MAX_MANTISSA_BIT_COUNT"] = {"HIPBLASLT_EMULATION_DESC_FIXEDPOINT_MAX_MANTISSA_BIT_COUNT", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_EMULATION_DESC_FIXEDPOINT_MANTISSA_BIT_OFFSET"] = {"HIPBLASLT_EMULATION_DESC_FIXEDPOINT_MANTISSA_BIT_OFFSET", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; m["CUBLASLT_EMULATION_DESC_FIXEDPOINT_MANTISSA_BIT_COUNT_POINTER"] = {"HIPBLASLT_EMULATION_DESC_FIXEDPOINT_MANTISSA_BIT_COUNT_POINTER", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["cublasLtIntegerWidth_t"] = {"hipblasLtIntegerWidth_t", "", CONV_TYPE, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_INTEGER_WIDTH_32"] = {"HIPBLASLT_INTEGER_WIDTH_32", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; + m["CUBLASLT_INTEGER_WIDTH_64"] = {"HIPBLASLT_INTEGER_WIDTH_64", "", CONV_NUMERIC_LITERAL, API_BLAS, SEC::BLAS_LT_DATA_TYPES, UNSUPPORTED}; return m; }(); @@ -2202,6 +2218,22 @@ const std::map CUDA_BLAS_TYPE_NAME_VER_MAP = [ m["CUBLASLT_EMULATION_DESC_FIXEDPOINT_MANTISSA_BIT_COUNT_POINTER"] = {CUDA_130, CUDA_0, CUDA_0 }; // CUBLAS_VERSION 130100 CUDA 13.0.2 m["CUBLAS_FP64_EMULATED_FIXEDPOINT_MATH"] = {CUDA_130, CUDA_0, CUDA_0 }; // CUBLAS_VERSION 130100 CUDA 13.0.2 m["CUBLAS_COMPUTE_64F_EMULATED_FIXEDPOINT"] = {CUDA_130, CUDA_0, CUDA_0 }; // CUBLAS_VERSION 130100 CUDA 13.0.2 + m["CUBLASLT_MATMUL_MATRIX_SCALE_PER_BATCH_SCALAR_32F"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_BATCH_MODE_GROUPED"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["cublasLtIntegerWidth_t"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_INTEGER_WIDTH_32"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_INTEGER_WIDTH_64"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_ARRAY"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_GROUPED_MATRIX_LAYOUT_COLS_ARRAY"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_GROUPED_MATRIX_LAYOUT_ROWS_COLS_ARRAY_INTEGER_WIDTH"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_GROUPED_MATRIX_LAYOUT_LD_ARRAY_INTEGER_WIDTH"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_MATMUL_DESC_ALPHA_BATCH_STRIDE"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_MATMUL_DESC_BETA_BATCH_STRIDE"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_MATMUL_PREF_GROUPED_AVERAGE_REDUCTION_DIM"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_ROWS"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_MATMUL_PREF_GROUPED_DESC_D_AVERAGE_COLS"] = {CUDA_131, CUDA_0, CUDA_0 }; + m["CUBLASLT_ALGO_CAP_POINTER_ARRAY_GROUPED_SUPPORT"] = {CUDA_131, CUDA_0, CUDA_0 }; return m; }(); @@ -2429,5 +2461,15 @@ const std::map HIP_BLAS_TYPE_NAME_VER_MAP = [] m["rocblas_xf32_xdl_math_op"] = {HIP_5070, HIP_0, HIP_0 }; m["rocblas_computetype"] = {HIP_5070, HIP_0, HIP_0 }; m["rocblas_compute_type_f32"] = {HIP_5070, HIP_0, HIP_0 }; + + return m; +}(); + +const std::map CUDA_BLAS_TYPE_CHANGED_VER_MAP = [] { + std::map m; + + m["cublasLtMatrixLayoutOpaque_t"] = {CUDA_131}; + m["cublasLtMatmulPreferenceOpaque_t"] = {CUDA_131}; + return m; }(); diff --git a/src/CUDA2HIP_Doc.cpp b/src/CUDA2HIP_Doc.cpp index 26a4de54..aee357fb 100644 --- a/src/CUDA2HIP_Doc.cpp +++ b/src/CUDA2HIP_Doc.cpp @@ -622,6 +622,7 @@ namespace doc { const hipVersionMap &getHipFunctionVersions() const override { return HIP_BLAS_FUNCTION_VER_MAP; } const hipChangedVersionMap &getHipChangedFunctionVersions() const override { return HIP_BLAS_FUNCTION_CHANGED_VER_MAP; } const cudaChangedVersionMap &getCudaChangedFunctionVersions() const override { return CUDA_BLAS_FUNCTION_CHANGED_VER_MAP; } + const cudaChangedVersionMap &getCudaChangedTypeVersions() const override { return CUDA_BLAS_TYPE_CHANGED_VER_MAP; } const versionMap &getTypeVersions() const override { return CUDA_BLAS_TYPE_NAME_VER_MAP; } const hipVersionMap &getHipTypeVersions() const override { return HIP_BLAS_TYPE_NAME_VER_MAP; } const string &getName() const override { return sCUBLAS; }