Wykres commitów

74 Commity

Autor SHA1 Wiadomość Data
Jatin 2d517fdcc6 Adding changes for hipExtLaunchKernel for rocCLR
Change-Id: Iba52bc3bde7c37f3fb375a55ba0947e87b3cdc9b
2020-06-02 14:16:41 -04:00
Tao Sang de4c173c6e support hipLaunchParm test with static lib of hip-vdi rt
Let hipMalloc() be called in main() so that global variable can be initialized.

Change-Id: I9aa1f0a0bb4fa0825d10af0b58c843e7b928e9a3
2020-04-21 13:55:42 -04:00
Lad, Aditya d80edf9541 Merge branch 'master' into amd-master-next
Conflicts:
	CMakeLists.txt
	tests/src/texture/simpleTexture2DLayered.cpp
	tests/src/texture/simpleTexture3D.cpp

Change-Id: I4aa4754d391b5f37ddf15fa0bcfc84d9da020119
2020-03-06 14:10:44 -05:00
agodavar 65ffaf82d8 Enable tests that are passing on hip-vdi
Change-Id: I7de965f7e8bb7e4d0fa61cd584f0cd118c1e212e
2020-03-05 16:08:51 +05:30
agodavar 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
Jatin Chaudhary d29ad50464 [dtests] __shfl_up and __shfl_down tests (#1899) 2020-02-28 16:48:15 +05:30
Tao Sang 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
Nick Curtis 797a929a65 Implement long / long long shuffles (#1829)
Implement additional data-types for shuffles (long and long long).
Based upon the double implementation.
2020-02-15 09:51:09 +05:30
Payam 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
Laurent Morichetti 258adce78e Merge branch 'master' into amd-master-next
Change-Id: Ib7e7824073f4dfc391fb3833fc90e11b327d3c22
2020-02-05 14:56:08 -08:00
Laurent Morichetti a8b81e96b4 Merge branch 'origin/pghafari/hip-vdi' into lmoriche/amd-master-next
Change-Id: I22c145d39f430ca571a981687bcb034ea6e3b8a2
2020-01-31 07:33:12 -08:00
Siu Chi Chan 6613a37b3b 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.
2020-01-24 16:22:49 +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
amd-lthakur e94c0592de [dtests] Fix build issues with hipLaunchParm.cpp on windows (#1293)
* Removed unwanted #include sys/time.h , gettimeofday() and timeval variables and this also helps avavoid compilation error in windows due to gettimeofday() call equivalent of which is not available in windows

* Changed the Macro name from GPU_PRINT_TIME to MY_LAUNCH_MACRO
2019-08-09 11:50:10 +00:00
Maneesh Gupta 9f2d1453fb [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074
2019-05-09 09:59:18 +05:30
Yaxun Sam Liu ec03a8b352 Add default arguments for hipConfigureCall 2018-12-18 15:48:21 -05:00
Alex Voicu fe959f7bd7 Re-sync with upstream. 2018-10-18 12:27:03 +01:00
Maneesh Gupta 52e320f396 Replace hipLaunchKernel -> hipLaunchKernelGGL
Change-Id: I4d99009e1199811d417becf1e1b934ec4d4e30be
2018-10-17 14:32:25 +05:30
Alex Voicu 5312336ce2 Minimal should mean minimal. 2018-10-11 00:21:41 +01:00
Alex Voicu 069bbbd7ed Use HIP math functions, stop using hipLaunchParm. 2018-10-10 11:56:54 +01:00
Alex Voicu ca375cb8c5 Re-sync with upstream. 2018-10-10 11:43:49 +01:00
Maneesh Gupta cca2c5afc8 [dests] Fix hipTestClock, hipTestNew & hipTestGlobalVariable tests for nvcc
nvcc does not support global kernels in struct/class

Change-Id: I2d7297e0c3725564215e20dbdd31c0bb8d7a07de
2018-09-17 15:32:05 +05:30
Alex Voicu c6720e882b Align with HC Next. 2018-09-17 11:50:29 +03:00
Yaxun Sam Liu a6c7aeed72 Add HIP directed test hipTestGlobalVariable.cpp 2018-08-10 08:15:36 -04:00
Maneesh Gupta 4c41d62435 [tests] Fixed hipLaunchParm test on nvcc path
- Uses c++11 features. Added it to nvcc options
- Arguments for some kernels exceeded 4096 bytes which is the limit
  imposed by nvcc. Reduced BLOCK_DIM_SIZE to 512 to handle this
- Fixed compilation issues on nvcc path

Change-Id: I14f6b28afcb7c6b24a085fd707b2104e2ed64627
2018-07-25 15:41:04 +05:30
Maneesh Gupta b1ca77147b Merge pull request #568 from Srinivasuluch/sprint2_9tests
Adding a few more struct scenarions and a ResultValidation()
2018-07-23 14:44:06 +05:30
Srinivasuluch b37c56efed Update hipLaunchParm.cpp
Added struct bit field test, test number#21
2018-07-20 12:38:06 +05:30
rohit pathania bf9832d957 Merge branch 'master' of https://github.com/rpathani/HIP
# Conflicts:
#	tests/src/kernel/hipLaunchParmFunctor.cpp
2018-07-19 12:11:23 +05:30
rohit pathania 8434f2ed6b Merge branch 'master' of https://github.com/rpathani/HIP
# Conflicts:
#	tests/src/kernel/hipLaunchParmFunctor.cpp
2018-07-19 12:02:42 +05:30
Srinivasuluch 4c707232b9 Update hipLaunchParm.cpp
submitting changes as per Sam review/suggestions
2018-07-18 12:41:51 +05:30
srinivas Charupally 19ace627a3 Adding more struct scenarions and a ResultValidation() 2018-07-12 17:08:41 +05:30
rohit pathania 131e2ee05a Adding functor unit tests for hip launch param 2018-07-10 15:23:10 +05:30
rohit pathania 3bbce754da Adding functor unit tests for hip launch param 2018-07-09 15:08:17 +05:30
Srinivasuluch 181ccebee6 Update hipLaunchParm.cpp
Changing macro name
2018-06-27 22:06:53 +05:30
Srinivasuluch 8b67625b65 Update hipLaunchParm.cpp
wrap up to 80 characters per line
2018-06-27 22:04:12 +05:30
Srinivasuluch 9e78ef99e5 Update hipLaunchParm.cpp
changing the condition, a = b, as Sam suggested
2018-06-27 21:48:37 +05:30
Srinivasuluch a9419098de Update hipLaunchParm.cpp 2018-06-27 20:49:07 +05:30
Srinivasuluch a76d8f5580 Update hipLaunchParm.cpp
Added a macro to disable the alignment test as it's broken
2018-06-27 19:57:44 +05:30
Srinivasuluch 6bd047fc47 Update hipLaunchParm.cpp
pass by value for struct
2018-06-27 16:45:51 +05:30
Srinivasuluch d8290f5a7b Update hipLaunchParm.cpp
Added validation part for struct, added two struct padding tests
2018-06-25 16:53:12 +05:30
Srinivasuluch ab07d7dbe6 Update hipLaunchParm.cpp
cleanup
2018-06-11 15:21:20 +05:30
srinivas Charupally 0e98aa4c78 Adding struct test for hipLaunchKernel() 2018-06-11 12:37:38 +05:30
Maneesh Gupta 1ba06f63c4 Apply .clangformat to all repo source files
Change-Id: I7e79c6058f0303f9a98911e3b7dd2e8596079344
2018-03-12 11:29:03 +05:30
Phaneendr-kumar Lanka 7cceebd9ed [nvccTests] Resubmit hipMemcpyDtoD & inline_asm_vadd 2017-12-18 14:46:19 +05:30
Phaneendr-kumar Lanka eea7d495c7 [nvccWarnings] Fix warnings seen with dtests on nvcc path 2017-12-14 14:10:37 +05:30
Maneesh Gupta 1174534e85 Merge pull request #265 from phani544/nvccTests
[nvccTests]Enabled inline_asm_vadd on nvcc
2017-11-20 07:28:29 +05:30
Ben Sander 59956a57ca Fix test on cuda 2017-11-19 15:31:02 -06:00
Alex Voicu cffd0e14eb This implements the trivial change needed to move back from the hip{Something}_{x, y, z} macros to the natural CUDA syntax of Something.{x, y, z}. This is contained in lines 384-404 in hip_runtime.h. All of the other changes have to do with changing unit tests to use this syntax. The macros are retained for backwards compatibility. 2017-11-19 01:54:12 +00:00
Phaneendr-kumar Lanka 18f6e31d1d [nvccTests]Enabled inline_asm_vadd on nvcc 2017-11-14 16:37:59 +05:30
Alex Voicu a619ac6f92 This corrects some interesting choices that were present in the HIP
unit tests such as e.g. de-allocating memory allocated with new[] using
free. All of these were identified via cppcheck.
2017-11-01 22:51:22 +00:00