Commit Graph

944 Commits

Author SHA1 Message Date
Tao Sang 6f25af095e Merge "Generating hiprtc lib with hcc+hip-clang" into amd-master-next
[ROCm/clr commit: 1d22c5b925]
2020-02-25 14:46:24 -05:00
Vladislav Sytchenko d4bb8d522d Reeanble texture tests for VDI
Enable hipBindTex2DPitch and hipBindTexRef1DFetch

Change-Id: I36a3252e25d1ed844967ec117e1f1951004cba11


[ROCm/clr commit: b1d2e581ff]
2020-02-24 15:24:00 -05:00
Jatin Chaudhary 97937573d4 Generating hiprtc lib with hcc+hip-clang
Review comments - generate hiprtc lib everytime when HIP_PLATFORM is hcc

Changes for hip-clang

Removing pre processor directive to simplify

Change-Id: Id38ab368362b58ee0458baeb8051fea709ae6bba


[ROCm/clr commit: 8bf287ef18]
2020-02-24 11:44:17 -05:00
Tao Sang 10021089af Add __hip_pinned_shadow__ for texture
Add missing __hip_pinned_shadow__ for texture in tex2d_kernel test.

Change-Id: Iefc96084fec8f84a1d1bb979998ffb95b4011f0b


[ROCm/clr commit: ba494c64cf]
2020-02-20 20:01:28 -05:00
Christophe Paquot 1f32dbad00 Merge "HIP-HCC + Clang fix failing texture tests(SWDEV-223622)" into amd-master-next
[ROCm/clr commit: 644dad178c]
2020-02-19 14:57:14 -05:00
Jatin Chaudhary 1b17cc297a Removing gcc test for clang
Change-Id: Iccf00221a07be920683207daa9ed0e0949259623


[ROCm/clr commit: e1024a249a]
2020-02-19 11:09:47 -05:00
agodavar 37745e6f1b HIP-HCC + Clang fix failing texture tests(SWDEV-223622)
Change-Id: I1c0a7059c6bba1ea2e39dc6634b32d006c07d1f5


[ROCm/clr commit: 63c1d28a4b]
2020-02-19 07:03:57 -05:00
Tao Sang 0292fd9991 Temporarily comment out Hcc-specific APIs for CLang compiler
Temporarily comment out Hcc-specific template functions
hipExtLaunchKernelGGL and hipOccupancyMaxPotentialBlockSize for CLang
compiler so that all test cases under hip/samples can be built
successfully for Clang + Hip/Hcc runtime.

Change-Id: Iafc761257be4a7b34eafa6759a01f369570cd6ce


[ROCm/clr commit: 15b91e9f1e]
2020-02-16 22:26:47 -05:00
Tao Sang 53e62f704d Support defaultDriver test with Clang+Hcc Runtime
Fix the following issues:
1.Ignore hidden arguments of kernel functions.
2.Look up both origial function name and function name with .kd postfix
when argments are retrived from module.
3.Addition, fix compiling issue of LaunchKernel test app.

Change-Id: I9400943f2f02433cb4409b19c0cac3626c2bc454


[ROCm/clr commit: eb8c4d1ce2]
2020-02-15 19:29:13 -05:00
Payam ca7c148089 removing oocupancy tests from hip-vdi for now
Change-Id: I06e966d07021af87fa2c195e4bbaf6bcc336658d


[ROCm/clr commit: 9bdc203a99]
2020-02-13 21:40:06 -05:00
Laurent Morichetti abe27cad61 Merge branch 'master' into amd-master-next
Change-Id: Ibb7775e7acd263d2ece40a241517bbd15976fdd4


