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

204 Коммитов

Автор SHA1 Сообщение Дата
Aaron En Ye Shi aee19bb761 Fix hipTestFMA to align with libcxx
The HIP-Clang math headers upstream have been updated
to perform type promotion on math function overloads.
If any argument has integral type, it will be cast to
double.

Change-Id: I38d9e6240c40c4092b946851469498b2ae6500ae


[ROCm/clr commit: 9c041b1984]
2020-12-08 10:48:29 -08:00
agodavar 9132d92ccd cmake hip-rocclr as default build,change HIP_PLATFORM to amd|nvidia
Change-Id: I59d2e15b297b6ca2d5eee1a6dee642bdb01a3839


[ROCm/clr commit: 8717a78bf7]
2020-10-21 07:26:14 -04:00
sumanthtg ceb9b66602 [dtest] Tests for atomicAdd/atomicAddnoRet
Positive and negative test cases for atomicAdd and
AtomicAddnoRet device functions

SWDEV-238517 for enhancing hip unit tests

Change-Id: Id20ba2550d20f224004f105cdcd087002cb80e56


[ROCm/clr commit: 00d46218b7]
2020-10-07 13:20:12 -04:00
Sarbojit Sarkar 8587ec2976 SWDEV:253548 : remove gfx-arch macros
Change-Id: I1ef0b4e080c15a9c6228f48ecd6a65b134d0a72d


[ROCm/clr commit: 3f0e33adb5]
2020-10-06 01:15:58 -04:00
Jatin Chaudhary 6c217e7f69 Fixing/Disabling tests on nvcc path
Change-Id: I7ed4a1246943867482ff595d5f98bb25bd79074b


[ROCm/clr commit: d251c2db57]
2020-07-30 00:39:07 -04:00
sushantkumar14 14e9205334 [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/clr commit: fe3cd6ca27]
2020-07-14 23:53:55 -04:00
mshivama 3b311d6c70 Add support for few CUDA compatible reduction operations like __syncthreads_count()
Change-Id: I0917820058f0edad5c0bdd42dea37f06353fc63c


[ROCm/clr commit: 1c5537dde4]
2020-07-14 12:03:14 -04:00
Yaxun (Sam) Liu aad28fd31d Add pow(float/double/_Float16,int)
Change-Id: Ie65d15cd3df9853a3bbd613d8c7188ae39c327c7


[ROCm/clr commit: b72e8b54e0]
2020-07-06 07:38:57 -04:00
Siu Chi Chan 1f7c745330 add constexpr constructor for vector types
Change-Id: I45bb0537d6a24ee50b548c2fd8b4f20518764813


[ROCm/clr commit: 4b56aaefd6]
2020-06-04 01:57:03 -04:00
Jatin 216873e9c8 Adding changes for hipExtLaunchKernel for rocCLR
Change-Id: Iba52bc3bde7c37f3fb375a55ba0947e87b3cdc9b


[ROCm/clr commit: 126573df4c]
2020-06-02 14:16:41 -04:00
Matt Arsenault 477012bf64 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/clr commit: 03ebfd2d49]
2020-05-11 15:20:58 -04:00
agodavar 7da11623bd find_package(hip) changes for clang
Change-Id: I9dc1be1dd5f9424e26ebcd2961207e1c4467550f


[ROCm/clr commit: ce8a5af666]
2020-05-01 20:48:32 +00:00
Yaxun (Sam) Liu c13a63bcff 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/clr commit: 29549ce4dc]
2020-04-24 12:30:28 -07:00
Yaxun (Sam) Liu 2406fa8a3d 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/clr commit: d556c3425b]
2020-04-14 16:07:14 +05:30
ansurya 6b18a8e068 Initial support for bfloat16 (#1980)
[ROCm/clr commit: ff7aaedca2]
2020-04-06 15:35:43 +05:30
Jatin Chaudhary b2615ca010 [dtest] Adding VectorTest (#1732)
Adding unit test for operations of device vector types

[ROCm/clr commit: b696451240]
2020-03-26 17:03:43 +05:30
Jatin Chaudhary 6d39b6fbb8 Adding Half Abs APIs (#1902)
[ROCm/clr commit: 8a3ce17ba6]
2020-03-17 14:13:19 +05:30
Yaxun (Sam) Liu 87887f6152 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/clr commit: 55525fa466]
2020-01-10 13:46:57 +05:30
Sarbojit2019 4d2ee146e1 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/clr commit: 4fd77f8336]
2019-12-30 12:44:24 +05:30
Maneesh Gupta 97850ae9a8 Revert changes for atomic FADD support when address is in LDS (#1701)
This reverts PR #1591 and follow-on PR #1695

[ROCm/clr commit: 4c92bd50c4]
2019-11-29 11:58:12 +05:30
Alex Voicu e1dca187c9 Use native support for atomic FADD when address is in LDS (#1591)
[ROCm/clr commit: 2ed3a0873c]
2019-11-22 07:53:48 +05:30
Alex Voicu 5c27a4f570 Extend vector type capabilities and add tests to reflect it. (#1656)
[ROCm/clr commit: c383f20691]
2019-11-20 21:32:32 +05:30
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