Commit Graph

1203 Commits

Author SHA1 Message Date
Tao Sang fe7d103d56 SWDEV-279657 - Fix hipMallocManaged-N256M failure
Add concurrentManagedAccess detection in hipMallocManaged test.
Skip test when device doesn't support concurrentManagedAccess.

Change-Id: Ie54046feef3baba857a7068972ec1fc1a60c2dfd


[ROCm/clr commit: 20fd6b8a66]
2021-04-20 09:07:31 -04:00
sumanthtg 9834c99bfc SWDEV-238517 - [dtest] Additional Tests for hipHostMalloc()
New Tests added for
 - hipHostMalloc() api.

SWDEV-238517 for enhancing hip unit tests

Change-Id: Id237ab6cd2445216cd7bd9b8189c22a36ad66b7c


[ROCm/clr commit: 248785e3d1]
2021-04-20 00:44:30 -04:00
Sourabh Betigeri eedde26cc9 SWDEV-256723 - Added group partitioning feature in ROCm CG.
Change-Id: Ie54046feef3baba857a7068972ec1fc0a60c2df9


[ROCm/clr commit: 0a0b026304]
2021-04-19 18:53:17 -04:00
DURGESH KROTTAPALLI c634c74f1b SWDEV-273550 - Tests for hipMemcpyAtoH and HtoA
[dtest] Tests for hipMemcpyAtoH & hipMemcpyHtoA APIs

1. hipMemcpyAtoH/hipMemcpyHtoA negative scenarios
2. hipMemcpyAtoH/hipMemcpyHtoA Functional scenarios

Change-Id: Iec5b339db7fdde2592390c1f56ab6cf31131d4c8


[ROCm/clr commit: 6d0d2aabd6]
2021-04-19 08:48:15 -04:00
sumanthtg 455fcfd330 SWDEV-278967 - Changes to handle dtest failures on cuda runtime version 11.2
Change-Id: I79c87d40b77b4e4beb7e3d0a9ea396ad918a81e8


[ROCm/clr commit: ee8b053a3e]
2021-04-14 12:38:46 -04:00
Aaron Enye Shi eb7035a7c1 SWDEV-261391 - Add Cache Coherency Tests for gfx90a
Add a test for fine-grained device to device coherency.
Add a test for fine-grained host to device coherency.

Change-Id: I62482cae917fa19feaa17adb53f3084527ad8fda


[ROCm/clr commit: 49696c568f]
2021-04-13 16:13:56 -04:00
Satyanvesh Dittakavi 954d7872f2 SWDEV-279486 - Fix hipMemcpyPeer/hipMemcpy APIs
Addresses the scenarios when the size passed is more than
the allocated size and when the deviceid is invalid
Change-Id: I6c9b62639096f655ffb61976905b1ce8c5f51ee7

Change-Id: I8a0d660924a8e2300c517aba6f9088626b8f6ef5


[ROCm/clr commit: 191ce1dd05]
2021-04-09 02:53:15 -04:00
Sarbojit Sarkar 4e5bf6268b SWDEV-280131 - Fix __half2 member access bug
Change-Id: Ic11750d18e4ba47446a7e494c3089a19cb4df783


[ROCm/clr commit: 9cbb283771]
2021-04-07 12:12:02 -04:00
Rupam Chetia 726547bca4 SWDEV-238517 - [dtest] Adding additional scenarios for block and grid dimension.
1. Corner case and negative test scenarios added for block and grid dimension.

Change-Id: I094faf02570fec101f688462712934b94ceb37e1


[ROCm/clr commit: c9ef2adf6a]
2021-04-07 01:44:39 -04:00
Rupam Chetia f896c3411d SWDEV-238517 - [dtest] Adding new test cases for hipComplex functions.
1. Added 21 test scenarios to test the hipComplex functions on both host and device.
2. Modified the floating point comparisons with precision check.

Change-Id: I9edfb0c635ced255935087c85b77d3cc6a1a82e3


[ROCm/clr commit: bbc933c914]
2021-04-06 07:54:29 -04:00
Sourabh Betigeri 9d4360b1ff SWDEV-274727 - Disabling tests temporarily
Change-Id: I695daebe15f592afdfee8e4efe4d8966b6e9922a


[ROCm/clr commit: 2ba421f784]
2021-03-30 13:02:19 -04:00
sumanthtg 5b48c40a55 SWDEV-278478 - hipDeviceGetPCIBusId-vs-lspci test enabled only for linux environment
Change-Id: Ia86174505d912a32b07e8e959adfba6391c3284d


[ROCm/clr commit: 5a84691e52]
2021-03-30 09:28:28 -04:00
sumanthtg d21f8da966 SWDEV-278478 - Fix for hipDeviceGetPCIBusId-vs-lspci test failure
Change-Id: I7c722633ba8023f03bb64f5fb32b31f10015c327


