From a57c2abaed3ca4d856822ad2b99a4a9d71b2e140 Mon Sep 17 00:00:00 2001 From: Evgeny Mankov Date: Sun, 24 Dec 2023 12:16:32 +0000 Subject: [PATCH] [HIPIFY][#675][#677][SOLVER][feature] `cuSOLVER` support - Step 56 - Functions (SP - Lowlevel Preview) + All `SP` APIs are not supported by both `hipSOLVER` and `rocSOLVER` + Updated the regenerated `hipify-perl`, and `SOLVER` `CUDA2HIP` documentation --- bin/hipify-perl | 39 ++++++++++++ docs/tables/CUSOLVER_API_supported_by_HIP.md | 39 ++++++++++++ .../CUSOLVER_API_supported_by_HIP_and_ROC.md | 39 ++++++++++++ docs/tables/CUSOLVER_API_supported_by_ROC.md | 39 ++++++++++++ src/CUDA2HIP_SOLVER_API_functions.cpp | 62 +++++++++++++++++++ src/CUDA2HIP_SOLVER_API_types.cpp | 16 +++++ 6 files changed, 234 insertions(+) diff --git a/bin/hipify-perl b/bin/hipify-perl index 42018704..8599f1ae 100755 --- a/bin/hipify-perl +++ b/bin/hipify-perl @@ -7661,7 +7661,13 @@ sub warnUnsupportedFunctions { "cusolverStorevMode_t", "cusolverSpZcsrzfdHost", "cusolverSpZcsrqrsvBatched", + "cusolverSpZcsrqrBufferInfoHost", "cusolverSpZcsrqrBufferInfoBatched", + "cusolverSpZcsrluZeroPivotHost", + "cusolverSpZcsrluSolveHost", + "cusolverSpZcsrluFactorHost", + "cusolverSpZcsrluExtractHost", + "cusolverSpZcsrluBufferInfoHost", "cusolverSpZcsrlsvqrHost", "cusolverSpZcsrlsvqr", "cusolverSpZcsrlsvluHost", @@ -7674,15 +7680,24 @@ sub warnUnsupportedFunctions { "cusolverSpXcsrsymrcmHost", "cusolverSpXcsrsymmdqHost", "cusolverSpXcsrsymamdHost", + "cusolverSpXcsrqrAnalysisHost", "cusolverSpXcsrqrAnalysisBatched", "cusolverSpXcsrperm_bufferSizeHost", "cusolverSpXcsrpermHost", "cusolverSpXcsrmetisndHost", + "cusolverSpXcsrluNnzHost", + "cusolverSpXcsrluAnalysisHost", "cusolverSpXcsrissymHost", "cusolverSpSetStream", "cusolverSpScsrzfdHost", "cusolverSpScsrqrsvBatched", + "cusolverSpScsrqrBufferInfoHost", "cusolverSpScsrqrBufferInfoBatched", + "cusolverSpScsrluZeroPivotHost", + "cusolverSpScsrluSolveHost", + "cusolverSpScsrluFactorHost", + "cusolverSpScsrluExtractHost", + "cusolverSpScsrluBufferInfoHost", "cusolverSpScsrlsvqrHost", "cusolverSpScsrlsvqr", "cusolverSpScsrlsvluHost", @@ -7694,11 +7709,19 @@ sub warnUnsupportedFunctions { "cusolverSpScsreigsHost", "cusolverSpHandle_t", "cusolverSpGetStream", + "cusolverSpDestroyCsrqrInfoHost", "cusolverSpDestroyCsrqrInfo", + "cusolverSpDestroyCsrluInfoHost", "cusolverSpDestroy", "cusolverSpDcsrzfdHost", "cusolverSpDcsrqrsvBatched", + "cusolverSpDcsrqrBufferInfoHost", "cusolverSpDcsrqrBufferInfoBatched", + "cusolverSpDcsrluZeroPivotHost", + "cusolverSpDcsrluSolveHost", + "cusolverSpDcsrluFactorHost", + "cusolverSpDcsrluExtractHost", + "cusolverSpDcsrluBufferInfoHost", "cusolverSpDcsrlsvqrHost", "cusolverSpDcsrlsvqr", "cusolverSpDcsrlsvluHost", @@ -7708,12 +7731,20 @@ sub warnUnsupportedFunctions { "cusolverSpDcsreigvsiHost", "cusolverSpDcsreigvsi", "cusolverSpDcsreigsHost", + "cusolverSpCreateCsrqrInfoHost", "cusolverSpCreateCsrqrInfo", + "cusolverSpCreateCsrluInfoHost", "cusolverSpCreate", "cusolverSpContext", "cusolverSpCcsrzfdHost", "cusolverSpCcsrqrsvBatched", + "cusolverSpCcsrqrBufferInfoHost", "cusolverSpCcsrqrBufferInfoBatched", + "cusolverSpCcsrluZeroPivotHost", + "cusolverSpCcsrluSolveHost", + "cusolverSpCcsrluFactorHost", + "cusolverSpCcsrluExtractHost", + "cusolverSpCcsrluBufferInfoHost", "cusolverSpCcsrlsvqrHost", "cusolverSpCcsrlsvqr", "cusolverSpCcsrlsvluHost", @@ -8920,7 +8951,15 @@ sub warnUnsupportedFunctions { "csrsv2Info", "csrsm2Info", "csrqrInfo_t", + "csrqrInfoHost_t", + "csrqrInfoHost", "csrqrInfo", + "csrluInfoHost_t", + "csrluInfoHost", + "csrcholInfo_t", + "csrcholInfoHost_t", + "csrcholInfoHost", + "csrcholInfo", "cl_event_flags_enum", "cl_event_flags", "cl_context_flags_enum", diff --git a/docs/tables/CUSOLVER_API_supported_by_HIP.md b/docs/tables/CUSOLVER_API_supported_by_HIP.md index 0c47c443..c6bf341d 100644 --- a/docs/tables/CUSOLVER_API_supported_by_HIP.md +++ b/docs/tables/CUSOLVER_API_supported_by_HIP.md @@ -96,7 +96,15 @@ |`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`|5.6.0| | | |6.1.0| +|`csrcholInfo`|7.5| | | | | | | | | | +|`csrcholInfoHost`|7.5| | | | | | | | | | +|`csrcholInfoHost_t`|7.5| | | | | | | | | | +|`csrcholInfo_t`|7.5| | | | | | | | | | +|`csrluInfoHost`|7.5| | | | | | | | | | +|`csrluInfoHost_t`|7.5| | | | | | | | | | |`csrqrInfo`| | | | | | | | | | | +|`csrqrInfoHost`|7.5| | | | | | | | | | +|`csrqrInfoHost_t`|7.5| | | | | | | | | | |`csrqrInfo_t`| | | | | | | | | | | |`cudaLibMgGrid_t`|10.1| | | | | | | | | | |`cudaLibMgMatrixDesc_t`|10.1| | | | | | | | | | @@ -578,11 +586,19 @@ |`cusolverSpCcsrlsvluHost`| | | | | | | | | | | |`cusolverSpCcsrlsvqr`| | | | | | | | | | | |`cusolverSpCcsrlsvqrHost`| | | | | | | | | | | +|`cusolverSpCcsrluBufferInfoHost`|7.5| | | | | | | | | | +|`cusolverSpCcsrluExtractHost`|7.5| | | | | | | | | | +|`cusolverSpCcsrluFactorHost`|7.5| | | | | | | | | | +|`cusolverSpCcsrluSolveHost`|7.5| | | | | | | | | | +|`cusolverSpCcsrluZeroPivotHost`|7.5| | | | | | | | | | |`cusolverSpCcsrqrBufferInfoBatched`| | | | | | | | | | | +|`cusolverSpCcsrqrBufferInfoHost`|7.5| | | | | | | | | | |`cusolverSpCcsrqrsvBatched`| | | | | | | | | | | |`cusolverSpCcsrzfdHost`|9.2| | | | | | | | | | |`cusolverSpCreate`| | | | | | | | | | | +|`cusolverSpCreateCsrluInfoHost`|7.5| | | | | | | | | | |`cusolverSpCreateCsrqrInfo`| | | | | | | | | | | +|`cusolverSpCreateCsrqrInfoHost`|7.5| | | | | | | | | | |`cusolverSpDcsreigsHost`| | | | | | | | | | | |`cusolverSpDcsreigvsi`| | | | | | | | | | | |`cusolverSpDcsreigvsiHost`| | | | | | | | | | | @@ -592,11 +608,19 @@ |`cusolverSpDcsrlsvluHost`| | | | | | | | | | | |`cusolverSpDcsrlsvqr`| | | | | | | | | | | |`cusolverSpDcsrlsvqrHost`| | | | | | | | | | | +|`cusolverSpDcsrluBufferInfoHost`|7.5| | | | | | | | | | +|`cusolverSpDcsrluExtractHost`|7.5| | | | | | | | | | +|`cusolverSpDcsrluFactorHost`|7.5| | | | | | | | | | +|`cusolverSpDcsrluSolveHost`|7.5| | | | | | | | | | +|`cusolverSpDcsrluZeroPivotHost`|7.5| | | | | | | | | | |`cusolverSpDcsrqrBufferInfoBatched`| | | | | | | | | | | +|`cusolverSpDcsrqrBufferInfoHost`|7.5| | | | | | | | | | |`cusolverSpDcsrqrsvBatched`| | | | | | | | | | | |`cusolverSpDcsrzfdHost`|9.2| | | | | | | | | | |`cusolverSpDestroy`| | | | | | | | | | | +|`cusolverSpDestroyCsrluInfoHost`|7.5| | | | | | | | | | |`cusolverSpDestroyCsrqrInfo`| | | | | | | | | | | +|`cusolverSpDestroyCsrqrInfoHost`|7.5| | | | | | | | | | |`cusolverSpGetStream`| | | | | | | | | | | |`cusolverSpScsreigsHost`| | | | | | | | | | | |`cusolverSpScsreigvsi`| | | | | | | | | | | @@ -607,15 +631,24 @@ |`cusolverSpScsrlsvluHost`| | | | | | | | | | | |`cusolverSpScsrlsvqr`| | | | | | | | | | | |`cusolverSpScsrlsvqrHost`| | | | | | | | | | | +|`cusolverSpScsrluBufferInfoHost`|7.5| | | | | | | | | | +|`cusolverSpScsrluExtractHost`|7.5| | | | | | | | | | +|`cusolverSpScsrluFactorHost`|7.5| | | | | | | | | | +|`cusolverSpScsrluSolveHost`|7.5| | | | | | | | | | +|`cusolverSpScsrluZeroPivotHost`|7.5| | | | | | | | | | |`cusolverSpScsrqrBufferInfoBatched`| | | | | | | | | | | +|`cusolverSpScsrqrBufferInfoHost`|7.5| | | | | | | | | | |`cusolverSpScsrqrsvBatched`| | | | | | | | | | | |`cusolverSpScsrzfdHost`|9.2| | | | | | | | | | |`cusolverSpSetStream`| | | | | | | | | | | |`cusolverSpXcsrissymHost`| | | | | | | | | | | +|`cusolverSpXcsrluAnalysisHost`|7.5| | | | | | | | | | +|`cusolverSpXcsrluNnzHost`|7.5| | | | | | | | | | |`cusolverSpXcsrmetisndHost`|9.2| | | | | | | | | | |`cusolverSpXcsrpermHost`| | | | | | | | | | | |`cusolverSpXcsrperm_bufferSizeHost`| | | | | | | | | | | |`cusolverSpXcsrqrAnalysisBatched`| | | | | | | | | | | +|`cusolverSpXcsrqrAnalysisHost`|7.5| | | | | | | | | | |`cusolverSpXcsrsymamdHost`|7.5| | | | | | | | | | |`cusolverSpXcsrsymmdqHost`|7.5| | | | | | | | | | |`cusolverSpXcsrsymrcmHost`| | | | | | | | | | | @@ -628,7 +661,13 @@ |`cusolverSpZcsrlsvluHost`| | | | | | | | | | | |`cusolverSpZcsrlsvqr`| | | | | | | | | | | |`cusolverSpZcsrlsvqrHost`| | | | | | | | | | | +|`cusolverSpZcsrluBufferInfoHost`|7.5| | | | | | | | | | +|`cusolverSpZcsrluExtractHost`|7.5| | | | | | | | | | +|`cusolverSpZcsrluFactorHost`|7.5| | | | | | | | | | +|`cusolverSpZcsrluSolveHost`|7.5| | | | | | | | | | +|`cusolverSpZcsrluZeroPivotHost`|7.5| | | | | | | | | | |`cusolverSpZcsrqrBufferInfoBatched`| | | | | | | | | | | +|`cusolverSpZcsrqrBufferInfoHost`|7.5| | | | | | | | | | |`cusolverSpZcsrqrsvBatched`| | | | | | | | | | | |`cusolverSpZcsrzfdHost`|9.2| | | | | | | | | | 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 c92170a1..326954ac 100644 --- a/docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md +++ b/docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md @@ -96,7 +96,15 @@ |`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`|5.6.0| | | |6.1.0|`rocblas_status_not_implemented`|1.5.0| | | |6.1.0| +|`csrcholInfo`|7.5| | | | | | | | | | | | | | | | +|`csrcholInfoHost`|7.5| | | | | | | | | | | | | | | | +|`csrcholInfoHost_t`|7.5| | | | | | | | | | | | | | | | +|`csrcholInfo_t`|7.5| | | | | | | | | | | | | | | | +|`csrluInfoHost`|7.5| | | | | | | | | | | | | | | | +|`csrluInfoHost_t`|7.5| | | | | | | | | | | | | | | | |`csrqrInfo`| | | | | | | | | | | | | | | | | +|`csrqrInfoHost`|7.5| | | | | | | | | | | | | | | | +|`csrqrInfoHost_t`|7.5| | | | | | | | | | | | | | | | |`csrqrInfo_t`| | | | | | | | | | | | | | | | | |`cudaLibMgGrid_t`|10.1| | | | | | | | | | | | | | | | |`cudaLibMgMatrixDesc_t`|10.1| | | | | | | | | | | | | | | | @@ -578,11 +586,19 @@ |`cusolverSpCcsrlsvluHost`| | | | | | | | | | | | | | | | | |`cusolverSpCcsrlsvqr`| | | | | | | | | | | | | | | | | |`cusolverSpCcsrlsvqrHost`| | | | | | | | | | | | | | | | | +|`cusolverSpCcsrluBufferInfoHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpCcsrluExtractHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpCcsrluFactorHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpCcsrluSolveHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpCcsrluZeroPivotHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpCcsrqrBufferInfoBatched`| | | | | | | | | | | | | | | | | +|`cusolverSpCcsrqrBufferInfoHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpCcsrqrsvBatched`| | | | | | | | | | | | | | | | | |`cusolverSpCcsrzfdHost`|9.2| | | | | | | | | | | | | | | | |`cusolverSpCreate`| | | | | | | | | | | | | | | | | +|`cusolverSpCreateCsrluInfoHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpCreateCsrqrInfo`| | | | | | | | | | | | | | | | | +|`cusolverSpCreateCsrqrInfoHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpDcsreigsHost`| | | | | | | | | | | | | | | | | |`cusolverSpDcsreigvsi`| | | | | | | | | | | | | | | | | |`cusolverSpDcsreigvsiHost`| | | | | | | | | | | | | | | | | @@ -592,11 +608,19 @@ |`cusolverSpDcsrlsvluHost`| | | | | | | | | | | | | | | | | |`cusolverSpDcsrlsvqr`| | | | | | | | | | | | | | | | | |`cusolverSpDcsrlsvqrHost`| | | | | | | | | | | | | | | | | +|`cusolverSpDcsrluBufferInfoHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpDcsrluExtractHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpDcsrluFactorHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpDcsrluSolveHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpDcsrluZeroPivotHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpDcsrqrBufferInfoBatched`| | | | | | | | | | | | | | | | | +|`cusolverSpDcsrqrBufferInfoHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpDcsrqrsvBatched`| | | | | | | | | | | | | | | | | |`cusolverSpDcsrzfdHost`|9.2| | | | | | | | | | | | | | | | |`cusolverSpDestroy`| | | | | | | | | | | | | | | | | +|`cusolverSpDestroyCsrluInfoHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpDestroyCsrqrInfo`| | | | | | | | | | | | | | | | | +|`cusolverSpDestroyCsrqrInfoHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpGetStream`| | | | | | | | | | | | | | | | | |`cusolverSpScsreigsHost`| | | | | | | | | | | | | | | | | |`cusolverSpScsreigvsi`| | | | | | | | | | | | | | | | | @@ -607,15 +631,24 @@ |`cusolverSpScsrlsvluHost`| | | | | | | | | | | | | | | | | |`cusolverSpScsrlsvqr`| | | | | | | | | | | | | | | | | |`cusolverSpScsrlsvqrHost`| | | | | | | | | | | | | | | | | +|`cusolverSpScsrluBufferInfoHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpScsrluExtractHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpScsrluFactorHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpScsrluSolveHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpScsrluZeroPivotHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpScsrqrBufferInfoBatched`| | | | | | | | | | | | | | | | | +|`cusolverSpScsrqrBufferInfoHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpScsrqrsvBatched`| | | | | | | | | | | | | | | | | |`cusolverSpScsrzfdHost`|9.2| | | | | | | | | | | | | | | | |`cusolverSpSetStream`| | | | | | | | | | | | | | | | | |`cusolverSpXcsrissymHost`| | | | | | | | | | | | | | | | | +|`cusolverSpXcsrluAnalysisHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpXcsrluNnzHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpXcsrmetisndHost`|9.2| | | | | | | | | | | | | | | | |`cusolverSpXcsrpermHost`| | | | | | | | | | | | | | | | | |`cusolverSpXcsrperm_bufferSizeHost`| | | | | | | | | | | | | | | | | |`cusolverSpXcsrqrAnalysisBatched`| | | | | | | | | | | | | | | | | +|`cusolverSpXcsrqrAnalysisHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpXcsrsymamdHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpXcsrsymmdqHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpXcsrsymrcmHost`| | | | | | | | | | | | | | | | | @@ -628,7 +661,13 @@ |`cusolverSpZcsrlsvluHost`| | | | | | | | | | | | | | | | | |`cusolverSpZcsrlsvqr`| | | | | | | | | | | | | | | | | |`cusolverSpZcsrlsvqrHost`| | | | | | | | | | | | | | | | | +|`cusolverSpZcsrluBufferInfoHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpZcsrluExtractHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpZcsrluFactorHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpZcsrluSolveHost`|7.5| | | | | | | | | | | | | | | | +|`cusolverSpZcsrluZeroPivotHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpZcsrqrBufferInfoBatched`| | | | | | | | | | | | | | | | | +|`cusolverSpZcsrqrBufferInfoHost`|7.5| | | | | | | | | | | | | | | | |`cusolverSpZcsrqrsvBatched`| | | | | | | | | | | | | | | | | |`cusolverSpZcsrzfdHost`|9.2| | | | | | | | | | | | | | | | diff --git a/docs/tables/CUSOLVER_API_supported_by_ROC.md b/docs/tables/CUSOLVER_API_supported_by_ROC.md index f7413fab..2bf4d806 100644 --- a/docs/tables/CUSOLVER_API_supported_by_ROC.md +++ b/docs/tables/CUSOLVER_API_supported_by_ROC.md @@ -96,7 +96,15 @@ |`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| +|`csrcholInfo`|7.5| | | | | | | | | | +|`csrcholInfoHost`|7.5| | | | | | | | | | +|`csrcholInfoHost_t`|7.5| | | | | | | | | | +|`csrcholInfo_t`|7.5| | | | | | | | | | +|`csrluInfoHost`|7.5| | | | | | | | | | +|`csrluInfoHost_t`|7.5| | | | | | | | | | |`csrqrInfo`| | | | | | | | | | | +|`csrqrInfoHost`|7.5| | | | | | | | | | +|`csrqrInfoHost_t`|7.5| | | | | | | | | | |`csrqrInfo_t`| | | | | | | | | | | |`cudaLibMgGrid_t`|10.1| | | | | | | | | | |`cudaLibMgMatrixDesc_t`|10.1| | | | | | | | | | @@ -578,11 +586,19 @@ |`cusolverSpCcsrlsvluHost`| | | | | | | | | | | |`cusolverSpCcsrlsvqr`| | | | | | | | | | | |`cusolverSpCcsrlsvqrHost`| | | | | | | | | | | +|`cusolverSpCcsrluBufferInfoHost`|7.5| | | | | | | | | | +|`cusolverSpCcsrluExtractHost`|7.5| | | | | | | | | | +|`cusolverSpCcsrluFactorHost`|7.5| | | | | | | | | | +|`cusolverSpCcsrluSolveHost`|7.5| | | | | | | | | | +|`cusolverSpCcsrluZeroPivotHost`|7.5| | | | | | | | | | |`cusolverSpCcsrqrBufferInfoBatched`| | | | | | | | | | | +|`cusolverSpCcsrqrBufferInfoHost`|7.5| | | | | | | | | | |`cusolverSpCcsrqrsvBatched`| | | | | | | | | | | |`cusolverSpCcsrzfdHost`|9.2| | | | | | | | | | |`cusolverSpCreate`| | | | | | | | | | | +|`cusolverSpCreateCsrluInfoHost`|7.5| | | | | | | | | | |`cusolverSpCreateCsrqrInfo`| | | | | | | | | | | +|`cusolverSpCreateCsrqrInfoHost`|7.5| | | | | | | | | | |`cusolverSpDcsreigsHost`| | | | | | | | | | | |`cusolverSpDcsreigvsi`| | | | | | | | | | | |`cusolverSpDcsreigvsiHost`| | | | | | | | | | | @@ -592,11 +608,19 @@ |`cusolverSpDcsrlsvluHost`| | | | | | | | | | | |`cusolverSpDcsrlsvqr`| | | | | | | | | | | |`cusolverSpDcsrlsvqrHost`| | | | | | | | | | | +|`cusolverSpDcsrluBufferInfoHost`|7.5| | | | | | | | | | +|`cusolverSpDcsrluExtractHost`|7.5| | | | | | | | | | +|`cusolverSpDcsrluFactorHost`|7.5| | | | | | | | | | +|`cusolverSpDcsrluSolveHost`|7.5| | | | | | | | | | +|`cusolverSpDcsrluZeroPivotHost`|7.5| | | | | | | | | | |`cusolverSpDcsrqrBufferInfoBatched`| | | | | | | | | | | +|`cusolverSpDcsrqrBufferInfoHost`|7.5| | | | | | | | | | |`cusolverSpDcsrqrsvBatched`| | | | | | | | | | | |`cusolverSpDcsrzfdHost`|9.2| | | | | | | | | | |`cusolverSpDestroy`| | | | | | | | | | | +|`cusolverSpDestroyCsrluInfoHost`|7.5| | | | | | | | | | |`cusolverSpDestroyCsrqrInfo`| | | | | | | | | | | +|`cusolverSpDestroyCsrqrInfoHost`|7.5| | | | | | | | | | |`cusolverSpGetStream`| | | | | | | | | | | |`cusolverSpScsreigsHost`| | | | | | | | | | | |`cusolverSpScsreigvsi`| | | | | | | | | | | @@ -607,15 +631,24 @@ |`cusolverSpScsrlsvluHost`| | | | | | | | | | | |`cusolverSpScsrlsvqr`| | | | | | | | | | | |`cusolverSpScsrlsvqrHost`| | | | | | | | | | | +|`cusolverSpScsrluBufferInfoHost`|7.5| | | | | | | | | | +|`cusolverSpScsrluExtractHost`|7.5| | | | | | | | | | +|`cusolverSpScsrluFactorHost`|7.5| | | | | | | | | | +|`cusolverSpScsrluSolveHost`|7.5| | | | | | | | | | +|`cusolverSpScsrluZeroPivotHost`|7.5| | | | | | | | | | |`cusolverSpScsrqrBufferInfoBatched`| | | | | | | | | | | +|`cusolverSpScsrqrBufferInfoHost`|7.5| | | | | | | | | | |`cusolverSpScsrqrsvBatched`| | | | | | | | | | | |`cusolverSpScsrzfdHost`|9.2| | | | | | | | | | |`cusolverSpSetStream`| | | | | | | | | | | |`cusolverSpXcsrissymHost`| | | | | | | | | | | +|`cusolverSpXcsrluAnalysisHost`|7.5| | | | | | | | | | +|`cusolverSpXcsrluNnzHost`|7.5| | | | | | | | | | |`cusolverSpXcsrmetisndHost`|9.2| | | | | | | | | | |`cusolverSpXcsrpermHost`| | | | | | | | | | | |`cusolverSpXcsrperm_bufferSizeHost`| | | | | | | | | | | |`cusolverSpXcsrqrAnalysisBatched`| | | | | | | | | | | +|`cusolverSpXcsrqrAnalysisHost`|7.5| | | | | | | | | | |`cusolverSpXcsrsymamdHost`|7.5| | | | | | | | | | |`cusolverSpXcsrsymmdqHost`|7.5| | | | | | | | | | |`cusolverSpXcsrsymrcmHost`| | | | | | | | | | | @@ -628,7 +661,13 @@ |`cusolverSpZcsrlsvluHost`| | | | | | | | | | | |`cusolverSpZcsrlsvqr`| | | | | | | | | | | |`cusolverSpZcsrlsvqrHost`| | | | | | | | | | | +|`cusolverSpZcsrluBufferInfoHost`|7.5| | | | | | | | | | +|`cusolverSpZcsrluExtractHost`|7.5| | | | | | | | | | +|`cusolverSpZcsrluFactorHost`|7.5| | | | | | | | | | +|`cusolverSpZcsrluSolveHost`|7.5| | | | | | | | | | +|`cusolverSpZcsrluZeroPivotHost`|7.5| | | | | | | | | | |`cusolverSpZcsrqrBufferInfoBatched`| | | | | | | | | | | +|`cusolverSpZcsrqrBufferInfoHost`|7.5| | | | | | | | | | |`cusolverSpZcsrqrsvBatched`| | | | | | | | | | | |`cusolverSpZcsrzfdHost`|9.2| | | | | | | | | | diff --git a/src/CUDA2HIP_SOLVER_API_functions.cpp b/src/CUDA2HIP_SOLVER_API_functions.cpp index 366bb550..e55cc38d 100644 --- a/src/CUDA2HIP_SOLVER_API_functions.cpp +++ b/src/CUDA2HIP_SOLVER_API_functions.cpp @@ -598,6 +598,37 @@ const std::map CUDA_SOLVER_FUNCTION_MAP { {"cusolverSpDcsrqrsvBatched", {"hipsolverSpDcsrqrsvBatched", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, {"cusolverSpCcsrqrsvBatched", {"hipsolverSpCcsrqrsvBatched", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, {"cusolverSpZcsrqrsvBatched", {"hipsolverSpZcsrqrsvBatched", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpCreateCsrluInfoHost", {"hipsolverSpCreateCsrluInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpDestroyCsrluInfoHost", {"hipsolverSpDestroyCsrluInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpXcsrluAnalysisHost", {"hipsolverSpXcsrluAnalysisHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpScsrluBufferInfoHost", {"hipsolverSpScsrluBufferInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpDcsrluBufferInfoHost", {"hipsolverSpDcsrluBufferInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpCcsrluBufferInfoHost", {"hipsolverSpCcsrluBufferInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpZcsrluBufferInfoHost", {"hipsolverSpZcsrluBufferInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpScsrluFactorHost", {"hipsolverSpScsrluFactorHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpDcsrluFactorHost", {"hipsolverSpDcsrluFactorHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpCcsrluFactorHost", {"hipsolverSpCcsrluFactorHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpZcsrluFactorHost", {"hipsolverSpZcsrluFactorHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpScsrluZeroPivotHost", {"hipsolverSpScsrluZeroPivotHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpDcsrluZeroPivotHost", {"hipsolverSpDcsrluZeroPivotHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpCcsrluZeroPivotHost", {"hipsolverSpCcsrluZeroPivotHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpZcsrluZeroPivotHost", {"hipsolverSpZcsrluZeroPivotHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpScsrluSolveHost", {"hipsolverSpScsrluSolveHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpDcsrluSolveHost", {"hipsolverSpDcsrluSolveHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpCcsrluSolveHost", {"hipsolverSpCcsrluSolveHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpZcsrluSolveHost", {"hipsolverSpZcsrluSolveHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpXcsrluNnzHost", {"hipsolverSpXcsrluNnzHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpScsrluExtractHost", {"hipsolverSpScsrluExtractHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpDcsrluExtractHost", {"hipsolverSpDcsrluExtractHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpCcsrluExtractHost", {"hipsolverSpCcsrluExtractHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpZcsrluExtractHost", {"hipsolverSpZcsrluExtractHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpCreateCsrqrInfoHost", {"hipsolverSpCreateCsrqrInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpDestroyCsrqrInfoHost", {"hipsolverSpDestroyCsrqrInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpXcsrqrAnalysisHost", {"hipsolverSpXcsrqrAnalysisHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpScsrqrBufferInfoHost", {"hipsolverSpScsrqrBufferInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpDcsrqrBufferInfoHost", {"hipsolverSpDcsrqrBufferInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpCcsrqrBufferInfoHost", {"hipsolverSpCcsrqrBufferInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverSpZcsrqrBufferInfoHost", {"hipsolverSpZcsrqrBufferInfoHost", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, }; const std::map CUDA_SOLVER_FUNCTION_VER_MAP { @@ -937,6 +968,37 @@ const std::map CUDA_SOLVER_FUNCTION_VER_MAP { {"cusolverSpDcsrzfdHost", {CUDA_92, CUDA_0, CUDA_0}}, {"cusolverSpCcsrzfdHost", {CUDA_92, CUDA_0, CUDA_0}}, {"cusolverSpZcsrzfdHost", {CUDA_92, CUDA_0, CUDA_0}}, + {"cusolverSpCreateCsrluInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpDestroyCsrluInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpXcsrluAnalysisHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpScsrluBufferInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpDcsrluBufferInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpCcsrluBufferInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpZcsrluBufferInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpScsrluFactorHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpDcsrluFactorHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpCcsrluFactorHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpZcsrluFactorHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpScsrluZeroPivotHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpDcsrluZeroPivotHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpCcsrluZeroPivotHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpZcsrluZeroPivotHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpScsrluSolveHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpDcsrluSolveHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpCcsrluSolveHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpZcsrluSolveHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpXcsrluNnzHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpScsrluExtractHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpDcsrluExtractHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpCcsrluExtractHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpZcsrluExtractHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpCreateCsrqrInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpDestroyCsrqrInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpXcsrqrAnalysisHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpScsrqrBufferInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpDcsrqrBufferInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpCcsrqrBufferInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"cusolverSpZcsrqrBufferInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, }; const std::map HIP_SOLVER_FUNCTION_VER_MAP { diff --git a/src/CUDA2HIP_SOLVER_API_types.cpp b/src/CUDA2HIP_SOLVER_API_types.cpp index 581ccb75..ed0fbd56 100644 --- a/src/CUDA2HIP_SOLVER_API_types.cpp +++ b/src/CUDA2HIP_SOLVER_API_types.cpp @@ -159,6 +159,14 @@ const std::map CUDA_SOLVER_TYPE_NAME_MAP { {"cusolverSpHandle_t", {"hipsolverSpHandle_t", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, {"csrqrInfo", {"hipsolvercsrqrInfo", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, {"csrqrInfo_t", {"hipsolvercsrqrInfo_t", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"csrluInfoHost", {"hipsolvercsrluInfoHost", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"csrluInfoHost_t", {"hipsolvercsrluInfoHost_t", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"csrqrInfoHost", {"hipsolvercsrqrInfoHost", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"csrqrInfoHost_t", {"hipsolvercsrqrInfoHost_t", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"csrcholInfoHost", {"hipsolvercsrcholInfoHost", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"csrcholInfoHost_t", {"hipsolvercsrcholInfoHost_t", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"csrcholInfo", {"hipsolvercsrcholInfo", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, + {"csrcholInfo_t", {"hipsolvercsrcholInfo_t", "", CONV_TYPE, API_SOLVER, 1, UNSUPPORTED}}, }; const std::map CUDA_SOLVER_TYPE_NAME_VER_MAP { @@ -254,6 +262,14 @@ const std::map CUDA_SOLVER_TYPE_NAME_VER_MAP { {"CUDALIBMG_GRID_MAPPING_COL_MAJOR", {CUDA_101, CUDA_0, CUDA_0}}, {"cudaLibMgGrid_t", {CUDA_101, CUDA_0, CUDA_0}}, {"cudaLibMgMatrixDesc_t", {CUDA_101, CUDA_0, CUDA_0}}, + {"csrluInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"csrluInfoHost_t", {CUDA_75, CUDA_0, CUDA_0}}, + {"csrqrInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"csrqrInfoHost_t", {CUDA_75, CUDA_0, CUDA_0}}, + {"csrcholInfoHost", {CUDA_75, CUDA_0, CUDA_0}}, + {"csrcholInfoHost_t", {CUDA_75, CUDA_0, CUDA_0}}, + {"csrcholInfo", {CUDA_75, CUDA_0, CUDA_0}}, + {"csrcholInfo_t", {CUDA_75, CUDA_0, CUDA_0}}, }; const std::map HIP_SOLVER_TYPE_NAME_VER_MAP {