[HIPIFY][ROCm#675][ROCm#677][SOLVER][feature] cuSOLVER support - St…

…ep 51 - Data Types (RF) + Updated `SOLVER` synthetic tests, the regenerated `hipify-perl`, and `SOLVER` `CUDA2HIP` documentation
emankov · Dec 20, 2023 · 0bfc264 · 0bfc264
1 parent 7e80296
commit 0bfc264
Show file tree

Hide file tree

Showing 6 changed files with 197 additions and 0 deletions.
diff --git a/bin/hipify-perl b/bin/hipify-perl
@@ -5185,6 +5185,13 @@ sub simpleSubstitutions {
     subst("curandState_t", "hiprandState_t", "type");
     subst("curandStatus", "hiprandStatus_t", "type");
     subst("curandStatus_t", "hiprandStatus_t", "type");
+    subst("cusolverRfFactorization_t", "hipsolverRfFactorization_t", "type");
+    subst("cusolverRfHandle_t", "hipsolverRfHandle_t", "type");
+    subst("cusolverRfMatrixFormat_t", "hipsolverRfMatrixFormat_t", "type");
+    subst("cusolverRfNumericBoostReport_t", "hipsolverRfNumericBoostReport_t", "type");
+    subst("cusolverRfResetValuesFastMode_t", "hipsolverRfResetValuesFastMode_t", "type");
+    subst("cusolverRfTriangularSolve_t", "hipsolverRfTriangularSolve_t", "type");
+    subst("cusolverRfUnitDiagonal_t", "hipsolverRfUnitDiagonal_t", "type");
     subst("cusparseAction_t", "hipsparseAction_t", "type");
     subst("cusparseColorInfo_t", "hipsparseColorInfo_t", "type");
     subst("cusparseConstDnMatDescr_t", "hipsparseConstDnMatDescr_t", "type");
@@ -5535,6 +5542,22 @@ sub simpleSubstitutions {
     subst("CURAND_STATUS_SUCCESS", "HIPRAND_STATUS_SUCCESS", "numeric_literal");
     subst("CURAND_STATUS_TYPE_ERROR", "HIPRAND_STATUS_TYPE_ERROR", "numeric_literal");
     subst("CURAND_STATUS_VERSION_MISMATCH", "HIPRAND_STATUS_VERSION_MISMATCH", "numeric_literal");
+    subst("CUSOLVERRF_FACTORIZATION_ALG0", "HIPSOLVERRF_FACTORIZATION_ALG0", "numeric_literal");
+    subst("CUSOLVERRF_FACTORIZATION_ALG1", "HIPSOLVERRF_FACTORIZATION_ALG1", "numeric_literal");
+    subst("CUSOLVERRF_FACTORIZATION_ALG2", "HIPSOLVERRF_FACTORIZATION_ALG2", "numeric_literal");
+    subst("CUSOLVERRF_MATRIX_FORMAT_CSC", "HIPSOLVERRF_MATRIX_FORMAT_CSC", "numeric_literal");
+    subst("CUSOLVERRF_MATRIX_FORMAT_CSR", "HIPSOLVERRF_MATRIX_FORMAT_CSR", "numeric_literal");
+    subst("CUSOLVERRF_NUMERIC_BOOST_NOT_USED", "HIPSOLVERRF_NUMERIC_BOOST_NOT_USED", "numeric_literal");
+    subst("CUSOLVERRF_NUMERIC_BOOST_USED", "HIPSOLVERRF_NUMERIC_BOOST_USED", "numeric_literal");
+    subst("CUSOLVERRF_RESET_VALUES_FAST_MODE_OFF", "HIPSOLVERRF_RESET_VALUES_FAST_MODE_OFF", "numeric_literal");
+    subst("CUSOLVERRF_RESET_VALUES_FAST_MODE_ON", "HIPSOLVERRF_RESET_VALUES_FAST_MODE_ON", "numeric_literal");
+    subst("CUSOLVERRF_TRIANGULAR_SOLVE_ALG1", "HIPSOLVERRF_TRIANGULAR_SOLVE_ALG1", "numeric_literal");
+    subst("CUSOLVERRF_TRIANGULAR_SOLVE_ALG2", "HIPSOLVERRF_TRIANGULAR_SOLVE_ALG2", "numeric_literal");
+    subst("CUSOLVERRF_TRIANGULAR_SOLVE_ALG3", "HIPSOLVERRF_TRIANGULAR_SOLVE_ALG3", "numeric_literal");
+    subst("CUSOLVERRF_UNIT_DIAGONAL_ASSUMED_L", "HIPSOLVERRF_UNIT_DIAGONAL_ASSUMED_L", "numeric_literal");
+    subst("CUSOLVERRF_UNIT_DIAGONAL_ASSUMED_U", "HIPSOLVERRF_UNIT_DIAGONAL_ASSUMED_U", "numeric_literal");
+    subst("CUSOLVERRF_UNIT_DIAGONAL_STORED_L", "HIPSOLVERRF_UNIT_DIAGONAL_STORED_L", "numeric_literal");
+    subst("CUSOLVERRF_UNIT_DIAGONAL_STORED_U", "HIPSOLVERRF_UNIT_DIAGONAL_STORED_U", "numeric_literal");
     subst("CUSOLVER_STATUS_IRS_INTERNAL_ERROR", "HIPSOLVER_STATUS_INTERNAL_ERROR", "numeric_literal");
     subst("CUSOLVER_STATUS_IRS_NOT_SUPPORTED", "HIPSOLVER_STATUS_NOT_SUPPORTED", "numeric_literal");
     subst("CUSOLVER_STATUS_IRS_PARAMS_INVALID", "HIPSOLVER_STATUS_INVALID_VALUE", "numeric_literal");
@@ -7585,6 +7608,7 @@ sub warnUnsupportedFunctions {
         "cusparseBsrSetStridedBatch",
         "cusparseAlgMode_t",
         "cusolverStorevMode_t",
+        "cusolverRfCommon",
         "cusolverPrecType_t",
         "cusolverNorm_t",
         "cusolverMgSyevd_bufferSize",

diff --git a/docs/tables/CUSOLVER_API_supported_by_HIP.md b/docs/tables/CUSOLVER_API_supported_by_HIP.md
@@ -12,6 +12,22 @@
 |`CUDALIBMG_GRID_MAPPING_ROW_MAJOR`|10.1| | | | | | | | | |
 |`CUSOLVERDN_GETRF`|11.0| | | | | | | | | |
 |`CUSOLVERDN_POTRF`|11.5| | | | | | | | | |
+|`CUSOLVERRF_FACTORIZATION_ALG0`| | | | |`HIPSOLVERRF_FACTORIZATION_ALG0`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_FACTORIZATION_ALG1`| | | | |`HIPSOLVERRF_FACTORIZATION_ALG1`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_FACTORIZATION_ALG2`| | | | |`HIPSOLVERRF_FACTORIZATION_ALG2`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_MATRIX_FORMAT_CSC`| | | | |`HIPSOLVERRF_MATRIX_FORMAT_CSC`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_MATRIX_FORMAT_CSR`| | | | |`HIPSOLVERRF_MATRIX_FORMAT_CSR`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_NUMERIC_BOOST_NOT_USED`| | | | |`HIPSOLVERRF_NUMERIC_BOOST_NOT_USED`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_NUMERIC_BOOST_USED`| | | | |`HIPSOLVERRF_NUMERIC_BOOST_USED`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_RESET_VALUES_FAST_MODE_OFF`| | | | |`HIPSOLVERRF_RESET_VALUES_FAST_MODE_OFF`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_RESET_VALUES_FAST_MODE_ON`| | | | |`HIPSOLVERRF_RESET_VALUES_FAST_MODE_ON`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_TRIANGULAR_SOLVE_ALG1`| | | | |`HIPSOLVERRF_TRIANGULAR_SOLVE_ALG1`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_TRIANGULAR_SOLVE_ALG2`| | | | |`HIPSOLVERRF_TRIANGULAR_SOLVE_ALG2`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_TRIANGULAR_SOLVE_ALG3`| | | | |`HIPSOLVERRF_TRIANGULAR_SOLVE_ALG3`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_UNIT_DIAGONAL_ASSUMED_L`| | | | |`HIPSOLVERRF_UNIT_DIAGONAL_ASSUMED_L`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_UNIT_DIAGONAL_ASSUMED_U`| | | | |`HIPSOLVERRF_UNIT_DIAGONAL_ASSUMED_U`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_UNIT_DIAGONAL_STORED_L`| | | | |`HIPSOLVERRF_UNIT_DIAGONAL_STORED_L`|5.6.0| | | |6.1.0|
+|`CUSOLVERRF_UNIT_DIAGONAL_STORED_U`| | | | |`HIPSOLVERRF_UNIT_DIAGONAL_STORED_U`|5.6.0| | | |6.1.0|
 |`CUSOLVER_ALG_0`|11.0| | | | | | | | | |
 |`CUSOLVER_ALG_1`|11.0| | | | | | | | | |
 |`CUSOLVER_ALG_2`|11.5| | | | | | | | | |
@@ -104,6 +120,14 @@
 |`cusolverMgHandle_t`|10.1| | | | | | | | | |
 |`cusolverNorm_t`|10.2| | | | | | | | | |
 |`cusolverPrecType_t`|11.0| | | | | | | | | |
+|`cusolverRfCommon`| | | | | | | | | | |
+|`cusolverRfFactorization_t`| | | | |`hipsolverRfFactorization_t`|5.6.0| | | |6.1.0|
+|`cusolverRfHandle_t`| | | | |`hipsolverRfHandle_t`|5.6.0| | | |6.1.0|
+|`cusolverRfMatrixFormat_t`| | | | |`hipsolverRfMatrixFormat_t`|5.6.0| | | |6.1.0|
+|`cusolverRfNumericBoostReport_t`| | | | |`hipsolverRfNumericBoostReport_t`|5.6.0| | | |6.1.0|
+|`cusolverRfResetValuesFastMode_t`| | | | |`hipsolverRfResetValuesFastMode_t`|5.6.0| | | |6.1.0|
+|`cusolverRfTriangularSolve_t`| | | | |`hipsolverRfTriangularSolve_t`|5.6.0| | | |6.1.0|
+|`cusolverRfUnitDiagonal_t`| | | | |`hipsolverRfUnitDiagonal_t`|5.6.0| | | |6.1.0|
 |`cusolverStatus_t`| | | | |`hipsolverStatus_t`|4.5.0| | | |6.1.0|
 |`cusolverStorevMode_t`|11.0| | | | | | | | | |
 |`cusolver_int_t`|10.1| | | |`int`| | | | | |

diff --git a/docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md b/docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md
@@ -12,6 +12,22 @@
 |`CUDALIBMG_GRID_MAPPING_ROW_MAJOR`|10.1| | | | | | | | | | | | | | | |
 |`CUSOLVERDN_GETRF`|11.0| | | | | | | | | | | | | | | |
 |`CUSOLVERDN_POTRF`|11.5| | | | | | | | | | | | | | | |
+|`CUSOLVERRF_FACTORIZATION_ALG0`| | | | |`HIPSOLVERRF_FACTORIZATION_ALG0`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_FACTORIZATION_ALG1`| | | | |`HIPSOLVERRF_FACTORIZATION_ALG1`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_FACTORIZATION_ALG2`| | | | |`HIPSOLVERRF_FACTORIZATION_ALG2`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_MATRIX_FORMAT_CSC`| | | | |`HIPSOLVERRF_MATRIX_FORMAT_CSC`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_MATRIX_FORMAT_CSR`| | | | |`HIPSOLVERRF_MATRIX_FORMAT_CSR`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_NUMERIC_BOOST_NOT_USED`| | | | |`HIPSOLVERRF_NUMERIC_BOOST_NOT_USED`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_NUMERIC_BOOST_USED`| | | | |`HIPSOLVERRF_NUMERIC_BOOST_USED`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_RESET_VALUES_FAST_MODE_OFF`| | | | |`HIPSOLVERRF_RESET_VALUES_FAST_MODE_OFF`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_RESET_VALUES_FAST_MODE_ON`| | | | |`HIPSOLVERRF_RESET_VALUES_FAST_MODE_ON`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_TRIANGULAR_SOLVE_ALG1`| | | | |`HIPSOLVERRF_TRIANGULAR_SOLVE_ALG1`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_TRIANGULAR_SOLVE_ALG2`| | | | |`HIPSOLVERRF_TRIANGULAR_SOLVE_ALG2`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_TRIANGULAR_SOLVE_ALG3`| | | | |`HIPSOLVERRF_TRIANGULAR_SOLVE_ALG3`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_UNIT_DIAGONAL_ASSUMED_L`| | | | |`HIPSOLVERRF_UNIT_DIAGONAL_ASSUMED_L`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_UNIT_DIAGONAL_ASSUMED_U`| | | | |`HIPSOLVERRF_UNIT_DIAGONAL_ASSUMED_U`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_UNIT_DIAGONAL_STORED_L`| | | | |`HIPSOLVERRF_UNIT_DIAGONAL_STORED_L`|5.6.0| | | |6.1.0| | | | | | |
+|`CUSOLVERRF_UNIT_DIAGONAL_STORED_U`| | | | |`HIPSOLVERRF_UNIT_DIAGONAL_STORED_U`|5.6.0| | | |6.1.0| | | | | | |
 |`CUSOLVER_ALG_0`|11.0| | | | | | | | | | | | | | | |
 |`CUSOLVER_ALG_1`|11.0| | | | | | | | | | | | | | | |
 |`CUSOLVER_ALG_2`|11.5| | | | | | | | | | | | | | | |
@@ -104,6 +120,14 @@
 |`cusolverMgHandle_t`|10.1| | | | | | | | | | | | | | | |
 |`cusolverNorm_t`|10.2| | | | | | | | | | | | | | | |
 |`cusolverPrecType_t`|11.0| | | | | | | | | | | | | | | |
+|`cusolverRfCommon`| | | | | | | | | | | | | | | | |
+|`cusolverRfFactorization_t`| | | | |`hipsolverRfFactorization_t`|5.6.0| | | |6.1.0| | | | | | |
+|`cusolverRfHandle_t`| | | | |`hipsolverRfHandle_t`|5.6.0| | | |6.1.0| | | | | | |
+|`cusolverRfMatrixFormat_t`| | | | |`hipsolverRfMatrixFormat_t`|5.6.0| | | |6.1.0| | | | | | |
+|`cusolverRfNumericBoostReport_t`| | | | |`hipsolverRfNumericBoostReport_t`|5.6.0| | | |6.1.0| | | | | | |
+|`cusolverRfResetValuesFastMode_t`| | | | |`hipsolverRfResetValuesFastMode_t`|5.6.0| | | |6.1.0| | | | | | |
+|`cusolverRfTriangularSolve_t`| | | | |`hipsolverRfTriangularSolve_t`|5.6.0| | | |6.1.0| | | | | | |
+|`cusolverRfUnitDiagonal_t`| | | | |`hipsolverRfUnitDiagonal_t`|5.6.0| | | |6.1.0| | | | | | |
 |`cusolverStatus_t`| | | | |`hipsolverStatus_t`|4.5.0| | | |6.1.0|`rocblas_status`|3.0.0| | | |6.1.0|
 |`cusolverStorevMode_t`|11.0| | | | | | | | | | | | | | | |
 |`cusolver_int_t`|10.1| | | |`int`| | | | | |`rocblas_int`|3.0.0| | | |6.1.0|

diff --git a/docs/tables/CUSOLVER_API_supported_by_ROC.md b/docs/tables/CUSOLVER_API_supported_by_ROC.md
@@ -12,6 +12,22 @@
 |`CUDALIBMG_GRID_MAPPING_ROW_MAJOR`|10.1| | | | | | | | | |
 |`CUSOLVERDN_GETRF`|11.0| | | | | | | | | |
 |`CUSOLVERDN_POTRF`|11.5| | | | | | | | | |
+|`CUSOLVERRF_FACTORIZATION_ALG0`| | | | | | | | | | |
+|`CUSOLVERRF_FACTORIZATION_ALG1`| | | | | | | | | | |
+|`CUSOLVERRF_FACTORIZATION_ALG2`| | | | | | | | | | |
+|`CUSOLVERRF_MATRIX_FORMAT_CSC`| | | | | | | | | | |
+|`CUSOLVERRF_MATRIX_FORMAT_CSR`| | | | | | | | | | |
+|`CUSOLVERRF_NUMERIC_BOOST_NOT_USED`| | | | | | | | | | |
+|`CUSOLVERRF_NUMERIC_BOOST_USED`| | | | | | | | | | |
+|`CUSOLVERRF_RESET_VALUES_FAST_MODE_OFF`| | | | | | | | | | |
+|`CUSOLVERRF_RESET_VALUES_FAST_MODE_ON`| | | | | | | | | | |
+|`CUSOLVERRF_TRIANGULAR_SOLVE_ALG1`| | | | | | | | | | |
+|`CUSOLVERRF_TRIANGULAR_SOLVE_ALG2`| | | | | | | | | | |
+|`CUSOLVERRF_TRIANGULAR_SOLVE_ALG3`| | | | | | | | | | |
+|`CUSOLVERRF_UNIT_DIAGONAL_ASSUMED_L`| | | | | | | | | | |
+|`CUSOLVERRF_UNIT_DIAGONAL_ASSUMED_U`| | | | | | | | | | |
+|`CUSOLVERRF_UNIT_DIAGONAL_STORED_L`| | | | | | | | | | |
+|`CUSOLVERRF_UNIT_DIAGONAL_STORED_U`| | | | | | | | | | |
 |`CUSOLVER_ALG_0`|11.0| | | | | | | | | |
 |`CUSOLVER_ALG_1`|11.0| | | | | | | | | |
 |`CUSOLVER_ALG_2`|11.5| | | | | | | | | |
@@ -104,6 +120,14 @@
 |`cusolverMgHandle_t`|10.1| | | | | | | | | |
 |`cusolverNorm_t`|10.2| | | | | | | | | |
 |`cusolverPrecType_t`|11.0| | | | | | | | | |
+|`cusolverRfCommon`| | | | | | | | | | |
+|`cusolverRfFactorization_t`| | | | | | | | | | |
+|`cusolverRfHandle_t`| | | | | | | | | | |
+|`cusolverRfMatrixFormat_t`| | | | | | | | | | |
+|`cusolverRfNumericBoostReport_t`| | | | | | | | | | |
+|`cusolverRfResetValuesFastMode_t`| | | | | | | | | | |
+|`cusolverRfTriangularSolve_t`| | | | | | | | | | |
+|`cusolverRfUnitDiagonal_t`| | | | | | | | | | |
 |`cusolverStatus_t`| | | | |`rocblas_status`|3.0.0| | | |6.1.0|
 |`cusolverStorevMode_t`|11.0| | | | | | | | | |
 |`cusolver_int_t`|10.1| | | |`rocblas_int`|3.0.0| | | |6.1.0|