Grafico dei commit
116 Commit
Autore SHA1 Messaggio Data
Tao Sang fd5ef38166 Make directed_test support static libs
1.Make directed_test apps linked against static libs
    of hip, rocclr, rocr, roct and amd_comgr.
    2.Remove custom_target amdhip64_static_combiner.
    3.Support EXCLUDE_HIP_LIB_TYPE <static|shared>.
    4.Simplify argument list parsing.
    5.Install rocclr when rocm is installed.
    6.Fix some original small bugs.

Revert "Revert "Make directed_test support static libs""
This reverts commit 4a8a95a8e9.

Change-Id: I918eeae94487e5e2ff5bfde083667ac65fb6e702


[ROCm/hip commit: bcd067f462]
2020-10-26 12:39:58 -04:00
agodavar 13436a7e1f cmake hip-rocclr as default build,change HIP_PLATFORM to amd|nvidia
Change-Id: I59d2e15b297b6ca2d5eee1a6dee642bdb01a3839


[ROCm/hip commit: d10124e1d7]
2020-10-21 07:26:14 -04:00
Tao Sang 4a8a95a8e9 Revert "Make directed_test support static libs"
This reverts commit 37282c6132.

Reason for revert: <INSERT REASONING HERE>

Change-Id: Ib2d1084ea21461f70f96f95c6025a08f88288357


[ROCm/hip commit: 5b7533e49f]
2020-10-12 00:01:13 -04:00
Tao Sang 37282c6132 Make directed_test support static libs
1.Make directed_test apps linked against static libs
of hip, rocclr, rocr, roct and amd_comgr.
2.Remove custom_target amdhip64_static_combiner.
3.Support EXCLUDE_HIP_LIB_TYPE <static|shared>.
4.Simplify argument list parsing.
5.Fix hip_pch.o missing issue in samples' build.
6.Fix some original small bugs.

Change-Id: I30f5e65367613152ce86b80b13e1c9f2a28da803


[ROCm/hip commit: b41a769517]
2020-10-08 22:46:58 -04:00
German Andryeyev 4577f0f1bb Use more managed memory interfaces
Add extra API calls for managed memory: hipMemAdvise, hipMemPrefetchAsync,
hipMemRangeGetAttribute

Change-Id: Ifb09744acdf7582d278453707373c89c30e3ed03


[ROCm/hip commit: 67c19cb10b]
2020-10-07 16:45:25 -04:00
Vladislav Sytchenko e4caaa2a77 Revert "Revert "Merge branch 'amd-master-next' into amd-npi-next""
This reverts commit 28b17d3dbd.

Reason for revert: <INSERT REASONING HERE>

Change-Id: I92ceb171e31026ed1864704cef2fc1497b883ef9


[ROCm/hip commit: ad2d55c144]
2020-10-05 13:20:58 -04:00
Vladislav Sytchenko 28b17d3dbd Revert "Merge branch 'amd-master-next' into amd-npi-next"
This reverts commit 258d79bca7.

Reason for revert: <INSERT REASONING HERE>

Change-Id: I53322718dadde2c98f96140b8e260ec7ee9ef721


[ROCm/hip commit: 374ead1d19]
2020-10-05 13:02:39 -04:00
Lakhan singh Thakur 0b3c2c3c27 [dtest] Additional tests for hipMallocManaged() api
5 scenarios were added for hipMallocManaged including negative
test.

SWDEV-238517 for enhancing hip unit tests

Change-Id: Ibba53fb64502d6df798e4e63100dcb8c5f94553f


[ROCm/hip commit: 8f4cc3017f]
2020-09-24 10:05:21 -04:00
kjayapra-amd 722bfd0a5d SWDEV-253349 - Add a SKIP state for hip directed tests when HIP_BRINGUP_SKIP macro is used.
Change-Id: If176cf775e568d4b32982127731223fe96a38f0d


[ROCm/hip commit: d1f82881f6]
2020-09-23 16:46:21 -04:00
Sumanth Tumbalam Gooty 7fde2122aa [dtest] Tests for hipMalloc
1. API validation
2. Validate the memory status after hipMalloc()
3. Test repeated hipMalloc() Calls, call in multiple threads
4. Parallel hipMalloc() from parent and child processes
5. hipMalloc() from multiple processes on multiple GPUs

SWDEV-238517 for enhancing hip unit tests

Change-Id: Ie152999d7a203a51704d2888ccc1ca866a2e1b05


