Commit Graph

434 Commits

Author SHA1 Message Date
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 6fd3d9fda5 identation change in hipPeekAtLastError
[ROCm/hip commit: e06c546283]
2017-11-07 09:51:32 +05:30
Alex Voicu c3fdb8ab8e Merge remote-tracking branch 'origin/master' into feature_use_module_based_dispatch_instead_of_pfe
[ROCm/hip commit: adaf6b8dff]
2017-11-07 00:01:22 +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
Maneesh Gupta 3746211481 Merge pull request #239 from phani544/newTests
[newTests]Adding tests for device APIs

[ROCm/hip commit: 2f4e1983e2]
2017-11-06 07:22:13 +05:30
Phaneendr-kumar Lanka 9d7c904529 [newTests]modified the test
[ROCm/hip commit: 0599d13b0d]
2017-11-03 14:52:19 +05:30
Phaneendr-kumar Lanka 0026b0a3d9 [newTests]Modified the test as per review comments
[ROCm/hip commit: a764a0980d]
2017-11-03 10:39:47 +05:30
Alex Voicu b8a81d2b75 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.


[ROCm/hip commit: a619ac6f92]
2017-11-01 22:51:22 +00:00
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
Maneesh Gupta e6e90e9cfa Merge pull request #197 from bensander/update_coherency_tests
Update coherency tests

[ROCm/hip commit: f27c2c1715]
2017-10-31 17:26:50 +05:30
Phaneendr-kumar Lanka a36c3c6d8b [newTests]Adding tests for device APIs
[ROCm/hip commit: 511de63bcb]
2017-10-30 14:34:24 +05:30
Ben Sander 68e571aa82 Clean up test to address review feedback.
[ROCm/hip commit: ca1230300a]
2017-10-25 16:08:16 -05:00
Siu Chi Chan 76f70bd60e add an unit test for printf
[ROCm/hip commit: b7b00fb281]
2017-10-23 18:31:13 -04:00
Ben Sander 05d5dd2d46 Test cleanup.
[ROCm/hip commit: 8e04b33c95]
2017-10-07 07:54:10 -07:00
Ben Sander 50ef165727 Add copy_coherency test
Test cache managemenent and synchronization between kernel and copy commands
in separate queues.


[ROCm/hip commit: 54d5b52d05]
2017-10-07 07:54:10 -07:00
Rahul Garg 5c9132056f Added HIT block
[ROCm/hip commit: ce13e4afbf]
2017-09-26 11:39:09 +05:30
Rahul Garg 990f85120a Added Texture 2D object and reference APIs tests
[ROCm/hip commit: 3b7a8fab5b]
2017-09-26 11:33:23 +05:30
Ben Sander 2a23d6dbe7 Refactor hipStreamWaitEvent
- Null streams use same flow as non-null.
- Add HIP_SYNC_STREAM_WAIT
- Resolve null stream.


[ROCm/hip commit: 882dab4536]
2017-08-31 03:00:14 +00:00
Rahul Garg 1d4213af20 Enable hipStreamSync2 and record_event dtests
[ROCm/hip commit: 4b98572f47]
2017-08-24 15:51:58 +05:30
Rahul Garg 82970c4dc1 PCI Bus ID related dtests
[ROCm/hip commit: 9441f3a50e]
2017-08-22 15:41:16 +05:30
Maneesh Gupta 52a97377ac [dtests] Fix hip_threadfence_system test's BUILD command
Change-Id: I037c523369e4bddd7a386ffe117fe97a178900fd


[ROCm/hip commit: 4bcb3372b5]
2017-08-11 14:49:17 +05:30
Siu Chi Chan 588ca89c92 add C++11 compilation flags and minor bug fixes
[ROCm/hip commit: 9a04c5cdd4]
2017-08-10 17:58:36 +00:00
Maneesh Gupta 0a25b3e972 Merge pull request #138 from scchan/threadfence_system
implement __threadfence_system

