From c1e34d006c1a8b8e98f497d2383a3f511e1a235d Mon Sep 17 00:00:00 2001
From: shadidashmiz <94885391+shadidashmiz@users.noreply.github.com>
Date: Thu, 2 Dec 2021 01:17:02 -0500
Subject: [PATCH] SWDEV-292011 - xgmi hip test not supported on windows (#2423)

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Ie78bea0f1507b0c103f9cc1cce941d35a9a88a9f
---
 .../runtimeApi/memory/hipMemcpy2DFromArray.cpp   |  9 +++++++++
 tests/src/runtimeApi/memory/hipMemcpyAtoH.cpp    |  2 ++
 .../runtimeApi/p2p/hipDeviceGetP2PAttribute.cpp  |  4 ++++
 .../runtimeApi/p2p/hipP2pLinkTypeAndHopFunc.cpp  | 16 ++++++++++++++++
 4 files changed, 31 insertions(+)

diff --git a/tests/src/runtimeApi/memory/hipMemcpy2DFromArray.cpp b/tests/src/runtimeApi/memory/hipMemcpy2DFromArray.cpp
index 076cfd12d8..c8ff891eba 100644
--- a/tests/src/runtimeApi/memory/hipMemcpy2DFromArray.cpp
+++ b/tests/src/runtimeApi/memory/hipMemcpy2DFromArray.cpp
@@ -173,6 +173,7 @@ bool Memcpy2DFromArray<T>::hipMemcpy2DFromArray_PeerDeviceContext() {
     err = hipMemcpy2DFromArray(A_h, width, A_d,
                                0, 0, width,
                                NUM_H, hipMemcpyDeviceToHost);
+
     if (err == hipSuccess) {
       TestPassed = ValidateResult(A_h, INITIAL_VAL);
     } else {
@@ -281,7 +282,11 @@ int main(int argc, char **argv) {
     TestPassed &= Array_obj.hipMemcpy2DFromArray_SizeCheck();
   } else if (p_tests == 3) {
     if (numDevices > 1) {
+#ifndef _WIN64
     TestPassed &= Array_obj.hipMemcpy2DFromArray_PeerDeviceContext();
+#else
+    printf("xgmi memory test not supported on windows\n");
+#endif
     } else {
       printf("skipped the testcase as noof devices <2\n");
     }
@@ -289,8 +294,12 @@ int main(int argc, char **argv) {
     TestPassed &= Array_obj.hipMemcpy2DFromArray_NegativeTests();
   } else if (p_tests == 5) {
     if (numDevices > 1) {
+#ifndef _WIN64
     TestPassed &= Array_obj.hipMemcpy2DFromArray_PinnedHostMemory_SameGPU();
     TestPassed &= Array_obj.hipMemcpy2DFromArray_PinnedHostMemory_PeerGPU();
+#else
+    printf("xgmi memory test not supported on windows\n");
+#endif
     } else {
       printf("skipped the testcases as noof devices <2\n");
     }
diff --git a/tests/src/runtimeApi/memory/hipMemcpyAtoH.cpp b/tests/src/runtimeApi/memory/hipMemcpyAtoH.cpp
index 0e5ba8e453..08d3e6b66f 100644
--- a/tests/src/runtimeApi/memory/hipMemcpyAtoH.cpp
+++ b/tests/src/runtimeApi/memory/hipMemcpyAtoH.cpp
@@ -209,7 +209,9 @@ int main(int argc, char **argv) {
   } else if (p_tests == 2) {
     TestPassed = AtoH_obj.hipMemcpyAtoH_ByteCountZero();
   } else if (p_tests == 3) {
+#ifndef _WIN64
     TestPassed = AtoH_obj.hipMemcpyAtoH_PeerDeviceContext();
+#endif
   } else if (p_tests == 4) {
     TestPassed = AtoH_obj.hipMemcpyAtoH_NegativeTests();
   } else if (p_tests == 5) {
diff --git a/tests/src/runtimeApi/p2p/hipDeviceGetP2PAttribute.cpp b/tests/src/runtimeApi/p2p/hipDeviceGetP2PAttribute.cpp
index 2d5b605de4..a1f2850320 100644
--- a/tests/src/runtimeApi/p2p/hipDeviceGetP2PAttribute.cpp
+++ b/tests/src/runtimeApi/p2p/hipDeviceGetP2PAttribute.cpp
@@ -42,8 +42,12 @@ int main() {
   HIPCHECK(hipGetDeviceCount(&count))
 
   if (count >= 2){
+#ifdef _WIN64
+    std::cout<<"XGMI p2p attribute test no supported on windows"<<std::endl;
+#else
     for (int dev_idx = 0; dev_idx < (count-1); ++dev_idx) {
       runTest(dev_idx, 1 + dev_idx);
+#endif
     }
   } else {
     std::cout<<"Not enough GPUs to run the single GPU tests"<<std::endl;
diff --git a/tests/src/runtimeApi/p2p/hipP2pLinkTypeAndHopFunc.cpp b/tests/src/runtimeApi/p2p/hipP2pLinkTypeAndHopFunc.cpp
index 4561c5537d..3cd5d915b5 100644
--- a/tests/src/runtimeApi/p2p/hipP2pLinkTypeAndHopFunc.cpp
+++ b/tests/src/runtimeApi/p2p/hipP2pLinkTypeAndHopFunc.cpp
@@ -393,13 +393,29 @@ int main(int argc, char* argv[]) {
     printf("This test is skipped due to non linux environment.\n");
 #endif
   } else if (p_tests == 0x3) {
+#ifdef __linux__
     TestPassed = testhipInvalidLinkType();
+#else
+    printf("This test is skipped due to non linux environment.\n");
+#endif
   } else if (p_tests == 0x4) {
+#ifdef __linux__
     TestPassed = testhipInvalidHopcount();
+#else
+    printf("This test is skipped due to non linux environment.\n");
+#endif
   } else if (p_tests == 0x5) {
+#ifdef __linux__
     TestPassed = testhipSameDevice(numDevices);
+#else
+    printf("This test is skipped due to non linux environment.\n");
+#endif
   } else if (p_tests == 0x6) {
+#ifdef __linux__
     TestPassed = testhipLinkTypeHopcountDeviceOrderRev(numDevices);
+#else
+    printf("This test is skipped due to non linux environment.\n");
+#endif
   } else if (p_tests == 0x7) {
     /*TODO:This test is currently ommited from directed test due to existing issues
     in rocm-smi. Once rocm-smi issues are resolved, this test will be enabled. */