[ROCm/hip commit: 3a4b74a3a0]
2020-09-23 09:20:01 -04:00
Lakhan singh Thakur 892b5046ff [dtest] Tests for hipIpcGetMemHandle()
Tests allocation of memory on various GPUs and pass on the IPC mem handle to child process.
Child process attaches to the mem handle and uses the memory on various GPUs

SWDEV-238517 for enhancing hip unit tests

Change-Id: I7babc7725813e05d651057beef6a8bec6f62a49b


[ROCm/hip commit: d623445c65]
2020-09-22 23:49:30 -04:00
mkumarmi 7f4fd6e62e [dtest] Disable few tests on NVCC platform
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]
2020-09-18 04:34:00 -04:00
Rahul Garg d0229930f9 Revert "[dtest] Additional tests for Memcpy"
This reverts commit fc61d76630.

Reason for revert: All the PSDBs on the CI are failing with the below error and its been root caused to this commit:
......................................................................................... Passed 0.59 sec 99% tests passed, 1 tests
failed out of 211 Total Test time (real) = 287.02 sec The following tests FAILED: 139 - directed_tests/runtimeApi/memory/hipMemcpyNegativeMThrdMSize_Negative_tests.tst
(Child aborted) Errors while running CTest Restoring clocks to: auto

Change-Id: I4ea0e14ba5f92cd61677f4a3b9482fea00902310


[ROCm/hip commit: 280d300320]
2020-09-01 00:48:20 -04:00
Lakhan singh Thakur fc61d76630 [dtest] Additional tests for Memcpy
APIs tested: hipMemcpy, hipMemcpyAsync, hipMemcpyHtoD, hipMemcpyHtoDAsync
             hipMemcpyDtoH, hipMemcpyDtoHAsync, hipMemcpyDtoD,
             hipMemcpyDtoDAsync

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

SWDEV-238517 for enhancing hip unit tests

Change-Id: Iace19cc54e865fae8450448d6f37abed88597f19


[ROCm/hip commit: 858b7e027e]
2020-08-20 16:41:57 -04:00
Jatin Chaudhary 2982f07b9c Fixing/Disabling tests on nvcc path
Change-Id: I7ed4a1246943867482ff595d5f98bb25bd79074b


[ROCm/hip commit: e7eaafe165]
2020-07-30 00:39:07 -04:00
Satyanvesh Dittakavi 74f13c1f9a SWDEV-244772 - Fix dtest hipMemcpyWithStreamMultiThread.cpp.
hipSetDevice is not used correctly to allocate on multiple devices in mGPU setup.
Due to which hipMalloc was called on the same device on multiple threads leading to out of memory issues on some devices with lesser memory.

Change-Id: I0e5b1bc028b9ecb11bd40c3a5edf715f8bd721ff


[ROCm/hip commit: 8fc4d64d2a]
2020-07-22 00:52:14 -04:00
Sudheer Kumar 877f2904a9 [dtest] Enhanced tests to cover multiple hipmemset and hipmemsetAsync apis
SWDEV-238517 for enhancing hip unit tests

Change-Id: Iba2c419a4487955f34b4f19abe174ef427d289d8


[ROCm/hip commit: 50f285ad67]
2020-07-15 01:13:07 -04:00
rohit pathania 1336a9de0b [dtest] hipMemcpyWithStream API multithreaded test scenarios
1.hipMemcpyWithStream with one stream
2.hipMemcpyWithStream with two streams
3.hipMemcpyWithStream multiGPU with one stream
4.hipMemcpyWithStream with kind DtoH
5.hipMemcpyWithStream with HtoH
6.hipMemcpyWithStream with DtoD
7.hipMemcpyWithStream with Default kind
8.hipMemcpyWithStream with Default kind on same device
9.hipMemcpyWithStream with DtoD on same device

SWDEV-238517 for enhancing hip unit tests

Change-Id: I5f55a12bdd7c8d28fcb06db94a491c2ad5ee3004


[ROCm/hip commit: 32a6e854b7]
2020-06-25 12:51:23 -04:00
kjayapra-amd b32c033585 SWDEV-209747 - Staging Copy will not be supported in HIP, adjust test case accordingly.
Change-Id: Iad616ef3990d539cdb82bbd8a22ea2124f7abe50


[ROCm/hip commit: 04b58e6e50]
2020-06-23 13:14:17 -04:00
rohit pathania 670a34e8e2 [ dtest ] Added different test scenario with hipMemcpyWithStream
- Test with one, two streams
- Test Multi-gpu (one stream per gpu)
- Test D-D (on same device/different devices).  Can discover issues
  when devices are on same or different root complexes.
- Test H-D/Default

