Commit Graph

1060 Commits

Author SHA1 Message Date
Aaron En Ye Shi 26cf8d399e SWDEV-292904 - Extend HIP coherency tests to gfx940
Change-Id: I54d57572d55c302ebaed29c7e11570e3d1b44a8e


[ROCm/hip commit: 9fbd19a675]
2021-07-19 12:13:53 -04:00
Tao Sang d33b577c95 SWDEV-266829 - Enable more NV DTests
Enable NV DTests as many as possible.

Change-Id: I3fe6dba35a7a140a9a19df197b7885df83d28044


[ROCm/hip commit: 4b5468e8e6]
2021-07-19 11:07:43 -04:00
Tao Sang f985ba8b26 SWDEV-295037 - Fix passed() in DTests
passed() should not call exit(0) which will prevent object
destructor being called.

Change-Id: Ibaee0d85cb616727dc5db557bb9422702670b688


[ROCm/hip commit: c74e2da333]
2021-07-19 10:59:04 -04:00
Tao Sang 65dbac4ec0 SWDEV-294582 - Fix hipStdComplex in NV
Use cuda::std instead of std name space for complex
operations.

Change-Id: I43b23384ac7a129fcd7f41204f796105576cd628


[ROCm/hip commit: 63586279ba]
2021-07-19 10:50:11 -04:00
Tao Sang 872b6abec3 SWDEV-295381 - Fix hipSimpleAtomicsTest
Fix hipSimpleAtomicsTest failure on amd and nvidia devices.

Change-Id: I43b23384ab70129ccd7f41204f796105576cd605


[ROCm/hip commit: a2fdc8cfbd]
2021-07-15 20:45:51 -04:00
Jatin Chaudhary d89d622678 SWDEV-283267 - Add rtc document and remove hip header from tests
Change-Id: I43a23384ab70128ccd7f41204f796105576cd604


[ROCm/hip commit: b337a5586b]
2021-07-14 11:00:38 -04:00
Anusha GodavarthySurya 73a73db651 SWDEV-240806 - Added Implementation for few more graph APIs
Change-Id: I1e443cf1b4e3a1e85f6fb9c1db8fdfa7c1fdfe06


[ROCm/hip commit: 6e7ea5b612]
2021-07-14 01:58:03 -04:00
Anusha GodavarthySurya 6bbe132eb7 SWDEV-240806 - Enable graph test on nvidia platform
Change-Id: Ia196dd7c650693155f786871671aec4dda0e886f


[ROCm/hip commit: 9c9b62f0b8]
2021-07-08 23:27:20 -04:00
Anusha GodavarthySurya 51a500812e SWDEV-240806 - updated hipMemcpyKind in nvidia tyes from enum to typedef
Change-Id: Id6a100257d47211cc9868ba84a2964302e4f069c


[ROCm/hip commit: 4025725ed6]
2021-07-08 02:54:36 -04:00
agunashe a4ff63a29b SWDEV-293742 - Update copyright end year
Change-Id: I2cb7bbd9a6d9da28116ba9dd9cec4e60525444e2


[ROCm/hip commit: d529637fbc]
2021-07-07 12:57:23 -04:00
Satyanvesh Dittakavi 49bdc84f41 SWDEV-293819 - Fix HIP Directed tests build failure
- add std=c++11 to the g++ test hipMalloc.cpp to avoid failure on centos
- Also, enabled gcc test hipMalloc.c on amd platform

Change-Id: I3ff6dba05a70140a9a19df107b7885df83d28041


[ROCm/hip commit: 966741a0b3]
2021-07-07 06:28:17 -04:00
Satyanvesh Dittakavi cac5c6a37c SWDEV-292618 - Enable/Fix more dtests on Nvidia Platform
Change-Id: I0fdac4ddefa693674dfce66ba29306f34ad886c9


[ROCm/hip commit: f5703d57cd]
2021-07-07 03:23:42 -04:00
Satyanvesh Dittakavi 7a49cdb7a0 SWDEV-292618 - Enable/Fix few of the dtests on Nvidia Platform
Change-Id: I6f4e37b293aac9054a768f9d692b914f52d42756


[ROCm/hip commit: 57569c62f4]
2021-06-30 01:23:29 -04:00
Anusha GodavarthySurya 1b0be33247 SWDEV-240806 - Enable hipgraph test on amd platform
Change-Id: I470a9c410704ec2074eb32030311df671da5e8bb


[ROCm/hip commit: 7c5afff964]
2021-06-22 01:41:25 -04:00
Tao Sang f37d157aaf SWDEV-291009 - Fix LaunchCoopMultiKernel on NV
Fix compiling error of hipLaunchCoopMultiKernel on
NV A100.
Fix test failure on all NV devices.

