diff --git a/tests/src/printf/hipPrintfFlags.cpp b/tests/src/printf/hipPrintfFlags.cpp index 33a7f1ae4d..558451d185 100644 --- a/tests/src/printf/hipPrintfFlags.cpp +++ b/tests/src/printf/hipPrintfFlags.cpp @@ -21,8 +21,8 @@ THE SOFTWARE. */ /* HIT_START - * BUILD: %t %s EXCLUDE_HIP_PLATFORM nvidia - * TEST: %t EXCLUDE_HIP_PLATFORM nvidia + * BUILD: %t %s + * TEST: %t * HIT_END */ diff --git a/tests/src/printf/hipPrintfWidthPrecision.cpp b/tests/src/printf/hipPrintfWidthPrecision.cpp index 132e249921..5ae9da6e9e 100644 --- a/tests/src/printf/hipPrintfWidthPrecision.cpp +++ b/tests/src/printf/hipPrintfWidthPrecision.cpp @@ -21,8 +21,8 @@ THE SOFTWARE. */ /* HIT_START - * BUILD: %t %s EXCLUDE_HIP_PLATFORM nvidia - * TEST: %t EXCLUDE_HIP_PLATFORM nvidia + * BUILD: %t %s + * TEST: %t * HIT_END */ diff --git a/tests/src/runtimeApi/memory/hipMemcpyWithStream.cpp b/tests/src/runtimeApi/memory/hipMemcpyWithStream.cpp index da46d51961..86d4c158c3 100755 --- a/tests/src/runtimeApi/memory/hipMemcpyWithStream.cpp +++ b/tests/src/runtimeApi/memory/hipMemcpyWithStream.cpp @@ -24,7 +24,7 @@ THE SOFTWARE. */ /* HIT_START - * BUILD: %t %s ../../test_common.cpp EXCLUDE_HIP_PLATFORM nvidia + * BUILD: %t %s ../../test_common.cpp * TEST: %t * HIT_END */ @@ -504,8 +504,10 @@ int main() { test_passed(TestOnMultiGPUwithOneStream); tests.TestkindDtoD(); test_passed(TestkindDtoD); +#ifndef __HIP_PLATFORM_NVIDIA__ tests.TestkindDefaultForDtoD(); test_passed(TestkindDefaultForDtoD); +#endif tests.TestkindHtoH(); test_passed(TestkindsHtoH); } diff --git a/tests/src/runtimeApi/memory/hipMemcpyWithStreamMultiThread.cpp b/tests/src/runtimeApi/memory/hipMemcpyWithStreamMultiThread.cpp index b5bb0a986e..c4462c06ef 100644 --- a/tests/src/runtimeApi/memory/hipMemcpyWithStreamMultiThread.cpp +++ b/tests/src/runtimeApi/memory/hipMemcpyWithStreamMultiThread.cpp @@ -24,7 +24,7 @@ THE SOFTWARE. */ /* HIT_START - * BUILD: %t %s ../../test_common.cpp NVCC_OPTIONS -std=c++11 EXCLUDE_HIP_PLATFORM nvidia + * BUILD: %t %s ../../test_common.cpp NVCC_OPTIONS -std=c++11 * TEST: %t * HIT_END */ @@ -53,7 +53,9 @@ enum class ops TestkindDtoD, TestkindHtoH, TestkindDefault, +#ifndef __HIP_PLATFORM_NVIDIA__ TestkindDefaultForDtoD, +#endif TestDtoDonSameDevice, END_OF_LIST }; @@ -601,9 +603,11 @@ void HipMemcpyWithStreamMultiThreadtests::TestwithMultiThreaded(ops op) { case ops::TestkindDefault: TestkindDefault(); break; +#ifndef __HIP_PLATFORM_NVIDIA__ case ops::TestkindDefaultForDtoD: TestkindDefaultForDtoD(); break; +#endif case ops::TestDtoDonSameDevice: TestDtoDonSameDevice(); break; @@ -648,10 +652,12 @@ int main() { test_passed(HipMemcpyWithStreamMultiThreadtests ::TestkindDefault); break; +#ifndef __HIP_PLATFORM_NVIDIA__ case ops::TestkindDefaultForDtoD: test_passed(HipMemcpyWithStreamMultiThreadtests ::TestkindDefaultForDtoD); break; +#endif case ops::TestDtoDonSameDevice: test_passed(HipMemcpyWithStreamMultiThreadtests ::TestDtoDonSameDevice); diff --git a/tests/src/runtimeApi/module/hipManagedKeyword.cpp b/tests/src/runtimeApi/module/hipManagedKeyword.cpp index c2b6b81691..d4b14f7489 100644 --- a/tests/src/runtimeApi/module/hipManagedKeyword.cpp +++ b/tests/src/runtimeApi/module/hipManagedKeyword.cpp @@ -22,7 +22,7 @@ THE SOFTWARE. /* HIT_START * BUILD_CMD: managed_kernel.code %hc --genco %S/managed_kernel.cpp -o managed_kernel.code EXCLUDE_HIP_PLATFORM amd - * BUILD: %t %s ../../test_common.cpp EXCLUDE_HIP_PLATFORM nvidia EXCLUDE_HIP_PLATFORM amd + * BUILD: %t %s ../../test_common.cpp EXCLUDE_HIP_PLATFORM amd * TEST: %t * HIT_END */ @@ -42,6 +42,10 @@ bool managedMultiGPUTest() { hipGetDeviceCount(&numDevices); for (int i = 0; i < numDevices; i++) { hipSetDevice(i); + hipDevice_t device; + hipCtx_t context; + hipDeviceGet(&device, i); + hipCtxCreate(&context, 0, device); hipModule_t Module; HIPCHECK(hipModuleLoad(&Module, fileName)); hipFunction_t Function; @@ -52,9 +56,11 @@ bool managedMultiGPUTest() { HIPCHECK(hipMemcpyDtoH(&data, hipDeviceptr_t(x), xSize)); if (data != (1 + MANAGED_VAR_INIT_VALUE)) { HIPCHECK(hipModuleUnload(Module)); + hipCtxDestroy(context); return false; } HIPCHECK(hipModuleUnload(Module)); + hipCtxDestroy(context); } return true; } diff --git a/tests/src/runtimeApi/module/hipModuleLoadDataMultThreaded.cpp b/tests/src/runtimeApi/module/hipModuleLoadDataMultThreaded.cpp index 51ea72fbe5..04da4ca1a7 100644 --- a/tests/src/runtimeApi/module/hipModuleLoadDataMultThreaded.cpp +++ b/tests/src/runtimeApi/module/hipModuleLoadDataMultThreaded.cpp @@ -18,7 +18,7 @@ THE SOFTWARE. */ /* HIT_START - * BUILD: %t %s ../../test_common.cpp NVCC_OPTIONS -std=c++11 EXCLUDE_HIP_RUNTIME rocclr EXCLUDE_HIP_PLATFORM nvidia + * BUILD: %t %s ../../test_common.cpp NVCC_OPTIONS -std=c++11 EXCLUDE_HIP_PLATFORM nvidia * TEST: %t * HIT_END */ @@ -131,7 +131,13 @@ void run_multi_threads(uint32_t n, const std::vector& buffer) { int main() { HIPCHECK(hipInit(0)); auto buffer = load_file(); - run_multi_threads(getThreadCount(), buffer); + auto file_size = buffer.size() / (1024 * 1024); + auto thread_count = getHostThreadCount(file_size + 10); + if(thread_count == 0) { + failed("Thread Count is zero"); + } + + run_multi_threads(thread_count, buffer); passed(); } diff --git a/tests/src/texture/simpleTexture3D.cpp b/tests/src/texture/simpleTexture3D.cpp index f5141eab7f..536d4af8b4 100644 --- a/tests/src/texture/simpleTexture3D.cpp +++ b/tests/src/texture/simpleTexture3D.cpp @@ -21,7 +21,7 @@ THE SOFTWARE. */ /* HIT_START - * BUILD: %t %s ../test_common.cpp EXCLUDE_HIP_PLATFORM nvidia EXCLUDE_HIP_RUNTIME rocclr + * BUILD: %t %s ../test_common.cpp * TEST: %t * HIT_END */ @@ -85,7 +85,11 @@ void runTest(int width,int height,int depth,texture