65ffaf82d8
Enable tests that are passing on hip-vdi
...
Change-Id: I7de965f7e8bb7e4d0fa61cd584f0cd118c1e212e
2020-03-05 16:08:51 +05:30
3d64a38953
reverting part of http://gerrit-git.amd.com/c/compute/ec/hip/+/326145
...
the test still fails
Change-Id: I2e5968115a717e8482be670d9fb8472e391922d7
2020-03-04 13:49:58 -05:00
3479847d16
Enable tests hipTestDeviceSymbol,hipTestConstant and p2p_copy_coherency on hip-vdi
...
SWDEV-225266: [HIP-VDI] HIP-VDI disabled tests (p2p_copy_coherency.cpp)
SWDEV-225388: hipTestDeviceSymbol.cpp & hipTestConstant.cpp failed to build on hip-vdi
For hipTestDeviceSymbol.cpp & hipTestConstant.cpp tests:
Currently "__HIP_VDI__" flag is enabled in CMakeLists.txt, but when application is compiled with hipcc,
__HIP_VDI__ is not defined to differentiate if compiled for VDI/HCC for headers.
For ./src/runtimeApi/memory/p2p_copy_coherency.cpp:
Fixed compilation issue to include only when compile for HCC runtime "<hc_am.hpp> not found"
Currently test is disabled to run on all platforms. When validated on multi-GPU machine,
memcpy between multiple GPUs via GPU synchronization is not working on hcc and vdi path.
Need to validate on nvidia machine to know if test is valid. Disabled GPU synchronization test for now.
For ./src/runtimeApi/module/hipModuleTexture2dDrv.cpp:
updated test to generate tex2d_kernel.code object in build directory. Currently ctest looks for it in build directory.
Change-Id: I629d395a919c2440d921422716944c7940ed6010
2020-03-04 10:07:09 -05:00
b910a7ff26
SWDEV-219799
...
Add missing __hip_pinned_shadow__ attribute to the hipModuleTexture2dDrv test.
Change-Id: I2c213a4108611c1af691388f268cac429b81a313
2020-03-03 11:49:00 -05:00
f4401ff2b5
removing 3 tests temporarily to enable hiptests
...
Change-Id: I8c45791aaf88628850462aff90979c147cb85f64
2020-02-25 19:01:34 -05:00
ed56e605d4
Add __hip_pinned_shadow__ for texture
...
Add missing __hip_pinned_shadow__ for texture in tex2d_kernel test.
Change-Id: Iefc96084fec8f84a1d1bb979998ffb95b4011f0b
2020-02-20 20:01:28 -05:00
b3f445c0f5
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
2020-02-16 22:26:47 -05:00
fabe62e31f
removing oocupancy tests from hip-vdi for now
...
Change-Id: I06e966d07021af87fa2c195e4bbaf6bcc336658d
2020-02-13 21:40:06 -05:00
2cf3257795
Merge branch 'master' into amd-master-next
...
Change-Id: Ibb7775e7acd263d2ece40a241517bbd15976fdd4
2020-02-12 00:14:07 -08:00
f8e1c01900
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 fa98798b63
2020-02-10 10:45:28 +05:30
e4e8c4b74b
Excluding vdi platform for now from the following tests so we can build
...
Change-Id: I651255c2515a62c8bdfdd17a3ac85c3d66a5761b
2020-02-07 02:16:05 -05:00
4d472b777f
[dtest] Update hipLaunchCoopMultiKernel.cpp ( #1844 )
...
used reinterpret_cast<uint32_t*> for numBlocks, as expected by hipOccupancyMaxActiveBlocksPerMultiprocessor() api.
2020-02-04 19:37:38 +05:30
48d1f766d5
[dtest] RCCL multi device launch test ( #1731 )
...
Simple test for hipLaunchCooperativeKernelMultiDevice API.
2020-02-04 08:53:43 +05:30
fa98798b63
Match Occupancy APIs syntax with CUDA ( #1625 )
...
* Match Occupancy APIs syntax with CUDA and fix tests using these APIs
2020-01-29 13:05:53 -08:00
0dadb23327
Merge pull request #1759 from emankov/master
...
[HIP] Unify hipError_t (Step 2)
2019-12-30 19:21:09 +03:00
4921678b6c
[HIP] Clean-up deprecated HIP error codes
...
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle
2019-12-23 17:01:35 +03:00
75a11330aa
Fix late-coming issues. ( #1724 )
...
Implementation for hipMemcpyWithStream.
2019-12-23 19:11:24 +05:30
bf3df9d7c0
Add comments explaining choice on the cap for system memory on Windows.
2019-12-13 21:38:27 -05:00
12634879e2
Add explicit cast when computing the available amount of system memory.
2019-12-13 21:37:30 -05:00
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
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
892d2a562e
Fix hipMemcpyWithStream ( #1707 )
...
* Fix hipMemcpyWithStream
* Add a dtest for the same.
2019-12-04 11:56:23 +05:30
153a959280
Revert [HIP] Fixed hipStreamAddCallback ( #1674 )
...
This reverts commit 45613311d7
2019-11-20 11:55:46 +05:30
188752b2cb
[dtest] Rename hipExtLaunchMultiKernelMultiDevice dtest ( #1671 )
2019-11-19 09:41:13 -08:00
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
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
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
cf92fae9e6
[hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel ( #1613 )
2019-11-05 12:32:46 +05:30
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
55f2a38120
Formatting changes
2019-10-30 18:12:51 -07:00
4ab71216b4
Formatting changes ,variable name and check update
2019-10-30 18:09:21 -07:00
e4a1e44162
Revert "Fix occupany APIs ( #1560 )"
...
This reverts commit af351d7e1b
2019-10-29 11:41:08 -07:00
4239c94fe5
Excluded the test case for nvcc platform
2019-10-25 15:52:11 +05:30
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
564418c308
Refactored the file as suggested
2019-10-25 10:44:38 +05:30
318df5c36b
Update matmul.cpp
2019-10-25 09:22:07 +05:30
cd25149225
Update hipExtModuleLaunchKernel.cpp
2019-10-25 09:19:49 +05:30
af351d7e1b
Fix occupany APIs ( #1560 )
...
Addresses SWDEV-205006
2019-10-24 17:44:47 +05:30
8b496e4715
Adding a directed test case for hipExtModuleLaunchKernel() api.
2019-10-24 15:06:28 +05:30
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
c747b77ac1
hipMemset2D and hipMemset3D tests should be passing by default.
2019-10-16 11:02:38 -04:00
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
346bfa90d6
Update indentation in the hipMemset3D test. Replace all tabs with four spaces.
2019-10-15 15:29:14 -04:00
00425bdf3d
Add async subtest to hipMemSet3D
2019-10-15 14:24:04 -04:00
3db2ecc52b
hipMemset2D test should pass only if both async and sync subtests pass.
2019-10-15 14:20:14 -04:00
87834500b9
Fix for directed tests failure ( #1511 )
...
directed_tests/runtimeApi/module/hipLaunchCooperativeKernel.tst - Disabling test temporarily until driver support is available.
directed_tests/runtimeApi/memory/hipArray.tst - Disabling test temporarily to reimplement it correctly.
2019-10-10 19:58:41 +05:30
ba9c6e13e4
Added new Memory API's ( #1399 )
...
Added new memory API's hipMemAllocPitch, hipMemAllocHost, hipMemsetD16, hipMemsetD16Async, hipMemsetD8Async
Modified to support all scenarios hipMemcpyParam2DAsync, hipMemcpyParam2D.
2019-10-04 13:36:31 +05:30
b3e6ba50c3
[hip] Added gfx803,gfx1010,gfx1012 kernel binary hipModule test. ( #1444 )
...
This is to address hipModule test seg fault in GFX1010
2019-09-30 10:38:37 +05:30
5ed1f3e2c8
[hip]Skip test when hipHostMallocCoherent is not supported by implementation ( #1380 )
2019-09-16 08:31:43 +00:00
ceb734b917
Added new device attributes ( #1377 )
...
* Added new device attributes
* updated comment
* updated with new device attributes supported
2019-09-16 08:31:30 +00:00
agodavar
Payam
Vladislav Sytchenko
Tao Sang
Laurent Morichetti
Maneesh Gupta
lthakur
gandryey
satyanveshd
Evgeny Mankov
Alex Voicu
Vladislav Sytchenko
Rahul Garg
Sarbojit2019
Aryan Salmanpour
amd-lthakur
amd-lthakur
ansurya
AlexBinXie