From 5759ef376faa4efd8d88fc09d69ff6b087512deb Mon Sep 17 00:00:00 2001 From: Evgeny Mankov Date: Tue, 19 Dec 2023 19:45:35 +0000 Subject: [PATCH] [HIPIFY][#675][#677][SOLVER][feature] `cuSOLVER` support - Step 49 - Functions (DN) + Added the rest of `UNSUPPORTED` DN functions + Updated `SOLVER` synthetic tests, the regenerated `hipify-perl`, and `SOLVER` `CUDA2HIP` documentation --- bin/hipify-perl | 19 +++++++++ docs/tables/CUSOLVER_API_supported_by_HIP.md | 25 +++++++++-- .../CUSOLVER_API_supported_by_HIP_and_ROC.md | 25 +++++++++-- docs/tables/CUSOLVER_API_supported_by_ROC.md | 25 +++++++++-- src/CUDA2HIP_SOLVER_API_functions.cpp | 42 +++++++++++++++++-- src/CUDA2HIP_SOLVER_API_types.cpp | 2 + 6 files changed, 126 insertions(+), 12 deletions(-) diff --git a/bin/hipify-perl b/bin/hipify-perl index df4dd34e..99c16fd3 100755 --- a/bin/hipify-perl +++ b/bin/hipify-perl @@ -7613,12 +7613,24 @@ sub warnUnsupportedFunctions { "cusolverDnXtrtri", "cusolverDnXsytrs_bufferSize", "cusolverDnXsytrs", + "cusolverDnXsyevdx_bufferSize", + "cusolverDnXsyevdx", + "cusolverDnXsyevd_bufferSize", + "cusolverDnXsyevd", "cusolverDnXpotrs", "cusolverDnXpotrf_bufferSize", "cusolverDnXpotrf", "cusolverDnXgetrs", "cusolverDnXgetrf_bufferSize", "cusolverDnXgetrf", + "cusolverDnXgesvdr_bufferSize", + "cusolverDnXgesvdr", + "cusolverDnXgesvdp_bufferSize", + "cusolverDnXgesvdp", + "cusolverDnXgesvd_bufferSize", + "cusolverDnXgesvd", + "cusolverDnXgeqrf_bufferSize", + "cusolverDnXgeqrf", "cusolverDnSyevdx_bufferSize", "cusolverDnSyevdx", "cusolverDnSyevd_bufferSize", @@ -7647,6 +7659,13 @@ sub warnUnsupportedFunctions { "cusolverDnPotrf", "cusolverDnParams_t", "cusolverDnParams", + "cusolverDnLoggerSetMask", + "cusolverDnLoggerSetLevel", + "cusolverDnLoggerSetFile", + "cusolverDnLoggerSetCallback", + "cusolverDnLoggerOpenFile", + "cusolverDnLoggerForceDisable", + "cusolverDnLoggerCallback_t", "cusolverDnIRSXgesv_bufferSize", "cusolverDnIRSXgesv", "cusolverDnIRSXgels_bufferSize", diff --git a/docs/tables/CUSOLVER_API_supported_by_HIP.md b/docs/tables/CUSOLVER_API_supported_by_HIP.md index 04d9b9c8..4dbddab0 100644 --- a/docs/tables/CUSOLVER_API_supported_by_HIP.md +++ b/docs/tables/CUSOLVER_API_supported_by_HIP.md @@ -88,6 +88,7 @@ |`cusolverDnIRSInfos_t`|10.2| | | | | | | | | | |`cusolverDnIRSParams`|10.2| | | | | | | | | | |`cusolverDnIRSParams_t`|10.2| | | | | | | | | | +|`cusolverDnLoggerCallback_t`|11.7| | | | | | | | | | |`cusolverDnParams`|11.0| | | | | | | | | | |`cusolverDnParams_t`|11.0| | | | | | | | | | |`cusolverEigMode_t`|8.0| | | |`hipsolverEigMode_t`|4.5.0| | | |6.1.0| @@ -295,6 +296,12 @@ |`cusolverDnIRSXgels_bufferSize`|11.0| | | | | | | | | | |`cusolverDnIRSXgesv`|10.2| | | | | | | | | | |`cusolverDnIRSXgesv_bufferSize`|10.2| | | | | | | | | | +|`cusolverDnLoggerForceDisable`|11.7| | | | | | | | | | +|`cusolverDnLoggerOpenFile`|11.7| | | | | | | | | | +|`cusolverDnLoggerSetCallback`|11.7| | | | | | | | | | +|`cusolverDnLoggerSetFile`|11.7| | | | | | | | | | +|`cusolverDnLoggerSetLevel`|11.7| | | | | | | | | | +|`cusolverDnLoggerSetMask`|11.7| | | | | | | | | | |`cusolverDnPotrf`|11.0|11.1| | | | | | | | | |`cusolverDnPotrf_bufferSize`|11.0|11.1| | | | | | | | | |`cusolverDnPotrs`|11.0|11.1| | | | | | | | | @@ -376,17 +383,29 @@ |`cusolverDnSyevd_bufferSize`|11.0|11.1| | | | | | | | | |`cusolverDnSyevdx`|11.0|11.1| | | | | | | | | |`cusolverDnSyevdx_bufferSize`|11.0|11.1| | | | | | | | | +|`cusolverDnXgeqrf`|11.1| | | | | | | | | | +|`cusolverDnXgeqrf_bufferSize`|11.1| | | | | | | | | | +|`cusolverDnXgesvd`|11.1| | | | | | | | | | +|`cusolverDnXgesvd_bufferSize`|11.1| | | | | | | | | | |`cusolverDnXgesvdjGetResidual`|9.0| | | |`hipsolverDnXgesvdjGetResidual`|5.1.0| | | |6.1.0| |`cusolverDnXgesvdjGetSweeps`|9.0| | | |`hipsolverDnXgesvdjGetSweeps`|5.1.0| | | |6.1.0| |`cusolverDnXgesvdjSetMaxSweeps`|9.0| | | |`hipsolverDnXgesvdjSetMaxSweeps`|5.1.0| | | |6.1.0| |`cusolverDnXgesvdjSetSortEig`|9.0| | | |`hipsolverDnXgesvdjSetSortEig`|5.1.0| | | |6.1.0| |`cusolverDnXgesvdjSetTolerance`|9.0| | | |`hipsolverDnXgesvdjSetTolerance`|5.1.0| | | |6.1.0| +|`cusolverDnXgesvdp`|11.1| | | | | | | | | | +|`cusolverDnXgesvdp_bufferSize`|11.1| | | | | | | | | | +|`cusolverDnXgesvdr`|11.2| | | | | | | | | | +|`cusolverDnXgesvdr_bufferSize`|11.2| | | | | | | | | | |`cusolverDnXgetrf`|11.1| | | | | | | | | | |`cusolverDnXgetrf_bufferSize`|11.1| | | | | | | | | | |`cusolverDnXgetrs`|11.1| | | | | | | | | | -|`cusolverDnXpotrf`|11.1|11.1| | | | | | | | | -|`cusolverDnXpotrf_bufferSize`|11.1|11.1| | | | | | | | | -|`cusolverDnXpotrs`|11.1|11.1| | | | | | | | | +|`cusolverDnXpotrf`|11.1| | | | | | | | | | +|`cusolverDnXpotrf_bufferSize`|11.1| | | | | | | | | | +|`cusolverDnXpotrs`|11.1| | | | | | | | | | +|`cusolverDnXsyevd`|11.1| | | | | | | | | | +|`cusolverDnXsyevd_bufferSize`|11.1| | | | | | | | | | +|`cusolverDnXsyevdx`|11.1| | | | | | | | | | +|`cusolverDnXsyevdx_bufferSize`|11.1| | | | | | | | | | |`cusolverDnXsyevjGetResidual`|9.0| | | |`hipsolverDnXsyevjGetResidual`|5.1.0| | | |6.1.0| |`cusolverDnXsyevjGetSweeps`|9.0| | | |`hipsolverDnXsyevjGetSweeps`|5.1.0| | | |6.1.0| |`cusolverDnXsyevjSetMaxSweeps`|9.0| | | |`hipsolverDnXsyevjSetMaxSweeps`|5.1.0| | | |6.1.0| 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 694bee89..45966f9d 100644 --- a/docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md +++ b/docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md @@ -88,6 +88,7 @@ |`cusolverDnIRSInfos_t`|10.2| | | | | | | | | | | | | | | | |`cusolverDnIRSParams`|10.2| | | | | | | | | | | | | | | | |`cusolverDnIRSParams_t`|10.2| | | | | | | | | | | | | | | | +|`cusolverDnLoggerCallback_t`|11.7| | | | | | | | | | | | | | | | |`cusolverDnParams`|11.0| | | | | | | | | | | | | | | | |`cusolverDnParams_t`|11.0| | | | | | | | | | | | | | | | |`cusolverEigMode_t`|8.0| | | |`hipsolverEigMode_t`|4.5.0| | | |6.1.0|`rocblas_evect`|4.1.0| | | |6.1.0| @@ -295,6 +296,12 @@ |`cusolverDnIRSXgels_bufferSize`|11.0| | | | | | | | | | | | | | | | |`cusolverDnIRSXgesv`|10.2| | | | | | | | | | | | | | | | |`cusolverDnIRSXgesv_bufferSize`|10.2| | | | | | | | | | | | | | | | +|`cusolverDnLoggerForceDisable`|11.7| | | | | | | | | | | | | | | | +|`cusolverDnLoggerOpenFile`|11.7| | | | | | | | | | | | | | | | +|`cusolverDnLoggerSetCallback`|11.7| | | | | | | | | | | | | | | | +|`cusolverDnLoggerSetFile`|11.7| | | | | | | | | | | | | | | | +|`cusolverDnLoggerSetLevel`|11.7| | | | | | | | | | | | | | | | +|`cusolverDnLoggerSetMask`|11.7| | | | | | | | | | | | | | | | |`cusolverDnPotrf`|11.0|11.1| | | | | | | | | | | | | | | |`cusolverDnPotrf_bufferSize`|11.0|11.1| | | | | | | | | | | | | | | |`cusolverDnPotrs`|11.0|11.1| | | | | | | | | | | | | | | @@ -376,17 +383,29 @@ |`cusolverDnSyevd_bufferSize`|11.0|11.1| | | | | | | | | | | | | | | |`cusolverDnSyevdx`|11.0|11.1| | | | | | | | | | | | | | | |`cusolverDnSyevdx_bufferSize`|11.0|11.1| | | | | | | | | | | | | | | +|`cusolverDnXgeqrf`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXgeqrf_bufferSize`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXgesvd`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXgesvd_bufferSize`|11.1| | | | | | | | | | | | | | | | |`cusolverDnXgesvdjGetResidual`|9.0| | | |`hipsolverDnXgesvdjGetResidual`|5.1.0| | | |6.1.0| | | | | | | |`cusolverDnXgesvdjGetSweeps`|9.0| | | |`hipsolverDnXgesvdjGetSweeps`|5.1.0| | | |6.1.0| | | | | | | |`cusolverDnXgesvdjSetMaxSweeps`|9.0| | | |`hipsolverDnXgesvdjSetMaxSweeps`|5.1.0| | | |6.1.0| | | | | | | |`cusolverDnXgesvdjSetSortEig`|9.0| | | |`hipsolverDnXgesvdjSetSortEig`|5.1.0| | | |6.1.0| | | | | | | |`cusolverDnXgesvdjSetTolerance`|9.0| | | |`hipsolverDnXgesvdjSetTolerance`|5.1.0| | | |6.1.0| | | | | | | +|`cusolverDnXgesvdp`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXgesvdp_bufferSize`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXgesvdr`|11.2| | | | | | | | | | | | | | | | +|`cusolverDnXgesvdr_bufferSize`|11.2| | | | | | | | | | | | | | | | |`cusolverDnXgetrf`|11.1| | | | | | | | | | | | | | | | |`cusolverDnXgetrf_bufferSize`|11.1| | | | | | | | | | | | | | | | |`cusolverDnXgetrs`|11.1| | | | | | | | | | | | | | | | -|`cusolverDnXpotrf`|11.1|11.1| | | | | | | | | | | | | | | -|`cusolverDnXpotrf_bufferSize`|11.1|11.1| | | | | | | | | | | | | | | -|`cusolverDnXpotrs`|11.1|11.1| | | | | | | | | | | | | | | +|`cusolverDnXpotrf`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXpotrf_bufferSize`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXpotrs`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXsyevd`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXsyevd_bufferSize`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXsyevdx`|11.1| | | | | | | | | | | | | | | | +|`cusolverDnXsyevdx_bufferSize`|11.1| | | | | | | | | | | | | | | | |`cusolverDnXsyevjGetResidual`|9.0| | | |`hipsolverDnXsyevjGetResidual`|5.1.0| | | |6.1.0| | | | | | | |`cusolverDnXsyevjGetSweeps`|9.0| | | |`hipsolverDnXsyevjGetSweeps`|5.1.0| | | |6.1.0| | | | | | | |`cusolverDnXsyevjSetMaxSweeps`|9.0| | | |`hipsolverDnXsyevjSetMaxSweeps`|5.1.0| | | |6.1.0| | | | | | | diff --git a/docs/tables/CUSOLVER_API_supported_by_ROC.md b/docs/tables/CUSOLVER_API_supported_by_ROC.md index 661480cc..d720a40c 100644 --- a/docs/tables/CUSOLVER_API_supported_by_ROC.md +++ b/docs/tables/CUSOLVER_API_supported_by_ROC.md @@ -88,6 +88,7 @@ |`cusolverDnIRSInfos_t`|10.2| | | | | | | | | | |`cusolverDnIRSParams`|10.2| | | | | | | | | | |`cusolverDnIRSParams_t`|10.2| | | | | | | | | | +|`cusolverDnLoggerCallback_t`|11.7| | | | | | | | | | |`cusolverDnParams`|11.0| | | | | | | | | | |`cusolverDnParams_t`|11.0| | | | | | | | | | |`cusolverEigMode_t`|8.0| | | |`rocblas_evect`|4.1.0| | | |6.1.0| @@ -295,6 +296,12 @@ |`cusolverDnIRSXgels_bufferSize`|11.0| | | | | | | | | | |`cusolverDnIRSXgesv`|10.2| | | | | | | | | | |`cusolverDnIRSXgesv_bufferSize`|10.2| | | | | | | | | | +|`cusolverDnLoggerForceDisable`|11.7| | | | | | | | | | +|`cusolverDnLoggerOpenFile`|11.7| | | | | | | | | | +|`cusolverDnLoggerSetCallback`|11.7| | | | | | | | | | +|`cusolverDnLoggerSetFile`|11.7| | | | | | | | | | +|`cusolverDnLoggerSetLevel`|11.7| | | | | | | | | | +|`cusolverDnLoggerSetMask`|11.7| | | | | | | | | | |`cusolverDnPotrf`|11.0|11.1| | | | | | | | | |`cusolverDnPotrf_bufferSize`|11.0|11.1| | | | | | | | | |`cusolverDnPotrs`|11.0|11.1| | | | | | | | | @@ -376,17 +383,29 @@ |`cusolverDnSyevd_bufferSize`|11.0|11.1| | | | | | | | | |`cusolverDnSyevdx`|11.0|11.1| | | | | | | | | |`cusolverDnSyevdx_bufferSize`|11.0|11.1| | | | | | | | | +|`cusolverDnXgeqrf`|11.1| | | | | | | | | | +|`cusolverDnXgeqrf_bufferSize`|11.1| | | | | | | | | | +|`cusolverDnXgesvd`|11.1| | | | | | | | | | +|`cusolverDnXgesvd_bufferSize`|11.1| | | | | | | | | | |`cusolverDnXgesvdjGetResidual`|9.0| | | | | | | | | | |`cusolverDnXgesvdjGetSweeps`|9.0| | | | | | | | | | |`cusolverDnXgesvdjSetMaxSweeps`|9.0| | | | | | | | | | |`cusolverDnXgesvdjSetSortEig`|9.0| | | | | | | | | | |`cusolverDnXgesvdjSetTolerance`|9.0| | | | | | | | | | +|`cusolverDnXgesvdp`|11.1| | | | | | | | | | +|`cusolverDnXgesvdp_bufferSize`|11.1| | | | | | | | | | +|`cusolverDnXgesvdr`|11.2| | | | | | | | | | +|`cusolverDnXgesvdr_bufferSize`|11.2| | | | | | | | | | |`cusolverDnXgetrf`|11.1| | | | | | | | | | |`cusolverDnXgetrf_bufferSize`|11.1| | | | | | | | | | |`cusolverDnXgetrs`|11.1| | | | | | | | | | -|`cusolverDnXpotrf`|11.1|11.1| | | | | | | | | -|`cusolverDnXpotrf_bufferSize`|11.1|11.1| | | | | | | | | -|`cusolverDnXpotrs`|11.1|11.1| | | | | | | | | +|`cusolverDnXpotrf`|11.1| | | | | | | | | | +|`cusolverDnXpotrf_bufferSize`|11.1| | | | | | | | | | +|`cusolverDnXpotrs`|11.1| | | | | | | | | | +|`cusolverDnXsyevd`|11.1| | | | | | | | | | +|`cusolverDnXsyevd_bufferSize`|11.1| | | | | | | | | | +|`cusolverDnXsyevdx`|11.1| | | | | | | | | | +|`cusolverDnXsyevdx_bufferSize`|11.1| | | | | | | | | | |`cusolverDnXsyevjGetResidual`|9.0| | | | | | | | | | |`cusolverDnXsyevjGetSweeps`|9.0| | | | | | | | | | |`cusolverDnXsyevjSetMaxSweeps`|9.0| | | | | | | | | | diff --git a/src/CUDA2HIP_SOLVER_API_functions.cpp b/src/CUDA2HIP_SOLVER_API_functions.cpp index 7d712192..dc8fe9b7 100644 --- a/src/CUDA2HIP_SOLVER_API_functions.cpp +++ b/src/CUDA2HIP_SOLVER_API_functions.cpp @@ -455,6 +455,24 @@ const std::map CUDA_SOLVER_FUNCTION_MAP { {"cusolverDnXpotrf_bufferSize", {"hipsolverDnXpotrf_bufferSize", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, {"cusolverDnXpotrf", {"hipsolverDnXpotrf", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, {"cusolverDnXpotrs", {"hipsolverDnXpotrs", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXgeqrf_bufferSize", {"hipsolverDnXgeqrf_bufferSize", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXgeqrf", {"hipsolverDnXgeqrf", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXsyevd_bufferSize", {"hipsolverDnXsyevd_bufferSize", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXsyevd", {"hipsolverDnXsyevd", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXsyevdx_bufferSize", {"hipsolverDnXsyevdx_bufferSize", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXsyevdx", {"hipsolverDnXsyevdx", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXgesvd_bufferSize", {"hipsolverDnXgesvd_bufferSize", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXgesvd", {"hipsolverDnXgesvd", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXgesvdp_bufferSize", {"hipsolverDnXgesvdp_bufferSize", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXgesvdp", {"hipsolverDnXgesvdp", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXgesvdr_bufferSize", {"hipsolverDnXgesvdr_bufferSize", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnXgesvdr", {"hipsolverDnXgesvdr", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnLoggerSetCallback", {"hipsolverDnLoggerSetCallback", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnLoggerSetFile", {"hipsolverDnLoggerSetFile", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnLoggerOpenFile", {"hipsolverDnLoggerOpenFile", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnLoggerSetLevel", {"hipsolverDnLoggerSetLevel", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnLoggerSetMask", {"hipsolverDnLoggerSetMask", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, + {"cusolverDnLoggerForceDisable", {"hipsolverDnLoggerForceDisable", "", CONV_LIB_FUNC, API_SOLVER, 2, UNSUPPORTED}}, }; const std::map CUDA_SOLVER_FUNCTION_VER_MAP { @@ -748,9 +766,27 @@ const std::map CUDA_SOLVER_FUNCTION_VER_MAP { {"cusolverDnSyevdx", {CUDA_110, CUDA_111, CUDA_0}}, {"cusolverDnGesvd_bufferSize", {CUDA_110, CUDA_111, CUDA_0}}, {"cusolverDnGesvd", {CUDA_110, CUDA_111, CUDA_0}}, - {"cusolverDnXpotrf_bufferSize", {CUDA_111, CUDA_111, CUDA_0}}, - {"cusolverDnXpotrf", {CUDA_111, CUDA_111, CUDA_0}}, - {"cusolverDnXpotrs", {CUDA_111, CUDA_111, CUDA_0}}, + {"cusolverDnXpotrf_bufferSize", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXpotrf", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXpotrs", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXgeqrf_bufferSize", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXgeqrf", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXsyevd_bufferSize", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXsyevd", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXsyevdx_bufferSize", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXsyevdx", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXgesvd_bufferSize", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXgesvd", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXgesvdp_bufferSize", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXgesvdp", {CUDA_111, CUDA_0, CUDA_0}}, + {"cusolverDnXgesvdr_bufferSize", {CUDA_112, CUDA_0, CUDA_0}}, + {"cusolverDnXgesvdr", {CUDA_112, CUDA_0, CUDA_0}}, + {"cusolverDnLoggerSetCallback", {CUDA_117, CUDA_0, CUDA_0}}, + {"cusolverDnLoggerSetFile", {CUDA_117, CUDA_0, CUDA_0}}, + {"cusolverDnLoggerOpenFile", {CUDA_117, CUDA_0, CUDA_0}}, + {"cusolverDnLoggerSetLevel", {CUDA_117, CUDA_0, CUDA_0}}, + {"cusolverDnLoggerSetMask", {CUDA_117, CUDA_0, CUDA_0}}, + {"cusolverDnLoggerForceDisable", {CUDA_117, 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 2c696904..b2770043 100644 --- a/src/CUDA2HIP_SOLVER_API_types.cpp +++ b/src/CUDA2HIP_SOLVER_API_types.cpp @@ -123,6 +123,7 @@ const std::map CUDA_SOLVER_TYPE_NAME_MAP { {"CUSOLVER_DETERMINISTIC_RESULTS", {"HIPSOLVER_DETERMINISTIC_RESULTS", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, {"CUSOLVER_ALLOW_NON_DETERMINISTIC_RESULTS", {"HIPSOLVER_ALLOW_NON_DETERMINISTIC_RESULTS", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, {"cusolver_int_t", {"int", "rocblas_int", CONV_NUMERIC_LITERAL, API_SOLVER, 1}}, + {"cusolverDnLoggerCallback_t", {"hipsolverDnLoggerCallback_t", "", CONV_NUMERIC_LITERAL, API_SOLVER, 1, UNSUPPORTED}}, }; const std::map CUDA_SOLVER_TYPE_NAME_VER_MAP { @@ -210,6 +211,7 @@ const std::map CUDA_SOLVER_TYPE_NAME_VER_MAP { {"cusolverDeterministicMode_t", {CUDA_122, CUDA_0, CUDA_0}}, {"CUSOLVER_DETERMINISTIC_RESULTS", {CUDA_122, CUDA_0, CUDA_0}}, {"CUSOLVER_ALLOW_NON_DETERMINISTIC_RESULTS", {CUDA_122, CUDA_0, CUDA_0}}, + {"cusolverDnLoggerCallback_t", {CUDA_117, CUDA_0, CUDA_0}}, }; const std::map HIP_SOLVER_TYPE_NAME_VER_MAP {