Граф коммитов

201 Коммитов

Автор SHA1 Сообщение Дата
Sarbojit Sarkar 0eebd71062 SWDEV:253548 : remove gfx-arch macros
Change-Id: I1ef0b4e080c15a9c6228f48ecd6a65b134d0a72d


[ROCm/hip commit: a2f9a2d469]
2020-10-06 01:15:58 -04:00
Jatin Chaudhary 2982f07b9c Fixing/Disabling tests on nvcc path
Change-Id: I7ed4a1246943867482ff595d5f98bb25bd79074b


[ROCm/hip commit: e7eaafe165]
2020-07-30 00:39:07 -04:00
sushantkumar14 4be568268b [dtest] Half2 comparison related tests
Tests heq2, hne2, hle2, hge2, hlt2, hgt2 APIs for functionality
and NaN tests

SWDEV-238517 for enhancing hip unit tests

Change-Id: I88a9a8ead0d00a1261f3d650361d655f2f397e48


[ROCm/hip commit: e590f20cbd]
2020-07-14 23:53:55 -04:00
mshivama 21b2538f90 Add support for few CUDA compatible reduction operations like __syncthreads_count()
Change-Id: I0917820058f0edad5c0bdd42dea37f06353fc63c


[ROCm/hip commit: 27e237ef48]
2020-07-14 12:03:14 -04:00
Yaxun (Sam) Liu 8cced93895 Add pow(float/double/_Float16,int)
Change-Id: Ie65d15cd3df9853a3bbd613d8c7188ae39c327c7


[ROCm/hip commit: 13316e2919]
2020-07-06 07:38:57 -04:00
Siu Chi Chan b8db8cac9b add constexpr constructor for vector types
Change-Id: I45bb0537d6a24ee50b548c2fd8b4f20518764813


[ROCm/hip commit: 784ca6f43c]
2020-06-04 01:57:03 -04:00
Jatin 7b52f0a1ea Adding changes for hipExtLaunchKernel for rocCLR
Change-Id: Iba52bc3bde7c37f3fb375a55ba0947e87b3cdc9b


[ROCm/hip commit: 2d517fdcc6]
2020-06-02 14:16:41 -04:00
Matt Arsenault 3a07d0e785 Remove some asm declarations for intrinsics
This technique should never be used, and only accessed through
__builtins.

There's currently no builtin for groupstaticsize. I left ds_swizzle
since for some reason it switches to the builtin based on __HCC__ or
not.

Change-Id: If1e1394221dba83ea4add6db5e94d6b715552044


[ROCm/hip commit: d2dd307c7d]
2020-05-11 15:20:58 -04:00
agodavar 41a1bb6733 find_package(hip) changes for clang
Change-Id: I9dc1be1dd5f9424e26ebcd2961207e1c4467550f


[ROCm/hip commit: 1468982f8a]
2020-05-01 20:48:32 +00:00
Yaxun (Sam) Liu f79898e90e Enable template max and min for HIP-Clang (#2028)
It was for HCC only. HIP-Clang also needs it for __fp16 since AMDMIGraphX uses it.

Change-Id: Id49322b7b89ef799accdf6b47627a6fce51d1ab5

[ROCm/hip commit: 808dae6813]
2020-04-24 12:30:28 -07:00
Yaxun (Sam) Liu 3207f06462 Disable device side malloc (#2009)
* Disable device side malloc

Currently device side malloc is not working and takes excessive
device memory.

Disable it for now until a working malloc is implemented.

Change-Id: I1ad908c1c53a83752383b4be96688a848642c699

[ROCm/hip commit: 8d83e95457]
2020-04-14 16:07:14 +05:30
ansurya f59ed79983 Initial support for bfloat16 (#1980)
[ROCm/hip commit: 770e76e752]
2020-04-06 15:35:43 +05:30
Jatin Chaudhary 26b7d3e2ee [dtest] Adding VectorTest (#1732)
Adding unit test for operations of device vector types

[ROCm/hip commit: ee5fa8977c]
2020-03-26 17:03:43 +05:30
Jatin Chaudhary 1bc892c6f2 Adding Half Abs APIs (#1902)
[ROCm/hip commit: 16a6a94fbf]
2020-03-17 14:13:19 +05:30
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