AI/rocm-systems
2
0
Rozštěpit 0
Zdrojový kód Úkoly Pull requesty Akce Balíčky Projekty Vydání Wiki Aktivita
3 991 Commity 3 Větve 0 Značky
aeba964a7e4c0815bf5a2713330cc2610f52f8f3
Graf commitů

75 Commity

Autor SHA1 Zpráva Datum
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
Maneesh Gupta 54c72c1079 Update hipMemset.cpp 
Address build issues on nvcc path.

[ROCm/hip commit: 51f29b9cee]
 2019-03-05 12:11:11 +05:30
Wen-Heng (Jack) Chung 085c6c15b2 Add direct test for hipMemsetD32 and hipMemsetD32Async 
[ROCm/hip commit: bfde8a7fab]
 2019-03-04 17:20:32 +00:00
Rahul Garg 7a9ebee08a Fix review comments 
[ROCm/hip commit: 131c0ea326]
 2019-03-02 23:38:37 +05:30
Rahul Garg 4093c03dd7 Fix hipMemset test for HIP/NVCC 
[ROCm/hip commit: 77c6d5451f]
 2019-03-01 03:46:57 +05:30
Rahul Garg fa0c9d8a73 Update hipMemset test 
[ROCm/hip commit: 026dc9457e]
 2019-02-28 06:54:49 +05:30
Rahul Garg 42a683e159 Remove redundant arguments from hipMemset3D test 
[ROCm/hip commit: 4272119eeb]
 2018-12-20 06:51:22 +05:30
Maneesh Gupta c4a93adb74 Replace hipLaunchKernel -> hipLaunchKernelGGL 
Change-Id: I4d99009e1199811d417becf1e1b934ec4d4e30be


[ROCm/hip commit: 52e320f396]
 2018-10-17 14:32:25 +05:30
