Commit Graph

182 Commits

Author SHA1 Message Date
vsytch eaa616bf6d Update hipMathFunctions, hipTestHalf and hipTestNativeHalf tests to support Navi10 and Navi14. (#1545)
[ROCm/hip commit: 2fb734ef5f]
2019-10-16 10:51:48 +05:30
ansurya 66e94b1b1f Added new Memory API's (#1399)
Added new memory API's hipMemAllocPitch, hipMemAllocHost, hipMemsetD16, hipMemsetD16Async, hipMemsetD8Async
Modified to support all scenarios hipMemcpyParam2DAsync, hipMemcpyParam2D.


[ROCm/hip commit: ba9c6e13e4]
2019-10-04 13:36:31 +05:30
Yaxun (Sam) Liu 21201779c6 Fix cast of __half for HIP-clang (#1475)
[ROCm/hip commit: 56193a7828]
2019-09-30 10:40:42 +05:30
AlexBinXie d86d4d674d [hip]Skip test when hipHostMallocCoherent is not supported by implementation (#1380)
[ROCm/hip commit: 5ed1f3e2c8]
2019-09-16 08:31:43 +00:00
Sameer Sahasrabuddhe 8afbecf687 remove obsolete test for OCKL Asynchronous Streams
The implementation for OCKL AS was recently removed from the device
library since that feature is now superseded by hostcall.


[ROCm/hip commit: 70023c9075]
2019-08-30 20:41:29 +05:30
amd-lthakur 2658921cfb [dtests] Fixed build issues with hipAsynchronousStreams.cpp on windows (#1292)
Changed the third arg of the functions __hip_as_write_block and __ockl_as_write_block from ulong to uint64_t so as to fix the compilation error in windows

[ROCm/hip commit: d3ffad7c83]
2019-08-09 11:49:31 +00:00
lthakur 68139db6b8 Resubmitting the fix so as to address the changed format in the last submission
[ROCm/hip commit: d18160920e]
2019-08-08 11:26:26 +05:30
lthakur aeb53881fb Fixed compilation errors being observed on windows
[ROCm/hip commit: 435badcb0e]
2019-08-07 15:54:46 +05:30
Vladislav Sytchenko 6837312da4 Don't use a hardcoded warp size, since it can be dynamically changed. Query it from the runtime instead.
[ROCm/hip commit: fd3b626386]
2019-07-31 17:04:31 -04:00
Aaron Enye Shi 2e45e37c51 Add GFX908 specific changes to HIP (#1229)
* Add GFX908 specific for HIP

* Fix missing __halfTest in hipTestNativeHalf


[ROCm/hip commit: b754de37c1]
2019-07-24 07:51:17 +00:00
Alex Voicu e474469213 Put 3-wide vector types on a ketogenic diet. (#1180)
* Put 3-wide vector types on a ketogenic diet.

* Remove needless include.

* Do not be narrow-minded.

* Do not be narrow-minded.

* Put the C people on a diet too.


[ROCm/hip commit: 67abac1365]
2019-06-25 06:32:09 +05:30
Maneesh Gupta fa07d40cdd [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074


[ROCm/hip commit: 9f2d1453fb]
2019-05-09 09:59:18 +05:30
Maneesh Gupta 5f54b7f9a6 Merge pull request #1075 from mhbliao/hliao/master/test_fix2
[test] Add device variant of `std::declval`.

[ROCm/hip commit: f931152280]
2019-05-07 16:15:01 +05:30
Maneesh Gupta 13d2c76d3d Merge pull request #1074 from mhbliao/hliao/master/test_fix
[test] Use explicit cast for address space cast.

[ROCm/hip commit: 1d4941e487]
2019-05-07 16:09:15 +05:30
Maneesh Gupta b6393eb059 Merge pull request #1069 from mhbliao/hliao/master/test_cleanup
[test] Remove unused common routines.

[ROCm/hip commit: 730763c817]
2019-05-07 16:02:57 +05:30
Michael LIAO d71327882c [test] Add device variant of std::declval.
- Current clang disallows any invocation of wrong-side functions even
  under context with type-inspection only. Work around that by adding a
  variant of `std::decl` with `__device__` attribute.


[ROCm/hip commit: 4fbfb646f6]
2019-05-03 15:58:31 -04:00
Michael LIAO cb55dc384a [test] Use explicit cast for address space cast.
[ROCm/hip commit: 2746d95906]
2019-05-03 14:56:00 -04:00
Michael LIAO b7ae0b6442 [test] Remove unused common routines.
- Remove used common routines, which variadic functions, not supported
  feature, are used.


[ROCm/hip commit: 16a27e06ee]
2019-05-02 12:34:07 -04:00
Michael LIAO e637e72364 [Device Function] Fix implementation of __bitinsert_u64
- It's a common mistake by assuming 1 << shamt would be promoted to
  64-bit, if shamt is a 64-bit integer. That's not the case. Replace
  that left shift to a 64-bit one to ensure it won't fall into undefined
  behavior.
- Fix the host-side implementation as well for device function testing.


[ROCm/hip commit: 9bd2d5746d]
2019-04-30 08:59:13 -04:00
Aaron Enye Shi ba1452b664 Fix mixed dot for Jenkins rocm_2_0
[ROCm/hip commit: ede494bd5f]
2019-01-24 22:48:35 +00:00
Aaron Enye Shi aabdf3a1b2 Exclude mixed dot functions from nvcc path
[ROCm/hip commit: 7e46f0639c]
2019-01-24 21:00:45 +00:00
Aaron Enye Shi 2ae4e21bb9 Fix mixed dot for Jenkins rocm_head
[ROCm/hip commit: f31aa946e7]
2019-01-23 16:39:25 +00:00
Aaron Enye Shi b1d61f076f Add tests for dot functions
[ROCm/hip commit: 1d70f4217e]
2019-01-22 22:32:28 +00:00
Maneesh Gupta cf7c7f2db2 Update hipAsynchronousStreams.cpp
This test needs to be excluded from nvcc platform

[ROCm/hip commit: 580c808400]
2019-01-07 09:26:21 +05:30
Sameer Sahasrabuddhe d1a7eb0cb5 introduce test for asynchronous streams
This test is identical to the HCC tests under
tests/Unit/OCKL/AsyncStreams, but only for synchronous operation.


[ROCm/hip commit: 8fe2a4b167]
2019-01-04 05:51:50 -05:00
Aaron Enye Shi 8e7b49d1cf Add *_rn functions back into HIP intrinsics
Add back the round-to-nearest-even intrinsics back to HIP math
intrinsics as it caused regression.


[ROCm/hip commit: 58dfeff27a]
2018-12-18 19:31:54 +00:00
Michael Kuron c35dfb71d5 Merge branch 'master' into getsymboladdress
[ROCm/hip commit: 8610128c3e]
2018-11-20 12:03:22 +01:00
Aaron Enye Shi 8bf2429663 Guard rcp rounded implementation as well
Since rcp implementations of non-default rounded versions are not correct or supported in OCML, guard them using the same macro OCML_BASIC_ROUNDED_OPERATIONS. Also update the docs and tests.


[ROCm/hip commit: 0cfaa52d15]
2018-11-06 19:53:28 +00:00
Aaron Enye Shi eb4053e3fe Guard the OCML rounded operations instead
Instead of commenting all these functions out, guard the functions with a macro OCML_BASIC_ROUNDED_OPERATIONS.


[ROCm/hip commit: e59c33250a]
2018-11-06 16:32:14 +00:00
Michael Kuron b23b30d373 Test for hipGetSymbolSize and hipGetSymbolAddress
[ROCm/hip commit: 49cc703d7a]
2018-11-06 11:39:34 +01:00
Aaron Enye Shi 1c6f47ef55 Remove non-working non-default-rounded math apis
In ROCm-Device-Libs, they have dropped the non-default-rounded versions of add, sub, mul, div, sqrt and fma. Therefore, ocml has removed the rte, rtp, rtn, and rtz counterparts. This will remove the same math APIs in HIP for _ru, _rd, _rn, and _rz.


[ROCm/hip commit: 2b108a2cfd]
2018-11-05 22:34:16 +00:00
Alex Voicu de15c6988d Re-sync with upstream.
[ROCm/hip commit: fe959f7bd7]
2018-10-18 12:27:03 +01:00
Maneesh Gupta c4a93adb74 Replace hipLaunchKernel -> hipLaunchKernelGGL
Change-Id: I4d99009e1199811d417becf1e1b934ec4d4e30be


[ROCm/hip commit: 52e320f396]
2018-10-17 14:32:25 +05:30
Alex Voicu 69b0baf37f Minimal should mean minimal.
[ROCm/hip commit: 5312336ce2]
2018-10-11 00:21:41 +01:00
Alex Voicu 62d7a132c8 Trailing whitespace is still not the final frontier.
[ROCm/hip commit: 50265028fc]
2018-10-11 00:08:09 +01:00
Alex Voicu 6d0b50e9b9 Re-sync with upstream.
[ROCm/hip commit: ca375cb8c5]
2018-10-10 11:43:49 +01:00
Maneesh Gupta 502fda5308 Merge pull request #685 from ROCm-Developer-Tools/hip-trig-return
Improve hip_trig test case

[ROCm/hip commit: 5c665acf74]
2018-09-26 09:50:48 +05:30
Aaron Enye Shi 93a84365ab Use trig functions from ocml instead
[ROCm/hip commit: 5179a72cda]
2018-09-25 15:58:36 +00:00
Aaron Enye Shi 9762215e54 Fix missing HIP_ASSERT in hip_trig
[ROCm/hip commit: 3d3820272a]
2018-09-24 15:01:24 +00:00
Maneesh Gupta a7c2d2ab08 Merge pull request #683 from ROCm-Developer-Tools/hip-float-rounded
Disable non-default-rounded functions

[ROCm/hip commit: ca6b916d15]
2018-09-24 09:32:52 +05:30
Aaron Enye Shi 8408bc5536 Improve hip_trig test case
Hip_trig is failing but returning a passing value on HIP-Clang.  Also update with debug output and free arrays used.

[ROCm/hip commit: 357b6844fa]
2018-09-21 15:28:10 -04:00
Maneesh Gupta d98ef3cc48 Update hipTestFMA.cpp
[ROCm/hip commit: 255589ae15]
2018-09-21 11:00:08 +05:30
Aaron Enye Shi 6efd97931c Disable non-default-rounded functions
Device library has removed the non-default-rounded functions, so hipFloatMath will fail to build. These include the removal of __ocml_sqrt_rte, __ocml_sqrt_rtn, __ocml_sqrt_rtp, and __ocml_sqrt_rtz. As seen here: https://github.com/RadeonOpenCompute/ROCm-Device-Libs/commit/2fc04e10e1354edee331ce700f98a60f8255effb . Disable these function tests for now, until they are re-enabled, or deleted completely.

[ROCm/hip commit: c11220f224]
2018-09-20 16:33:32 -04:00
Maneesh Gupta 8431e3620a Update hipTestFMA.cpp
Fix the test so that it works on nvcc path as well.

[ROCm/hip commit: ecd6a212c7]
2018-09-20 11:23:51 +05:30
Yaxun Sam Liu 2d4040f75d Add fma function with float and _Float16 arguments
[ROCm/hip commit: bd622a4b4a]
2018-09-19 09:59:33 -04:00
Maneesh Gupta 5947c0e94d [dests] Fix hipTestClock, hipTestNew & hipTestGlobalVariable tests for nvcc
nvcc does not support global kernels in struct/class

Change-Id: I2d7297e0c3725564215e20dbdd31c0bb8d7a07de


[ROCm/hip commit: cca2c5afc8]
2018-09-17 15:32:05 +05:30
Maneesh Gupta e14fc1c65e [dtests] Fix deviceLib/hipSimpleAtomicsTest for nvcc
Change-Id: I23cbea2820d41da6f6a1bcab4bc3b59ac21799dd


[ROCm/hip commit: 94a0589eb5]
2018-09-17 15:26:45 +05:30
Maneesh Gupta 6b8913d4e5 [dtests] Fix deviceLib/hipTestIncludeMath on nvcc path
Change-Id: Ifb121886bec6c1134e98bd194ff1713f28454d33


[ROCm/hip commit: 0b211bb429]
2018-09-17 15:15:49 +05:30
Alex Voicu 312d29ebaf Align with HC Next.
[ROCm/hip commit: c6720e882b]
2018-09-17 11:50:29 +03:00
Maneesh Gupta 4a671abf13 Merge branch 'master' into support-malloc
[ROCm/hip commit: 66f863d1f3]
2018-09-17 10:17:25 +05:30