Change-Id: Iba20caa0e9021480378625506197384c275a3289


[ROCm/hip commit: f70b109cc3]
2021-06-18 09:07:17 -04:00
Tao Sang 5000aa0f9b SWDEV-291011 - Fix ModuleLaunchKernel on NV
Should not add extra for non-parameter dummyKernel()
in hipModuleLaunchKernel()

Change-Id: If6f881ebb027bd3e8435d3de5295b00277e96a6a


[ROCm/hip commit: 87ba31e596]
2021-06-16 11:52:38 -04:00
Tao Sang 3a7e5a87ca SWDEV-291001 - Disable sincos() for NV
Disable sincos() for NV temporarily in order
to prevent kernel launch failure for NVA100.

Change-Id: Ic9ec976c5c486c4e1d3b83e1578081673f97efa3


[ROCm/hip commit: fd50af8c77]
2021-06-15 13:31:20 -04:00
cjatin 96abeb55fa SWDEV-245414 - Add Copyright and exlude mipmap test on Nvidia platform
Change-Id: Iba29caa0e9021488378625506197384c275a3282


[ROCm/hip commit: 575be36c2e]
2021-06-07 11:15:00 -04:00
Tao Sang 7a932782e2 SWDEV-287768 - Fix hipTestClock test
Use long long instead of int as clock64() return.

Change-Id: Id3e4645c05959e13f58efd88bc43f3a1d3e50d59


[ROCm/hip commit: 792415f960]
2021-06-04 15:45:07 -04:00
Vladislav Sytchenko f112ad301e Revert "SWDEV-255979 - Enable __managed__ test for amd platform"
This reverts commit bbd07b0bd9.

Change-Id: Ib1be007535dcfb24d9e4eddbdb706d3be4acc20c


[ROCm/hip commit: 88242ad446]
2021-06-01 17:37:30 -04:00
Joseph Greathouse 9f962f4d74 SWDEV-288361 - Implement funnel shift operators
Change-Id: I0c73809366f2d21e75f98fdeac7fed0c7591ee34


[ROCm/hip commit: bec284b26a]
2021-06-01 11:10:11 -04:00
Anusha GodavarthySurya 878ce92905 SWDEV-255979 - Add support for dynamic __managed__ variables
Change-Id: I62b790853ea3ab3b7ac57bab389046c627fdecce


[ROCm/hip commit: d9fffacfb3]
2021-06-01 05:09:51 -04:00
Tao Sang 230088d790 SWDEV-276853 - Add kernelVerify
Add kernelVerify for data verification and memory
reading performance checking in kernel.

Change-Id: Id3f9bcad75d643f493daf9d5f47b3a012a427179


[ROCm/hip commit: 9ba66fc157]
2021-05-31 12:45:10 -04:00
Anusha GodavarthySurya bbd07b0bd9 SWDEV-255979 - Enable __managed__ test for amd platform
Change-Id: I0cb31c1983e68e9010340770a56fc45b2a619dcd


[ROCm/hip commit: e519600383]
2021-05-31 05:35:05 -04:00
Satyanvesh Dittakavi c61110559f SWDEV-286231 - Fix hipMallocManaged tests failure
Test is modified as hipMemAttachHost is accepted now by hipMallocManaged

Change-Id: If73d210297cde7a92960eef57a902dbd6402a173


[ROCm/hip commit: da9564e302]
2021-05-31 04:10:47 -04:00
Tao Sang 62d33a3b96 SWDEV-288106 - Fix g++/hipMalloc
Fix a typo

Change-Id: I71328687b2dd4a3f563571f2b755079d83dca63e


[ROCm/hip commit: adf58d4ef1]
2021-05-25 17:23:36 -04:00
Satyanvesh Dittakavi a951797224 SWDEV-286830 - Fix hipStreamACb_ThrdBehaviour on windows
use sleep_for which works cross-platform
for other tests as well

Change-Id: I915444d620e9fad0b9eda93bcdd244f9956ab8d5


[ROCm/hip commit: 03ae7251de]
2021-05-24 03:18:36 -04:00
Satyanvesh Dittakavi cbc620f5e7 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


[ROCm/hip commit: f300d11931]
2021-05-21 02:57:14 -04:00
Satyanvesh Dittakavi 802fee3078 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


[ROCm/hip commit: acafb344c0]
2021-05-21 02:54:22 -04:00
Julia Jiang 6bef7b2b86 SWDEV-286322 - Fix EOL in files
Change-Id: I1746e80aceeeaa4fc5df65c858f4816d99010186


[ROCm/hip commit: f8a08e2429]
2021-05-19 14:48:53 -04:00
Sourabh Betigeri 31089e6ce9 SWDEV-282354 - Some AMD GPUs cause clock64() to roll over faster, this changeset prevents infinite loops due to that.
Change-Id: I19d026073afa16104ffbee4705b74d37003a04d9


