From e10fa5852881657d904282e8f3f800f69d9e2aed Mon Sep 17 00:00:00 2001 From: Evgeny Mankov Date: Wed, 15 Nov 2023 20:24:48 +0100 Subject: [PATCH] [HIPIFY][#675][#677][SOLVER][feature] `cuSOLVER` support - Step 9 - Data types (common) + `cusolverStorevMode_t`, `cusolverAlgMode_t`, and `cusolverPrecType_t` are `UNSUPPORTED` + Updated the regenerated hipify-perl and `SOLVER` `CUDA2HIP` documentation --- bin/hipify-perl | 24 +++++++++ docs/tables/CUSOLVER_API_supported_by_HIP.md | 24 +++++++++ .../CUSOLVER_API_supported_by_HIP_and_ROC.md | 24 +++++++++ docs/tables/CUSOLVER_API_supported_by_ROC.md | 24 +++++++++ src/CUDA2HIP_SOLVER_API_types.cpp | 49 ++++++++++++++++++- 5 files changed, 144 insertions(+), 1 deletion(-) diff --git a/bin/hipify-perl b/bin/hipify-perl index 6490232e..1fda8035 100755 --- 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 index 82288f99..fa7e7c9d 100644 --- 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,6 +74,7 @@ |`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| @@ -60,7 +82,9 @@ |`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 index b2809a86..b2ca3fdc 100644 --- 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,6 +74,7 @@ |`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| @@ -60,7 +82,9 @@ |`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 index 1d052795..51a03d6c 100644 --- 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,6 +74,7 @@ |`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| @@ -60,7 +82,9 @@ |`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** diff --git a/src/CUDA2HIP_SOLVER_API_types.cpp b/src/CUDA2HIP_SOLVER_API_types.cpp index b0a5a38c..3be25f5d 100644 --- a/src/CUDA2HIP_SOLVER_API_types.cpp +++ b/src/CUDA2HIP_SOLVER_API_types.cpp @@ -81,6 +81,30 @@ const std::map CUDA_SOLVER_TYPE_NAME_MAP { {"cusolverDirectMode_t", {"hipsolverDirectMode_t", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, {"CUBLAS_DIRECT_FORWARD", {"HIPBLAS_DIRECT_FORWARD", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, {"CUBLAS_DIRECT_BACKWARD", {"HIPBLAS_DIRECT_BACKWARD", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"cusolverStorevMode_t", {"hipsolverStorevMode_t", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"CUBLAS_STOREV_COLUMNWISE", {"HIPBLAS_STOREV_COLUMNWISE", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUBLAS_STOREV_ROWWISE", {"HIPBLAS_STOREV_ROWWISE", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"cusolverAlgMode_t", {"hipsolverAlgMode_t", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_ALG_0", {"HIPSOLVER_ALG_0", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_ALG_1", {"HIPSOLVER_ALG_1", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_ALG_2", {"HIPSOLVER_ALG_2", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"cusolverPrecType_t", {"hipsolverPrecType_t", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_R_8I", {"HIPSOLVER_R_8I", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_R_8U", {"HIPSOLVER_R_8U", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_R_64F", {"HIPSOLVER_R_64F", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_R_32F", {"HIPSOLVER_R_32F", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_R_16F", {"HIPSOLVER_R_16F", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_R_16BF", {"HIPSOLVER_R_16BF", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_R_TF32", {"HIPSOLVER_R_TF32", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_R_AP", {"HIPSOLVER_R_AP", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_C_8I", {"HIPSOLVER_C_8I", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_C_8U", {"HIPSOLVER_C_8U", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_C_64F", {"HIPSOLVER_C_64F", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_C_32F", {"HIPSOLVER_C_32F", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_C_16F", {"HIPSOLVER_C_16F", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_C_16BF", {"HIPSOLVER_C_16BF", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_C_TF32", {"HIPSOLVER_C_TF32", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, + {"CUSOLVER_C_AP", {"HIPSOLVER_C_AP", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, }; const std::map CUDA_SOLVER_TYPE_NAME_VER_MAP { @@ -127,6 +151,30 @@ const std::map CUDA_SOLVER_TYPE_NAME_VER_MAP { {"cusolverDirectMode_t", {CUDA_110, CUDA_0, CUDA_0}}, {"CUBLAS_DIRECT_FORWARD", {CUDA_110, CUDA_0, CUDA_0}}, {"CUBLAS_DIRECT_BACKWARD", {CUDA_110, CUDA_0, CUDA_0}}, + {"cusolverStorevMode_t", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUBLAS_STOREV_COLUMNWISE", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUBLAS_STOREV_ROWWISE", {CUDA_110, CUDA_0, CUDA_0}}, + {"cusolverAlgMode_t", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_ALG_0", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_ALG_1", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_ALG_2", {CUDA_115, CUDA_0, CUDA_0}}, + {"cusolverPrecType_t", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_R_8I", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_R_8U", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_R_64F", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_R_32F", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_R_16F", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_R_16BF", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_R_TF32", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_R_AP", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_C_8I", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_C_8U", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_C_64F", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_C_32F", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_C_16F", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_C_16BF", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_C_TF32", {CUDA_110, CUDA_0, CUDA_0}}, + {"CUSOLVER_C_AP", {CUDA_110, CUDA_0, CUDA_0}}, }; const std::map HIP_SOLVER_TYPE_NAME_VER_MAP { @@ -152,7 +200,6 @@ const std::map HIP_SOLVER_TYPE_NAME_VER_MAP { {"HIPSOLVER_EIG_RANGE_ALL", {HIP_5030, HIP_0, HIP_0, HIP_LATEST}}, {"HIPSOLVER_EIG_RANGE_I", {HIP_5030, HIP_0, HIP_0, HIP_LATEST}}, {"HIPSOLVER_EIG_RANGE_V", {HIP_5030, HIP_0, HIP_0, HIP_LATEST}}, - {"rocblas_status", {HIP_3000, HIP_0, HIP_0, HIP_LATEST}}, {"rocblas_status_success", {HIP_3000, HIP_0, HIP_0, HIP_LATEST}}, {"rocblas_status_invalid_handle", {HIP_5060, HIP_0, HIP_0, HIP_LATEST}},