[ROCm/hip commit: f14e31d9d7]
2017-08-10 12:51:05 +05:30
Maneesh Gupta 7390368693 [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


[ROCm/hip commit: 69e431f035]
2017-08-10 12:05:58 +05:30
Rahul Garg 63456bfea0 Disable failing test p2p_copy_coherency
[ROCm/hip commit: 2f617bac6d]
2017-08-02 14:47:13 +05:30
Siu Chi Chan 21c1d69e77 implement __threadfence_system
[ROCm/hip commit: 96e79f97e2]
2017-08-02 08:50:18 +00:00
Ben Sander a9dce0cfe8 Merge pull request #110 from sunway513/fix_hipEnvVar_test
Fix hipEnvVar test

[ROCm/hip commit: 9cede50942]
2017-07-27 13:03:43 -05:00
sunway513 014f1797d9 Change to use hipDeviceGetPCIBusId api for hipEnvVarDriver test
[ROCm/hip commit: ed0d6cf745]
2017-07-27 17:41:49 +00:00
Ben Sander 9ec4b0b66f Merge pull request #100 from weixingzhang/texture
HIP Texture Support

[ROCm/hip commit: 4f93b99f23]
2017-07-26 19:28:15 -05:00
sunway513 286ab981a9 Fix indentation, binary path and add wait on popen calls to hipEnvVar test
[ROCm/hip commit: 81bc82d166]
2017-07-24 17:16:13 +00:00
Maneesh Gupta 9ce8abb1ed Renable frexp(f) device math function
Change-Id: I53c022b8ddf38cd17ddb42eba457b9020db66395


[ROCm/hip commit: 7a446dcbc5]
2017-07-20 14:41:30 +05:30
Maneesh Gupta 60293c4c42 [dt] hip_texture.h -> hip_texture_types.h
Change-Id: If106efa0a2e52105d4025706fdbc291c27352a74


[ROCm/hip commit: 9d5d4f9abb]
2017-07-19 12:46:18 +05:30
Rahul Garg 298fa00e8c Enable memcpytosymbol family functions test
[ROCm/hip commit: 039f62213b]
2017-07-18 12:37:37 +05:30
Maneesh Gupta 3e230cfcc6 [dt] temporarily disable broken tests
Change-Id: I3ce23e410dc36e06d460263d768412f8368a6699


[ROCm/hip commit: b3a9e202b1]
2017-07-18 11:17:02 +05:30
Wen-Heng (Jack) Chung f28a1365f8 Remove explicit address spaces declarations
[ROCm/hip commit: 30ee797dd4]
2017-07-07 12:46:29 -05:00
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 ee92e19e7a hipDeviceMemcpy test: make it functional on nvcc path
Change-Id: Id10c79b48747ed701adbd0a233c53cd60cfa743b


[ROCm/hip commit: e6cafbf342]
2017-06-07 15:24:44 +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 445042f916 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


[ROCm/hip commit: 39c18e5e5f]
2017-06-05 08:50:22 -05:00
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
Maneesh Gupta be2c61b72a Disable rcbrtf, scalblnf, scalbnf in single precision device test
Change-Id: I8a250a64a0cb05132d022a11d9766ced9cdf11a7


[ROCm/hip commit: 5cdd1b2bf5]
2017-05-31 10:16:19 +05:30
Maneesh Gupta ed41fcd51a Disable rcbrt, scalbln and scalbn double precision device test
Change-Id: I46bd895701c46d3592b553090cafba99e41a2e2d


[ROCm/hip commit: 4919863d3e]
2017-05-31 10:15:41 +05:30
Sandeep Kumar 96a7f1853e Add inline asm hip directed tests for v_add and v_mac
Change-Id: Ie5ace2e42d5da89b16e040537df2bb13d3883c6d


[ROCm/hip commit: 830f2b100d]
2017-05-31 09:25:40 +05:30