Wykres commitów

823 Commity

Autor SHA1 Wiadomość Data
Rahul Garg 971b75588e [dtests] refactor windows specific changes (#1313)
* [dtests] refactor windows specific changes

* Refactor hipMemoryAllocateCoherentDriver - PR- 1309

* Fix missing z in _putenv_s

* Revert "Fix missing z in _putenv_s"

This reverts commit 099a1b20a5c75c5f122d57c0ad2bca01745cdc9c.

* Refactor changes from PR 1299

* Update hipEnvVarDriver.cpp


[ROCm/hip commit: 44422065a1]
2019-08-16 02:13:00 +00:00
Maneesh Gupta a1b3e902d4 [hit] Add support for specifying dependencies in HIT syntax (#1323)
[ROCm/hip commit: d3e2bbc791]
2019-08-14 11:30:42 +00:00
Evgeny Mankov bddcbdeeb6 [HIPIFY] Add cudaMallocManaged -> hipMallocManaged
+ Add mapping for corresponding data types
+ Add a test
+ Update docs


[ROCm/hip commit: d20ae3b50a]
2019-08-13 17:56:06 +03:00
Evgeny Mankov f0789e57e6 [HIPIFY][cuRAND][#1257] Fix
+ Update CURAND_API_supported_by_HIP.md and test accordingly


[ROCm/hip commit: 3ac3b2800b]
2019-08-09 21:27:16 +03:00
amd-lthakur 07ee0e825b [dtests] Fix build issues with hipMemoryAllocateCoherentDriver.cpp on windows (#1309)
Compilation error being observed due to popen(), pclose() and setenv() linux calls on windows. Replaced with appropriate calls on windows.

[ROCm/hip commit: 9b31d26237]
2019-08-09 11:53:16 +00:00
amd-lthakur 45652a1fba [dtests] Fix build issue with hipMemcpy_simple.cpp on windows (#1306)
Compilation error being observed on windows due to aligned_alloc() call. Mapped the call to _aligned_malloc() for windows.

[ROCm/hip commit: 9abae7114c]
2019-08-09 11:52:46 +00:00
ansurya 83e95631cf [dtests[ Fix build issues with hipEnvVar*.cpp on windows (#1299)
* replace getopt with clara based command line options

* Removed header getopt.h

[ROCm/hip commit: cbe9f8dc6b]
2019-08-09 11:52:10 +00:00
amd-lthakur eacee18c37 [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


[ROCm/hip commit: e94c0592de]
2019-08-09 11:50:10 +00:00
amd-lthakur 2658921cfb [dtests] Fixed build issues with hipAsynchronousStreams.cpp on windows (#1292)
Changed the third arg of the functions __hip_as_write_block and __ockl_as_write_block from ulong to uint64_t so as to fix the compilation error in windows

[ROCm/hip commit: d3ffad7c83]
2019-08-09 11:49:31 +00:00
lthakur 68139db6b8 Resubmitting the fix so as to address the changed format in the last submission
[ROCm/hip commit: d18160920e]
2019-08-08 11:26:26 +05:30
lthakur aeb53881fb Fixed compilation errors being observed on windows
[ROCm/hip commit: 435badcb0e]
2019-08-07 15:54:46 +05:30
Sarbojit2019 b72170d037 Enabled gcc for hip host code (#1214)
* Enabled gcc for hip host code

* Adding tests for hip code + (gcc & g++), without kernels

* Excluding nvcc platforms for gcc and g++ tests + Addressing review comments

* minor code clean-up

* Add rocm include path

* Added relative path for library

* Hiding non supported functions for gcc

* Incorporating review comments


[ROCm/hip commit: 3bfff0a23d]
2019-08-05 09:51:36 +00:00
Evgeny Mankov 728b2f5843 [HIPIFY][fix][#211] Taking into account include guard controlling macro
...while including HIP main header file, which is inserted now after #indef controlling macro, or after #pragma once, if it's occurred earlier.

+ Add a couple of unit tests.
ToDo: Check backward compatibility on older clang versions.


[ROCm/hip commit: 25075729f9]
2019-08-02 16:46:45 +03:00
wkwchau b663dbc5ce Added CooperativeLaunch and CooperativeMultiDeviceLaunch flag and property for hipDeviceGetAttribute() and hipGetDeviceProperties() (#1247)
[ROCm/hip commit: aaec4f73a6]
2019-08-02 10:00:25 +00:00
wkwchau c666fdaa08 Added query of hipDeviceAttributeHdpMemFlushCntl and hipDeviceAttribu… (#1238)
* Added query of hipDeviceAttributeHdpMemFlushCntl and hipDeviceAttributeHdpRegFlushCntl

* Added NVCC blocker for the hip*FlushCntl test cases


[ROCm/hip commit: e7447d5809]
2019-08-01 16:03:35 +00:00
Maneesh Gupta bcd4ffb953 Merge pull request #1276 from vsytch/SWDEV-197675
[hip][tests] Don't use a hardcoded warp size, since it can be dynamically changed.…

[ROCm/hip commit: 79358e086a]
2019-08-01 08:59:43 +00:00
wkwchau 7676b86f12 Added support of hipOccupancyMaxActiveBlocksPerMultiprocessor & hipOc… (#1240)
* Added support of hipOccupancyMaxActiveBlocksPerMultiprocessor & hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags APIs

* Taking into account of SGPR usage to determine the max active blocks in hipOccupancyMaxActiveBlocksPerMultiprocessor()


[ROCm/hip commit: 4b18b321f7]
2019-08-01 08:58:48 +00:00
Vladislav Sytchenko 6837312da4 Don't use a hardcoded warp size, since it can be dynamically changed. Query it from the runtime instead.
[ROCm/hip commit: fd3b626386]
2019-07-31 17:04:31 -04:00
Rahul Garg d7973153ca Add HIP init in hipFuncGetAttributes (#1262)
* Add HIP init in hipFuncGetAttributes

* [dtest]Remove explicit hip init call in hipFuncGetAttributes dtest


[ROCm/hip commit: 0517c30507]
2019-07-31 15:42:08 +00:00
ansurya 1aee311e6a Testcase to validate signed/unsigned char,short as normalized float (#1267)
* Testcase to validate signed/unsigned char,short as normalized float

* corrected test_common.cpp file path


[ROCm/hip commit: 0f0b60f57d]
2019-07-31 05:02:35 +00:00
Aryan Salmanpour 563b385ad6 [hip][tests] add a unit test for using hipExtLaunchMultiKernelMultiDevice API (#1250)
[ROCm/hip commit: f3c4952f80]
2019-07-24 07:57:39 +00:00
Aaron Enye Shi 2e45e37c51 Add GFX908 specific changes to HIP (#1229)
* Add GFX908 specific for HIP

* Fix missing __halfTest in hipTestNativeHalf


[ROCm/hip commit: b754de37c1]
2019-07-24 07:51:17 +00:00
Maneesh Gupta 57289b2d4c [dtests] Fix complex_loading_behavior.cpp build issues on nvcc path (#1242)
[ROCm/hip commit: 75abc65e12]
2019-07-24 07:49:39 +00:00
Aaron Enye Shi 85fa58c117 Fix hipMemcpy-size test running out of Host Mem (#1224)
* Fix hipMemcpy-size test running out of Host Mem

The hipMemcpy-size uses a maxElem calculated from the total GPU mem /8. Then it will allocate 4 times that amount of host memory. This tests begins failing when there is not enough host memory, such as on systems with 32GB GPU mem, and 16GB RAM. This fixes the test if not enough host memory is available on the system.

* Add windows support to hipMemcpy-size fix

* avoid linking extra libs for windows

* HIPMemcpy-size Remove freeCPU including swap


[ROCm/hip commit: 0de4caa085]
2019-07-24 07:49:20 +00:00
Maneesh Gupta 4db7b0526c [hit] Workaround for %cc and %cxx mappings. (#1233)
* [hit] Workaround for %cc and %cxx mappings.

HIP CMakeLists.txt modifies CMAKE_C_COMPILER and CMAKE_CXX_COMPILER.
This messes up any dtests that want to test against cc/c++.

So hardcode %cc to /usr/bin/cc and %cxx to /usr/bin/c++ for now till
we come up with a better solution.

Change-Id: I7dce93ce8360191e612a94e3a735e5612ac27ab5

* [hit] Add auto-variable %hip-path to syntax for BUILD_CMD

Change-Id: Id097a183fbce2b2c9691d0180d3304dd17a4e016


[ROCm/hip commit: 888ccbc205]
2019-07-19 04:45:56 +00:00
ansurya de3a7dfe43 [HIP][Tests] Added new testcases for Module API (#1150)
* [HIP][tests] New testcases for module api

* [HIP][Tests]Support for CUDA devices

* Updated tests as per latest master & test GetGlobal to work on all platforms


[ROCm/hip commit: fa4d6b353a]
2019-07-19 04:45:20 +00:00
ansurya df4dee39f4 Add Max Texture 1D,2D,3D device properties (#1226)
* Add Max Texture 1D,2D,3D device properties

* Corrected testcase to use enums defined in hipDeviceAttribute_t

* Added texture 1D,2D and 3D support for NVIDIA path


[ROCm/hip commit: 8e496c09d9]
2019-07-18 03:18:50 +00:00
Maneesh Gupta 7f41814190 [dtests] Fix typo in hipAPIStreamDisable.cpp (#1227)
Change-Id: Ib88a6be49ba192578129bb88ad09817839981398

[ROCm/hip commit: 8a28afeb84]
2019-07-17 07:28:38 +00:00
Maneesh Gupta d4040e8e9c [dtests] Temporarily disable failing tests (#1218)
Change-Id: I7bb36a964c635bfbdf67484f3454d8fff7168eb2

[ROCm/hip commit: f7bb4f233c]
2019-07-17 07:28:21 +00:00
Evgeny Mankov 1ccb6ea65e Merge pull request #1220 from emankov/master
[HIP][HIPIFY] Split HIP_ARRAY_DESCRIPTOR struct to HIP_ARRAY_DESCRIPTOR and HIP_ARRAY3D_DESCRIPTOR

[ROCm/hip commit: 7a87fc6c04]
2019-07-16 18:15:44 +03:00
kpyzhov 5b1910d140 Added gfx906 kernel binary to the HIPFB file for hipModule test. (#1215)
[ROCm/hip commit: e6a8d1daee]
2019-07-12 03:13:45 +00:00
Evgeny Mankov 96801f7b3a [HIP][HIPIFY] Split HIP_ARRAY_DESCRIPTOR struct to HIP_ARRAY_DESCRIPTOR and HIP_ARRAY3D_DESCRIPTOR
[Reason] To be compatible with CUDA [#1133]

Update HIP code, hipify-clang, tests and docs

[TODO] Add support of the corresponding functions on nvcc fallback path


[ROCm/hip commit: c7117df91b]
2019-07-11 14:58:16 +03:00
Yaxun (Sam) Liu 4d2f0de651 Add __hip_pinned_shadow__ for hip-clang and fix texture reference tests (#1200)
[ROCm/hip commit: 85c3b903df]
2019-07-03 08:51:59 +00:00
Alex Voicu e474469213 Put 3-wide vector types on a ketogenic diet. (#1180)
* Put 3-wide vector types on a ketogenic diet.

* Remove needless include.

* Do not be narrow-minded.

* Do not be narrow-minded.

* Put the C people on a diet too.


[ROCm/hip commit: 67abac1365]
2019-06-25 06:32:09 +05:30
wkwchau 40bd111519 Implement the hipOccupancyMaxPotentialBlockSize function (#1162)
* Implement the hipOccupancyMaxPotentialBlockSize function

* Replaced hipGetDeviceProperties() call by ihipGetDeviceProperties() in ihipOccupancyMaxPotentialBlockSize()

* Add test for hipOccupancyMaxPotentialBlockSize in Module API

* Added extern declaration for ihipGetDeviceProperties() to be accessed inside ihipOccupancyMaxPotentialBlockSize()

* fixed hipOccupancyMaxPotentialBlockSize test build issue

* Fix hipOccupancyMaxPotentialBlockSize dtest

* Add BUILD_CMD in hipOccupancyMaxPotentialBlockSize dtest

* Revert "Add BUILD_CMD in hipOccupancyMaxPotentialBlockSize dtest"

This reverts commit 0480ff56f1441fc515d2c26ce33783e303423938.

* Disable hipOccupancyMaxPotentialBlockSize dtest on NVCC

* move extern declaration of ihipGetDeviceProperties to hip_module.cpp

* Update the limiation of 32 wavefronts per CU and 800/512 SGPRs for VI/pre-VI chips to calculate the occupancy


[ROCm/hip commit: d492f1fd6b]
2019-06-20 05:58:29 +05:30
Maneesh Gupta 2f957147c9 [dtests] Temporarily disable hiprtc tests
Change-Id: I87c0c01837e7b59b11d99fb94d679a765f914da5


[ROCm/hip commit: bd4d1838f2]
2019-05-31 16:39:33 +05:30
Maneesh Gupta 4b19bd3736 Merge pull request #1124 from kpyzhov/hipModule-test
Updated kernel binary file for hipModule test.

[ROCm/hip commit: 35aac8e8ce]
2019-05-24 14:16:03 +05:30
Maneesh Gupta bc2f291f49 Merge pull request #1121 from kpyzhov/hipStreamSync2-test
Disable hipStreamSync2 test for hip-clang.

[ROCm/hip commit: d840268636]
2019-05-24 14:15:54 +05:30
Evgeny Mankov 6ba67c4a81 [HIPIFY] Add device texture fetch functions support
+ Add a corresponding reverse engineered sample tex2dKernel with texture template


[ROCm/hip commit: c7a2b4e492]
2019-05-23 12:47:08 +03:00
Konstantin Pyzhov a4202d5ce6 Updated kernel binary file for hipModule test.
[ROCm/hip commit: a8b07ada2f]
2019-05-21 13:21:48 -04:00
Evgeny Mankov 87aa888175 [HIPIFY][tests] Add reverse engineered HIP sample "peer2peer"
+ Fix typo in sample "stream"


[ROCm/hip commit: 29d8e10112]
2019-05-20 17:16:11 +03:00
Konstantin Pyzhov 993f323887 Disable hipStreamSync2 test for hip-clang.
[ROCm/hip commit: 7cbaa5082b]
2019-05-20 02:13:30 -04:00
Evgeny Mankov fa872ef65d Merge pull request #1115 from emankov/master
[HIPIFY][cuDNN] Add cudnnGetFilter4dDescriptor support

[ROCm/hip commit: 390db35dfb]
2019-05-16 16:39:34 +03:00
Evgeny Mankov ce28dc83e4 [HIPIFY][cuDNN] Add cudnnGetFilter4dDescriptor support
+ Update cudnn_convolution_forward test accordingly


[ROCm/hip commit: aed2affda2]
2019-05-16 16:36:23 +03:00
Alex Voicu d5a3acfd69 Add HIPRTC, glorious ersatz for NVRTC (#1097)
* Add ersatz for NVRTC.

* Fix extraneous paren and use correct namespace.

* Use lowerCamelCase (yuck, yuck) consistently.

* Link against FS when building hiprtc lib.

* Correctly mark Manipulators. Fix dual compile.

* Add unit tests. Extend HIT to accept linker options.

* Make sure the HIPRTC library is installed.

* Better logging. Try to auto-detect the target.

* Stop specifying the target explicitly.

* Add missing flavour of `hipModuleLaunchKernel`.

* Program was already destroyed.

* Don't use `--genco`. Fix mangled name trimming.

* Fix HIPRTC breakage due to upstream noise.

* [dtests] Replace RUN -> TEST in hiprtc tests

Change-Id: Ie499e92dfe4e5c94634b1c2b76cf52d241bcfea3

* [hit] Set HIP_PATH to HIP_ROOT_DIR for all tests

Change-Id: Ib0ad1f99bc71c03e363e055dd508a7a4a210680a


[ROCm/hip commit: ccfb764a59]
2019-05-16 18:28:54 +05:30
Evgeny Mankov 75adf32213 [HIPIFY][tests] Add reverse engineered HIP sample "stream"
+ Add additional checks for extern __shared__ due to [#1109]


[ROCm/hip commit: 64eeeca6ce]
2019-05-15 20:17:03 +03:00
Evgeny Mankov 2472ece71d [HIPIFY][fix][#1109] Do not preserve extern __shared__ for IncompleteArrayType
+ Update tests accordingly


[ROCm/hip commit: fa3dda9107]
2019-05-15 20:05:56 +03:00
Konstantin Pyzhov 769171e2bb Upload pre-built kernel binary for hipModule test.
[ROCm/hip commit: c8f92bebf3]
2019-05-15 07:19:40 -04:00
Evgeny Mankov 265f9336f5 [HIPIFY][tests] Add reverse engineered HIP sample Profiler
+ Add missing cuda_profiler_api.h to hip/hip_profile.h transformation.
NOTE: HIP Profiler API is under development. This is NOT WORKING example.
TODO: Find out a way to generate HIP_SCOPED_MARKER, HIP_BEGIN_MARKER, HIP_END_MARKER, declared in hip/hip_profile.h in particular place (signatures are to obtain).


[ROCm/hip commit: d74d03aa74]
2019-05-14 16:43:44 +03:00
Evgeny Mankov 3d00f22ccc [HIPIFY][tests] Add reverse engineered HIP sample hipEvent
[ROCm/hip commit: 3bc3b61fb4]
2019-05-13 22:12:43 +03:00