* SWDEV-266829 - Enable more tests on AMD and NV devices
1. Enable tests on AMD and NV devices
tests/src/runtimeApi/event/hipEventMultiThreaded.cpp
Loops and threads per core are changed smaller so that test can
finish in a shorter time.
tests/src/runtimeApi/stream/hipStreamCreateWithPriority.cpp
Fix logic error on how to get priority_normal
2. Simply enable test on AMD device
tests/src/runtimeApi/memory/hipManagedKeyword.cpp
tests/src/runtimeApi/module/hipManagedKeyword.cpp
tests/src/runtimeApi/stream/hipStreamACb_MultiThread.cpp
tests/src/runtimeApi/memory/p2p_copy_coherency.cpp
3. Simply enable test on NV device
tests/src/runtimeApi/module/hipModuleLoadDataMultThreaded.cpp
4. Fix typo
tests/src/runtimeApi/stream/hipStreamAddCallbackCatch.cpp
5. Remove useless tests
tests/src/hipC.c
tests/src/hipHcc.cpp
Change-Id: Ia4406353e64d69bd34c58ebb56185701f7ce1caa
* Remove tests/src/runtimeApi/module/hipModuleLoadDataMultThreaded.cpp for cuda test
Co-authored-by: anusha GodavarthySurya <Anusha.GodavarthySurya@amd.com>
Co-authored-by: Jenkins <jenkins-compute@amd.com>
[ROCm/hip commit: 3fd16c0b5b]
1.Fix hipModuleNegative failure on all NV GPUs
a.Add signal handler for signal sent by cuda functions.
b.Make hipModuleGetGlobal match cuModuleGetGlobal behavour.
That is, if one of the first two parameters is nullptr, ignore it.
2.Fix hipModuleLoadDataMultThreaded failure on NV RTX5000
Improve lamda function.
Change-Id: I3fe6dbc35a7a14aa9119df197b7885df83d28047
[ROCm/hip commit: ae30c5cd6b]
passed() should not call exit(0) which will prevent object
destructor being called.
Change-Id: Ibaee0d85cb616727dc5db557bb9422702670b688
[ROCm/hip commit: c74e2da333]
Should not add extra for non-parameter dummyKernel()
in hipModuleLaunchKernel()
Change-Id: If6f881ebb027bd3e8435d3de5295b00277e96a6a
[ROCm/hip commit: 87ba31e596]
Fix wrong mixing of current device and stream device in
ihipModuleLaunchKernel() and hipLaunchCooperativeKernel().
Fix missing hipSetDevice() in hipMemcpyWithStream* tests.
Change-Id: I09333bb40d239bb42c832df5ea16d17eeaeff5e7
[ROCm/hip commit: a95ff95bf7]
1. Corner case and negative test scenarios added for block and grid dimension.
Change-Id: I094faf02570fec101f688462712934b94ceb37e1
[ROCm/hip commit: b1d78e4096]
Added a test to generate a code object for multiple target
architectures (including for the current device),
load and execute the kernel.
SWDEV-238517 for enhancing hip unit tests
Change-Id: I509d01124abdc0495cfc770ab5508738f108c91c
[ROCm/hip commit: 7c20d3e4e4]
tests/src/runtimeApi/module/hipModuleLaunchKernel.cpp doesn't
need hip_ext.h which will fail cuda building. So remove it
Change-Id: Icf5763449ccec839d9efda90ffe3a86fb53bdb85
[ROCm/hip commit: 9996ebb641]
Fix for kernel execution time using clock rate
SWDEV-238517 for enhancing hip unit tests
Change-Id: Id06df31387ecab96f219e0c1fbcdda1609f75605
[ROCm/hip commit: 0b871a24f6]
Added test scenarios for hipExtLaunchKernelGGL
1. verify kernel execution time using events
passed through argument
2. Verify the API by disabling time flag in
event creation.
SWDEV-238517 for enhancing hip unit tests
Change-Id: I755adc34a25c58b68041fc927bbffd2a9e6eafde
[ROCm/hip commit: d1c921ffca]
Added test scenarios for hipExtModuleLaunchKernel/hipModuleLaunchKernel APIs
1. Negative Test Scenarios for hipExtModuleLaunchKernel API
2. Negative Test Scenarios for hipModuleLaunchKernel API
3. hipExtModuleLaunchKernel API Concurrency Verification
using global variable
4. hipExtModuleLaunchKernel API Concurrency Verification
using total time taken by kernels.
5. hipExtModuleLaunchKernel API verifying the kernel execution time
of a particular kernel
6. hipExtModuleLaunchKernel API verifying by disabling the
time flag during event creation
SWDEV-238517 for enhancing hip unit tests
Change-Id: I33bbab152d47beba62065c461a07cbcacdc01d97
[ROCm/hip commit: ba3fff4fcd]
Enabling all negative test cases for amd as they are functional now
SWDEV-238517 for enhancing hip unit tests
Change-Id: I0bdbf8c192ef94588403c8f027c0399dd5480a00
[ROCm/hip commit: a6d7c7c8ff]
- Added test for V3 Static Lds code object with sramecc/xnack settings.
- Added test for V4 Static Lds code object.
SWDEV-238517 for enhancing hip unit tests
Change-Id: Ibc4f7e12033dec231d6834ccdd983e3b9e001d60
[ROCm/hip commit: 4c2e91c772]
1.Rename include/hip/hcc_detail/ as include/hip/amd_detail/
2.Rename include/hip/nvcc_detail/ as include/hip/nvidia_detail/
3.Create __HIP_PLATFORM_AMD__ to replace __HIP_PLATFORM_HCC__
4.Create __HIP_PLATFORM_NVIDIA__ to replace __HIP_PLATFORM_NVCC__
After hcc_detail, nvcc_detail, __HIP_PLATFORM_HCC__ and __HIP_PLATFORM_NVCC__
have been removed from upstream, they will be removed from hip runtime.
Change-Id: I1ae457effd739d6c25bca203c1724b026be21fce
[ROCm/hip commit: c2adc70d4d]
1. Negative Test Cases
2. API functionality test using multiple streams.
3. API functionality validation using multiple GPUs.
4. Setting hipTexRefSetFlags() with HIP_TRSF_READ_AS_INTEGER flag instead of 0 as suggested in SWDEV-256096.
5. Enabling test cases 0x03 (short) and 0x04 (char).
6. Implemented external code review comments.
SWDEV-238517 for enhancing hip unit tests
Change-Id: If42796047ec1cf2e3695dc2b7f40a2d9dd50f5bd
[ROCm/hip commit: 9d92c90b55]
APIs: hipModuleLoad, hipModuleLoadData and hipModuleLoadDataEx,
hipModuleGetGlobal(), hipModuleGetFunction
Functional and negative tests
Repeated call to ModuleLoadXX/ModuleUnloadXX
Few tests are disabled now, will be enabled when functional
SWDEV-238517 for enhancing hip unit tests
Change-Id: I65c12027e32db80213468fdee1c5cc1aa3e60bfd
[ROCm/hip commit: 71ba35eb2c]
hipStreamDestroy() by definition doesn't guarantee waiting for all stream operations.
Change-Id: Ibfd21c48d71741ebcbcb9898c8b5ac235bdc570b
[ROCm/hip commit: 2299459ce0]
Few of the tests are being validated in nvcc platform. Till then
these tests are disabled.
SWDEV-238517 for enhancing hip unit tests
Change-Id: I1acbfe90c6ea39f3de676e98f0e3c33cbac97888
[ROCm/hip commit: 5bf2a70382]
1.Added hipModuleLaunchKernel multithreaded multi GPU scenario.
2.removed hipCtxCreate API from earlier test as it is deprecated.
SWDEV-238517 for enhancing hip unit tests
Change-Id: Id102d80887b6ff61a59938dbeb9fa2a26a3275b2
[ROCm/hip commit: cc6a87e9e3]
When the original size is devided accross all GPUs rounding can
occur, causing incorrect validation. Readjust the final value
for comparison to the new size accordingly.
Change-Id: I9b42149e33dfcb328de7419e546a0202a69a8610
[ROCm/hip commit: 20f0e36041]
* Use deque instead of vector for code readers so that the iterators and references will be stable
* Fix compile error
* Assign the iterator
* Add multithreaded test
* Make threads a multiple of hardware concurrency
* Output on failure
* Add setDevice to try and initialize the context on cuda
* Create context for cuda
* Set context on each thread
* Reduce threads on cuda
* Skip test on cuda
* Try to initialize the primary context on cuda
* Push ctx to the stack as current
* Revert "Push ctx to the stack as current"
This reverts commit 0fb72d9e7f.
* Revert "Try to initialize the primary context on cuda"
This reverts commit 44e3908680.
* updated test for nvidia path
* Add c++11 option for nvcc
Co-authored-by: satyanveshd <53337087+satyanveshd@users.noreply.github.com>
[ROCm/hip commit: e7120dd876]
Julia Jiang
TomSang
arjun-raj-kuppala
agunashe
Satyanvesh Dittakavi
Anusha GodavarthySurya
sumanthtg
Rupam Chetia
cjatin
DURGESH KROTTAPALLI
Lakhan singh Thakur
Jason Tang
Vladislav Sytchenko
Aryan Salmanpour
Todd tiantuo Li
mkumarmi
kjayapra-amd
rohit pathania
German Andryeyev
Payam
Maneesh Gupta
Rahul Garg
Sarbojit2019
Paul