f7919a8321
Merge remote-tracking branch 'origin/master' into feature_use_module_based_dispatch_instead_of_pfe
...
# Conflicts:
# tests/src/runtimeApi/stream/hipStreamSync2.cpp
2017-11-08 10:26:30 +00:00
0ad1308efd
Clean up trailing whitespace so as to reduce noise in #246 .
2017-11-08 00:08:55 +00:00
2a1d7db371
identation change in hipPeekAtLastError
2017-11-07 09:51:32 +05:30
8854dec897
Merge remote-tracking branch 'origin/master' into feature_use_module_based_dispatch_instead_of_pfe
2017-11-07 00:01:22 +00:00
e18f4239b6
Modified tests as per review
2017-11-06 15:13:36 +05:30
7427abba04
More tests for memory,stream & error APIs
2017-11-06 11:31:52 +05:30
544538fd88
Merge pull request #239 from phani544/newTests
...
[newTests]Adding tests for device APIs
2017-11-06 07:22:13 +05:30
fa32a1924a
[newTests]modified the test
2017-11-03 14:52:19 +05:30
19946ca43d
[newTests]Modified the test as per review comments
2017-11-03 10:39:47 +05:30
58a18eaf0c
This corrects some interesting choices that were present in the HIP
...
unit tests such as e.g. de-allocating memory allocated with new[] using
free. All of these were identified via cppcheck.
2017-11-01 22:51:22 +00:00
28f87f7d2e
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.
2017-11-01 15:09:59 +00:00
a6458616f5
Merge pull request #197 from bensander/update_coherency_tests
...
Update coherency tests
2017-10-31 17:26:50 +05:30
71434383a3
[newTests]Adding tests for device APIs
2017-10-30 14:34:24 +05:30
cc2bcbcbcf
Clean up test to address review feedback.
2017-10-25 16:08:16 -05:00
f1992c5b11
add an unit test for printf
2017-10-23 18:31:13 -04:00
c4612f3dc9
Test cleanup.
2017-10-07 07:54:10 -07:00
cb613bb6a8
Add copy_coherency test
...
Test cache managemenent and synchronization between kernel and copy commands
in separate queues.
2017-10-07 07:54:10 -07:00
05070fe824
Added HIT block
2017-09-26 11:39:09 +05:30
36db84a68f
Added Texture 2D object and reference APIs tests
2017-09-26 11:33:23 +05:30
ed8c3ba7e7
Refactor hipStreamWaitEvent
...
- Null streams use same flow as non-null.
- Add HIP_SYNC_STREAM_WAIT
- Resolve null stream.
2017-08-31 03:00:14 +00:00
3e4df05632
Enable hipStreamSync2 and record_event dtests
2017-08-24 15:51:58 +05:30
5a49396e3e
PCI Bus ID related dtests
2017-08-22 15:41:16 +05:30
88ff8d9da4
[dtests] Fix hip_threadfence_system test's BUILD command
...
Change-Id: I037c523369e4bddd7a386ffe117fe97a178900fd
2017-08-11 14:49:17 +05:30
8c2cda8f9e
add C++11 compilation flags and minor bug fixes
2017-08-10 17:58:36 +00:00
2bd79ab9f5
Merge pull request #138 from scchan/threadfence_system
...
implement __threadfence_system
2017-08-10 12:51:05 +05:30
0d537f9966
[dtests] Disable hip_threadfence_system.tst on nvcc
...
The test needs some more modifications before it is ready for building
on nvcc path. Disabling it for now so that the pull request can be
merged.
Change-Id: I19a894fcda7b2159f86a4e4e95a409c5655d3760
2017-08-10 12:05:58 +05:30
f916a7654e
Disable failing test p2p_copy_coherency
2017-08-02 14:47:13 +05:30
b6e22b5c93
implement __threadfence_system
2017-08-02 08:50:18 +00:00
bd563bf761
Merge pull request #110 from sunway513/fix_hipEnvVar_test
...
Fix hipEnvVar test
2017-07-27 13:03:43 -05:00
b7c34fb80f
Change to use hipDeviceGetPCIBusId api for hipEnvVarDriver test
2017-07-27 17:41:49 +00:00
702651fc85
Merge pull request #100 from weixingzhang/texture
...
HIP Texture Support
2017-07-26 19:28:15 -05:00
046e9c570d
Fix indentation, binary path and add wait on popen calls to hipEnvVar test
2017-07-24 17:16:13 +00:00
1bd1c6bea8
Renable frexp(f) device math function
...
Change-Id: I53c022b8ddf38cd17ddb42eba457b9020db66395
2017-07-20 14:41:30 +05:30
2448b6ee90
[dt] hip_texture.h -> hip_texture_types.h
...
Change-Id: If106efa0a2e52105d4025706fdbc291c27352a74
2017-07-19 12:46:18 +05:30
f2d6da3e34
Enable memcpytosymbol family functions test
2017-07-18 12:37:37 +05:30
814eddcd96
[dt] temporarily disable broken tests
...
Change-Id: I3ce23e410dc36e06d460263d768412f8368a6699
2017-07-18 11:17:02 +05:30
0237aeab06
Remove explicit address spaces declarations
2017-07-07 12:46:29 -05:00
42882ddf9c
Clean up old USE_* and RELEASE.md notes.
2017-06-23 18:05:30 -05:00
ce6e455677
Update P2P test for using memcpy and kernel tests
...
Change-Id: Ib0f8fc9425e6e85fd11d7d02395c52bc713dcb37
2017-06-12 11:53:25 +05:30
ff8ade59aa
hipMemcpy-size test: reduce max size to make it work correctly on nvcc path
...
Change-Id: I9ce9f5a9e141ffd8ddf961269010b33358e02771
2017-06-07 15:25:54 +05:30
a50f5ca0ac
hipDeviceMemcpy test: make it functional on nvcc path
...
Change-Id: Id10c79b48747ed701adbd0a233c53cd60cfa743b
2017-06-07 15:24:44 +05:30
a7dc938ec0
p2p_copy_coherency test: gracefully handle single gpu case
...
Change-Id: I216663f67ef58c673136332635dab8b57079b909
2017-06-07 15:23:37 +05:30
823281dcba
Fix HIP_SYNC_NULL_STREAM=0 mode.
...
- Fix null-stream sync
- hipStreamDestroy of null stream returns hipErrorInvalidResourceHandle
- Update documentation.
- Add tests for null stream sync, hipEventElapsedTime.
- Rename internal enum hipEventStatusRecorded to hipEventStatusComplete
- refactor hipStreamWaitEvent to streamline control-flow
2017-06-05 08:50:22 -05:00
863b7c3f56
Update tests.
...
Fix some NVCC issues.
Add hipStreamSync2, record_event tests.
2017-06-04 20:18:37 -05:00
15f54fb943
Update tests, add p2p coherency test.
2017-06-03 17:11:34 -05:00
06ee0d3704
Fix hipMemoryAllocate test for single GPU
...
Change-Id: If121c18ab490ba125dc689ffc08a8839fd280c38
2017-05-31 10:16:57 +05:30
2145e94049
Disable rcbrtf, scalblnf, scalbnf in single precision device test
...
Change-Id: I8a250a64a0cb05132d022a11d9766ced9cdf11a7
2017-05-31 10:16:19 +05:30
da19087ae2
Disable rcbrt, scalbln and scalbn double precision device test
...
Change-Id: I46bd895701c46d3592b553090cafba99e41a2e2d
2017-05-31 10:15:41 +05:30
c964a5f208
Add inline asm hip directed tests for v_add and v_mac
...
Change-Id: Ie5ace2e42d5da89b16e040537df2bb13d3883c6d
2017-05-31 09:25:40 +05:30
942ec0eff8
Add event controls for release fences.
...
Env var : HIP_EVENT_SYS_RELEASE
Event allocation flags : hipEventReleaseToDevice, hipEventReleaseToSystem
(remove hipEventDisableSystemRelease)
Update test for new functionality.
2017-05-27 16:02:34 -05:00
Alex Voicu
Phaneendr-kumar Lanka
Maneesh Gupta
Ben Sander
Siu Chi Chan
Rahul Garg
sunway513
Wen-Heng (Jack) Chung
Sandeep Kumar