Wykres commitów

218 Commity

Autor SHA1 Wiadomość Data
TomSang 588a6c250e SWDEV-299960 - Fix .hipTestAtomicAdd test on NV (#2338)
1. Add --gpu-architecture=compute_60 to fully support AtomicAdd()
2. Add atomicAddNoRet() for NV.

Change-Id: I5add28ebabcfa21fb3ef99d09004c5d13423a290

[ROCm/hip commit: 7dba6dc28e]
2021-09-14 13:37:30 +05:30
Tao Sang 65dbac4ec0 SWDEV-294582 - Fix hipStdComplex in NV
Use cuda::std instead of std name space for complex
operations.

Change-Id: I43b23384ac7a129fcd7f41204f796105576cd628


[ROCm/hip commit: 63586279ba]
2021-07-19 10:50:11 -04:00
Tao Sang 872b6abec3 SWDEV-295381 - Fix hipSimpleAtomicsTest
Fix hipSimpleAtomicsTest failure on amd and nvidia devices.

Change-Id: I43b23384ab70129ccd7f41204f796105576cd605


[ROCm/hip commit: a2fdc8cfbd]
2021-07-15 20:45:51 -04:00
agunashe a4ff63a29b SWDEV-293742 - Update copyright end year
Change-Id: I2cb7bbd9a6d9da28116ba9dd9cec4e60525444e2


[ROCm/hip commit: d529637fbc]
2021-07-07 12:57:23 -04:00
Satyanvesh Dittakavi 7a49cdb7a0 SWDEV-292618 - Enable/Fix few of the dtests on Nvidia Platform
Change-Id: I6f4e37b293aac9054a768f9d692b914f52d42756


[ROCm/hip commit: 57569c62f4]
2021-06-30 01:23:29 -04:00
Tao Sang 3a7e5a87ca SWDEV-291001 - Disable sincos() for NV
Disable sincos() for NV temporarily in order
to prevent kernel launch failure for NVA100.

Change-Id: Ic9ec976c5c486c4e1d3b83e1578081673f97efa3


[ROCm/hip commit: fd50af8c77]
2021-06-15 13:31:20 -04:00
Tao Sang 7a932782e2 SWDEV-287768 - Fix hipTestClock test
Use long long instead of int as clock64() return.

Change-Id: Id3e4645c05959e13f58efd88bc43f3a1d3e50d59


[ROCm/hip commit: 792415f960]
2021-06-04 15:45:07 -04:00
Joseph Greathouse 9f962f4d74 SWDEV-288361 - Implement funnel shift operators
Change-Id: I0c73809366f2d21e75f98fdeac7fed0c7591ee34


[ROCm/hip commit: bec284b26a]
2021-06-01 11:10:11 -04:00
Yaxun (Sam) Liu 416d9fbfb6 SWDEV-283048 - Fix hipTestFMA
This test is incorrect about _Float16 overloading. Need to keep the test
passing for both old and new compiler until the compiler change is in
mainline.

Change-Id: I2f9be8957282fd0579c74f1e9f23e65c4484f3a2


[ROCm/hip commit: 6eabbc83f7]
2021-04-22 15:07:16 -04:00
Sarbojit Sarkar 47c83726a4 SWDEV-280131 - Fix __half2 member access bug
Change-Id: Ic11750d18e4ba47446a7e494c3089a19cb4df783


[ROCm/hip commit: 83a25eb5b5]
2021-04-07 12:12:02 -04:00
Rupam Chetia db7803ee5d SWDEV-238517 - [dtest] Adding new test cases for hipComplex functions.
1. Added 21 test scenarios to test the hipComplex functions on both host and device.
2. Modified the floating point comparisons with precision check.

Change-Id: I9edfb0c635ced255935087c85b77d3cc6a1a82e3


[ROCm/hip commit: 366f0462f2]
2021-04-06 07:54:29 -04:00
Tao Sang 2820f91c90 Remove hip-hcc codes: Part four
Remove __HCC__, __HCC_ONLY__, __HCC_CPP__, __HCC_C__,
__HCC_OR_HIP_CLANG__, __HIP_ROCclr__ and their guarded codes.

Remove Hcc codes from directed_tests and samples.

Remove __HIP_PLATFORM_HCC__ and __HIP_PLATFORM_NVCC__ from
some files where they are not necessary.

Add deprecation notice.

Change-Id: I1ae467eafd749d6c25bca204c1724b026be21fce


[ROCm/hip commit: b34dd95124]
2021-01-08 10:53:34 -05:00
Tao Sang c618b6aeff Remove hip-hcc codes: Part three
1.Rename include/hip/hcc_detail/ as include/hip/amd_detail/

2.Rename include/hip/nvcc_detail/ as include/hip/nvidia_detail/

3.Create __HIP_PLATFORM_AMD__ to replace __HIP_PLATFORM_HCC__

4.Create __HIP_PLATFORM_NVIDIA__ to replace __HIP_PLATFORM_NVCC__

After hcc_detail, nvcc_detail, __HIP_PLATFORM_HCC__ and __HIP_PLATFORM_NVCC__
have been removed from upstream, they will be removed from hip runtime.

Change-Id: I1ae457effd739d6c25bca203c1724b026be21fce


[ROCm/hip commit: c2adc70d4d]
2021-01-05 10:39:31 -05:00
Aaron En Ye Shi e2f8d46749 Fix hipTestFMA to support older compiler
The older compiler does not promote integral
arguments to double, instead it uses float.
This patch tries to support the old compiler
headers, and also the newer one.

Change-Id: I01e0b96a82ecddc6230cb5baf2573a318b25445b


[ROCm/hip commit: 09a1c22208]
2020-12-10 14:27:42 -05:00
Aaron En Ye Shi 9db34cbdd9 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/hip commit: 1f0037eefc]
2020-12-08 10:48:29 -08:00
agodavar 13436a7e1f cmake hip-rocclr as default build,change HIP_PLATFORM to amd|nvidia
Change-Id: I59d2e15b297b6ca2d5eee1a6dee642bdb01a3839


[ROCm/hip commit: d10124e1d7]
2020-10-21 07:26:14 -04:00
sumanthtg b92a369a11 [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/hip commit: 543dc8cea5]
2020-10-07 13:20:12 -04:00
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