saleelk 428120f219 Fix hipHostRegister mem leak and copy kind in hipMemcpyAsync (#587) 
[ROCm/hip commit: 8bc73424d1]
 2018-07-23 11:04:14 +05:30
Rahul Garg 14c424827b Cleaned up hipMemset3D test 
[ROCm/hip commit: 18944113ed]
 2018-07-06 14:54:08 +05:30
Rahul Garg e2a2b5bdcf Added hipMemset3D 
[ROCm/hip commit: da302c3e93]
 2018-05-07 10:24:30 +05:30
Rahul Garg e1e88f3bff Added hipMemset2DAsync support 
[ROCm/hip commit: 3cfb9c0d40]
 2018-04-17 18:27:27 +05:30
Maneesh Gupta 4f42ee762d Apply .clangformat to all repo source files 
Change-Id: I7e79c6058f0303f9a98911e3b7dd2e8596079344


[ROCm/hip commit: 1ba06f63c4]
 2018-03-12 11:29:03 +05:30
Phaneendr-kumar Lanka e2487a261e [nvccTests] Resubmit hipMemcpyDtoD & inline_asm_vadd 
[ROCm/hip commit: 7cceebd9ed]
 2017-12-18 14:46:19 +05:30
Phaneendr-kumar Lanka f8d610cf61 [nvccWarnings] Fix warnings seen with dtests on nvcc path 
[ROCm/hip commit: eea7d495c7]
 2017-12-14 14:10:37 +05:30
Alex Voicu 8d51eaafb6 Revert "Revert adoption of CUDA indexing in general - this can only work with later versions of the compiler, just like module based dispatch, and thus must be guarded against usage in earlier (e.g. 1.6) versions." 
This reverts commit 1c50968


[ROCm/hip commit: 32e11e7dc6]
 2017-11-29 21:49:10 +00:00
Alex Voicu fcc42f035e Revert "Revert adoption of CUDA indexing in general - this can only work with later versions of the compiler, just like module based dispatch, and thus must be guarded against usage in earlier (e.g. 1.6) versions." 
This reverts commit d2fd1f5


[ROCm/hip commit: fbaf729f88]
 2017-11-29 21:36:29 +00:00
Alex Voicu 3c936777aa Re-sync with upstream. 
[ROCm/hip commit: c5f2b22d0d]
 2017-11-20 15:34:50 +00:00
Ben Sander 64a169fd5c Merge branch 'feature_natural_indexing' of https://github.com/AlexVlx/HIP 
[ROCm/hip commit: 5a7a28ad29]
 2017-11-19 15:25:17 -06:00
Ben Sander dde41ae0aa Temporarily disable P2P on nvidia (fails on dual GPU) 
[ROCm/hip commit: e0c3f684ae]
 2017-11-19 15:21:37 -06:00
Alex Voicu 962bf7bfda This implements the trivial change needed to move back from the hip{Something}_{x, y, z} macros to the natural CUDA syntax of Something.{x, y, z}. This is contained in lines 384-404 in hip_runtime.h. All of the other changes have to do with changing unit tests to use this syntax. The macros are retained for backwards compatibility. 
[ROCm/hip commit: cffd0e14eb]
 2017-11-19 01:54:12 +00:00
Alex Voicu 7bc5d01aaa Update new tests so as to make them work with new variadic based launch mechanisms. 
[ROCm/hip commit: bd78459690]
 2017-11-10 00:14:34 +00:00
Alex Voicu 4950373967 Merge remote-tracking branch 'origin/master' into feature_use_module_based_dispatch_instead_of_pfe 
# Conflicts:
#	tests/src/runtimeApi/stream/hipStreamSync2.cpp


[ROCm/hip commit: 3d248927e4]
 2017-11-08 10:26:30 +00:00
Alex Voicu 35d8af2001 Clean up trailing whitespace so as to reduce noise in #246. 
[ROCm/hip commit: d8e323d4b5]
 2017-11-08 00:08:55 +00:00
Phaneendr-kumar Lanka 2f4b59a9b9 Modified tests as per review 
[ROCm/hip commit: 9ee330451a]
 2017-11-06 15:13:36 +05:30
Phaneendr-kumar Lanka a8da9c1c3b More tests for memory,stream & error APIs 
[ROCm/hip commit: 093279b10b]
 2017-11-06 11:31:52 +05:30
Alex Voicu 70a41e7dac This switches HIP from its currently convoluted macro + pfe based dispatch mechanism to a more natural one partially based on the existing module API. The basic idea is that HCC will always correctly emit __global__ functions: as empty-bodied stubs, on host, and as kernels, on device. It then becomes trivial to obtain the mangled name on host, at dispatch, from the function's address, and then to use the mangled name to retrieve the kernel. This should address all problems stemming from serialisation, dubious mismatches due to the manufactured functor, macro-isms et al. It also immediately enables support for generalised globals as a consequence of that being available in the module API. Finally, it will make debug much easier, since the actual names of the __global__ functions will automatically be used in traces etc. One detail is that due to how dispatch works now (hipLaunchKernel and hipLaunchKernelGGL are themselves variadic function templates which deduce the function type of the callee), in certain cases it may be necesssary to insert explicit casts to ensure that the variadic argument list selects a viable overload - this can be observed in some unit tests. Eventually we may be able to remove this limitation, but for now it does not appear terribly onerous. The code is not extremely HIPpie, nor is it fully optimised, but rather is intended as a starting point for the HIP team to make its own. 
[ROCm/hip commit: c2482d1255]
 2017-11-01 15:09:59 +00:00
Ben Sander 68e571aa82 Clean up test to address review feedback. 
[ROCm/hip commit: ca1230300a]
 2017-10-25 16:08:16 -05:00
Ben Sander 05d5dd2d46 Test cleanup. 
[ROCm/hip commit: 8e04b33c95]
 2017-10-07 07:54:10 -07:00
Rahul Garg 63456bfea0 Disable failing test p2p_copy_coherency 
[ROCm/hip commit: 2f617bac6d]
 2017-08-02 14:47:13 +05:30
Ben Sander ed1f242c60 Clean up old USE_* and RELEASE.md notes. 
[ROCm/hip commit: 7912e61502]
 2017-06-23 18:05:30 -05:00
Rahul Garg aaa09cbf1c Update P2P test for using memcpy and kernel tests 
Change-Id: Ib0f8fc9425e6e85fd11d7d02395c52bc713dcb37


[ROCm/hip commit: a9449533a1]
 2017-06-12 11:53:25 +05:30
Maneesh Gupta 59a792d892 hipMemcpy-size test: reduce max size to make it work correctly on nvcc path 
Change-Id: I9ce9f5a9e141ffd8ddf961269010b33358e02771


[ROCm/hip commit: 1c93d8592e]
 2017-06-07 15:25:54 +05:30
Maneesh Gupta 7213c7a1ad p2p_copy_coherency test: gracefully handle single gpu case 
Change-Id: I216663f67ef58c673136332635dab8b57079b909


[ROCm/hip commit: 1efb6ce994]
 2017-06-07 15:23:37 +05:30
Ben Sander f3950e0748 Update tests. 
Fix some NVCC issues.
Add hipStreamSync2, record_event tests.


[ROCm/hip commit: 8ce6d17983]
 2017-06-04 20:18:37 -05:00
Ben Sander a1bdd5f585 Update tests, add p2p coherency test. 
[ROCm/hip commit: d5c1616324]
 2017-06-03 17:11:34 -05:00
Maneesh Gupta 404c3f6751 Fix hipMemoryAllocate test for single GPU 
Change-Id: If121c18ab490ba125dc689ffc08a8839fd280c38


[ROCm/hip commit: 502a74fcd6]
 2017-05-31 10:16:57 +05:30
Ben Sander b3e01ed74f Add event controls for release fences. 
Env var : HIP_EVENT_SYS_RELEASE
Event allocation flags : hipEventReleaseToDevice, hipEventReleaseToSystem
   (remove hipEventDisableSystemRelease)

Update test for new functionality.


[ROCm/hip commit: ec7102f461]
 2017-05-27 16:02:34 -05:00
Ben Sander e24627aa80 Cleanup hipEvent. (Intermediate checkpoint) 
Support hipEventDisableSystemRelease flag.
Update test.
Remove stray printf


[ROCm/hip commit: 620eb30691]
 2017-05-27 16:02:34 -05:00
Ben Sander 5b9ce41633 Add hipHostMallocCoherent, hipHostMallocNonCoherent 
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.


[ROCm/hip commit: 75f691ec2f]
 2017-05-24 00:48:10 -05:00
Ben Sander ff72a701b7 hipHostMalloc allocation are mapped to all devices by default. 
Support hipHostMallocPortable flag.
Default flags are hipHostMallocPortable | hipHostMallocMapped.

Also:
-refactor tests to move addCount and addCountReverse into HipTest
namespace.
-test multi-GPU host memory.


[ROCm/hip commit: c3ccaa01e5]
 2017-05-10 17:34:36 -05:00
Ben Sander 639d152ff8 Refactor hipHostRegister test. 
Run all tests in one command.
Run 128 offsets.


[ROCm/hip commit: 6437f5d2b2]
 2017-05-05 17:29:04 -05:00