AI/rocm-systems
2
0
Forka 0
Codice Problemi Pull Request Actions Pacchetti Progetti Rilasci Wiki Attività
2.003 Commit 3 Rami (Branch) 0 Tag
51df93cf25bb024a5447e1d4b93db8ba05d30dde
Grafico dei commit

446 Commit

Autore SHA1 Messaggio Data
Chris Kitching 6491c2c3eb Greatly enhance handling of macros in kernel launches 
All but the most contrived use of macros is now properly handled -
have a look at the new testcases this commit adds. You can have
macros in kernel calls, macros spanning chunks of your arguments,
the call, call parameters, or callee can all be macros or
partially macros.
 2017-10-26 17:28:46 +01:00
Chris Kitching 8d91579dcf Don't use now-defunct cmake variable in lit test config 2017-10-24 20:52:51 +01:00
Chris Kitching 2c65d0da37 Add concurentKernels.cu to the testsuite 2017-10-23 13:39:37 +01:00
Chris Kitching 64d5f07050 Add the CUDA samples include dir to the path for tests 
Means we get to easily steal CUDA examples for tests
 2017-10-23 13:39:37 +01:00
Chris Kitching 2437b31939 Add cudaRegister.cu lit test 2017-10-23 13:39:37 +01:00
Chris Kitching ead79e5bf4 Add square.cu to lit testsuite 2017-10-23 13:39:37 +01:00
Chris Kitching c99dcbba8d Introduce a test runner script to simplify invocation 
... And to use a standard, highly amusing trick for making
coloured output work.
 2017-10-23 13:39:37 +01:00
Chris Kitching 5912f465bd Adapt lit test for the hipLaunchKernelGGL changes from before... 2017-10-23 13:39:37 +01:00
Chris Kitching 74fd64d5c1 Migrate lit test to using FileCheck, so failures are readable 
It seems the test is already broken, but look how awesome the
error message is now:

/home/chris/HIP/tests/hipify-clang/axpy.cu:31:12: error: expected string not found in input
 // CHECK: hipLaunchKernel(HIP_KERNEL_NAME(axpy), dim3(1), dim3(kDataLen), 0, 0, a, device_x, device_y);
           ^
<stdin>:31:2: note: scanning from here
 //
 ^
<stdin>:33:2: note: possible intended match here
 hipLaunchKernelGGL(axpy, dim3(1), dim3(kDataLen), 0, 0, a, device_x, device_y);
 ^
 2017-10-23 13:39:37 +01:00
Chris Kitching 9747578d09 Propagate the CUDA toolkit directory into the lit tests 
Allows the tests to actually run... :D
 2017-10-23 13:39:36 +01:00
Rahul Garg 05070fe824 Added HIT block 2017-09-26 11:39:09 +05:30
Rahul Garg 36db84a68f Added Texture 2D object and reference APIs tests 2017-09-26 11:33:23 +05:30
Ben Sander 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
Rahul Garg 3e4df05632 Enable hipStreamSync2 and record_event dtests 2017-08-24 15:51:58 +05:30
Rahul Garg 5a49396e3e PCI Bus ID related dtests 2017-08-22 15:41:16 +05:30
Maneesh Gupta 88ff8d9da4 [dtests] Fix hip_threadfence_system test's BUILD command 
Change-Id: I037c523369e4bddd7a386ffe117fe97a178900fd
 2017-08-11 14:49:17 +05:30
Siu Chi Chan 8c2cda8f9e add C++11 compilation flags and minor bug fixes 2017-08-10 17:58:36 +00:00
Maneesh Gupta 2bd79ab9f5 Merge pull request #138 from scchan/threadfence_system 
implement __threadfence_system
 2017-08-10 12:51:05 +05:30
Maneesh Gupta 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
Rahul Garg f916a7654e Disable failing test p2p_copy_coherency 2017-08-02 14:47:13 +05:30
Siu Chi Chan b6e22b5c93 implement __threadfence_system 2017-08-02 08:50:18 +00:00
Ben Sander bd563bf761 Merge pull request #110 from sunway513/fix_hipEnvVar_test 
Fix hipEnvVar test
 2017-07-27 13:03:43 -05:00
sunway513 b7c34fb80f Change to use hipDeviceGetPCIBusId api for hipEnvVarDriver test 2017-07-27 17:41:49 +00:00
Ben Sander 702651fc85 Merge pull request #100 from weixingzhang/texture 
HIP Texture Support
 2017-07-26 19:28:15 -05:00
