Merge pull request #1141 from emankov/HIPIFY

[HIPIFY][#675][#677][SOLVER][feature] `cuSOLVER` support - Step 9 - Data types (common)
ROCm · Nov 15, 2023 · e719710 · e719710
2 parents a5b5de8 + e10fa58
commit e719710
Show file tree

Hide file tree

Showing 5 changed files with 144 additions and 1 deletion.
diff --git a/bin/hipify-perl b/bin/hipify-perl
@@ -7053,6 +7053,8 @@ sub warnUnsupportedFunctions {
         "cusparseCbsric02_bufferSizeExt",
         "cusparseBsrSetStridedBatch",
         "cusparseAlgMode_t",
+        "cusolverStorevMode_t",
+        "cusolverPrecType_t",
         "cusolverNorm_t",
         "cusolverIRSRefinement_t",
         "cusolverDnXgetrs",
@@ -7061,6 +7063,7 @@ sub warnUnsupportedFunctions {
         "cusolverDnSetAdvOptions",
         "cusolverDnCreateParams",
         "cusolverDirectMode_t",
+        "cusolverAlgMode_t",
         "curand_mtgp32_specific",
         "curand_mtgp32_single_specific",
         "curand_mtgp32_single",
@@ -8674,6 +8677,14 @@ sub warnUnsupportedFunctions {
         "CUSOLVER_STATUS_IRS_INFOS_NOT_DESTROYED",
         "CUSOLVER_STATUS_INVALID_WORKSPACE",
         "CUSOLVER_STATUS_INVALID_LICENSE",
+        "CUSOLVER_R_TF32",
+        "CUSOLVER_R_AP",
+        "CUSOLVER_R_8U",
+        "CUSOLVER_R_8I",
+        "CUSOLVER_R_64F",
+        "CUSOLVER_R_32F",
+        "CUSOLVER_R_16F",
+        "CUSOLVER_R_16BF",
         "CUSOLVER_PREC_SS",
         "CUSOLVER_PREC_SHT",
         "CUSOLVER_PREC_DD",
@@ -8688,6 +8699,17 @@ sub warnUnsupportedFunctions {
         "CUSOLVER_IRS_REFINE_CLASSICAL",
         "CUSOLVER_INF_NORM",
         "CUSOLVER_FRO_NORM",
+        "CUSOLVER_C_TF32",
+        "CUSOLVER_C_AP",
+        "CUSOLVER_C_8U",
+        "CUSOLVER_C_8I",
+        "CUSOLVER_C_64F",
+        "CUSOLVER_C_32F",
+        "CUSOLVER_C_16F",
+        "CUSOLVER_C_16BF",
+        "CUSOLVER_ALG_2",
+        "CUSOLVER_ALG_1",
+        "CUSOLVER_ALG_0",
         "CURAND_REJECTION",
         "CURAND_POISSON",
         "CURAND_ORDERING_QUASI_DEFAULT",
@@ -9452,6 +9474,8 @@ sub warnUnsupportedFunctions {
         "CUB_CAT_",
         "CUB_CAT",
         "CUB_ALIGN",
+        "CUBLAS_STOREV_ROWWISE",
+        "CUBLAS_STOREV_COLUMNWISE",
         "CUBLAS_DIRECT_FORWARD",
         "CUBLAS_DIRECT_BACKWARD"
     )

diff --git a/docs/tables/CUSOLVER_API_supported_by_HIP.md b/docs/tables/CUSOLVER_API_supported_by_HIP.md
@@ -6,6 +6,19 @@
 |:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
 |`CUBLAS_DIRECT_BACKWARD`|11.0| | | | | | | | | |
 |`CUBLAS_DIRECT_FORWARD`|11.0| | | | | | | | | |
+|`CUBLAS_STOREV_COLUMNWISE`|11.0| | | | | | | | | |
+|`CUBLAS_STOREV_ROWWISE`|11.0| | | | | | | | | |
+|`CUSOLVER_ALG_0`|11.0| | | | | | | | | |
+|`CUSOLVER_ALG_1`|11.0| | | | | | | | | |
+|`CUSOLVER_ALG_2`|11.5| | | | | | | | | |
+|`CUSOLVER_C_16BF`|11.0| | | | | | | | | |
+|`CUSOLVER_C_16F`|11.0| | | | | | | | | |
+|`CUSOLVER_C_32F`|11.0| | | | | | | | | |
+|`CUSOLVER_C_64F`|11.0| | | | | | | | | |
+|`CUSOLVER_C_8I`|11.0| | | | | | | | | |
+|`CUSOLVER_C_8U`|11.0| | | | | | | | | |
+|`CUSOLVER_C_AP`|11.0| | | | | | | | | |
+|`CUSOLVER_C_TF32`|11.0| | | | | | | | | |
 |`CUSOLVER_EIG_MODE_NOVECTOR`|8.0| | | |`HIPSOLVER_EIG_MODE_NOVECTOR`|4.5.0| | | |6.1.0|
 |`CUSOLVER_EIG_MODE_VECTOR`|8.0| | | |`HIPSOLVER_EIG_MODE_VECTOR`|4.5.0| | | |6.1.0|
 |`CUSOLVER_EIG_RANGE_ALL`|10.1| | | |`HIPSOLVER_EIG_RANGE_ALL`|5.3.0| | | |6.1.0|
@@ -28,6 +41,14 @@
 |`CUSOLVER_PREC_DD`|10.2| | | | | | | | | |
 |`CUSOLVER_PREC_SHT`|10.2| | | | | | | | | |
 |`CUSOLVER_PREC_SS`|10.2| | | | | | | | | |
+|`CUSOLVER_R_16BF`|11.0| | | | | | | | | |
+|`CUSOLVER_R_16F`|11.0| | | | | | | | | |
+|`CUSOLVER_R_32F`|11.0| | | | | | | | | |
+|`CUSOLVER_R_64F`|11.0| | | | | | | | | |
+|`CUSOLVER_R_8I`|11.0| | | | | | | | | |
+|`CUSOLVER_R_8U`|11.0| | | | | | | | | |
+|`CUSOLVER_R_AP`|11.0| | | | | | | | | |
+|`CUSOLVER_R_TF32`|11.0| | | | | | | | | |
 |`CUSOLVER_STATUS_ALLOC_FAILED`| | | | |`HIPSOLVER_STATUS_ALLOC_FAILED`|4.5.0| | | |6.1.0|
 |`CUSOLVER_STATUS_ARCH_MISMATCH`| | | | |`HIPSOLVER_STATUS_ARCH_MISMATCH`|4.5.0| | | |6.1.0|
 |`CUSOLVER_STATUS_EXECUTION_FAILED`| | | | |`HIPSOLVER_STATUS_EXECUTION_FAILED`|4.5.0| | | |6.1.0|
@@ -53,14 +74,17 @@
 |`CUSOLVER_STATUS_NOT_SUPPORTED`| | | | |`HIPSOLVER_STATUS_NOT_SUPPORTED`|4.5.0| | | |6.1.0|
 |`CUSOLVER_STATUS_SUCCESS`| | | | |`HIPSOLVER_STATUS_SUCCESS`|4.5.0| | | |6.1.0|
 |`CUSOLVER_STATUS_ZERO_PIVOT`| | | | |`HIPSOLVER_STATUS_ZERO_PIVOT`| | | | | |
+|`cusolverAlgMode_t`|11.0| | | | | | | | | |
 |`cusolverDirectMode_t`|11.0| | | | | | | | | |
 |`cusolverDnHandle_t`| | | | |`hipsolverHandle_t`|4.5.0| | | |6.1.0|
 |`cusolverEigMode_t`|8.0| | | |`hipsolverEigMode_t`|4.5.0| | | |6.1.0|
 |`cusolverEigRange_t`|10.1| | | |`hipsolverEigRange_t`|5.3.0| | | |6.1.0|
 |`cusolverEigType_t`|8.0| | | |`hipsolverEigType_t`|4.5.0| | | |6.1.0|
 |`cusolverIRSRefinement_t`|10.2| | | | | | | | | |
 |`cusolverNorm_t`|10.2| | | | | | | | | |
+|`cusolverPrecType_t`|11.0| | | | | | | | | |
 |`cusolverStatus_t`| | | | |`hipsolverStatus_t`|4.5.0| | | |6.1.0|
+|`cusolverStorevMode_t`|11.0| | | | | | | | | |
 
 ## **2. CUSOLVER Function Reference**
 

diff --git a/docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md b/docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md
@@ -6,6 +6,19 @@
 |:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
 |`CUBLAS_DIRECT_BACKWARD`|11.0| | | | | | | | | | | | | | | |
 |`CUBLAS_DIRECT_FORWARD`|11.0| | | | | | | | | | | | | | | |
+|`CUBLAS_STOREV_COLUMNWISE`|11.0| | | | | | | | | | | | | | | |
+|`CUBLAS_STOREV_ROWWISE`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_ALG_0`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_ALG_1`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_ALG_2`|11.5| | | | | | | | | | | | | | | |
+|`CUSOLVER_C_16BF`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_C_16F`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_C_32F`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_C_64F`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_C_8I`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_C_8U`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_C_AP`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_C_TF32`|11.0| | | | | | | | | | | | | | | |
 |`CUSOLVER_EIG_MODE_NOVECTOR`|8.0| | | |`HIPSOLVER_EIG_MODE_NOVECTOR`|4.5.0| | | |6.1.0|`rocblas_evect_none`|4.1.0| | | |6.1.0|
 |`CUSOLVER_EIG_MODE_VECTOR`|8.0| | | |`HIPSOLVER_EIG_MODE_VECTOR`|4.5.0| | | |6.1.0|`rocblas_evect_original`|4.1.0| | | |6.1.0|
 |`CUSOLVER_EIG_RANGE_ALL`|10.1| | | |`HIPSOLVER_EIG_RANGE_ALL`|5.3.0| | | |6.1.0|`rocblas_erange_all`|5.2.0| | | |6.1.0|
@@ -28,6 +41,14 @@
 |`CUSOLVER_PREC_DD`|10.2| | | | | | | | | | | | | | | |
 |`CUSOLVER_PREC_SHT`|10.2| | | | | | | | | | | | | | | |
 |`CUSOLVER_PREC_SS`|10.2| | | | | | | | | | | | | | | |
+|`CUSOLVER_R_16BF`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_R_16F`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_R_32F`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_R_64F`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_R_8I`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_R_8U`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_R_AP`|11.0| | | | | | | | | | | | | | | |
+|`CUSOLVER_R_TF32`|11.0| | | | | | | | | | | | | | | |
 |`CUSOLVER_STATUS_ALLOC_FAILED`| | | | |`HIPSOLVER_STATUS_ALLOC_FAILED`|4.5.0| | | |6.1.0|`rocblas_status_memory_error`|5.6.0| | | |6.1.0|
 |`CUSOLVER_STATUS_ARCH_MISMATCH`| | | | |`HIPSOLVER_STATUS_ARCH_MISMATCH`|4.5.0| | | |6.1.0|`rocblas_status_arch_mismatch`|5.7.0| | | |6.1.0|
 |`CUSOLVER_STATUS_EXECUTION_FAILED`| | | | |`HIPSOLVER_STATUS_EXECUTION_FAILED`|4.5.0| | | |6.1.0|`rocblas_status_not_implemented`|1.5.0| | | |6.1.0|
@@ -53,14 +74,17 @@
 |`CUSOLVER_STATUS_NOT_SUPPORTED`| | | | |`HIPSOLVER_STATUS_NOT_SUPPORTED`|4.5.0| | | |6.1.0|`rocblas_status_not_implemented`|1.5.0| | | |6.1.0|
 |`CUSOLVER_STATUS_SUCCESS`| | | | |`HIPSOLVER_STATUS_SUCCESS`|4.5.0| | | |6.1.0|`rocblas_status_success`|3.0.0| | | |6.1.0|
 |`CUSOLVER_STATUS_ZERO_PIVOT`| | | | |`HIPSOLVER_STATUS_ZERO_PIVOT`| | | | | |`rocblas_status_not_implemented`|1.5.0| | | |6.1.0|
+|`cusolverAlgMode_t`|11.0| | | | | | | | | | | | | | | |
 |`cusolverDirectMode_t`|11.0| | | | | | | | | | | | | | | |
 |`cusolverDnHandle_t`| | | | |`hipsolverHandle_t`|4.5.0| | | |6.1.0|`rocblas_handle`|1.5.0| | | |6.1.0|
 |`cusolverEigMode_t`|8.0| | | |`hipsolverEigMode_t`|4.5.0| | | |6.1.0|`rocblas_evect`|4.1.0| | | |6.1.0|
 |`cusolverEigRange_t`|10.1| | | |`hipsolverEigRange_t`|5.3.0| | | |6.1.0|`rocblas_erange`|5.2.0| | | |6.1.0|
 |`cusolverEigType_t`|8.0| | | |`hipsolverEigType_t`|4.5.0| | | |6.1.0|`rocblas_eform`|4.2.0| | | |6.1.0|
 |`cusolverIRSRefinement_t`|10.2| | | | | | | | | | | | | | | |
 |`cusolverNorm_t`|10.2| | | | | | | | | | | | | | | |
+|`cusolverPrecType_t`|11.0| | | | | | | | | | | | | | | |
 |`cusolverStatus_t`| | | | |`hipsolverStatus_t`|4.5.0| | | |6.1.0|`rocblas_status`|3.0.0| | | |6.1.0|
+|`cusolverStorevMode_t`|11.0| | | | | | | | | | | | | | | |
 
 ## **2. CUSOLVER Function Reference**
 

diff --git a/docs/tables/CUSOLVER_API_supported_by_ROC.md b/docs/tables/CUSOLVER_API_supported_by_ROC.md
@@ -6,6 +6,19 @@
 |:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|
 |`CUBLAS_DIRECT_BACKWARD`|11.0| | | | | | | | | |
 |`CUBLAS_DIRECT_FORWARD`|11.0| | | | | | | | | |
+|`CUBLAS_STOREV_COLUMNWISE`|11.0| | | | | | | | | |
+|`CUBLAS_STOREV_ROWWISE`|11.0| | | | | | | | | |
+|`CUSOLVER_ALG_0`|11.0| | | | | | | | | |
+|`CUSOLVER_ALG_1`|11.0| | | | | | | | | |
+|`CUSOLVER_ALG_2`|11.5| | | | | | | | | |
+|`CUSOLVER_C_16BF`|11.0| | | | | | | | | |
+|`CUSOLVER_C_16F`|11.0| | | | | | | | | |
+|`CUSOLVER_C_32F`|11.0| | | | | | | | | |
+|`CUSOLVER_C_64F`|11.0| | | | | | | | | |
+|`CUSOLVER_C_8I`|11.0| | | | | | | | | |
+|`CUSOLVER_C_8U`|11.0| | | | | | | | | |
+|`CUSOLVER_C_AP`|11.0| | | | | | | | | |
+|`CUSOLVER_C_TF32`|11.0| | | | | | | | | |
 |`CUSOLVER_EIG_MODE_NOVECTOR`|8.0| | | |`rocblas_evect_none`|4.1.0| | | |6.1.0|
 |`CUSOLVER_EIG_MODE_VECTOR`|8.0| | | |`rocblas_evect_original`|4.1.0| | | |6.1.0|
 |`CUSOLVER_EIG_RANGE_ALL`|10.1| | | |`rocblas_erange_all`|5.2.0| | | |6.1.0|
@@ -28,6 +41,14 @@
 |`CUSOLVER_PREC_DD`|10.2| | | | | | | | | |
 |`CUSOLVER_PREC_SHT`|10.2| | | | | | | | | |
 |`CUSOLVER_PREC_SS`|10.2| | | | | | | | | |
+|`CUSOLVER_R_16BF`|11.0| | | | | | | | | |
+|`CUSOLVER_R_16F`|11.0| | | | | | | | | |
+|`CUSOLVER_R_32F`|11.0| | | | | | | | | |
+|`CUSOLVER_R_64F`|11.0| | | | | | | | | |
+|`CUSOLVER_R_8I`|11.0| | | | | | | | | |
+|`CUSOLVER_R_8U`|11.0| | | | | | | | | |
+|`CUSOLVER_R_AP`|11.0| | | | | | | | | |
+|`CUSOLVER_R_TF32`|11.0| | | | | | | | | |
 |`CUSOLVER_STATUS_ALLOC_FAILED`| | | | |`rocblas_status_memory_error`|5.6.0| | | |6.1.0|
 |`CUSOLVER_STATUS_ARCH_MISMATCH`| | | | |`rocblas_status_arch_mismatch`|5.7.0| | | |6.1.0|
 |`CUSOLVER_STATUS_EXECUTION_FAILED`| | | | |`rocblas_status_not_implemented`|1.5.0| | | |6.1.0|
@@ -53,14 +74,17 @@
 |`CUSOLVER_STATUS_NOT_SUPPORTED`| | | | |`rocblas_status_not_implemented`|1.5.0| | | |6.1.0|
 |`CUSOLVER_STATUS_SUCCESS`| | | | |`rocblas_status_success`|3.0.0| | | |6.1.0|
 |`CUSOLVER_STATUS_ZERO_PIVOT`| | | | |`rocblas_status_not_implemented`|1.5.0| | | |6.1.0|
+|`cusolverAlgMode_t`|11.0| | | | | | | | | |
 |`cusolverDirectMode_t`|11.0| | | | | | | | | |
 |`cusolverDnHandle_t`| | | | |`rocblas_handle`|1.5.0| | | |6.1.0|
 |`cusolverEigMode_t`|8.0| | | |`rocblas_evect`|4.1.0| | | |6.1.0|
 |`cusolverEigRange_t`|10.1| | | |`rocblas_erange`|5.2.0| | | |6.1.0|
 |`cusolverEigType_t`|8.0| | | |`rocblas_eform`|4.2.0| | | |6.1.0|
 |`cusolverIRSRefinement_t`|10.2| | | | | | | | | |
 |`cusolverNorm_t`|10.2| | | | | | | | | |
+|`cusolverPrecType_t`|11.0| | | | | | | | | |
 |`cusolverStatus_t`| | | | |`rocblas_status`|3.0.0| | | |6.1.0|
+|`cusolverStorevMode_t`|11.0| | | | | | | | | |
 
 ## **2. CUSOLVER Function Reference**