[ROCm/hip commit: 6bcbb61e5f]
2021-05-11 20:40:23 -04:00
Anusha Godavarthy Surya a76f840701 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


[ROCm/hip commit: c35ba37287]
2021-05-07 17:38:16 -04:00
Ravi C Akkenapally d5ee250204 SWDEV-281998 - TEST: StreamOperations : Split StreamWait and Update into two seperate threads
Change-Id: I0fda25857dd9f097f36ce1bafedb7689ca2beecc


[ROCm/hip commit: db7421cb10]
2021-05-07 11:11:28 -07:00
Aaron En Ye Shi 34625c7a88 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


[ROCm/hip commit: 9edd31100d]
2021-04-30 21:38:45 +00:00
kjayapra-amd 06e4e7ee8f SWDEV-245533 - Implementing Mipmap array APIs
Change-Id: I222c8d0fcbd50cdefd702462e689463bb36366d2


[ROCm/hip commit: 9c07201c6b]
2021-04-30 16:33:43 -04:00
Satyanvesh Dittakavi a2b81ae792 SWDEV-278464 - Unit Test For Suspected race condition
Change-Id: I561ec3073a6e6813c5f7aa50983fcf098c6ac54a


[ROCm/hip commit: 98d1acf1f2]
2021-04-29 23:40:43 -04:00
Tao Sang bed2381766 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


[ROCm/hip commit: a95ff95bf7]
2021-04-29 14:46:47 -04:00
Satyanvesh Dittakavi 1b4f397904 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


[ROCm/hip commit: 3a6324f5d1]
2021-04-27 01:19:08 -04:00
German Andryeyev c7e4a8c30a SWDEV-240804 - Check the managed capability
Some system have HMM disabled. Check the capability before running the test.

Change-Id: I098d04d87c12ec317b4cb57e121e702b6bba03bc


[ROCm/hip commit: b777f4f010]
2021-04-26 14:10:57 -04:00
DURGESH KROTTAPALLI 88ca345e3a 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


[ROCm/hip commit: b36936645d]
2021-04-23 13:07:08 -04:00
Yaxun (Sam) Liu 416d9fbfb6 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


[ROCm/hip commit: 6eabbc83f7]
2021-04-22 15:07:16 -04:00
Rahul Garg b384753745 SWDEV-229520 - Reenable hipEventIpc test
Change-Id: Ib40fb07a07cc447182e23664573c5e37a1194a32


[ROCm/hip commit: f2c96993e1]
2021-04-21 13:55:15 -04:00
Tao Sang abcbcee510 SWDEV-279657 - Fix hipMallocManaged-N256M failure
Add concurrentManagedAccess detection in hipMallocManaged test.
Skip test when device doesn't support concurrentManagedAccess.

Change-Id: Ie54046feef3baba857a7068972ec1fc1a60c2dfd


[ROCm/hip commit: 60e2b1299c]
2021-04-20 09:07:31 -04:00
sumanthtg 63ae7621ae SWDEV-238517 - [dtest] Additional Tests for hipHostMalloc()
New Tests added for
 - hipHostMalloc() api.

SWDEV-238517 for enhancing hip unit tests

Change-Id: Id237ab6cd2445216cd7bd9b8189c22a36ad66b7c


[ROCm/hip commit: 9c86e4a8f5]
2021-04-20 00:44:30 -04:00
Sourabh Betigeri 4c043fc89f SWDEV-256723 - Added group partitioning feature in ROCm CG.
Change-Id: Ie54046feef3baba857a7068972ec1fc0a60c2df9


[ROCm/hip commit: 70af64121b]
2021-04-19 18:53:17 -04:00
DURGESH KROTTAPALLI 38ddfaefbb 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/hip commit: 03a0c84ad4]
2021-04-19 08:48:15 -04:00
sumanthtg 578ce42bc5 SWDEV-278967 - Changes to handle dtest failures on cuda runtime version 11.2
Change-Id: I79c87d40b77b4e4beb7e3d0a9ea396ad918a81e8


[ROCm/hip commit: 5476c9877b]
2021-04-14 12:38:46 -04:00
Aaron Enye Shi c7cc093f1a 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/hip commit: eed3fe6da9]
2021-04-13 16:13:56 -04:00
Satyanvesh Dittakavi d7ce1b93ea 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/hip commit: 68161ff0dd]
2021-04-09 02:53:15 -04:00
Sarbojit Sarkar 47c83726a4 SWDEV-280131 - Fix __half2 member access bug
Change-Id: Ic11750d18e4ba47446a7e494c3089a19cb4df783


[ROCm/hip commit: 83a25eb5b5]
2021-04-07 12:12:02 -04:00