sunway513 046e9c570d Fix indentation, binary path and add wait on popen calls to hipEnvVar test 2017-07-24 17:16:13 +00:00
Maneesh Gupta 1bd1c6bea8 Renable frexp(f) device math function 
Change-Id: I53c022b8ddf38cd17ddb42eba457b9020db66395
 2017-07-20 14:41:30 +05:30
Maneesh Gupta 2448b6ee90 [dt] hip_texture.h -> hip_texture_types.h 
Change-Id: If106efa0a2e52105d4025706fdbc291c27352a74
 2017-07-19 12:46:18 +05:30
Rahul Garg f2d6da3e34 Enable memcpytosymbol family functions test 2017-07-18 12:37:37 +05:30
Maneesh Gupta 814eddcd96 [dt] temporarily disable broken tests 
Change-Id: I3ce23e410dc36e06d460263d768412f8368a6699
 2017-07-18 11:17:02 +05:30
Wen-Heng (Jack) Chung 0237aeab06 Remove explicit address spaces declarations 2017-07-07 12:46:29 -05:00
Ben Sander 42882ddf9c Clean up old USE_* and RELEASE.md notes. 2017-06-23 18:05:30 -05:00
Rahul Garg ce6e455677 Update P2P test for using memcpy and kernel tests 
Change-Id: Ib0f8fc9425e6e85fd11d7d02395c52bc713dcb37
 2017-06-12 11:53:25 +05:30
Maneesh Gupta 15a3464630 Update directed tests README.md 
Change-Id: I395245454d376508f04e5a4a62c8933895cb3867
 2017-06-12 11:19:55 +05:30
Maneesh Gupta 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
Maneesh Gupta a50f5ca0ac hipDeviceMemcpy test: make it functional on nvcc path 
Change-Id: Id10c79b48747ed701adbd0a233c53cd60cfa743b
 2017-06-07 15:24:44 +05:30
Maneesh Gupta a7dc938ec0 p2p_copy_coherency test: gracefully handle single gpu case 
Change-Id: I216663f67ef58c673136332635dab8b57079b909
 2017-06-07 15:23:37 +05:30
Ben Sander 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
Ben Sander 863b7c3f56 Update tests. 
Fix some NVCC issues.
Add hipStreamSync2, record_event tests.
 2017-06-04 20:18:37 -05:00
Ben Sander 15f54fb943 Update tests, add p2p coherency test. 2017-06-03 17:11:34 -05:00
Maneesh Gupta 06ee0d3704 Fix hipMemoryAllocate test for single GPU 
Change-Id: If121c18ab490ba125dc689ffc08a8839fd280c38
 2017-05-31 10:16:57 +05:30
Maneesh Gupta 2145e94049 Disable rcbrtf, scalblnf, scalbnf in single precision device test 
Change-Id: I8a250a64a0cb05132d022a11d9766ced9cdf11a7
 2017-05-31 10:16:19 +05:30
Maneesh Gupta da19087ae2 Disable rcbrt, scalbln and scalbn double precision device test 
Change-Id: I46bd895701c46d3592b553090cafba99e41a2e2d
 2017-05-31 10:15:41 +05:30
Sandeep Kumar c964a5f208 Add inline asm hip directed tests for v_add and v_mac 
Change-Id: Ie5ace2e42d5da89b16e040537df2bb13d3883c6d
 2017-05-31 09:25:40 +05:30
Ben Sander 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
Ben Sander c8178c6838 Cleanup hipEvent. (Intermediate checkpoint) 
Support hipEventDisableSystemRelease flag.
Update test.
Remove stray printf
 2017-05-27 16:02:34 -05:00
Ben Sander 8dc968f036 Updates so hip compiles on CUDA. 2017-05-27 15:55:07 -05:00
Ben Sander dda70ae514 Add hipHostMallocCoherent, hipHostMallocNonCoherent 
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.
 2017-05-24 00:48:10 -05:00
Ben Sander 92bd54d7b3 Expand test to cover copy followed by event sync 2017-05-23 23:15:45 -05:00
Ben Sander 848d77ebb5 Make hipMultiThreadStreams1 test a little harsher. 
Fail faster if synchronization rules are violated.
Run vectorAddRevers to read last elements of array first - if the
vector add kernel starts before preceding copy finishes we
will read stale data and flag the error.

Increase default array sizes, so synchronization errors more easily
exposed.
 2017-05-16 19:04:25 -05:00
Ben Sander fad9104b5f Fix HIP_TRACE_API so kernel launch only printed when requested. 2017-05-16 19:04:25 -05:00