SWDEV-238517 for enhancing hip unit tests

Change-Id: I8031a7eebe2f9c8c0e0996e2c7accb09ac0b96d4


[ROCm/hip commit: d701632e01]
2020-06-18 10:31:01 -04:00
Lakhan Singh Thakur 55f368c3a0 [dtest] merge 'Adding the two test cases to cover scenarios observed in SWDEV-181598.'
SWDEV-238517 for enhancing hip unit tests

Change-Id: Ie61145b46c89b2e970af0ab11e22b6f6286ec90f


[ROCm/hip commit: fb77b2497c]
2020-06-05 09:10:23 -04:00
German Andryeyev 20e64e1450 Add a test case for async double memset
Change-Id: I8a1df610c8d3d942651f258e7812e8697067c347


[ROCm/hip commit: 4503d44e12]
2020-05-20 12:52:29 -04:00
agodavar e5c6555eee Fix hipMemset for unaligned ptr, correct offset required by ROCclr per aligment and testcase to validate unaligned ptr
Change-Id: Ib1a0f9d1556d09cf72a12a90cad2e27c6d9c6a1c


[ROCm/hip commit: 458a966aa1]
2020-05-16 02:38:14 -04:00
Payam 0c8b343931 name change vdi to rocclr
Change-Id: I06d198bbb4a499e153b290b73a92afed3553b252


