Forward into fetch

Author: davschneller

interfaces/cuda/Control.cu

@@ -38,6 +38,14 @@ ConcreteAPI::ConcreteAPI() {
 
   CHECK_ERR;
 
+  int numDevices{};
+  APIWRAP(cudaGetDeviceCount(&numDevices));
+
+  properties.resize(numDevices);
+  for (int i = 0; i < numDevices; ++i) {
+    APIWRAP(cudaGetDeviceProperties(&properties[i], i));
+  }
+
   status[StatusID::DriverApiInitialized] = true;
 }
 
@@ -63,14 +71,6 @@ void ConcreteAPI::initialize() {
     status[StatusID::InterfaceInitialized] = true;
     APIWRAP(cudaStreamCreateWithFlags(&defaultStream, cudaStreamNonBlocking));
 
-    int numDevices{};
-    APIWRAP(cudaGetDeviceCount(&numDevices));
-
-    properties.resize(numDevices);
-    for (int i = 0; i < numDevices; ++i) {
-      APIWRAP(cudaGetDeviceProperties(&properties[i], i));
-    }
-
     allowedConcurrentManagedAccess = properties[getDeviceId()].concurrentManagedAccess != 0;
 
     usmDefault = properties[getDeviceId()].directManagedMemAccessFromHost != 0;

interfaces/hip/Control.cpp

@@ -35,6 +35,14 @@ ConcreteAPI::ConcreteAPI() {
 
   CHECK_ERR;
 
+  int numDevices{};
+  APIWRAP(hipGetDeviceCount(&numDevices));
+
+  properties.resize(numDevices);
+  for (int i = 0; i < numDevices; ++i) {
+    APIWRAP(hipGetDeviceProperties(&properties[i], i));
+  }
+
   status[StatusID::DriverApiInitialized] = true;
 }
 
@@ -61,14 +69,6 @@ void ConcreteAPI::initialize() {
     status[StatusID::InterfaceInitialized] = true;
     APIWRAP(hipStreamCreateWithFlags(&defaultStream, hipStreamNonBlocking));
 
-    int numDevices{};
-    APIWRAP(hipGetDeviceCount(&numDevices));
-
-    properties.resize(numDevices);
-    for (int i = 0; i < numDevices; ++i) {
-      APIWRAP(hipGetDeviceProperties(&properties[i], i));
-    }
-
     // NOTE: hipDeviceGetAttribute internally calls hipGetDeviceProperties; hence it doesn't make
     // sense to use it here