e2487a261e
[nvccTests] Resubmit hipMemcpyDtoD & inline_asm_vadd
...
[ROCm/hip commit: 7cceebd9ed
2017-12-18 14:46:19 +05:30
f8d610cf61
[nvccWarnings] Fix warnings seen with dtests on nvcc path
...
[ROCm/hip commit: eea7d495c7
2017-12-14 14:10:37 +05:30
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 1c5096832e11e7dc6
2017-11-29 21:49:10 +00:00
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 d2fd1f5fbaf729f88
2017-11-29 21:36:29 +00:00
3c936777aa
Re-sync with upstream.
...
[ROCm/hip commit: c5f2b22d0d
2017-11-20 15:34:50 +00:00
64a169fd5c
Merge branch 'feature_natural_indexing' of https://github.com/AlexVlx/HIP
...
[ROCm/hip commit: 5a7a28ad29
2017-11-19 15:25:17 -06:00
dde41ae0aa
Temporarily disable P2P on nvidia (fails on dual GPU)
...
[ROCm/hip commit: e0c3f684ae
2017-11-19 15:21:37 -06:00
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
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
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
35d8af2001
Clean up trailing whitespace so as to reduce noise in #246 .
...
[ROCm/hip commit: d8e323d4b5
2017-11-08 00:08:55 +00:00
2f4b59a9b9
Modified tests as per review
...
[ROCm/hip commit: 9ee330451a
2017-11-06 15:13:36 +05:30
a8da9c1c3b
More tests for memory,stream & error APIs
...
[ROCm/hip commit: 093279b10b
2017-11-06 11:31:52 +05:30
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
68e571aa82
Clean up test to address review feedback.
...
[ROCm/hip commit: ca1230300a
2017-10-25 16:08:16 -05:00
05d5dd2d46
Test cleanup.
...
[ROCm/hip commit: 8e04b33c95
2017-10-07 07:54:10 -07:00
63456bfea0
Disable failing test p2p_copy_coherency
...
[ROCm/hip commit: 2f617bac6d
2017-08-02 14:47:13 +05:30
ed1f242c60
Clean up old USE_* and RELEASE.md notes.
...
[ROCm/hip commit: 7912e61502
2017-06-23 18:05:30 -05:00
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
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
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
f3950e0748
Update tests.
...
Fix some NVCC issues.
Add hipStreamSync2, record_event tests.
[ROCm/hip commit: 8ce6d17983
2017-06-04 20:18:37 -05:00
a1bdd5f585
Update tests, add p2p coherency test.
...
[ROCm/hip commit: d5c1616324
2017-06-03 17:11:34 -05:00
404c3f6751
Fix hipMemoryAllocate test for single GPU
...
Change-Id: If121c18ab490ba125dc689ffc08a8839fd280c38
[ROCm/hip commit: 502a74fcd6
2017-05-31 10:16:57 +05:30
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
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
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
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
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
0e14f7f58e
Add host offset checking
...
[ROCm/hip commit: cd93a2f229
2017-04-24 22:30:54 -05:00
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
244e79d54d
Refactor hipHostRegister to cover misaligned cases.
...
[ROCm/hip commit: 8ba993e36c
2017-04-24 22:30:54 -05:00
ed7b16786a
Add test for non-page-aligned mem copies.
...
[ROCm/hip commit: ab410add5c
2017-04-24 22:30:54 -05:00
70ed508153
Add corrected test for offsets
...
[ROCm/hip commit: c5d89d9e7f
2017-04-24 22:30:54 -05:00
9699bcc3da
Refactor hipMemcpy test to share mem alloc for multiple copies.
...
[ROCm/hip commit: 2bc0a6030e
2017-04-24 22:30:54 -05:00
3ef01532b9
Add negative testing for memory full condition.
...
[ROCm/hip commit: dc001ef9b4
2017-04-24 22:30:54 -05:00
86e2a5d11d
Disable broken tests on hcc path
...
Change-Id: Id6234da576566faa32d5fdf42dca6d6267596823
[ROCm/hip commit: 65bb22eefc
2017-03-15 12:03:44 +05:30
3b768fb36c
Update hiphostregister test.
...
Move check to correct place.
[ROCm/hip commit: e7d6a34327
2017-03-12 09:51:33 -05:00
a735ffa947
Update hipHostRegister debug and pointerTracker debug and notes
...
[ROCm/hip commit: 0a554f4dc1
2017-03-11 09:18:27 -06:00
3297a65b8f
Fix copying of registered memory.
...
Set device properly so copying can recover context.
Enhance test to catch this case.
[ROCm/hip commit: 94c85fd4fc
2017-03-11 09:18:27 -06:00
a1ecc551aa
Disable hipMemPtrGetInfo test on nvcc path
...
Change-Id: I864e571314abfe5ae614e6792c86d7b457c920ee
[ROCm/hip commit: 7a59103cea
2017-03-08 16:16:08 +05:30
fe81d08987
Added new API, hipMemPtrGetInfo
...
1. This API returns memory allocation size of pointer
2. Added test to check its functionality
Change-Id: I87976d817b5a6ca5530336c09e7cb0420601cb2c
[ROCm/hip commit: 1546732604
2017-03-07 13:46:29 -06:00
2799863a54
Fix compilation of some broken tests on nvcc path
...
Change-Id: I92406af00c2de09d728e9b7f661c1f3873470560
[ROCm/hip commit: f1c3dd0dff
2017-02-27 13:17:51 +05:30
6d5992d445
changed __global__ attribute
...
1. Moved around tests and added them to HIT
Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b
[ROCm/hip commit: 5e3d63c0a3
2017-02-03 10:53:36 -06:00
a446102fcc
Add direct test case for threadfence_system workaround
...
Change-Id: I5b21b590e957c901044741ac94e816cd8b1426f9
[ROCm/hip commit: 50867efa10
2016-11-11 15:09:43 -06:00
70b6885995
Remove deprecated make and cmake files
...
Change-Id: I8cac0ec9cb997214559627425af207bbb9be0ddf
[ROCm/hip commit: 66f810ebaa
2016-10-07 11:44:26 +05:30
724a024bb6
directed tests: Updated to use new hip include path
...
Change-Id: Iab1aee638b7158eb9674a19625dedf6471947e51
[ROCm/hip commit: 7e04884d0f
2016-10-04 22:20:50 +05:30
c3034c06df
fix test args
...
Change-Id: If18eb2a5e504accb72a25716aafb6867002fefb2
[ROCm/hip commit: 3bda7532cf
2016-10-01 14:39:22 -05:00
a826689145
directed tests: Enable remaining tests in HIT infrastructure
...
Change-Id: I800ee00d6f7d339bb5d2ed898a16362a8541ed3a
[ROCm/hip commit: 4807279988
2016-09-27 17:24:33 +05:30
1b40622143
Doc and test updates.
...
Change-Id: I44cbd2c0de7cb692d0194d1bb8b8ae25c58d4e00
[ROCm/hip commit: 84b14aa9d6
2016-09-02 09:46:59 -05:00
Phaneendr-kumar Lanka
Phaneendr-kumar Lanka
Alex Voicu
Ben Sander
Rahul Garg
Maneesh Gupta
Aditya Atluri
pensun