[HIPIFY][ROCm#675][ROCm#677][SOLVER][feature] cuSOLVER support - Step…

… 7 - Data types (common) + `cusolverEigMode_t` and `cusolverEigRange_t` support + Updated the synthetic tests and the regenerated hipify-perl
emankov · Nov 13, 2023 · 0847e42 · 0847e42
1 parent 992c2f2
commit 0847e42
Show file tree

Hide file tree

Showing 7 changed files with 108 additions and 1 deletion.
diff --git 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
@@ -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
@@ -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
@@ -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
@@ -55,6 +55,13 @@ const std::map<llvm::StringRef, hipCounter> 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<llvm::StringRef, cudaAPIversions> CUDA_SOLVER_TYPE_NAME_VER_MAP {
@@ -75,6 +82,13 @@ const std::map<llvm::StringRef, cudaAPIversions> 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<llvm::StringRef, hipAPIversions> HIP_SOLVER_TYPE_NAME_VER_MAP {
@@ -93,6 +107,14 @@ const std::map<llvm::StringRef, hipAPIversions> 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<llvm::StringRef, hipAPIversions> 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
@@ -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
@@ -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;