Commit Graph

182 Commits

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


[ROCm/clr commit: 96890792b0]
2019-10-04 13:36:31 +05:30
Yaxun (Sam) Liu 2ed78f20a2 Fix cast of __half for HIP-clang (#1475)
[ROCm/clr commit: 7b3b82bd0d]
2019-09-30 10:40:42 +05:30
AlexBinXie cc921b35be [hip]Skip test when hipHostMallocCoherent is not supported by implementation (#1380)
[ROCm/clr commit: 313726a457]
2019-09-16 08:31:43 +00:00
Sameer Sahasrabuddhe 929b6d5f34 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/clr commit: 68c133bd78]
2019-08-30 20:41:29 +05:30
amd-lthakur 421f940def [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/clr commit: c212c484af]
2019-08-09 11:49:31 +00:00
lthakur b62254608c Resubmitting the fix so as to address the changed format in the last submission
[ROCm/clr commit: 80acd13ba7]
2019-08-08 11:26:26 +05:30
lthakur 6a15871e91 Fixed compilation errors being observed on windows
[ROCm/clr commit: c4f6d58354]
2019-08-07 15:54:46 +05:30
Vladislav Sytchenko 5b201fe854 Don't use a hardcoded warp size, since it can be dynamically changed. Query it from the runtime instead.
[ROCm/clr commit: 9a1835ddc3]
2019-07-31 17:04:31 -04:00
Aaron Enye Shi 73af1ac4bd Add GFX908 specific changes to HIP (#1229)
* Add GFX908 specific for HIP

* Fix missing __halfTest in hipTestNativeHalf


[ROCm/clr commit: 8c82f9db77]
2019-07-24 07:51:17 +00:00
Alex Voicu 1e12e00009 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/clr commit: 87eac86298]
2019-06-25 06:32:09 +05:30
Maneesh Gupta 74110bbd43 [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074


[ROCm/clr commit: 53dd1df3fa]
2019-05-09 09:59:18 +05:30
Maneesh Gupta 532725c9c8 Merge pull request #1075 from mhbliao/hliao/master/test_fix2
[test] Add device variant of `std::declval`.

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

[ROCm/clr commit: 7f759750d1]
2019-05-07 16:09:15 +05:30
Maneesh Gupta 4a4745e466 Merge pull request #1069 from mhbliao/hliao/master/test_cleanup
[test] Remove unused common routines.

[ROCm/clr commit: 0fffbbe67a]
2019-05-07 16:02:57 +05:30
Michael LIAO f644d4daaa [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/clr commit: 32f69c8bc4]
2019-05-03 15:58:31 -04:00
Michael LIAO fa74e75fc1 [test] Use explicit cast for address space cast.
[ROCm/clr commit: a27877794f]
2019-05-03 14:56:00 -04:00
Michael LIAO 9823184397 [test] Remove unused common routines.
- Remove used common routines, which variadic functions, not supported
  feature, are used.


[ROCm/clr commit: aad19f6171]
2019-05-02 12:34:07 -04:00
Michael LIAO eb43303d0b [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/clr commit: 2380eb8ecc]
2019-04-30 08:59:13 -04:00
Aaron Enye Shi 859c3bc699 Fix mixed dot for Jenkins rocm_2_0
[ROCm/clr commit: 2ab6fd374c]
2019-01-24 22:48:35 +00:00
Aaron Enye Shi d54135c38d Exclude mixed dot functions from nvcc path
[ROCm/clr commit: 77de87d0cd]
2019-01-24 21:00:45 +00:00
Aaron Enye Shi 5024e71039 Fix mixed dot for Jenkins rocm_head
[ROCm/clr commit: a014668d3a]
2019-01-23 16:39:25 +00:00
Aaron Enye Shi 0e1860dd53 Add tests for dot functions
[ROCm/clr commit: bbe5a0381f]
2019-01-22 22:32:28 +00:00
Maneesh Gupta e7195f7dc2 Update hipAsynchronousStreams.cpp
This test needs to be excluded from nvcc platform

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


[ROCm/clr commit: 39574dba4c]
2019-01-04 05:51:50 -05:00
Aaron Enye Shi 56262f0970 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/clr commit: 2d50392c17]
2018-12-18 19:31:54 +00:00
Michael Kuron 4b77b5c1ba Merge branch 'master' into getsymboladdress
[ROCm/clr commit: e9b88711e2]
2018-11-20 12:03:22 +01:00
Aaron Enye Shi 890beb81d6 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/clr commit: 7b3bbc85c5]
2018-11-06 19:53:28 +00:00
Aaron Enye Shi 4480bb6d06 Guard the OCML rounded operations instead
Instead of commenting all these functions out, guard the functions with a macro OCML_BASIC_ROUNDED_OPERATIONS.


