Gráfico de commits

1230 Commits

Autor SHA1 Mensaje Fecha
Vladislav Sytchenko 59b98a3949 Revert "SWDEV-255979 - Enable __managed__ test for amd platform"
This reverts commit 25f190a645.

Change-Id: Ib1be007535dcfb24d9e4eddbdb706d3be4acc20c
2021-06-01 17:37:30 -04:00
Joseph Greathouse 3212fdf4d6 SWDEV-288361 - Implement funnel shift operators
Change-Id: I0c73809366f2d21e75f98fdeac7fed0c7591ee34
2021-06-01 11:10:11 -04:00
cjatin 895e83851c SWDEV-277697 - [CatchTest] Disable CXX Extensions (gnu++11 etc) on CMake
Change-Id: I17abd329c16cf0a61316186558828d0524b98281
2021-06-01 06:48:05 -04:00
Anusha GodavarthySurya 995e6bff13 SWDEV-255979 - Add support for dynamic __managed__ variables
Change-Id: I62b790853ea3ab3b7ac57bab389046c627fdecce
2021-06-01 05:09:51 -04:00
Tao Sang f7e3347215 SWDEV-276853 - Add kernelVerify
Add kernelVerify for data verification and memory
reading performance checking in kernel.

Change-Id: Id3f9bcad75d643f493daf9d5f47b3a012a427179
2021-05-31 12:45:10 -04:00
Anusha GodavarthySurya 25f190a645 SWDEV-255979 - Enable __managed__ test for amd platform
Change-Id: I0cb31c1983e68e9010340770a56fc45b2a619dcd
2021-05-31 05:35:05 -04:00
Satyanvesh Dittakavi 3488785a89 SWDEV-286231 - Fix hipMallocManaged tests failure
Test is modified as hipMemAttachHost is accepted now by hipMallocManaged

Change-Id: If73d210297cde7a92960eef57a902dbd6402a173
2021-05-31 04:10:47 -04:00
Tao Sang b9d70a3da9 SWDEV-288106 - Fix g++/hipMalloc
Fix a typo

Change-Id: I71328687b2dd4a3f563571f2b755079d83dca63e
2021-05-25 17:23:36 -04:00
Tao Sang e594ae6581 SWDEV-276853 - Add test for mem perf
Add memory filling performance test for large bar device memory,
hip managed memory, conherent/non-coherent host memory and fine
grained device memory

Change-Id: Id3f9bcad45d643e493daf9d5f47b3a012a427178
2021-05-25 12:32:44 -04:00
Jatin Chaudhary 8749e231e6 SWDEV-277697 - [CatchTest] Fix Documentation, Add test to AMD specific, Add HIP Macros, New Binary for multiproc tests
Change-Id: I3783caf85c694b724ed55b778220b8ef9a39f84b
2021-05-25 07:12:54 -04:00
Satyanvesh Dittakavi 5738bf4a29 SWDEV-286830 - Fix hipStreamACb_ThrdBehaviour on windows
use sleep_for which works cross-platform
for other tests as well

Change-Id: I915444d620e9fad0b9eda93bcdd244f9956ab8d5
2021-05-24 03:18:36 -04:00
Satyanvesh Dittakavi 247a1e1fee SWDEV-278464 - Update unit test hipEventMultiThreaded
Run with multiple threads to catch possible race condition
Disable running the test by default on CI as this takes lot of time

Change-Id: I1c1a66fd5c72f8d2bf7ad120461384488b46abbd
2021-05-21 02:57:14 -04:00
Satyanvesh Dittakavi e9ac835e0e SWDEV-285521 - SWDEV-284626 - Fix P2P and Caffe2 test failures
- waitList was released before the awaitcompletion
causing stream sync after the async copies fail

- Enable the hipPeerToPeer_simple test

Change-Id: I1eeaa7e6320ab38c106902078f034dfec4c3f3ea
2021-05-21 02:54:22 -04:00
Julia Jiang e1a640bfc2 SWDEV-286322 - Fix EOL in files
Change-Id: I1746e80aceeeaa4fc5df65c858f4816d99010186
2021-05-19 14:48:53 -04:00
cjatin 93bd76672e SWDEV-277697 - Adding Infra and dependent libs: Catch2 and json parser, for new HIP Testing framework
Change-Id: Iedfa041ec9acc13eeb631ff67e1677e2fe29463d
2021-05-19 00:47:00 -04:00
Sourabh Betigeri 66b9a34f06 SWDEV-282354 - Some AMD GPUs cause clock64() to roll over faster, this changeset prevents infinite loops due to that.
Change-Id: I19d026073afa16104ffbee4705b74d37003a04d9
2021-05-11 20:40:23 -04:00
Anusha Godavarthy Surya 8cc0e04239 SWDEV-240806 - Initial commit for hipGraph and stream capture infrastructure
On StreamBegincapture captures the parameters passed to APIs and respective node will be created and added to graph
All parameters are passed to STREAM_CAPTURE macro, it checks if stream in capture mode and redirects the call to the capture function and returns
Updated hipStream and hipEvent with capture parameters
Added handling for hipStreamBeginCapture & hipStreamEndCapture

