Added 64-bit geqrf (#310)

* Added 64-bit geqrf APIs
* Testing for 64-bit geqrf APIs
* Updated documentation
* Fixed failing cuda build

CHANGELOG.md

@@ -7,6 +7,10 @@ Full documentation for hipSOLVER is available at the [hipSOLVER Documentation](h
 - Added functions
   - auxiliary
     - hipsolverSetDeterministicMode, hipsolverGetDeterministicMode
+- Added compatibility-only functions
+  - geqrf
+    - hipsolverDnXgeqrf_bufferSize
+    - hipsolverDnXgeqrf
 
 ### Optimized
 ### Changed

clients/gtest/geqrf_gtest.cpp

@@ -83,7 +83,7 @@ Arguments geqrf_setup_arguments(geqrf_tuple tup)
     return arg;
 }
 
-template <testAPI_t API>
+template <testAPI_t API, typename I, typename SIZE>
 class GEQRF_BASE : public ::TestWithParam<geqrf_tuple>
 {
 protected:
@@ -98,18 +98,26 @@ class GEQRF_BASE : public ::TestWithParam<geqrf_tuple>
         Arguments arg = geqrf_setup_arguments(GetParam());
 
         if(arg.peek<rocblas_int>("m") == -1 && arg.peek<rocblas_int>("n") == -1)
-            testing_geqrf_bad_arg<API, BATCHED, STRIDED, T>();
+            testing_geqrf_bad_arg<API, BATCHED, STRIDED, T, I, SIZE>();
 
         arg.batch_count = 1;
-        testing_geqrf<API, BATCHED, STRIDED, T>(arg);
+        testing_geqrf<API, BATCHED, STRIDED, T, I, SIZE>(arg);
     }
 };
 
-class GEQRF : public GEQRF_BASE<API_NORMAL>
+class GEQRF : public GEQRF_BASE<API_NORMAL, int, int>
 {
 };
 
-class GEQRF_FORTRAN : public GEQRF_BASE<API_FORTRAN>
+class GEQRF_FORTRAN : public GEQRF_BASE<API_FORTRAN, int, int>
+{
+};
+
+class GEQRF_COMPAT : public GEQRF_BASE<API_COMPAT, int64_t, size_t>
+{
+};
+
+class GEQRF_COMPAT_64 : public GEQRF_BASE<API_COMPAT, int64_t, size_t>
 {
 };
 
@@ -155,6 +163,46 @@ TEST_P(GEQRF_FORTRAN, __double_complex)
     run_tests<false, false, rocblas_double_complex>();
 }
 
+TEST_P(GEQRF_COMPAT, __float)
+{
+    run_tests<false, false, float>();
+}
+
+TEST_P(GEQRF_COMPAT, __double)
+{
+    run_tests<false, false, double>();
+}
+
+TEST_P(GEQRF_COMPAT, __float_complex)
+{
+    run_tests<false, false, rocblas_float_complex>();
+}
+
+TEST_P(GEQRF_COMPAT, __double_complex)
+{
+    run_tests<false, false, rocblas_double_complex>();
+}
+
+TEST_P(GEQRF_COMPAT_64, __float)
+{
+    run_tests<false, false, float>();
+}
+
+TEST_P(GEQRF_COMPAT_64, __double)
+{
+    run_tests<false, false, double>();
+}
+
+TEST_P(GEQRF_COMPAT_64, __float_complex)
+{
+    run_tests<false, false, rocblas_float_complex>();
+}
+
+TEST_P(GEQRF_COMPAT_64, __double_complex)
+{
+    run_tests<false, false, rocblas_double_complex>();
+}
+
 // INSTANTIATE_TEST_SUITE_P(daily_lapack,
 //                          GEQRF,
 //                          Combine(ValuesIn(large_matrix_size_range), ValuesIn(large_n_size_range)));
@@ -170,3 +218,19 @@ INSTANTIATE_TEST_SUITE_P(checkin_lapack,
 INSTANTIATE_TEST_SUITE_P(checkin_lapack,
                          GEQRF_FORTRAN,
                          Combine(ValuesIn(matrix_size_range), ValuesIn(n_size_range)));
+
+// INSTANTIATE_TEST_SUITE_P(daily_lapack,
+//                          GEQRF_COMPAT,
+//                          Combine(ValuesIn(large_matrix_size_range), ValuesIn(large_n_size_range)));
+
+INSTANTIATE_TEST_SUITE_P(checkin_lapack,
+                         GEQRF_COMPAT,
+                         Combine(ValuesIn(matrix_size_range), ValuesIn(n_size_range)));
+
+// INSTANTIATE_TEST_SUITE_P(daily_lapack,
+//                          GEQRF_COMPAT_64,
+//                          Combine(ValuesIn(large_matrix_size_range), ValuesIn(large_n_size_range)));
+
+INSTANTIATE_TEST_SUITE_P(checkin_lapack,
+                         GEQRF_COMPAT_64,
+                         Combine(ValuesIn(matrix_size_range), ValuesIn(n_size_range)));