Yaxun (Sam) Liu
02848e0b80
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.
2020-01-10 13:46:57 +05:30
Rahul Garg
a5d7e7d8d3
Add hipBindTexture2D on NVCC path ( #1773 )
2020-01-06 12:33:50 +05:30
Evgeny Mankov
0dadb23327
Merge pull request #1759 from emankov/master
...
[HIP] Unify hipError_t (Step 2)
2019-12-30 19:21:09 +03:00
Sarbojit2019
aa4aea0754
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.
2019-12-30 12:44:24 +05:30
Evgeny Mankov
4921678b6c
[HIP] Clean-up deprecated HIP error codes
...
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle
2019-12-23 17:01:35 +03:00
Alex Voicu
75a11330aa
Fix late-coming issues. ( #1724 )
...
Implementation for hipMemcpyWithStream.
2019-12-23 19:11:24 +05:30
Vladislav Sytchenko
bf3df9d7c0
Add comments explaining choice on the cap for system memory on Windows.
2019-12-13 21:38:27 -05:00
Vladislav Sytchenko
12634879e2
Add explicit cast when computing the available amount of system memory.
2019-12-13 21:37:30 -05:00
Vladislav Sytchenko
b12c53cceb
Reduce the amount of free host memory to 40% of what is reported on Windows, otherwise we can run into OOM situations.
2019-12-11 20:21:12 -05:00
Rahul Garg
e53fc316f1
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.
2019-12-06 09:51:53 +05:30
Rahul Garg
892d2a562e
Fix hipMemcpyWithStream ( #1707 )
...
* Fix hipMemcpyWithStream
* Add a dtest for the same.
2019-12-04 11:56:23 +05:30
Maneesh Gupta
32442c6506
Revert changes for atomic FADD support when address is in LDS ( #1701 )
...
This reverts PR #1591 and follow-on PR #1695
2019-11-29 11:58:12 +05:30
Alex Voicu
d597e7ca20
Use native support for atomic FADD when address is in LDS ( #1591 )
2019-11-22 07:53:48 +05:30
Paul Fultz II
8519a1411c
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 .
2019-11-20 21:33:42 +05:30
Alex Voicu
b5b3d1bbaa
Extend vector type capabilities and add tests to reflect it. ( #1656 )
2019-11-20 21:32:32 +05:30
Sarbojit2019
153a959280
Revert [HIP] Fixed hipStreamAddCallback ( #1674 )
...
This reverts commit 45613311d7 .
Addresses SWDEV#212675.
2019-11-20 11:55:46 +05:30
Rahul Garg
188752b2cb
[dtest] Rename hipExtLaunchMultiKernelMultiDevice dtest ( #1671 )
2019-11-19 09:41:13 -08:00
Sameer Sahasrabuddhe
363caf29c6
hostcall: add tests that are only used by the VDI build ( #1664 )
2019-11-18 19:52:40 -08:00
Rahul Garg
e39d7497ec
Fix gcc build on NVCC path ( #1661 )
...
* Fix gcc build on NVCC path
* Fix CI build errors
* [dtest] Fix texture and surface obj2D tests
2019-11-18 12:19:22 +05:30
jiabaxie
e73927caee
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
2019-11-18 12:18:29 +05:30
kjayapra-amd
0a68be8b5b
[dtests] Fixing compilation error in saxpy.cpp ( #1608 )
2019-11-18 12:18:11 +05:30
Alex Voicu
69e74c3e96
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
2019-11-16 22:24:07 -08:00
Maneesh Gupta
f9fec8fdca
[ci] Fix failures on nvcc path ( #1654 )
...
Change-Id: I97f6b51314e14965618ab510bf57a2b034183e78
2019-11-15 07:58:40 +05:30
Sarbojit2019
45613311d7
[HIP] Fixed hipStreamAddCallback [SWDEV#165185] ( #1425 )
...
Fixed hipStreamAddCallback() as requested in SWDEV#165185
Added unit test to test the behavior
2019-11-07 13:18:12 +05:30
ansurya
e07926ce0f
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
2019-11-07 13:17:46 +05:30
Rahul Garg
579a4f36fa
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
2019-11-07 13:17:10 +05:30
Aryan Salmanpour
cf92fae9e6
[hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel ( #1613 )
2019-11-05 12:32:46 +05:30
Rahul Garg
4739e68bbe
Merge pull request #1582 from amd-lthakur/hipExtMLK
...
Adding a directed test case for hipExtModuleLaunchKernel() api.
2019-10-31 17:13:26 -07:00
Rahul Garg
55f2a38120
Formatting changes
2019-10-30 18:12:51 -07:00
Rahul Garg
4ab71216b4
Formatting changes ,variable name and check update
2019-10-30 18:09:21 -07:00
Rahul Garg
ba8105e0cd
Merge pull request #1515 from ansurya/tex_unbind_issue_fix
...
Fix undefined ref to hipUnbindTexture for texture types
2019-10-30 17:54:15 -07:00
Rahul Garg
e4a1e44162
Revert "Fix occupany APIs ( #1560 )"
...
This reverts commit af351d7e1b .
2019-10-29 11:41:08 -07:00
Anusha Godavarthy Surya
03623cc3f1
Merge branch 'master' into tex_unbind_issue_fix
2019-10-25 15:54:25 +05:30
amd-lthakur
4239c94fe5
Excluded the test case for nvcc platform
2019-10-25 15:52:11 +05:30
Anusha Godavarthy Surya
5f47e99ffe
merge from master
2019-10-25 15:52:09 +05:30
Rahul Garg
12e1a86ec1
[dtest] Fix hipMemset2D test ( #1579 )
...
Reverts changes made in #1399 . This is a RT api test. For testing hipMemAllocPitch , a new test should be written and that should use correct memset API.
2019-10-25 15:44:05 +05:30
Anusha Godavarthy Surya
259d8b4cdf
Merge branch 'master' into tex_unbind_issue_fix
2019-10-25 15:36:55 +05:30
amd-lthakur
564418c308
Refactored the file as suggested
2019-10-25 10:44:38 +05:30
amd-lthakur
318df5c36b
Update matmul.cpp
2019-10-25 09:22:07 +05:30
amd-lthakur
cd25149225
Update hipExtModuleLaunchKernel.cpp
2019-10-25 09:19:49 +05:30
satyanveshd
af351d7e1b
Fix occupany APIs ( #1560 )
...
Addresses SWDEV-205006
2019-10-24 17:44:47 +05:30
amd-lthakur
8b496e4715
Adding a directed test case for hipExtModuleLaunchKernel() api.
2019-10-24 15:06:28 +05:30
Vladislav Sytchenko
664b115c44
Remove extra #endif.
2019-10-18 16:40:29 -04:00
Vladislav Sytchenko
8f0a226660
_aligned_malloc() on Windows first takes size, then alignment, which is the opposite of how the similar function behaves on Linux. Memory allocated by it also has to be freed using _aligned_free(), unlike Linux where we can use regular free().
...
Edit aligned_alloc() macro and add a aligned_free() one to align with the above behaviour.
2019-10-17 18:58:32 -04:00
Rahul Garg
e1aac060da
Merge pull request #1544 from vsytch/master
...
QoL changes to the hipMemset family
2019-10-16 18:54:20 -07:00
Vladislav Sytchenko
c747b77ac1
hipMemset2D and hipMemset3D tests should be passing by default.
2019-10-16 11:02:38 -04:00
vsytch
2fb734ef5f
Update hipMathFunctions, hipTestHalf and hipTestNativeHalf tests to support Navi10 and Navi14. ( #1545 )
2019-10-16 10:51:48 +05:30
Vladislav Sytchenko
f5af263aba
In the hipMemset2D and hipMemset3D tests synchronize with the default stream after performing an async memset.
2019-10-15 17:15:49 -04:00
Vladislav Sytchenko
346bfa90d6
Update indentation in the hipMemset3D test. Replace all tabs with four spaces.
2019-10-15 15:29:14 -04:00
Vladislav Sytchenko
00425bdf3d
Add async subtest to hipMemSet3D
2019-10-15 14:24:04 -04:00