Commit Graph

190 Commits

Author SHA1 Message Date
agodavar de0b92948e Enable tests that are passing on hip-vdi
Change-Id: I7de965f7e8bb7e4d0fa61cd584f0cd118c1e212e


[ROCm/hip commit: 65ffaf82d8]
2020-03-05 16:08:51 +05:30
agodavar 428d4842ae Enable tests hipTestDeviceSymbol,hipTestConstant and p2p_copy_coherency on hip-vdi
SWDEV-225266: [HIP-VDI] HIP-VDI disabled tests (p2p_copy_coherency.cpp)
SWDEV-225388: hipTestDeviceSymbol.cpp & hipTestConstant.cpp failed to build on hip-vdi

For hipTestDeviceSymbol.cpp & hipTestConstant.cpp tests:
Currently "__HIP_VDI__" flag is enabled in CMakeLists.txt, but when application is compiled with hipcc,  
__HIP_VDI__ is not defined to differentiate if compiled for VDI/HCC for headers.

For ./src/runtimeApi/memory/p2p_copy_coherency.cpp:
Fixed compilation issue to include only when compile for HCC runtime "<hc_am.hpp> not found"
Currently test is disabled to run on all platforms. When validated on multi-GPU machine,
memcpy between multiple GPUs via GPU synchronization is not working on hcc and vdi path.
Need to validate on nvidia machine to know if test is valid. Disabled GPU synchronization test for now.

For ./src/runtimeApi/module/hipModuleTexture2dDrv.cpp:
updated test to generate tex2d_kernel.code object in build directory. Currently ctest looks for it in build directory.

Change-Id: I629d395a919c2440d921422716944c7940ed6010


[ROCm/hip commit: 3479847d16]
2020-03-04 10:07:09 -05:00
Payam 5cf8d742cb Excluding vdi platform for now from the following tests so we can build
Change-Id: I651255c2515a62c8bdfdd17a3ac85c3d66a5761b


[ROCm/hip commit: e4e8c4b74b]
2020-02-07 02:16:05 -05:00
Yaxun (Sam) Liu 5d17d5b029 Fix test hip_bitextract.cpp (#1784)
The randomly generated offset+width may exceeds 32, which causes
a left shift operation with 32-offset-width. As an unsigned number
that is greater than 32 and causes undefined behavior. When the
test is compiled without -mavx it is still OK. However when
the test is compiled with -mavx, the undefined behavior causes
wrong results and test failure.

This patch adjusts width so that offset+width<=32 always.

[ROCm/hip commit: 02848e0b80]
2020-01-10 13:46:57 +05:30
Sarbojit2019 6d2ec032fe Change to generate hipVersion.h (#1726)
HIP_VERSION_MAJOR, HIP_VERSION_MINOR, HIP_VERSION_PATCH and HIP_VERSION pre-processor macros are now defined in hipVersion.h instead of being set by hipcc.

[ROCm/hip commit: aa4aea0754]
2019-12-30 12:44:24 +05:30
Maneesh Gupta 4e564f783e Revert changes for atomic FADD support when address is in LDS (#1701)
This reverts PR #1591 and follow-on PR #1695

[ROCm/hip commit: 32442c6506]
2019-11-29 11:58:12 +05:30
Alex Voicu fd08d068c7 Use native support for atomic FADD when address is in LDS (#1591)
[ROCm/hip commit: d597e7ca20]
2019-11-22 07:53:48 +05:30
Alex Voicu 4ec70a7e03 Extend vector type capabilities and add tests to reflect it. (#1656)
[ROCm/hip commit: b5b3d1bbaa]
2019-11-20 21:32:32 +05:30
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