Skip to content

Commit

Permalink
[HIPIFY][BLAS][6.2.0] cuBLAS support - Step 2 - 64-bit functions
Browse files Browse the repository at this point in the history 
+ Updated synthetic tests, the regenerated `hipify-perl`, and `BLAS` `CUDA2HIP` documentation
  • Loading branch information
@emankov
emankov committed Jun 11, 2024
1 parent 8ff6a66 commit 8ece9bf
Show file tree
Hide file tree
Showing 5 changed files with 102 additions and 48 deletions.
36 changes: 26 additions & 10 deletions bin/hipify-perl
View file
Original file line number Diff line number Diff line change
Expand Up @@ -1444,12 +1444,20 @@ my %experimental_funcs = (
"cudaDriverEntryPointSymbolNotFound" => "6.2.0",
"cudaDriverEntryPointSuccess" => "6.2.0",
"cudaDriverEntryPointQueryResult" => "6.2.0",
"cublasZgemv_v2_64" => "6.2.0",
"cublasZgemv_64" => "6.2.0",
"cublasZgbmv_v2_64" => "6.2.0",
"cublasZgbmv_64" => "6.2.0",
"cublasSgemv_v2_64" => "6.2.0",
"cublasSgemv_64" => "6.2.0",
"cublasSgbmv_v2_64" => "6.2.0",
"cublasSgbmv_64" => "6.2.0",
"cublasDgemv_v2_64" => "6.2.0",
"cublasDgemv_64" => "6.2.0",
"cublasDgbmv_v2_64" => "6.2.0",
"cublasDgbmv_64" => "6.2.0",
"cublasCgemv_v2_64" => "6.2.0",
"cublasCgemv_64" => "6.2.0",
"cublasCgbmv_v2_64" => "6.2.0",
"cublasCgbmv_64" => "6.2.0",
"cuStreamBeginCaptureToGraph" => "6.2.0",
Expand Down Expand Up @@ -1653,13 +1661,21 @@ sub experimentalSubstitutions {
subst("cudaGetDriverEntryPoint", "hipGetProcAddress", "driver_entry_point");
subst("cudaGetFuncBySymbol", "hipGetFuncBySymbol", "driver_interact");
subst("cublasCgbmv_64", "hipblasCgbmv_64", "library");
subst("cublasCgbmv_v2_64", "hipblasCgbmv_64", "library");
subst("cublasCgbmv_v2_64", "hipblasCgbmv_v2_64", "library");
subst("cublasCgemv_64", "hipblasCgemv_64", "library");
subst("cublasCgemv_v2_64", "hipblasCgemv_v2_64", "library");
subst("cublasDgbmv_64", "hipblasDgbmv_64", "library");
subst("cublasDgbmv_v2_64", "hipblasDgbmv_64", "library");
subst("cublasDgemv_64", "hipblasDgemv_64", "library");
subst("cublasDgemv_v2_64", "hipblasDgemv_64", "library");
subst("cublasSgbmv_64", "hipblasSgbmv_64", "library");
subst("cublasSgbmv_v2_64", "hipblasSgbmv_64", "library");
subst("cublasSgemv_64", "hipblasSgemv_64", "library");
subst("cublasSgemv_v2_64", "hipblasSgemv_64", "library");
subst("cublasZgbmv_64", "hipblasZgbmv_64", "library");
subst("cublasZgbmv_v2_64", "hipblasZgbmv_64", "library");
subst("cublasZgbmv_v2_64", "hipblasZgbmv_v2_64", "library");
subst("cublasZgemv_64", "hipblasZgemv_64", "library");
subst("cublasZgemv_v2_64", "hipblasZgemv_v2_64", "library");
subst("curandSetGeneratorOrdering", "hiprandSetGeneratorOrdering", "library");
subst("cusolverDnCreateParams", "hipsolverDnCreateParams", "library");
subst("cusolverDnDestroyParams", "hipsolverDnDestroyParams", "library");
Expand Down Expand Up @@ -11318,8 +11334,6 @@ sub warnHipOnlyUnsupportedFunctions {
"cublasZgeru_64",
"cublasZgerc_v2_64",
"cublasZgerc_64",
"cublasZgemv_v2_64",
"cublasZgemv_64",
"cublasZgemvStridedBatched_64",
"cublasZgemvBatched_64",
"cublasZgemm_v2_64",
Expand Down Expand Up @@ -11386,8 +11400,6 @@ sub warnHipOnlyUnsupportedFunctions {
"cublasShutdown",
"cublasSger_v2_64",
"cublasSger_64",
"cublasSgemv_v2_64",
"cublasSgemv_64",
"cublasSgemvStridedBatched_64",
"cublasSgemvStridedBatched",
"cublasSgemvBatched_64",
Expand Down Expand Up @@ -11533,8 +11545,6 @@ sub warnHipOnlyUnsupportedFunctions {
"cublasDmatinvBatched",
"cublasDger_v2_64",
"cublasDger_64",
"cublasDgemv_v2_64",
"cublasDgemv_64",
"cublasDgemvStridedBatched_64",
"cublasDgemvStridedBatched",
"cublasDgemvBatched_64",
Expand Down Expand Up @@ -11616,8 +11626,6 @@ sub warnHipOnlyUnsupportedFunctions {
"cublasCgeru_64",
"cublasCgerc_v2_64",
"cublasCgerc_64",
"cublasCgemv_v2_64",
"cublasCgemv_64",
"cublasCgemvStridedBatched_64",
"cublasCgemvBatched_64",
"cublasCgemm_v2_64",
Expand Down Expand Up @@ -12013,6 +12021,8 @@ sub warnRocOnlyUnsupportedFunctions {
"cublasZgemm3m",
"cublasZgelsBatched",
"cublasZgeam_64",
"cublasZgbmv_v2_64",
"cublasZgbmv_64",
"cublasZdgmm_64",
"cublasXerbla",
"cublasUint8gemmBias",
Expand Down Expand Up @@ -12086,6 +12096,8 @@ sub warnRocOnlyUnsupportedFunctions {
"cublasSgemmBatched_64",
"cublasSgelsBatched",
"cublasSgeam_64",
"cublasSgbmv_v2_64",
"cublasSgbmv_64",
"cublasSetVector_64",
"cublasSetVectorAsync_64",
"cublasSetSmCountTarget",
Expand Down Expand Up @@ -12252,6 +12264,8 @@ sub warnRocOnlyUnsupportedFunctions {
"cublasDgemmBatched_64",
"cublasDgelsBatched",
"cublasDgeam_64",
"cublasDgbmv_v2_64",
"cublasDgbmv_64",
"cublasDdgmm_64",
"cublasCtrttp",
"cublasCtrsv_v2_64",
Expand Down Expand Up @@ -12345,6 +12359,8 @@ sub warnRocOnlyUnsupportedFunctions {
"cublasCgemm3m",
"cublasCgelsBatched",
"cublasCgeam_64",
"cublasCgbmv_v2_64",
"cublasCgbmv_64",
"cublasCdgmm_64",
"cublasAsumEx_64",
"cublasAsumEx",
Expand Down
20 changes: 10 additions & 10 deletions docs/tables/CUBLAS_API_supported_by_HIP.md
View file
Original file line number Diff line number Diff line change
Expand Up @@ -725,11 +725,11 @@
|`cublasCgbmv`| | | | |`hipblasCgbmv_v2`|6.0.0| | | | |
|`cublasCgbmv_64`|12.0| | | |`hipblasCgbmv_64`|6.2.0| | | |6.2.0|
|`cublasCgbmv_v2`| | | | |`hipblasCgbmv_v2`|6.0.0| | | | |
|`cublasCgbmv_v2_64`|12.0| | | |`hipblasCgbmv_64`|6.2.0| | | |6.2.0|
|`cublasCgbmv_v2_64`|12.0| | | |`hipblasCgbmv_v2_64`|6.2.0| | | |6.2.0|
|`cublasCgemv`| | | | |`hipblasCgemv_v2`|6.0.0| | | | |
|`cublasCgemv_64`|12.0| | | | | | | | | |
|`cublasCgemv_64`|12.0| | | |`hipblasCgemv_64`|6.2.0| | | |6.2.0|
|`cublasCgemv_v2`| | | | |`hipblasCgemv_v2`|6.0.0| | | | |
|`cublasCgemv_v2_64`|12.0| | | | | | | | | |
|`cublasCgemv_v2_64`|12.0| | | |`hipblasCgemv_v2_64`|6.2.0| | | |6.2.0|
|`cublasCgerc`| | | | |`hipblasCgerc_v2`|6.0.0| | | | |
|`cublasCgerc_64`|12.0| | | | | | | | | |
|`cublasCgerc_v2`| | | | |`hipblasCgerc_v2`|6.0.0| | | | |
Expand Down Expand Up @@ -807,9 +807,9 @@
|`cublasDgbmv_v2`| | | | |`hipblasDgbmv`|3.5.0| | | | |
|`cublasDgbmv_v2_64`|12.0| | | |`hipblasDgbmv_64`|6.2.0| | | |6.2.0|
|`cublasDgemv`| | | | |`hipblasDgemv`|1.8.2| | | | |
|`cublasDgemv_64`|12.0| | | | | | | | | |
|`cublasDgemv_64`|12.0| | | |`hipblasDgemv_64`|6.2.0| | | |6.2.0|
|`cublasDgemv_v2`| | | | |`hipblasDgemv`|1.8.2| | | | |
|`cublasDgemv_v2_64`|12.0| | | | | | | | | |
|`cublasDgemv_v2_64`|12.0| | | |`hipblasDgemv_64`|6.2.0| | | |6.2.0|
|`cublasDger`| | | | |`hipblasDger`|1.8.2| | | | |
|`cublasDger_64`|12.0| | | | | | | | | |
|`cublasDger_v2`| | | | |`hipblasDger`|1.8.2| | | | |
Expand Down Expand Up @@ -871,9 +871,9 @@
|`cublasSgbmv_v2`| | | | |`hipblasSgbmv`|3.5.0| | | | |
|`cublasSgbmv_v2_64`|12.0| | | |`hipblasSgbmv_64`|6.2.0| | | |6.2.0|
|`cublasSgemv`| | | | |`hipblasSgemv`|1.8.2| | | | |
|`cublasSgemv_64`|12.0| | | | | | | | | |
|`cublasSgemv_64`|12.0| | | |`hipblasSgemv_64`|6.2.0| | | |6.2.0|
|`cublasSgemv_v2`| | | | |`hipblasSgemv`|1.8.2| | | | |
|`cublasSgemv_v2_64`|12.0| | | | | | | | | |
|`cublasSgemv_v2_64`|12.0| | | |`hipblasSgemv_64`|6.2.0| | | |6.2.0|
|`cublasSger`| | | | |`hipblasSger`|1.8.2| | | | |
|`cublasSger_64`|12.0| | | | | | | | | |
|`cublasSger_v2`| | | | |`hipblasSger`|1.8.2| | | | |
Expand Down Expand Up @@ -933,11 +933,11 @@
|`cublasZgbmv`| | | | |`hipblasZgbmv_v2`|6.0.0| | | | |
|`cublasZgbmv_64`|12.0| | | |`hipblasZgbmv_64`|6.2.0| | | |6.2.0|
|`cublasZgbmv_v2`| | | | |`hipblasZgbmv_v2`|6.0.0| | | | |
|`cublasZgbmv_v2_64`|12.0| | | |`hipblasZgbmv_64`|6.2.0| | | |6.2.0|
|`cublasZgbmv_v2_64`|12.0| | | |`hipblasZgbmv_v2_64`|6.2.0| | | |6.2.0|
|`cublasZgemv`| | | | |`hipblasZgemv_v2`|6.0.0| | | | |
|`cublasZgemv_64`|12.0| | | | | | | | | |
|`cublasZgemv_64`|12.0| | | |`hipblasZgemv_64`|6.2.0| | | |6.2.0|
|`cublasZgemv_v2`| | | | |`hipblasZgemv_v2`|6.0.0| | | | |
|`cublasZgemv_v2_64`|12.0| | | | | | | | | |
|`cublasZgemv_v2_64`|12.0| | | |`hipblasZgemv_v2_64`|6.2.0| | | |6.2.0|
|`cublasZgerc`| | | | |`hipblasZgerc_v2`|6.0.0| | | | |
|`cublasZgerc_64`|12.0| | | | | | | | | |
|`cublasZgerc_v2`| | | | |`hipblasZgerc_v2`|6.0.0| | | | |
Expand Down
20 changes: 10 additions & 10 deletions docs/tables/CUBLAS_API_supported_by_HIP_and_ROC.md
View file
Original file line number Diff line number Diff line change
Expand Up @@ -725,11 +725,11 @@
|`cublasCgbmv`| | | | |`hipblasCgbmv_v2`|6.0.0| | | | |`rocblas_cgbmv`|3.5.0| | | | |
|`cublasCgbmv_64`|12.0| | | |`hipblasCgbmv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasCgbmv_v2`| | | | |`hipblasCgbmv_v2`|6.0.0| | | | |`rocblas_cgbmv`|3.5.0| | | | |
|`cublasCgbmv_v2_64`|12.0| | | |`hipblasCgbmv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasCgbmv_v2_64`|12.0| | | |`hipblasCgbmv_v2_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasCgemv`| | | | |`hipblasCgemv_v2`|6.0.0| | | | |`rocblas_cgemv`|1.5.0| | | | |
|`cublasCgemv_64`|12.0| | | | | | | | | | | | | | | |
|`cublasCgemv_64`|12.0| | | |`hipblasCgemv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasCgemv_v2`| | | | |`hipblasCgemv_v2`|6.0.0| | | | |`rocblas_cgemv`|1.5.0| | | | |
|`cublasCgemv_v2_64`|12.0| | | | | | | | | | | | | | | |
|`cublasCgemv_v2_64`|12.0| | | |`hipblasCgemv_v2_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasCgerc`| | | | |`hipblasCgerc_v2`|6.0.0| | | | |`rocblas_cgerc`|3.5.0| | | | |
|`cublasCgerc_64`|12.0| | | | | | | | | | | | | | | |
|`cublasCgerc_v2`| | | | |`hipblasCgerc_v2`|6.0.0| | | | |`rocblas_cgerc`|3.5.0| | | | |
Expand Down Expand Up @@ -807,9 +807,9 @@
|`cublasDgbmv_v2`| | | | |`hipblasDgbmv`|3.5.0| | | | |`rocblas_dgbmv`|3.5.0| | | | |
|`cublasDgbmv_v2_64`|12.0| | | |`hipblasDgbmv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasDgemv`| | | | |`hipblasDgemv`|1.8.2| | | | |`rocblas_dgemv`|1.5.0| | | | |
|`cublasDgemv_64`|12.0| | | | | | | | | | | | | | | |
|`cublasDgemv_64`|12.0| | | |`hipblasDgemv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasDgemv_v2`| | | | |`hipblasDgemv`|1.8.2| | | | |`rocblas_dgemv`|1.5.0| | | | |
|`cublasDgemv_v2_64`|12.0| | | | | | | | | | | | | | | |
|`cublasDgemv_v2_64`|12.0| | | |`hipblasDgemv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasDger`| | | | |`hipblasDger`|1.8.2| | | | |`rocblas_dger`|1.5.0| | | | |
|`cublasDger_64`|12.0| | | | | | | | | | | | | | | |
|`cublasDger_v2`| | | | |`hipblasDger`|1.8.2| | | | |`rocblas_dger`|1.5.0| | | | |
Expand Down Expand Up @@ -871,9 +871,9 @@
|`cublasSgbmv_v2`| | | | |`hipblasSgbmv`|3.5.0| | | | |`rocblas_sgbmv`|3.5.0| | | | |
|`cublasSgbmv_v2_64`|12.0| | | |`hipblasSgbmv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasSgemv`| | | | |`hipblasSgemv`|1.8.2| | | | |`rocblas_sgemv`|1.5.0| | | | |
|`cublasSgemv_64`|12.0| | | | | | | | | | | | | | | |
|`cublasSgemv_64`|12.0| | | |`hipblasSgemv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasSgemv_v2`| | | | |`hipblasSgemv`|1.8.2| | | | |`rocblas_sgemv`|1.5.0| | | | |
|`cublasSgemv_v2_64`|12.0| | | | | | | | | | | | | | | |
|`cublasSgemv_v2_64`|12.0| | | |`hipblasSgemv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasSger`| | | | |`hipblasSger`|1.8.2| | | | |`rocblas_sger`|1.5.0| | | | |
|`cublasSger_64`|12.0| | | | | | | | | | | | | | | |
|`cublasSger_v2`| | | | |`hipblasSger`|1.8.2| | | | |`rocblas_sger`|1.5.0| | | | |
Expand Down Expand Up @@ -933,11 +933,11 @@
|`cublasZgbmv`| | | | |`hipblasZgbmv_v2`|6.0.0| | | | |`rocblas_zgbmv`|3.5.0| | | | |
|`cublasZgbmv_64`|12.0| | | |`hipblasZgbmv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasZgbmv_v2`| | | | |`hipblasZgbmv_v2`|6.0.0| | | | |`rocblas_zgbmv`|3.5.0| | | | |
|`cublasZgbmv_v2_64`|12.0| | | |`hipblasZgbmv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasZgbmv_v2_64`|12.0| | | |`hipblasZgbmv_v2_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasZgemv`| | | | |`hipblasZgemv_v2`|6.0.0| | | | |`rocblas_zgemv`|1.5.0| | | | |
|`cublasZgemv_64`|12.0| | | | | | | | | | | | | | | |
|`cublasZgemv_64`|12.0| | | |`hipblasZgemv_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasZgemv_v2`| | | | |`hipblasZgemv_v2`|6.0.0| | | | |`rocblas_zgemv`|1.5.0| | | | |
|`cublasZgemv_v2_64`|12.0| | | | | | | | | | | | | | | |
|`cublasZgemv_v2_64`|12.0| | | |`hipblasZgemv_v2_64`|6.2.0| | | |6.2.0| | | | | | |
|`cublasZgerc`| | | | |`hipblasZgerc_v2`|6.0.0| | | | |`rocblas_zgerc`|3.5.0| | | | |
|`cublasZgerc_64`|12.0| | | | | | | | | | | | | | | |
|`cublasZgerc_v2`| | | | |`hipblasZgerc_v2`|6.0.0| | | | |`rocblas_zgerc`|3.5.0| | | | |
Expand Down
Loading

0 comments on commit 8ece9bf

Please sign in to comment.