Skip to content

Commit

Permalink
[HIPIFY][ROCm#675][ROCm#677][SOLVER][feature] cuSOLVER support - St…
Browse files Browse the repository at this point in the history 
…ep 49 - Functions (DN)

+ Added the rest of `UNSUPPORTED` DN functions
+ Updated `SOLVER` synthetic tests, the regenerated `hipify-perl`, and `SOLVER` `CUDA2HIP` documentation
  • Loading branch information
@emankov
emankov committed Dec 19, 2023
1 parent c9573e1 commit 5759ef3
Show file tree
Hide file tree
Showing 6 changed files with 126 additions and 12 deletions.
19 changes: 19 additions & 0 deletions bin/hipify-perl
View file
Original file line number Diff line number Diff line change
Expand Up @@ -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",
Expand Down Expand Up @@ -7647,6 +7659,13 @@ sub warnUnsupportedFunctions {
"cusolverDnPotrf",
"cusolverDnParams_t",
"cusolverDnParams",
"cusolverDnLoggerSetMask",
"cusolverDnLoggerSetLevel",
"cusolverDnLoggerSetFile",
"cusolverDnLoggerSetCallback",
"cusolverDnLoggerOpenFile",
"cusolverDnLoggerForceDisable",
"cusolverDnLoggerCallback_t",
"cusolverDnIRSXgesv_bufferSize",
"cusolverDnIRSXgesv",
"cusolverDnIRSXgels_bufferSize",
Expand Down
25 changes: 22 additions & 3 deletions docs/tables/CUSOLVER_API_supported_by_HIP.md
View file
Original file line number Diff line number Diff line change
Expand Up @@ -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|
Expand Down Expand Up @@ -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| | | | | | | | |
Expand Down Expand Up @@ -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|
Expand Down
25 changes: 22 additions & 3 deletions docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md
View file
Original file line number Diff line number Diff line change
Expand Up @@ -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|
Expand Down Expand Up @@ -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| | | | | | | | | | | | | | |
Expand Down Expand Up @@ -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| | | | | | |
Expand Down
25 changes: 22 additions & 3 deletions docs/tables/CUSOLVER_API_supported_by_ROC.md
View file
Original file line number Diff line number Diff line change
Expand Up @@ -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|
Expand Down Expand Up @@ -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| | | | | | | | |
Expand Down Expand Up @@ -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| | | | | | | | | |
Expand Down
42 changes: 39 additions & 3 deletions src/CUDA2HIP_SOLVER_API_functions.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -455,6 +455,24 @@ const std::map<llvm::StringRef, hipCounter> 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<llvm::StringRef, cudaAPIversions> CUDA_SOLVER_FUNCTION_VER_MAP {
Expand Down Expand Up @@ -748,9 +766,27 @@ const std::map<llvm::StringRef, cudaAPIversions> 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<llvm::StringRef, hipAPIversions> HIP_SOLVER_FUNCTION_VER_MAP {
Expand Down
2 changes: 2 additions & 0 deletions src/CUDA2HIP_SOLVER_API_types.cpp
View file
Original file line number Diff line number Diff line change
Expand Up @@ -123,6 +123,7 @@ const std::map<llvm::StringRef, hipCounter> 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<llvm::StringRef, cudaAPIversions> CUDA_SOLVER_TYPE_NAME_VER_MAP {
Expand Down Expand Up @@ -210,6 +211,7 @@ const std::map<llvm::StringRef, cudaAPIversions> 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<llvm::StringRef, hipAPIversions> HIP_SOLVER_TYPE_NAME_VER_MAP {
Expand Down

0 comments on commit 5759ef3

Please sign in to comment.