[ROCm/hip commit: c5f76c3de3]
2020-05-06 09:14:30 -04:00
Maneesh Gupta 8e137a6ec1 Merge in the rocclr based hip runtime (#2032)
* Merge master-next changes in master (include vdi development in master branch)



[ROCm/hip commit: a0b5dfd625]
2020-04-23 09:12:06 -07:00
Sarbojit2019 9e98e69b7a Fix for segfault seen if invalid kind is passed to hipMemcpy (#1937)
Fixes SWDEV-224941

[ROCm/hip commit: 3e363047d5]
2020-03-26 17:04:43 +05:30
Rahul Garg f1746197c7 Fix hipMemcpy3D (#1798)
Fixes #1790 and #1791. hipMemcpy3D still requires further refactoring for different input and output combinations.

[ROCm/hip commit: 8c5e5e435b]
2020-02-17 19:35:35 +05:30
Alex Voicu 1f5ecc0f6a Fix late-coming issues. (#1724)
Implementation for hipMemcpyWithStream.


[ROCm/hip commit: 75a11330aa]
2019-12-23 19:11:24 +05:30
Vladislav Sytchenko 6015efe6f5 Add comments explaining choice on the cap for system memory on Windows.
[ROCm/hip commit: bf3df9d7c0]
2019-12-13 21:38:27 -05:00
Vladislav Sytchenko 29ca9f7d53 Add explicit cast when computing the available amount of system memory.
[ROCm/hip commit: 12634879e2]
2019-12-13 21:37:30 -05:00
Vladislav Sytchenko 9dade23425 Reduce the amount of free host memory to 40% of what is reported on Windows, otherwise we can run into OOM situations.
[ROCm/hip commit: b12c53cceb]
2019-12-11 20:21:12 -05:00
Rahul Garg ebdd811632 Revert - Changes related to hipMemcpyWithStream (#1718)
Reverting #1673, #1697 and #1707.
Support for hipMemcpyWithStream and memcpy optimizations, will be brought in again once issues seen with these are resolved independently.

[ROCm/hip commit: e53fc316f1]
2019-12-06 09:51:53 +05:30
Rahul Garg fa87abd58a Fix hipMemcpyWithStream (#1707)
* Fix hipMemcpyWithStream
* Add a dtest for the same.


[ROCm/hip commit: 892d2a562e]
2019-12-04 11:56:23 +05:30
Rahul Garg 849ae2bff0 [dtest] Fix hipMemset2D test (#1579)
Reverts changes made in #1399. This is a RT api test. For testing hipMemAllocPitch , a new test should be written and that should use correct memset API.

[ROCm/hip commit: 12e1a86ec1]
2019-10-25 15:44:05 +05:30
Vladislav Sytchenko fd17d3b737 _aligned_malloc() on Windows first takes size, then alignment, which is the opposite of how the similar function behaves on Linux. Memory allocated by it also has to be freed using _aligned_free(), unlike Linux where we can use regular free().
Edit aligned_alloc() macro and add a aligned_free() one to align with the above behaviour.


[ROCm/hip commit: 8f0a226660]
2019-10-17 18:58:32 -04:00
Vladislav Sytchenko 779d723ac2 hipMemset2D and hipMemset3D tests should be passing by default.
[ROCm/hip commit: c747b77ac1]
2019-10-16 11:02:38 -04:00
Vladislav Sytchenko 948dd510eb In the hipMemset2D and hipMemset3D tests synchronize with the default stream after performing an async memset.
[ROCm/hip commit: f5af263aba]
2019-10-15 17:15:49 -04:00
Vladislav Sytchenko 6180a9edb3 Update indentation in the hipMemset3D test. Replace all tabs with four spaces.
[ROCm/hip commit: 346bfa90d6]
2019-10-15 15:29:14 -04:00
Vladislav Sytchenko 5a29d10dbb Add async subtest to hipMemSet3D
[ROCm/hip commit: 00425bdf3d]
2019-10-15 14:24:04 -04:00
Vladislav Sytchenko 28089f61b6 hipMemset2D test should pass only if both async and sync subtests pass.
[ROCm/hip commit: 3db2ecc52b]
2019-10-15 14:20:14 -04:00
ansurya b37210badc Fix for directed tests failure (#1511)
directed_tests/runtimeApi/module/hipLaunchCooperativeKernel.tst - Disabling test temporarily until driver support is available.
directed_tests/runtimeApi/memory/hipArray.tst - Disabling test temporarily to reimplement it correctly.

[ROCm/hip commit: 87834500b9]
2019-10-10 19:58:41 +05:30
ansurya 66e94b1b1f Added new Memory API's (#1399)
Added new memory API's hipMemAllocPitch, hipMemAllocHost, hipMemsetD16, hipMemsetD16Async, hipMemsetD8Async
Modified to support all scenarios hipMemcpyParam2DAsync, hipMemcpyParam2D.


[ROCm/hip commit: ba9c6e13e4]
2019-10-04 13:36:31 +05:30
AlexBinXie d86d4d674d [hip]Skip test when hipHostMallocCoherent is not supported by implementation (#1380)
[ROCm/hip commit: 5ed1f3e2c8]
2019-09-16 08:31:43 +00:00
Rahul Garg 971b75588e [dtests] refactor windows specific changes (#1313)
* [dtests] refactor windows specific changes

* Refactor hipMemoryAllocateCoherentDriver - PR- 1309

* Fix missing z in _putenv_s

* Revert "Fix missing z in _putenv_s"

This reverts commit 099a1b20a5c75c5f122d57c0ad2bca01745cdc9c.

* Refactor changes from PR 1299

* Update hipEnvVarDriver.cpp


[ROCm/hip commit: 44422065a1]
2019-08-16 02:13:00 +00:00
amd-lthakur 07ee0e825b [dtests] Fix build issues with hipMemoryAllocateCoherentDriver.cpp on windows (#1309)
Compilation error being observed due to popen(), pclose() and setenv() linux calls on windows. Replaced with appropriate calls on windows.

[ROCm/hip commit: 9b31d26237]
2019-08-09 11:53:16 +00:00
amd-lthakur 45652a1fba [dtests] Fix build issue with hipMemcpy_simple.cpp on windows (#1306)
Compilation error being observed on windows due to aligned_alloc() call. Mapped the call to _aligned_malloc() for windows.

[ROCm/hip commit: 9abae7114c]
2019-08-09 11:52:46 +00:00
Aaron Enye Shi 85fa58c117 Fix hipMemcpy-size test running out of Host Mem (#1224)
* Fix hipMemcpy-size test running out of Host Mem

The hipMemcpy-size uses a maxElem calculated from the total GPU mem /8. Then it will allocate 4 times that amount of host memory. This tests begins failing when there is not enough host memory, such as on systems with 32GB GPU mem, and 16GB RAM. This fixes the test if not enough host memory is available on the system.

* Add windows support to hipMemcpy-size fix

* avoid linking extra libs for windows

* HIPMemcpy-size Remove freeCPU including swap


[ROCm/hip commit: 0de4caa085]
2019-07-24 07:49:20 +00:00
Maneesh Gupta fa07d40cdd [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074


[ROCm/hip commit: 9f2d1453fb]
2019-05-09 09:59:18 +05:30
Rahul Garg c01236f679 Add hipMallocManaged default functional support (#1036)
* Add hipMallocManaged default functional support

* Fix build error

* Add dtest


[ROCm/hip commit: 2bc2c46d4d]
2019-04-24 16:50:03 +05:30
Rahul Garg d0951a9c20 Fix D2DAsync test
[ROCm/hip commit: e5e7651a4a]
2019-04-18 07:35:06 +05:30