[ROCm/clr commit: e7ee877a50]
2021-03-23 21:49:17 +05:30
Sourabh Betigeri 58f30f3174 SWDEV-274727 - The callback associated with the event was being processed after the event is destroyed. Commit after resolving merge conflict.
Change-Id: Ia7383c83318ca0c2a4f21f7aaf22b1cebd828cf0


[ROCm/clr commit: c90c7a5cf1]
2021-03-18 15:08:58 -04:00
Ravi C Akkenapally 212cc49ed6 SWDEV-276827 - Stream Operations: match API with CUDA
Change-Id: Ia79a950561e97df3b2229f76f5512dede2babf98


[ROCm/clr commit: 397bac37a3]
2021-03-18 07:52:29 -07:00
Tao Sang e212e1a947 SWDEV-273943 - Enable runtimeApi.event dtest
Add device_id_ in hip::event to match cuda behaviour in
hipEventQuery() and hipEventRecord().
Enable hipEventElapsedTime test on AMD platform.
Workarround sporadic crash of hipEventIpc test due to
some bug of event ipc.
Add missing hipEventDestroy() in some event tests.
Fix some logic code errors.
Fix typo in comment.

Change-Id: I9ec74c475161b3e31df48d193449023e921f2924


[ROCm/clr commit: 629ea5fe19]
2021-03-16 17:12:08 -04:00
jujiang a2ded8ffca SWDEV-271283, SWDEV-274749 - Fix hipLaunchParmFUnctor test failure
Change-Id: I568eba45403feae6f50eceab4a6bcc76756fd5bd


[ROCm/clr commit: 3dea940498]
2021-03-15 14:42:41 -04:00
Saleel Kudchadker 49d2182dc7 SWDEV-271010 - Add 512KB transfer size for test
Add a new transfer to hipPerfBufferCopySpeed test

Change-Id: Ia7ec9a89e8789bf16fd5f86b08521287049c1e77


[ROCm/clr commit: 47e44117cd]
2021-03-11 11:01:54 -08:00
kjayapra-amd 449cc5096e SWDEV-276169 - Multiprocess IPC tests for Events and Memory.
Change-Id: I4a7af60e732de234a535574aa8597a7abd0b899b


[ROCm/clr commit: 57615530a7]
2021-03-11 11:16:23 -05:00
Lakhan singh Thakur 3064521743 SWDEV-238517 - Enhancing hip unit tests
[dtest] Additional tests for Memcpy

APIs tested:
      hipMemcpy, hipMemcpyAsync,
      hipMemcpyHtoD, hipMemcpyHtoDAsync,
      hipMemcpyDtoH, hipMemcpyDtoHAsync,
      hipMemcpyDtoD, hipMemcpyDtoDAsync

1: The aim of this test case is to cover all
   the negative test cases for 8 hipMemcpy apis
2: This test launches NUM_THREADS threads.
   Each thread in turn tests the working of
   8 hipmemcpy apis
3: This test case verifies the working of
   Memcpy apis for range of memory sizes from
   smallest one unit transfer to 1GB.

Change-Id: If5c99527a78e817bafab2e1bd9b686a9ff916184


[ROCm/clr commit: d4041fae4a]
2021-03-10 10:14:36 -05:00
Vladislav Sytchenko 11ad5689db SWDEV-232428 - Fix HIP printf tests on Windows
On Windows there's something fundamentally broken about redirecting IO
into a file and then restoring that said IO to it's original state. Even
though no syscalls would fail, the output would sometimes either go into
CLI or straight up nowhere.

Simply using pipes instead of a temporary file magically resolves the
above issue ¯\_(ツ)_/¯

Unfortunately the max pipe size on Linux is 1Mb, which is not enough to
store all the data printed by the kernel. This leads to a softhang in
vprintf().

Stick to using a temporary file on Linux, but switch to pipes on
Windows. Slightly refactor the CaptureStream struct to accomadate this
difference.

Change-Id: Id8e68f150df47815a4f652ee2bcd6cfb7c3e3bac


[ROCm/clr commit: 55377dfee2]
2021-03-08 18:12:42 -05:00
Vladislav Sytchenko a38929b879 SWDEV-232428 - Fix hipPrintSpecifiers test failure on Windows
The following snippets has different behaviour based on platform.

printf("%p", 0x123abc);
Linux   -> 0x123abc
Windows -> 123ABC

printf("%p", nullptr);
Linux   -> (nil)
Windows -> 0000000000000000

%p specifier according to C spec is implementation defined, so we need
to adjust the reference string to be correct on Windows.

Change-Id: I7059fa0f6cde611718bd76655637670fcbccf43c