[ROCm/clr commit: 9aa92238ab]
2018-11-06 16:32:14 +00:00
Michael Kuron 35227acd6d Test for hipGetSymbolSize and hipGetSymbolAddress
[ROCm/clr commit: fe2281f101]
2018-11-06 11:39:34 +01:00
Aaron Enye Shi 5c1dc7a071 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/clr commit: cef6e8ef1f]
2018-11-05 22:34:16 +00:00
Alex Voicu c505c2be38 Re-sync with upstream.
[ROCm/clr commit: 602280eb8b]
2018-10-18 12:27:03 +01:00
Maneesh Gupta 50e89b0a30 Replace hipLaunchKernel -> hipLaunchKernelGGL
Change-Id: I4d99009e1199811d417becf1e1b934ec4d4e30be


[ROCm/clr commit: e1fe095471]
2018-10-17 14:32:25 +05:30
Alex Voicu f3495964ea Minimal should mean minimal.
[ROCm/clr commit: 217fe345ca]
2018-10-11 00:21:41 +01:00
Alex Voicu 0e5f21c96b Trailing whitespace is still not the final frontier.
[ROCm/clr commit: 7874ec8aaf]
2018-10-11 00:08:09 +01:00
Alex Voicu 50388a3bd1 Re-sync with upstream.
[ROCm/clr commit: 9ec697c620]
2018-10-10 11:43:49 +01:00
Maneesh Gupta 27986e6788 Merge pull request #685 from ROCm-Developer-Tools/hip-trig-return
Improve hip_trig test case

[ROCm/clr commit: 802520f5f1]
2018-09-26 09:50:48 +05:30
Aaron Enye Shi 20e9391cfb Use trig functions from ocml instead
[ROCm/clr commit: 04ed44f074]
2018-09-25 15:58:36 +00:00
Aaron Enye Shi 4bbfaf06b5 Fix missing HIP_ASSERT in hip_trig
[ROCm/clr commit: bc5de031a5]
2018-09-24 15:01:24 +00:00
Maneesh Gupta 0d75b78a5a Merge pull request #683 from ROCm-Developer-Tools/hip-float-rounded
Disable non-default-rounded functions

[ROCm/clr commit: ad008c5e3f]
2018-09-24 09:32:52 +05:30
Aaron Enye Shi f4fc30ccc7 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/clr commit: afef6a3ece]
2018-09-21 15:28:10 -04:00
Maneesh Gupta 203e3dd5d5 Update hipTestFMA.cpp
[ROCm/clr commit: a4bdbe0aaf]
2018-09-21 11:00:08 +05:30
Aaron Enye Shi 646de2e876 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/clr commit: a3dea28c9d]
2018-09-20 16:33:32 -04:00
Maneesh Gupta f742125288 Update hipTestFMA.cpp
Fix the test so that it works on nvcc path as well.

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

Change-Id: I2d7297e0c3725564215e20dbdd31c0bb8d7a07de


[ROCm/clr commit: f63ffaf6e5]
2018-09-17 15:32:05 +05:30
Maneesh Gupta 6e7f871105 [dtests] Fix deviceLib/hipSimpleAtomicsTest for nvcc
Change-Id: I23cbea2820d41da6f6a1bcab4bc3b59ac21799dd


[ROCm/clr commit: 7066147760]
2018-09-17 15:26:45 +05:30
Maneesh Gupta 51f5e9ea04 [dtests] Fix deviceLib/hipTestIncludeMath on nvcc path
Change-Id: Ifb121886bec6c1134e98bd194ff1713f28454d33


[ROCm/clr commit: 644fc85a37]
2018-09-17 15:15:49 +05:30
Alex Voicu f5d204450c Align with HC Next.
[ROCm/clr commit: 26c26f63cb]
2018-09-17 11:50:29 +03:00
Maneesh Gupta 20abaa15c4 Merge branch 'master' into support-malloc
[ROCm/clr commit: b23609ad42]
2018-09-17 10:17:25 +05:30