[ROCm/clr commit: 9b3e214952]
2020-02-12 00:14:07 -08:00
Maneesh Gupta a21b1f84cb Revert "Match Occupancy APIs syntax with CUDA (#1625)" (#1857)
Reverting this for now till we figure out how to avoid the build
breakage.

This reverts commit 2c6e880e05.

[ROCm/clr commit: d032637934]
2020-02-10 10:45:28 +05:30
Payam a5fdb0c135 Excluding vdi platform for now from the following tests so we can build
Change-Id: I651255c2515a62c8bdfdd17a3ac85c3d66a5761b


[ROCm/clr commit: 141aa8e5dc]
2020-02-07 02:16:05 -05:00
Laurent Morichetti 3cfd9b4f6a Merge branch 'master' into amd-master-next
Change-Id: Ib7e7824073f4dfc391fb3833fc90e11b327d3c22


[ROCm/clr commit: c33903b5da]
2020-02-05 14:56:08 -08:00
vsytch e2b6794a07 Device texture functions should not normalize the sampled pixel (#1826)
* Device texture functions should not normalize the sampled pixel. This is already done by HW.
* Add support to use h/w capability for normalized float data convertion for driver API's

Co-authored-by: ansurya <50609411+ansurya@users.noreply.github.com>


[ROCm/clr commit: fa363ae721]
2020-02-05 20:56:17 +05:30
lthakur a5409a5556 [dtest] Update hipLaunchCoopMultiKernel.cpp (#1844)
used reinterpret_cast<uint32_t*> for numBlocks, as expected by hipOccupancyMaxActiveBlocksPerMultiprocessor() api.

[ROCm/clr commit: 2ef4dead24]
2020-02-04 19:37:38 +05:30
Siu Chi Chan 30f09a1435 Fix C-style hipLaunchKernel (#1835)
* Fix bug in LaunchKernel test
Instead of passing the address of the gpu buffer, pass the address
of the pointer that holds the address of the gpu buffer

* Fix hipLaunchKernel's kernarg buffer construction.
The hipLaunchKernel implementation should rely on ihipModuleLaunchKernel
to construct the kernarg buffer correctly based on kernel metadata.

* Fix a bug in get_functions where the Kernel_descriptor wasn't constructed with the correct kernarg layout information.

* Fix a bug in kernarg layout parsing dealing with kernel without any arg

* teach ihipModuleLaunchKernel to handle kernel without any arg

* Add a more interesting test

[ROCm/clr commit: 14e235378f]
2020-02-04 19:37:16 +05:30
ansurya 0c87c8639d [hit] Syntax support for EXCLUDE_HIP_RUNTIME and EXCLUDE_HIP_COMPILER (#1800)
* Added support to disable test based on HIP Runtime(HCC/VDI) and Compiler(hcc/clang)
* Updated README.md, HIT.cmake for new options EXCLUDE_HIP_RUNTIME and EXCLUDE_HIP_COMPILER


[ROCm/clr commit: 696c85aec9]
2020-02-04 08:56:02 +05:30
gandryey f33fa4ab31 [dtest] RCCL multi device launch test (#1731)
Simple test for hipLaunchCooperativeKernelMultiDevice API.


[ROCm/clr commit: 3c718ebe15]
2020-02-04 08:53:43 +05:30
Laurent Morichetti 540a8d6337 Merge branch 'origin/pghafari/hip-vdi' into lmoriche/amd-master-next
Change-Id: I22c145d39f430ca571a981687bcb034ea6e3b8a2


[ROCm/clr commit: 2f1305b9a4]
2020-01-31 07:33:12 -08:00
jujiang-del a6012c4bfb [dtest] Avoid resViewDesc for non-array resource in texture creation (#1823)
[ROCm/clr commit: cb632005bc]
2020-01-30 14:04:41 -08:00
satyanveshd 2c6e880e05 Match Occupancy APIs syntax with CUDA (#1625)
* Match Occupancy APIs syntax with CUDA and fix tests using these APIs


[ROCm/clr commit: 262ad13dd5]
2020-01-29 13:05:53 -08:00
Siu Chi Chan adb93af8c3 Fix associate code object symbols with host allocation bug (#1799)
The current implementation skips this procedure for a given device
object when a global symbol is found in the cache.  This is incorrect:

 - There could be other undefined globals that have not been previously
encountered further down the list
 - If a symbol is found in the cache, it doesn't need to be pinned again
but it still need to be defined for the current executable

Added special case for the printf buffer symbol (already pinned by HCC)

The bug was exposed by running printf on different GPUs.

[ROCm/clr commit: 8fc7cad90f]
2020-01-24 16:22:49 +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
Rahul Garg 1e78733f53 Add hipBindTexture2D on NVCC path (#1773)
[ROCm/clr commit: 534376cb41]
2020-01-06 12:33:50 +05:30
Evgeny Mankov 8c58286a9b Merge pull request #1759 from emankov/master
[HIP] Unify hipError_t (Step 2)

[ROCm/clr commit: ed43699a3a]
2019-12-30 19:21:09 +03:00
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
Evgeny Mankov d191980c6a [HIP] Clean-up deprecated HIP error codes
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle


[ROCm/clr commit: 4aaa2336a8]
2019-12-23 17:01:35 +03:00
Alex Voicu 1f762e3970 Fix late-coming issues. (#1724)
Implementation for hipMemcpyWithStream.


[ROCm/clr commit: 150e690a3a]
2019-12-23 19:11:24 +05:30
Evgeny Mankov e25a6a39a3 [HIP] Unify hipError_t (Step 2)
Step 2. Make a few hipError codes deprecated
Update hipify-clang, hipify-perl, docs and samples accordingly


[ROCm/clr commit: 9ae76609a1]
2019-12-22 02:05:31 +03:00
Vladislav Sytchenko dc12f8017e Add comments explaining choice on the cap for system memory on Windows.
[ROCm/clr commit: a91bafca40]
2019-12-13 21:38:27 -05:00
Vladislav Sytchenko 014f068e2f Add explicit cast when computing the available amount of system memory.
[ROCm/clr commit: 4c21eed68b]
2019-12-13 21:37:30 -05:00
Vladislav Sytchenko d2be30f0e0 Reduce the amount of free host memory to 40% of what is reported on Windows, otherwise we can run into OOM situations.
[ROCm/clr commit: 282367ed6d]
2019-12-11 20:21:12 -05:00
Rahul Garg 48faf7423a Revert - Changes related to hipMemcpyWithStream (#1718)
Reverting #1673, #1697 and #1707.
Support for hipMemcpyWithStream and memcpy optimizations, will be brought in again once issues seen with these are resolved independently.

[ROCm/clr commit: a369bd4418]
2019-12-06 09:51:53 +05:30
Rahul Garg 6c7a338471 Fix hipMemcpyWithStream (#1707)
* Fix hipMemcpyWithStream
* Add a dtest for the same.


[ROCm/clr commit: 261a04580f]
2019-12-04 11:56:23 +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
Paul Fultz II 29bb65f6e0 Fix helper header when using c++17 (#1666)
This will fix issue #1621. It also adds tests for is_callable with c++11, c++14, and c++17.

The fallback implementation was completely broken so I rewrote it so it pass the tests as well. This should be used instead of PR #1631.

[ROCm/clr commit: 57b1b03261]
2019-11-20 21:33:42 +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
Sarbojit2019 2c00d66995 Revert [HIP] Fixed hipStreamAddCallback (#1674)
This reverts commit 4d0b7e65bb.
Addresses SWDEV#212675.

[ROCm/clr commit: 8a3c36a424]
2019-11-20 11:55:46 +05:30
Rahul Garg 6813f0436c [dtest] Rename hipExtLaunchMultiKernelMultiDevice dtest (#1671)
[ROCm/clr commit: fa1335f419]
2019-11-19 09:41:13 -08:00
Sameer Sahasrabuddhe 82aa679a6d hostcall: add tests that are only used by the VDI build (#1664)
[ROCm/clr commit: e158b0b255]
2019-11-18 19:52:40 -08:00
Rahul Garg f524f75b69 Fix gcc build on NVCC path (#1661)
* Fix gcc build on NVCC path

* Fix CI build errors

* [dtest] Fix texture and surface obj2D tests


[ROCm/clr commit: ff31f734fe]
2019-11-18 12:19:22 +05:30
jiabaxie de260a6d60 Updated hipEnvVarDriver to work with Windows (#1614)
* Updated hipEnvVarDriver to work with Windows

* Cleaned up a bit of code

* Fixed a part where putenv was used for both win and linux

* Defines moved to test_common.h and cleaned up code

* Cleaned up some macro defines and used const char instead

* Got rid of some excess commenting

* directory paths are unconditional

* Cleaned some duplicate code, and variables are now declared and defined together


[ROCm/clr commit: 7bbd420068]
2019-11-18 12:18:29 +05:30
kjayapra-amd fffdd3da8d [dtests] Fixing compilation error in saxpy.cpp (#1608)
[ROCm/clr commit: 99da905509]
2019-11-18 12:18:11 +05:30
Alex Voicu f48b38b0ed Add support for extended launch syntax. (#1530)
* Add support for extended launch syntax.

* Add unit test.

* Fix typo

* hipExtLaunchKernelGGL lives in hip_ext.h

Change-Id: Ice32dab0d43475fda65c6a910c11416871a8f2ff

* [dtest] remove redundant include from hipModuleGetGlobal dtest


[ROCm/clr commit: 355d0bdf95]
2019-11-16 22:24:07 -08:00
Maneesh Gupta 57225de63f [ci] Fix failures on nvcc path (#1654)
Change-Id: I97f6b51314e14965618ab510bf57a2b034183e78

[ROCm/clr commit: 4d0a234183]
2019-11-15 07:58:40 +05:30
Sarbojit2019 4d0b7e65bb [HIP] Fixed hipStreamAddCallback [SWDEV#165185] (#1425)
Fixed hipStreamAddCallback() as requested in SWDEV#165185
Added unit test to test the behavior


[ROCm/clr commit: 97fca3439d]
2019-11-07 13:18:12 +05:30
ansurya f5a92e5cb6 Fixed texture 2D mapping for pitched arrays & 3D Texture read (#1415)
Texture 2D image mapping for pitched arrays:
github issue: Texture Object's Buffer seems to be Misaligned #886
JIRA ticket: SWDEV-199313

SWDEV-151670 : Fixed issue with 3D texture with 4 components
SWDEV-151671 : Issue with 2D layered texture with 4 components

[ROCm/clr commit: dc8f556460]
2019-11-07 13:17:46 +05:30
Rahul Garg cf648f7dbe Rename hip/hip_hcc.h to hip/hip_ext.h (#1341)
* Rename hip/hip_hcc.h to hip/hip_ext.h

* Deprecate hip_hcc.h


[ROCm/clr commit: dfee3ae279]
2019-11-07 13:17:10 +05:30