[ROCm/clr commit: 4dd4d8c05f]
2021-03-08 18:11:33 -05:00
Tao Sang 7c5373dbdc SWDEV-274725 - Enable hiprtc test
Enable hiprtc test for Rocclr.
Remove unnecessary LINK_OPTIONS hiprtc.

Change-Id: I9ec74c475161b3e31df47d193449023e921f2923


[ROCm/clr commit: cc086cb08c]
2021-03-04 15:07:38 -05:00
kjayapra-amd 2b715e4826 SWDEV-259566 - Adding support to retrieve handle for offsetted pointer.
Change-Id: I5da5ab6a24c6df915950637feb486b8c288e60e0


[ROCm/clr commit: 8ef68df3a8]
2021-03-04 12:28:56 -05:00
Sarbojit Sarkar dcca6fe956 SWDEV-267199 - hipMalloc test issue on centOS
Change-Id: I789516e2bf921ffd3577f97571e33bcc08047849


[ROCm/clr commit: 7d6bf9fb97]
2021-03-03 11:47:13 -05:00
Ravi C Akkenapally 4cf7a5799a SWDEV-179105 - Stream Operations: Add swqupport for Wait and Write
Change-Id: I9d6d0665d12b62fe705ce1569a0e8264a4f23ab7


[ROCm/clr commit: fd0f49503f]
2021-03-02 12:15:46 -08:00
Tao Sang 2a6f45533d SWDEV-270973 - Add missing copyright headers
Change-Id: I6bb27650f74372dae6e29c79fd6bb2022cc062fe


[ROCm/clr commit: 4048db950c]
2021-03-01 19:46:24 -05:00
Satyanvesh Dittakavi 4f7df3c396 SWDEV-272082 - Fix Cooperative groups tests on HIP CUDA path
Change-Id: Icc68bc1e48c01ee120aaab17c928ffbbb96eae96


[ROCm/clr commit: 3abd25b1e9]
2021-02-25 04:54:27 -05:00
DURGESH KROTTAPALLI 781a11c2ae SWDEV-238517 - Enhancing hip unit tests
[dtest] Tests for hipEvent related APIs

Added Negative scenarios for hipEvent related APIs

1. Verifying all hipEvent related APIs by passing nullptr.
2. Pass illegal/unknown flag to hipEventCreateWithFlags API

Change-Id: Ia0a24065d16fe0f5ee28a88e280c25c1be0c3590


[ROCm/clr commit: 2a0593258c]
2021-02-24 06:29:26 -05:00
Tao Sang 06a085377d SWDEV-272088 - Fix runtimeApi/event/hipEventElapsedTime issue
runtimeApi/event/hipEventElapsedTime will report invalid resource error
on cuda due to wrong calling sequence. The fix will arrange the calling
in right sequence.

Change-Id: I3db28a962888566ea135e3cbdefa68d373e2d369


[ROCm/clr commit: b9cf12e920]
2021-02-23 12:36:40 -05:00
Tao Sang ae1db33145 SWDEV-272089 - Shorten memory test time
memory/hipMalloc_MultiThreaded_MultiGpu costs too much time to finish.
    1 GPU: about 1000s, 2 GPUs: about 2200s
But Jenkin build need quick return and ctest will kill test that last
1500+s. So we need shorten the test time.

Change-Id: I3db27a962808566ea135e3cbdefa66d373e2d369


[ROCm/clr commit: 657a515e60]
2021-02-22 18:01:00 -05:00
Tao Sang fc6ff00574 SWDEV-273484 - Fix static lib build failure
Exclude gcc/LaunchKernel from static lib as
it's shared lib test case only

Change-Id: I3db17a962808565ea135e3cbcefa66d373e2d364


[ROCm/clr commit: f055582473]
2021-02-19 17:11:26 -05:00
agodavar 601d2453be SWDEV-255979 - Added support of __managed__ static variable
Change-Id: I9d5cbbecc8c19ec38a95c94ab4130465ba76c102


[ROCm/clr commit: d5b4762d96]
2021-02-17 13:01:29 -05:00
Rupam Chetia 322818430d SWDEV-238517 - [dtest] Adding new test case to validate hipDeviceProp_t arch values
1. Added 1 scenario to validate value of deviceProp.arch.has* with
value of __HIP_ARCH_HAS_* device flag.

SWDEV-238517 - Enhancing hip unit tests

Change-Id: Idb237a76b75180ce77808853a5351f19077a0d33


[ROCm/clr commit: a28c367ed0]
2021-02-17 03:23:42 -05:00
Sarbojit Sarkar e919fb467d SWDEV-272769 - Enabled gcc based hip test
Change-Id: I48bc850df00848bf11de71e3f614273111d31b47