Change-Id: Ic8926a7b4336c2cc81f0b3a9a224aa392c474134
2021-05-07 17:38:16 -04:00
Ravi C Akkenapally 44ac926b08 SWDEV-281998 - TEST: StreamOperations : Split StreamWait and Update into two seperate threads
Change-Id: I0fda25857dd9f097f36ce1bafedb7689ca2beecc
2021-05-07 11:11:28 -07:00
Aaron En Ye Shi bacb89c086 SWDEV-283930 - Fix bugs in HIP Tests on Windows
Windows doesn't have headers unistd.h, sys/wait.h, so
remove them for _WIN64. Also, Windows doesn't have rand_r
so define it. Fixes builds for HIP tests:
d2dMemCpyWithPinnedHostMemory, hipMemset3DFunctional,
hipModuleLoadMultProcessOnMultGPU,
hipModuleLoadUnloadStress, hipModuleNegative,
hipStreamACb_ThrdBehaviour, hipMemcpyNegativeMThrdMSize,
hipStreamACb_MStrm_Mgpu, StreamAddCallback,
hipStreamACb_StrmSyncTiming, hipStreamACb_MultiCalls,
hipMallocConcurrency, hipMemset3DRegressMultiThread,
and hipSetGetDevice.

Change-Id: Id2f98d664716026c590d879e464ba467d4c071be
2021-04-30 21:38:45 +00:00
kjayapra-amd 31d412c292 SWDEV-245533 - Implementing Mipmap array APIs
Change-Id: I222c8d0fcbd50cdefd702462e689463bb36366d2
2021-04-30 16:33:43 -04:00
Satyanvesh Dittakavi 710b0a904b SWDEV-278464 - Unit Test For Suspected race condition
Change-Id: I561ec3073a6e6813c5f7aa50983fcf098c6ac54a
2021-04-29 23:40:43 -04:00
Tao Sang b99efb9d67 SWDEV-283515 - Fix crashing in kernel launch on MGPUS
Fix wrong mixing of current device and stream device in
ihipModuleLaunchKernel() and hipLaunchCooperativeKernel().

Fix missing hipSetDevice() in hipMemcpyWithStream* tests.

Change-Id: I09333bb40d239bb42c832df5ea16d17eeaeff5e7
2021-04-29 14:46:47 -04:00
Satyanvesh Dittakavi 991ab72d5f SWDEV-281062 - Modify the IPC tests
Remove hipSimpleIpcMem.cpp as the IPC APIs are expected to work
with different processes and not the same process. Also, modify
the hipMultiProcIpcMem.cpp to test the offset scenarios
Change-Id: Ia161fc9ab39e27f22d8ef7268e0d7669ece5cdce

Change-Id: Ic3cb79ef4aca40b4a504483eb81fd83bb8a201d9
2021-04-27 01:19:08 -04:00
German Andryeyev 17f32d4508 SWDEV-240804 - Check the managed capability
Some system have HMM disabled. Check the capability before running the test.

Change-Id: I098d04d87c12ec317b4cb57e121e702b6bba03bc
2021-04-26 14:10:57 -04:00
DURGESH KROTTAPALLI f9d422bcbd SWDEV-273550 - Add Directed Tests for HIP APIs
[dtest] Tests for hipMemcpy2DFromArray
        and hipMemcpy2DFromArrayAsync APIs

1. Negative scenarios for both the APIs
2. Functional size check scenarios for both APIs
3. Invoke the API from Peer Device Context
4. Simple scenarios for both APIs
5. Pinned Host Memory from same & multi GPU

Change-Id: I80c84ec3f9722d18683d31be65caa1bd64054da6
2021-04-23 13:07:08 -04:00
Yaxun (Sam) Liu 932d34dc6e SWDEV-283048 - Fix hipTestFMA
This test is incorrect about _Float16 overloading. Need to keep the test
passing for both old and new compiler until the compiler change is in
mainline.

Change-Id: I2f9be8957282fd0579c74f1e9f23e65c4484f3a2
2021-04-22 15:07:16 -04:00
Rahul Garg 22fe144b08 SWDEV-229520 - Reenable hipEventIpc test
Change-Id: Ib40fb07a07cc447182e23664573c5e37a1194a32
2021-04-21 13:55:15 -04:00
Tao Sang 20fd6b8a66 SWDEV-279657 - Fix hipMallocManaged-N256M failure
Add concurrentManagedAccess detection in hipMallocManaged test.
Skip test when device doesn't support concurrentManagedAccess.

