Commit Graph

61 Commits

Author SHA1 Message Date
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
Siu Chi Chan b7b00fb281 add an unit test for printf 2017-10-23 18:31:13 -04:00
Ben Sander 8ce6d17983 Update tests.
Fix some NVCC issues.
Add hipStreamSync2, record_event tests.
2017-06-04 20:18:37 -05:00
Sandeep Kumar 830f2b100d Add inline asm hip directed tests for v_add and v_mac
Change-Id: Ie5ace2e42d5da89b16e040537df2bb13d3883c6d
2017-05-31 09:25:40 +05:30
Maneesh Gupta 65bb22eefc Disable broken tests on hcc path
Change-Id: Id6234da576566faa32d5fdf42dca6d6267596823
2017-03-15 12:03:44 +05:30
Wen-Heng (Jack) Chung 77e21dc09f Revert "Changes to HIP to cope with Promote-free HCC"
This reverts commit efb9b9e86c.

Change-Id: I20a9bab3883ad09913b320210344d37599cb8fcd
2017-03-14 22:59:27 +08:00
Wen-Heng (Jack) Chung efb9b9e86c Changes to HIP to cope with Promote-free HCC
Squashed commit of the following:

commit c111b5bd10d7c2a5b0b1ad8b07f6e81185b47b39
Author: Wen-Heng (Jack) Chung <whchung@gmail.com>
Date:   Sat Mar 4 17:06:46 2017 +0800

    Use __device__ for all variables and functions to be used in kernel path

    Abolish __device and adopt [[hc]] in HIP implementation, so __device__ can be
    used on all HIP applications, no matter they are variables or functions.

    Change-Id: I20ca25857ce3bc3e42a5ebf65cafea2c8492f4c7

commit 30c0e4e4701bbf6bd9a7182e0320a71ff73d3a83
Author: Wen-Heng (Jack) Chung <whchung@gmail.com>
Date:   Thu Mar 2 12:14:11 2017 +0800

    XXX FIXME get around LDS spills caused in Promote-free HCC

    hipDynamicShared2 uses all 64KB of LDS for computation. But in Promote-free HCC
    there are cases where LDS spills would occur, which would make the test case to
    hang.

    In this workaround commit we reduce the size of dynamic LDS used to get around
    this known issue, and will revert this commit when LDS spills are resolved in
    HCC.

    Change-Id: If648b36200a4f9143951a8129192bcb7ed0bef5e

commit e803173be2d73e2f132a7ff7f61e7a20b4083d34
Author: Wen-Heng (Jack) Chung <whchung@gmail.com>
Date:   Wed Mar 1 21:41:41 2017 +0800

    Fix math functions which take pointer arguments

    Change-Id: I332c997e640edbc44824691e2a9434c6b3dadefa

commit de590c469e213c42090ff83dbd060f25bb1d6047
Author: Wen-Heng (Jack) Chung <whchung@gmail.com>
Date:   Wed Mar 1 18:38:54 2017 +0800

    Changes to cope with Promote-free HCC

    - abolish usage of address_space GNU attribute
    - use __device in file-scope global variables which would be accessed by GPU kernels
    - temporarily disable some math functions which take pointer arguments

    Change-Id: I730311dee848e20e763e35cd3980317fce0dce0d

Change-Id: I1f6b970b53b9401eeaaab08f04a7b9fed0fb8cf0
2017-03-08 01:32:59 +08:00
Aditya Atluri d52c5867f2 Enable symbol tests
Change-Id: I6bd036bf00c8051c8ff728ee60562c4ebd222160
2017-02-22 13:42:03 -06:00
Siu Chi Chan 806deeb476 Squashed commit of the following:
commit 931d3de6c1c903cfd47842bc5026a9294ac492b4
Author: Siu Chi Chan <siuchi.chan@amd.com>
Date:   Mon Feb 13 10:54:06 2017 -0500

    only force to libstdc++ if the g++ is older than version 5 since hcc already defaults to libstdc++ with newer g++

commit 1ef8d71aa788de7b9eead4906fe56186f06d7d3f
Author: scchan <siuchi.chan@amd.com>
Date:   Sun Feb 12 14:44:11 2017 -0500

    remove hardcoded -lc++ in tests

commit 5d99ef338eb3a66523cc9ddd139e86c6fd707b9c
Author: scchan <siuchi.chan@amd.com>
Date:   Sun Feb 12 14:35:46 2017 -0500

    force include libstdc++ headers and stdc++ only if g++ version < 5 since hcc uses libstdc++ by default if g++ > 5 is present

commit a2bc21b24d100feefe91cd3cb2271238bda0738a
Author: scchan <siuchi.chan@amd.com>
Date:   Fri Feb 10 04:36:27 2017 -0500

    use hcc-config to generate compiler and linker flags

Change-Id: I13a79629c0adfd75439a47d0488ff4fd619c55ba
(cherry picked from commit 866e744e40cf1378af8a679b54959bf5226c340f)
2017-02-16 13:12:32 +05:30
Aditya Atluri 28871ddd5b fixed shared memory usage implementation for hipDynamicShared2.cpp test
Change-Id: I34c72cb905f78de0f37e94174382e8be5c532028
2017-02-09 18:17:42 -06:00
Aditya Atluri 2a064cfcc5 added new dynamic shared mem test
Change-Id: Ic2a12fc9bc5b67e85f1e6c6008f10c7c66388377
2017-02-09 18:07:48 -06:00
Maneesh Gupta 5754d641e0 Disable failing directed tests
- hipTestDeviceSymbol
- hipTestConstant
- hipTestMallocKernel

Change-Id: Ibfe9fc0b8a59882f1de64b42e18777a7bd56ee97
2017-02-09 14:48:22 +05:30
Aditya Atluri 05c8aa1cf5 Fixed HIP for C runtime
1. fixed constant memory test
2. added runtime gcc/g++ test
3. added fix for runtime with gcc/g++

Change-Id: Ie14dad6633411b188bdeea044e140b6d5beabe16
2017-02-07 13:15:36 -06:00
Aditya Atluri 5e3d63c0a3 changed __global__ attribute
1. Moved around tests and added them to HIT

Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b
2017-02-03 10:53:36 -06:00