SWDEV-273138 - Update canUseStreamWaitValue retrieving

Remove canUseStreamWaitValue from hipDeviceProp_t.
Update canUseStreamWaitValue retrieving in hipDeviceGetAttribute().

Change-Id: I275bd42d8b03e141caaf9f1bc6b714e51ca72dfb

hipamd/include/hip/hip_runtime_api.h

@@ -147,8 +147,6 @@ typedef struct hipDeviceProp_t {
     int pageableMemoryAccess;        ///< Device supports coherently accessing pageable memory
                                      ///< without calling hipHostRegister on it
     int pageableMemoryAccessUsesHostPageTables; ///< Device accesses pageable memory via the host's page tables
-    int canUseStreamWaitValue;  ///< '1' if Device supports hipStreamWaitValue32() and
-                                ///< hipStreamWaitValue64() , '0' otherwise.
 } hipDeviceProp_t;
 
 

hipamd/rocclr/hip_device.cpp

@@ -235,9 +235,6 @@ hipError_t hipGetDeviceProperties ( hipDeviceProp_t* props, hipDevice_t device )
   deviceProps.pageableMemoryAccess = info.hmmCpuMemoryAccessible_;
   deviceProps.pageableMemoryAccessUsesHostPageTables = info.hostUnifiedMemory_;
 
-  // hipStreamWaitValue64() and hipStreamWaitValue32() support
-  deviceProps.canUseStreamWaitValue = info.aqlBarrierValue_;
-
   *props = deviceProps;
   HIP_RETURN(hipSuccess);
 }

hipamd/rocclr/hip_device_runtime.cpp

@@ -315,7 +315,8 @@ hipError_t hipDeviceGetAttribute(int* pi, hipDeviceAttribute_t attr, int device)
     *pi = prop.pageableMemoryAccessUsesHostPageTables;
     break;
   case hipDeviceAttributeCanUseStreamWaitValue:
-    *pi = prop.canUseStreamWaitValue;
+    // hipStreamWaitValue64() and hipStreamWaitValue32() support
+    *pi = g_devices[device]->devices()[0]->info().aqlBarrierValue_;
     break;
   default:
     HIP_RETURN(hipErrorInvalidValue);