Change-Id: Ie54046feef3baba857a7068972ec1fc1a60c2dfd
2021-04-20 09:07:31 -04:00
sumanthtg 248785e3d1 SWDEV-238517 - [dtest] Additional Tests for hipHostMalloc()
New Tests added for
 - hipHostMalloc() api.

SWDEV-238517 for enhancing hip unit tests

Change-Id: Id237ab6cd2445216cd7bd9b8189c22a36ad66b7c
2021-04-20 00:44:30 -04:00
Sourabh Betigeri 0a0b026304 SWDEV-256723 - Added group partitioning feature in ROCm CG.
Change-Id: Ie54046feef3baba857a7068972ec1fc0a60c2df9
2021-04-19 18:53:17 -04:00
DURGESH KROTTAPALLI 6d0d2aabd6 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
2021-04-19 08:48:15 -04:00
sumanthtg ee8b053a3e SWDEV-278967 - Changes to handle dtest failures on cuda runtime version 11.2
Change-Id: I79c87d40b77b4e4beb7e3d0a9ea396ad918a81e8
2021-04-14 12:38:46 -04:00
Aaron Enye Shi 49696c568f 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
2021-04-13 16:13:56 -04:00
Satyanvesh Dittakavi 191ce1dd05 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
2021-04-09 02:53:15 -04:00
Sarbojit Sarkar 9cbb283771 SWDEV-280131 - Fix __half2 member access bug
Change-Id: Ic11750d18e4ba47446a7e494c3089a19cb4df783
2021-04-07 12:12:02 -04:00
Rupam Chetia c9ef2adf6a 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
2021-04-07 01:44:39 -04:00
Rupam Chetia bbc933c914 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
2021-04-06 07:54:29 -04:00
Sourabh Betigeri 2ba421f784 SWDEV-274727 - Disabling tests temporarily
Change-Id: I695daebe15f592afdfee8e4efe4d8966b6e9922a
2021-03-30 13:02:19 -04:00
sumanthtg 5a84691e52 SWDEV-278478 - hipDeviceGetPCIBusId-vs-lspci test enabled only for linux environment
Change-Id: Ia86174505d912a32b07e8e959adfba6391c3284d
2021-03-30 09:28:28 -04:00
sumanthtg e7ee877a50 SWDEV-278478 - Fix for hipDeviceGetPCIBusId-vs-lspci test failure
Change-Id: I7c722633ba8023f03bb64f5fb32b31f10015c327
2021-03-23 21:49:17 +05:30
Sourabh Betigeri c90c7a5cf1 SWDEV-274727 - The callback associated with the event was being processed after the event is destroyed. Commit after resolving merge conflict.
Change-Id: Ia7383c83318ca0c2a4f21f7aaf22b1cebd828cf0
2021-03-18 15:08:58 -04:00
Ravi C Akkenapally 397bac37a3 SWDEV-276827 - Stream Operations: match API with CUDA
Change-Id: Ia79a950561e97df3b2229f76f5512dede2babf98
2021-03-18 07:52:29 -07:00
Tao Sang 629ea5fe19 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
2021-03-16 17:12:08 -04:00
jujiang 3dea940498 SWDEV-271283, SWDEV-274749 - Fix hipLaunchParmFUnctor test failure
Change-Id: I568eba45403feae6f50eceab4a6bcc76756fd5bd
2021-03-15 14:42:41 -04:00
Saleel Kudchadker 47e44117cd SWDEV-271010 - Add 512KB transfer size for test
Add a new transfer to hipPerfBufferCopySpeed test

Change-Id: Ia7ec9a89e8789bf16fd5f86b08521287049c1e77
2021-03-11 11:01:54 -08:00
kjayapra-amd 57615530a7 SWDEV-276169 - Multiprocess IPC tests for Events and Memory.
Change-Id: I4a7af60e732de234a535574aa8597a7abd0b899b
2021-03-11 11:16:23 -05:00
Lakhan singh Thakur d4041fae4a 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
2021-03-10 10:14:36 -05:00
Vladislav Sytchenko 55377dfee2 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
2021-03-08 18:12:42 -05:00
Vladislav Sytchenko 4dd4d8c05f 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
2021-03-08 18:11:33 -05:00
Tao Sang cc086cb08c SWDEV-274725 - Enable hiprtc test
Enable hiprtc test for Rocclr.
Remove unnecessary LINK_OPTIONS hiprtc.

Change-Id: I9ec74c475161b3e31df47d193449023e921f2923
2021-03-04 15:07:38 -05:00