[HIPIFY] Sync with CUDA 12.5.0 - Step 5 - BLAS API

+ Updated the regenerated `hipify-perl` and `BLAS` `CUDA2HIP` docs accordingly
emankov · Jun 22, 2024 · 2866564 · 2866564
1 parent 636e038
commit 2866564
Show file tree

Hide file tree

Showing 5 changed files with 14 additions and 0 deletions.
diff --git a/bin/hipify-perl b/bin/hipify-perl
@@ -11535,6 +11535,8 @@ sub warnHipOnlyUnsupportedFunctions {
         "cublasGetError",
         "cublasGetCudartVersion",
         "cublasGemmStridedBatchedEx_64",
+        "cublasGemmGroupedBatchedEx_64",
+        "cublasGemmGroupedBatchedEx",
         "cublasGemmEx_64",
         "cublasGemmBatchedEx_64",
         "cublasFree",
@@ -12235,6 +12237,8 @@ sub warnRocOnlyUnsupportedFunctions {
         "cublasGetError",
         "cublasGetCudartVersion",
         "cublasGemmStridedBatchedEx_64",
+        "cublasGemmGroupedBatchedEx_64",
+        "cublasGemmGroupedBatchedEx",
         "cublasGemmEx_64",
         "cublasGemmBatchedEx_64",
         "cublasFree",

diff --git a/docs/tables/CUBLAS_API_supported_by_HIP.md b/docs/tables/CUBLAS_API_supported_by_HIP.md
@@ -1107,6 +1107,8 @@
 |`cublasDtrsm_64`|12.0| | | | | | | | | |
 |`cublasDtrsm_v2`| | | | |`hipblasDtrsm`|1.8.2| | | | |
 |`cublasDtrsm_v2_64`|12.0| | | | | | | | | |
+|`cublasGemmGroupedBatchedEx`|12.5| | | | | | | | | |
+|`cublasGemmGroupedBatchedEx_64`|12.5| | | | | | | | | |
 |`cublasHSHgemvBatched`|11.6| | | | | | | | | |
 |`cublasHSHgemvBatched_64`|12.0| | | | | | | | | |
 |`cublasHSHgemvStridedBatched`|11.6| | | | | | | | | |

diff --git a/docs/tables/CUBLAS_API_supported_by_HIP_and_ROC.md b/docs/tables/CUBLAS_API_supported_by_HIP_and_ROC.md
@@ -1107,6 +1107,8 @@
 |`cublasDtrsm_64`|12.0| | | | | | | | | | | | | | | |
 |`cublasDtrsm_v2`| | | | |`hipblasDtrsm`|1.8.2| | | | |`rocblas_dtrsm`|1.5.0| | | | |
 |`cublasDtrsm_v2_64`|12.0| | | | | | | | | | | | | | | |
+|`cublasGemmGroupedBatchedEx`|12.5| | | | | | | | | | | | | | | |
+|`cublasGemmGroupedBatchedEx_64`|12.5| | | | | | | | | | | | | | | |
 |`cublasHSHgemvBatched`|11.6| | | | | | | | | |`rocblas_hshgemv_batched`|6.0.0| | | | |
 |`cublasHSHgemvBatched_64`|12.0| | | | | | | | | | | | | | | |
 |`cublasHSHgemvStridedBatched`|11.6| | | | | | | | | |`rocblas_hshgemv_strided_batched`|6.0.0| | | | |

diff --git a/docs/tables/CUBLAS_API_supported_by_ROC.md b/docs/tables/CUBLAS_API_supported_by_ROC.md
@@ -1107,6 +1107,8 @@
 |`cublasDtrsm_64`|12.0| | | | | | | | | |
 |`cublasDtrsm_v2`| | | | |`rocblas_dtrsm`|1.5.0| | | | |
 |`cublasDtrsm_v2_64`|12.0| | | | | | | | | |
+|`cublasGemmGroupedBatchedEx`|12.5| | | | | | | | | |
+|`cublasGemmGroupedBatchedEx_64`|12.5| | | | | | | | | |
 |`cublasHSHgemvBatched`|11.6| | | |`rocblas_hshgemv_batched`|6.0.0| | | | |
 |`cublasHSHgemvBatched_64`|12.0| | | | | | | | | |
 |`cublasHSHgemvStridedBatched`|11.6| | | |`rocblas_hshgemv_strided_batched`|6.0.0| | | | |

diff --git a/src/CUDA2HIP_BLAS_API_functions.cpp b/src/CUDA2HIP_BLAS_API_functions.cpp
@@ -438,6 +438,8 @@ const std::map<llvm::StringRef, hipCounter> CUDA_BLAS_FUNCTION_MAP {
   {"cublasZgemmStridedBatched_64",                         {"hipblasZgemmStridedBatched_64",                             "",                                                   CONV_LIB_FUNC, API_BLAS, SEC::BLAS_LEVEL_3, UNSUPPORTED}},
   {"cublasHgemmStridedBatched",                            {"hipblasHgemmStridedBatched",                                "rocblas_hgemm_strided_batched",                      CONV_LIB_FUNC, API_BLAS, SEC::BLAS_LEVEL_3}},
   {"cublasHgemmStridedBatched_64",                         {"hipblasHgemmStridedBatched_64",                             "",                                                   CONV_LIB_FUNC, API_BLAS, SEC::BLAS_LEVEL_3, UNSUPPORTED}},
+  {"cublasGemmGroupedBatchedEx",                           {"hipblasGemmGroupedBatchedEx",                               "",                                                   CONV_LIB_FUNC, API_BLAS, SEC::BLAS_LEVEL_3, UNSUPPORTED}},
+  {"cublasGemmGroupedBatchedEx_64",                        {"hipblasGemmGroupedBatchedEx_64",                            "",                                                   CONV_LIB_FUNC, API_BLAS, SEC::BLAS_LEVEL_3, UNSUPPORTED}},
 
   // BATCH GEMV
   {"cublasSgemvBatched",                                   {"hipblasSgemvBatched",                                       "",                                                   CONV_LIB_FUNC, API_BLAS, SEC::BLAS_LEVEL_3, UNSUPPORTED}},
@@ -1623,6 +1625,8 @@ const std::map<llvm::StringRef, cudaAPIversions> CUDA_BLAS_FUNCTION_VER_MAP {
   {"cublasLtLoggerSetLevel",                               {CUDA_110, CUDA_0,   CUDA_0   }}, // A: CUDA_VERSION 11003, CUBLAS_VERSION 11200, CUBLAS_VER_MAJOR 11 CUBLAS_VER_MINOR 2
   {"cublasLtLoggerSetMask",                                {CUDA_110, CUDA_0,   CUDA_0   }}, // A: CUDA_VERSION 11003, CUBLAS_VERSION 11200, CUBLAS_VER_MAJOR 11 CUBLAS_VER_MINOR 2
   {"cublasLtLoggerForceDisable",                           {CUDA_110, CUDA_0,   CUDA_0   }}, // A: CUDA_VERSION 11003, CUBLAS_VERSION 11200, CUBLAS_VER_MAJOR 11 CUBLAS_VER_MINOR 2
+  {"cublasGemmGroupedBatchedEx",                           {CUDA_125, CUDA_0,   CUDA_0   }},
+  {"cublasGemmGroupedBatchedEx_64",                        {CUDA_125, CUDA_0,   CUDA_0   }},
 };
 
 const std::map<llvm::StringRef, hipAPIversions> HIP_BLAS_FUNCTION_VER_MAP {