[ROCm/clr commit: ed7f4560cf]
2021-02-16 21:20:00 -05:00
Tao Sang 18ec4c7268 SWDEV-272089 - Fix concurrent memory test failure on CUDA
Change-Id: Ibf35c789d6bd4279bdcedba1a6e057639c258489


[ROCm/clr commit: 5039649dd4]
2021-02-16 10:00:23 -05:00
Rupam Chetia 22c580bac8 SWDEV-238517 - [dtest] Test for Multiple Target Architecture Code Object
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/clr commit: 05409f05d0]
2021-02-15 06:41:24 -05:00
cjatin c31897edcf SWDEV-252745 - Adding rtc options transformer
Change-Id: Ib250689906a35f81255398e53da979774361dbfa


[ROCm/clr commit: caf9b2b108]
2021-02-09 13:35:30 -05:00
cjatin c2216ca46f SWDEV-269879 - Adding function that recommends optimal thread count
Change-Id: I42eb94a058c1b7f9253182e16ff1c3389a836d61


[ROCm/clr commit: d9496c149b]
2021-02-09 13:34:08 -05:00
Satyanvesh Dittakavi 7e95883cfc SWDEV-269439 - Fix dtests build failure on HIP CUDA
Change-Id: Ibdba5d364df1bcd3b9e158e22a602dd993044d7a


[ROCm/clr commit: 45e5d6aa67]
2021-02-08 17:09:49 -05:00
Tao Sang a1c44ebfac SWDEV-271406 - Remove unecessary hip_ext.h
tests/src/runtimeApi/module/hipModuleLaunchKernel.cpp doesn't
need hip_ext.h which will fail cuda building. So remove it

Change-Id: Icf5763449ccec839d9efda90ffe3a86fb53bdb85


[ROCm/clr commit: a6176099cf]
2021-02-08 14:33:04 -05:00
Julia Jiang 0e20fbfbec SWDEV-271416 - Remove HIP_DYNAMIC_SHARED macro in hip
Change-Id: I12f39ea8438eb7ce76d8ffb2151b4faa93689048


[ROCm/clr commit: e4fdbfcf5b]
2021-02-08 13:17:46 -05:00
kjayapra-amd 81c1c29bc4 SWDEV-270007 - Fixing the hipMemoryAllocateCoherent test binary path for hipMemoryAllocateCoherentDriver test path.
Change-Id: Iae5363685d10fce32ff80ac5d6bfba460dc2b574


[ROCm/clr commit: d13124d90f]
2021-01-28 09:47:01 -05:00
agodavar 53a0b62f82 SWDEV-268552 - HIP sample segfaults during hipModuleLoad, fix mmap bug
Change-Id: I51c6061e7ac6b2524586d96fdd69b9f084b1906a


[ROCm/clr commit: 2d2f127b8a]
2021-01-27 23:39:50 -05:00
DURGESH KROTTAPALLI 80f1fdb5b7 [dtest] Kernel Execution time fix for hipExtLaunchKernelGGL and hipExtModuleLaunchKernel API's
Fix for kernel execution time using clock rate

SWDEV-238517 for enhancing hip unit tests

Change-Id: Id06df31387ecab96f219e0c1fbcdda1609f75605


[ROCm/clr commit: d27db0f038]
2021-01-15 01:58:22 -05:00
Tao Sang c42df761a3 Fix failure for g++/hipMalloc test
Fix hardcoded /opt/rocm

Change-Id: I1ae48567eafd749d6c25bca204c1724b026be21f


[ROCm/clr commit: 12c976ef63]
2021-01-11 11:46:17 -05:00
Rahul Garg f169546403 Add IPC Events support
Change-Id: Iac2bf3d5e1d9a993bebbb066c20d300d6f05558b


[ROCm/clr commit: 3829645039]
2021-01-08 20:09:26 +00:00
Tao Sang eeb275d643 Remove hip-hcc codes: Part four
Remove __HCC__, __HCC_ONLY__, __HCC_CPP__, __HCC_C__,
__HCC_OR_HIP_CLANG__, __HIP_ROCclr__ and their guarded codes.

Remove Hcc codes from directed_tests and samples.

Remove __HIP_PLATFORM_HCC__ and __HIP_PLATFORM_NVCC__ from
some files where they are not necessary.

Add deprecation notice.

Change-Id: I1ae467eafd749d6c25bca204c1724b026be21fce


[ROCm/clr commit: d504a761ad]
2021-01-08 10:53:34 -05:00
DURGESH KROTTAPALLI da309a2db5 [dtest] Tests for hipExtLaunchKernelGGL APIs
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/clr commit: ec794ae051]
2021-01-08 00:16:54 -05:00
DURGESH KROTTAPALLI 04e34656af [dtest] Tests for hipExtModuleLaunchKernel APIs
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/clr commit: a57968fba9]
2021-01-08 00:05:57 -05:00