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
Ben Sander
0e14f7f58e
Add host offset checking
...
[ROCm/hip commit: cd93a2f229 ]
2017-04-24 22:30:54 -05:00
Ben Sander
e0bd60a22f
Refactor hipHostRegister test.
...
- Add more testing for offsets.
- Parse cmdline options and use --tests.
[ROCm/hip commit: b7b17c3841 ]
2017-04-24 22:30:54 -05:00
Ben Sander
244e79d54d
Refactor hipHostRegister to cover misaligned cases.
...
[ROCm/hip commit: 8ba993e36c ]
2017-04-24 22:30:54 -05:00
Ben Sander
ed7b16786a
Add test for non-page-aligned mem copies.
...
[ROCm/hip commit: ab410add5c ]
2017-04-24 22:30:54 -05:00
Ben Sander
70ed508153
Add corrected test for offsets
...
[ROCm/hip commit: c5d89d9e7f ]
2017-04-24 22:30:54 -05:00
Ben Sander
9699bcc3da
Refactor hipMemcpy test to share mem alloc for multiple copies.
...
[ROCm/hip commit: 2bc0a6030e ]
2017-04-24 22:30:54 -05:00
Ben Sander
3ef01532b9
Add negative testing for memory full condition.
...
[ROCm/hip commit: dc001ef9b4 ]
2017-04-24 22:30:54 -05:00
Maneesh Gupta
86e2a5d11d
Disable broken tests on hcc path
...
Change-Id: Id6234da576566faa32d5fdf42dca6d6267596823
[ROCm/hip commit: 65bb22eefc ]
2017-03-15 12:03:44 +05:30