diff --git a/bin/hipify-perl b/bin/hipify-perl index 5118737a..26e29b03 100755 --- a/bin/hipify-perl +++ b/bin/hipify-perl @@ -1078,6 +1078,8 @@ my %removed_funcs = ( my %experimental_funcs = ( "cusolverStatus_t" => "6.1.0", "cusolverEigType_t" => "6.1.0", + "cusolverEigRange_t" => "6.1.0", + "cusolverEigMode_t" => "6.1.0", "cusolverDnSgetrs" => "6.1.0", "cusolverDnSgetrf_bufferSize" => "6.1.0", "cusolverDnSgetrf" => "6.1.0", @@ -1098,7 +1100,12 @@ my %experimental_funcs = ( "CUSOLVER_STATUS_ALLOC_FAILED" => "6.1.0", "CUSOLVER_EIG_TYPE_3" => "6.1.0", "CUSOLVER_EIG_TYPE_2" => "6.1.0", - "CUSOLVER_EIG_TYPE_1" => "6.1.0" + "CUSOLVER_EIG_TYPE_1" => "6.1.0", + "CUSOLVER_EIG_RANGE_V" => "6.1.0", + "CUSOLVER_EIG_RANGE_I" => "6.1.0", + "CUSOLVER_EIG_RANGE_ALL" => "6.1.0", + "CUSOLVER_EIG_MODE_VECTOR" => "6.1.0", + "CUSOLVER_EIG_MODE_NOVECTOR" => "6.1.0" ); $print_stats = 1 if $examine; @@ -1245,8 +1252,15 @@ sub experimentalSubstitutions { subst("cusolverDnSgetrf_bufferSize", "hipsolverDnSgetrf_bufferSize", "library"); subst("cusolverDnSgetrs", "hipsolverDnSgetrs", "library"); subst("cusolverDnHandle_t", "hipsolverHandle_t", "type"); + subst("cusolverEigMode_t", "hipsolverEigMode_t", "type"); + subst("cusolverEigRange_t", "hipsolverEigRange_t", "type"); subst("cusolverEigType_t", "hipsolverEigType_t", "type"); subst("cusolverStatus_t", "hipsolverStatus_t", "type"); + subst("CUSOLVER_EIG_MODE_NOVECTOR", "HIPSOLVER_EIG_MODE_NOVECTOR", "numeric_literal"); + subst("CUSOLVER_EIG_MODE_VECTOR", "HIPSOLVER_EIG_MODE_VECTOR", "numeric_literal"); + subst("CUSOLVER_EIG_RANGE_ALL", "HIPSOLVER_EIG_RANGE_ALL", "numeric_literal"); + subst("CUSOLVER_EIG_RANGE_I", "HIPSOLVER_EIG_RANGE_I", "numeric_literal"); + subst("CUSOLVER_EIG_RANGE_V", "HIPSOLVER_EIG_RANGE_V", "numeric_literal"); subst("CUSOLVER_EIG_TYPE_1", "HIPSOLVER_EIG_TYPE_1", "numeric_literal"); subst("CUSOLVER_EIG_TYPE_2", "HIPSOLVER_EIG_TYPE_2", "numeric_literal"); subst("CUSOLVER_EIG_TYPE_3", "HIPSOLVER_EIG_TYPE_3", "numeric_literal"); @@ -2119,6 +2133,8 @@ sub rocSubstitutions { subst("cudnnStatus_t", "miopenStatus_t", "type"); subst("cudnnTensorDescriptor_t", "miopenTensorDescriptor_t", "type"); subst("cusolverDnHandle_t", "rocblas_handle", "type"); + subst("cusolverEigMode_t", "rocblas_evect", "type"); + subst("cusolverEigRange_t", "rocblas_erange", "type"); subst("cusolverEigType_t", "rocblas_eform", "type"); subst("cusolverStatus_t", "rocblas_status", "type"); subst("cusparseAction_t", "rocsparse_action", "type"); @@ -2278,6 +2294,11 @@ sub rocSubstitutions { subst("CUDNN_STATUS_NOT_SUPPORTED", "miopenStatusUnsupportedOp", "numeric_literal"); subst("CUDNN_STATUS_SUCCESS", "miopenStatusSuccess", "numeric_literal"); subst("CUDNN_UNIDIRECTIONAL", "miopenRNNunidirection", "numeric_literal"); + subst("CUSOLVER_EIG_MODE_NOVECTOR", "rocblas_evect_none", "numeric_literal"); + subst("CUSOLVER_EIG_MODE_VECTOR", "rocblas_evect_original", "numeric_literal"); + subst("CUSOLVER_EIG_RANGE_ALL", "rocblas_erange_all", "numeric_literal"); + subst("CUSOLVER_EIG_RANGE_I", "rocblas_erange_index", "numeric_literal"); + subst("CUSOLVER_EIG_RANGE_V", "rocblas_erange_value", "numeric_literal"); subst("CUSOLVER_EIG_TYPE_1", "rocblas_eform_ax", "numeric_literal"); subst("CUSOLVER_EIG_TYPE_2", "rocblas_eform_abx", "numeric_literal"); subst("CUSOLVER_EIG_TYPE_3", "rocblas_eform_bax", "numeric_literal"); diff --git a/docs/tables/CUSOLVER_API_supported_by_HIP.md b/docs/tables/CUSOLVER_API_supported_by_HIP.md index 3ec7da0c..d14e28e8 100644 --- a/docs/tables/CUSOLVER_API_supported_by_HIP.md +++ b/docs/tables/CUSOLVER_API_supported_by_HIP.md @@ -4,6 +4,11 @@ |**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**| |:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:| +|`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| +|`CUSOLVER_EIG_RANGE_I`|10.1| | | |`HIPSOLVER_EIG_RANGE_I`|5.3.0| | | |6.1.0| +|`CUSOLVER_EIG_RANGE_V`|10.1| | | |`HIPSOLVER_EIG_RANGE_V`|5.3.0| | | |6.1.0| |`CUSOLVER_EIG_TYPE_1`|8.0| | | |`HIPSOLVER_EIG_TYPE_1`|4.5.0| | | |6.1.0| |`CUSOLVER_EIG_TYPE_2`|8.0| | | |`HIPSOLVER_EIG_TYPE_2`|4.5.0| | | |6.1.0| |`CUSOLVER_EIG_TYPE_3`|8.0| | | |`HIPSOLVER_EIG_TYPE_3`|4.5.0| | | |6.1.0| @@ -33,6 +38,8 @@ |`CUSOLVER_STATUS_SUCCESS`| | | | |`HIPSOLVER_STATUS_SUCCESS`|4.5.0| | | |6.1.0| |`CUSOLVER_STATUS_ZERO_PIVOT`| | | | |`HIPSOLVER_STATUS_ZERO_PIVOT`| | | | | | |`cusolverDnHandle_t`| | | | |`hipsolverHandle_t`|4.5.0| | | |6.1.0| +|`cusolverEigMode_t`|8.0| | | |`hipsolverEigMode_t`|4.5.0| | | |6.1.0| +|`cusolverEigRange_t`|10.1| | | |`hipsolverEigRange_t`|5.3.0| | | |6.1.0| |`cusolverEigType_t`|8.0| | | |`hipsolverEigType_t`|4.5.0| | | |6.1.0| |`cusolverStatus_t`| | | | |`hipsolverStatus_t`|4.5.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 6faea800..8a2b7b93 100644 --- a/docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md +++ b/docs/tables/CUSOLVER_API_supported_by_HIP_and_ROC.md @@ -4,6 +4,11 @@ |**CUDA**|**A**|**D**|**C**|**R**|**HIP**|**A**|**D**|**C**|**R**|**E**|**ROC**|**A**|**D**|**C**|**R**|**E**| |:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:| +|`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| +|`CUSOLVER_EIG_RANGE_I`|10.1| | | |`HIPSOLVER_EIG_RANGE_I`|5.3.0| | | |6.1.0|`rocblas_erange_index`|5.2.0| | | |6.1.0| +|`CUSOLVER_EIG_RANGE_V`|10.1| | | |`HIPSOLVER_EIG_RANGE_V`|5.3.0| | | |6.1.0|`rocblas_erange_value`|5.2.0| | | |6.1.0| |`CUSOLVER_EIG_TYPE_1`|8.0| | | |`HIPSOLVER_EIG_TYPE_1`|4.5.0| | | |6.1.0|`rocblas_eform_ax`|4.2.0| | | |6.1.0| |`CUSOLVER_EIG_TYPE_2`|8.0| | | |`HIPSOLVER_EIG_TYPE_2`|4.5.0| | | |6.1.0|`rocblas_eform_abx`|4.2.0| | | |6.1.0| |`CUSOLVER_EIG_TYPE_3`|8.0| | | |`HIPSOLVER_EIG_TYPE_3`|4.5.0| | | |6.1.0|`rocblas_eform_bax`|4.2.0| | | |6.1.0| @@ -33,6 +38,8 @@ |`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| |`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| +|`cusolverEigRange_t`|10.1| | | |`hipsolverEigRange_t`|5.3.0| | | |6.1.0|`rocblas_erange`|5.2.0| | | |6.1.0| |`cusolverEigType_t`|8.0| | | |`hipsolverEigType_t`|4.5.0| | | |6.1.0|`rocblas_eform`|4.2.0| | | |6.1.0| |`cusolverStatus_t`| | | | |`hipsolverStatus_t`|4.5.0| | | |6.1.0|`rocblas_status`|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 index f9972d8a..b50e6763 100644 --- a/docs/tables/CUSOLVER_API_supported_by_ROC.md +++ b/docs/tables/CUSOLVER_API_supported_by_ROC.md @@ -4,6 +4,11 @@ |**CUDA**|**A**|**D**|**C**|**R**|**ROC**|**A**|**D**|**C**|**R**|**E**| |:--|:-:|:-:|:-:|:-:|:--|:-:|:-:|:-:|:-:|:-:| +|`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| +|`CUSOLVER_EIG_RANGE_I`|10.1| | | |`rocblas_erange_index`|5.2.0| | | |6.1.0| +|`CUSOLVER_EIG_RANGE_V`|10.1| | | |`rocblas_erange_value`|5.2.0| | | |6.1.0| |`CUSOLVER_EIG_TYPE_1`|8.0| | | |`rocblas_eform_ax`|4.2.0| | | |6.1.0| |`CUSOLVER_EIG_TYPE_2`|8.0| | | |`rocblas_eform_abx`|4.2.0| | | |6.1.0| |`CUSOLVER_EIG_TYPE_3`|8.0| | | |`rocblas_eform_bax`|4.2.0| | | |6.1.0| @@ -33,6 +38,8 @@ |`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| |`cusolverDnHandle_t`| | | | |`rocblas_handle`|1.5.0| | | |6.1.0| +|`cusolverEigMode_t`|8.0| | | |`rocblas_evect`|4.1.0| | | |6.1.0| +|`cusolverEigRange_t`|10.1| | | |`rocblas_erange`|5.2.0| | | |6.1.0| |`cusolverEigType_t`|8.0| | | |`rocblas_eform`|4.2.0| | | |6.1.0| |`cusolverStatus_t`| | | | |`rocblas_status`|3.0.0| | | |6.1.0| diff --git a/src/CUDA2HIP_SOLVER_API_types.cpp b/src/CUDA2HIP_SOLVER_API_types.cpp index 7b5ae9de..c75e6a3a 100644 --- a/src/CUDA2HIP_SOLVER_API_types.cpp +++ b/src/CUDA2HIP_SOLVER_API_types.cpp @@ -55,6 +55,13 @@ const std::map CUDA_SOLVER_TYPE_NAME_MAP { {"CUSOLVER_EIG_TYPE_1", {"HIPSOLVER_EIG_TYPE_1", "rocblas_eform_ax", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}}, {"CUSOLVER_EIG_TYPE_2", {"HIPSOLVER_EIG_TYPE_2", "rocblas_eform_abx", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}}, {"CUSOLVER_EIG_TYPE_3", {"HIPSOLVER_EIG_TYPE_3", "rocblas_eform_bax", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}}, + {"cusolverEigMode_t", {"hipsolverEigMode_t", "rocblas_evect", CONV_TYPE, API_SOLVER, 1, HIP_EXPERIMENTAL}}, + {"CUSOLVER_EIG_MODE_NOVECTOR", {"HIPSOLVER_EIG_MODE_NOVECTOR", "rocblas_evect_none", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}}, + {"CUSOLVER_EIG_MODE_VECTOR", {"HIPSOLVER_EIG_MODE_VECTOR", "rocblas_evect_original", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}}, + {"cusolverEigRange_t", {"hipsolverEigRange_t", "rocblas_erange", CONV_TYPE, API_SOLVER, 1, HIP_EXPERIMENTAL}}, + {"CUSOLVER_EIG_RANGE_ALL", {"HIPSOLVER_EIG_RANGE_ALL", "rocblas_erange_all", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}}, + {"CUSOLVER_EIG_RANGE_I", {"HIPSOLVER_EIG_RANGE_I", "rocblas_erange_index", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}}, + {"CUSOLVER_EIG_RANGE_V", {"HIPSOLVER_EIG_RANGE_V", "rocblas_erange_value", CONV_NUMERIC_LITERAL, API_SOLVER, 1, HIP_EXPERIMENTAL}}, }; const std::map CUDA_SOLVER_TYPE_NAME_VER_MAP { @@ -75,6 +82,13 @@ const std::map CUDA_SOLVER_TYPE_NAME_VER_MAP { {"CUSOLVER_EIG_TYPE_1", {CUDA_80, CUDA_0, CUDA_0}}, {"CUSOLVER_EIG_TYPE_2", {CUDA_80, CUDA_0, CUDA_0}}, {"CUSOLVER_EIG_TYPE_3", {CUDA_80, CUDA_0, CUDA_0}}, + {"cusolverEigMode_t", {CUDA_80, CUDA_0, CUDA_0}}, + {"CUSOLVER_EIG_MODE_NOVECTOR", {CUDA_80, CUDA_0, CUDA_0}}, + {"CUSOLVER_EIG_MODE_VECTOR", {CUDA_80, CUDA_0, CUDA_0}}, + {"cusolverEigRange_t", {CUDA_101, CUDA_0, CUDA_0}}, + {"CUSOLVER_EIG_RANGE_ALL", {CUDA_101, CUDA_0, CUDA_0}}, + {"CUSOLVER_EIG_RANGE_I", {CUDA_101, CUDA_0, CUDA_0}}, + {"CUSOLVER_EIG_RANGE_V", {CUDA_101, CUDA_0, CUDA_0}}, }; const std::map HIP_SOLVER_TYPE_NAME_VER_MAP { @@ -93,6 +107,14 @@ const std::map HIP_SOLVER_TYPE_NAME_VER_MAP { {"HIPSOLVER_EIG_TYPE_1", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}}, {"HIPSOLVER_EIG_TYPE_2", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}}, {"HIPSOLVER_EIG_TYPE_3", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}}, + {"hipsolverEigMode_t", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}}, + {"HIPSOLVER_EIG_MODE_NOVECTOR", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}}, + {"HIPSOLVER_EIG_MODE_VECTOR", {HIP_4050, HIP_0, HIP_0, HIP_LATEST}}, + {"hipsolverEigRange_t", {HIP_5030, HIP_0, HIP_0, HIP_LATEST}}, + {"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}}, @@ -106,4 +128,11 @@ const std::map HIP_SOLVER_TYPE_NAME_VER_MAP { {"rocblas_eform_ax", {HIP_4020, HIP_0, HIP_0, HIP_LATEST}}, {"rocblas_eform_abx", {HIP_4020, HIP_0, HIP_0, HIP_LATEST}}, {"rocblas_eform_bax", {HIP_4020, HIP_0, HIP_0, HIP_LATEST}}, + {"rocblas_evect", {HIP_4010, HIP_0, HIP_0, HIP_LATEST}}, + {"rocblas_evect_none", {HIP_4010, HIP_0, HIP_0, HIP_LATEST}}, + {"rocblas_evect_original", {HIP_4010, HIP_0, HIP_0, HIP_LATEST}}, + {"rocblas_erange", {HIP_5020, HIP_0, HIP_0, HIP_LATEST}}, + {"rocblas_erange_all", {HIP_5020, HIP_0, HIP_0, HIP_LATEST}}, + {"rocblas_erange_index", {HIP_5020, HIP_0, HIP_0, HIP_LATEST}}, + {"rocblas_erange_value", {HIP_5020, HIP_0, HIP_0, HIP_LATEST}}, }; diff --git a/tests/unit_tests/synthetic/libraries/cusolver2hipsolver.cu b/tests/unit_tests/synthetic/libraries/cusolver2hipsolver.cu index cd4ec697..c3e455bd 100644 --- a/tests/unit_tests/synthetic/libraries/cusolver2hipsolver.cu +++ b/tests/unit_tests/synthetic/libraries/cusolver2hipsolver.cu @@ -102,6 +102,24 @@ int main() { cusolverEigType_t EIG_TYPE_1 = CUSOLVER_EIG_TYPE_1; cusolverEigType_t EIG_TYPE_2 = CUSOLVER_EIG_TYPE_2; cusolverEigType_t EIG_TYPE_3 = CUSOLVER_EIG_TYPE_3; + + // CHECK: hipsolverEigMode_t eigMode; + // CHECK-NEXT: hipsolverEigMode_t SOLVER_EIG_MODE_NOVECTOR = HIPSOLVER_EIG_MODE_NOVECTOR; + // CHECK-NEXT: hipsolverEigMode_t SOLVER_EIG_MODE_VECTOR = HIPSOLVER_EIG_MODE_VECTOR; + cusolverEigMode_t eigMode; + cusolverEigMode_t SOLVER_EIG_MODE_NOVECTOR = CUSOLVER_EIG_MODE_NOVECTOR; + cusolverEigMode_t SOLVER_EIG_MODE_VECTOR = CUSOLVER_EIG_MODE_VECTOR; +#endif + +#if CUDA_VERSION >= 10010 + // CHECK: hipsolverEigRange_t eigRange; + // CHECK-NEXT: hipsolverEigRange_t EIG_RANGE_ALL = HIPSOLVER_EIG_RANGE_ALL; + // CHECK-NEXT: hipsolverEigRange_t EIG_RANGE_I = HIPSOLVER_EIG_RANGE_I; + // CHECK-NEXT: hipsolverEigRange_t EIG_RANGE_V = HIPSOLVER_EIG_RANGE_V; + cusolverEigRange_t eigRange; + cusolverEigRange_t EIG_RANGE_ALL = CUSOLVER_EIG_RANGE_ALL; + cusolverEigRange_t EIG_RANGE_I = CUSOLVER_EIG_RANGE_I; + cusolverEigRange_t EIG_RANGE_V = CUSOLVER_EIG_RANGE_V; #endif return 0; diff --git a/tests/unit_tests/synthetic/libraries/cusolver2rocsolver.cu b/tests/unit_tests/synthetic/libraries/cusolver2rocsolver.cu index c2007734..a32afcd7 100644 --- a/tests/unit_tests/synthetic/libraries/cusolver2rocsolver.cu +++ b/tests/unit_tests/synthetic/libraries/cusolver2rocsolver.cu @@ -54,6 +54,24 @@ int main() { cusolverEigType_t EIG_TYPE_1 = CUSOLVER_EIG_TYPE_1; cusolverEigType_t EIG_TYPE_2 = CUSOLVER_EIG_TYPE_2; cusolverEigType_t EIG_TYPE_3 = CUSOLVER_EIG_TYPE_3; + + // CHECK: rocblas_evect eigMode; + // CHECK-NEXT: rocblas_evect SOLVER_EIG_MODE_NOVECTOR = rocblas_evect_none; + // CHECK-NEXT: rocblas_evect SOLVER_EIG_MODE_VECTOR = rocblas_evect_original; + cusolverEigMode_t eigMode; + cusolverEigMode_t SOLVER_EIG_MODE_NOVECTOR = CUSOLVER_EIG_MODE_NOVECTOR; + cusolverEigMode_t SOLVER_EIG_MODE_VECTOR = CUSOLVER_EIG_MODE_VECTOR; +#endif + +#if CUDA_VERSION >= 10010 + // CHECK: rocblas_erange eigRange; + // CHECK-NEXT: rocblas_erange EIG_RANGE_ALL = rocblas_erange_all; + // CHECK-NEXT: rocblas_erange EIG_RANGE_I = rocblas_erange_index; + // CHECK-NEXT: rocblas_erange EIG_RANGE_V = rocblas_erange_value; + cusolverEigRange_t eigRange; + cusolverEigRange_t EIG_RANGE_ALL = CUSOLVER_EIG_RANGE_ALL; + cusolverEigRange_t EIG_RANGE_I = CUSOLVER_EIG_RANGE_I; + cusolverEigRange_t EIG_RANGE_V = CUSOLVER_EIG_RANGE_V; #endif return 0;