AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
4,094 Commits 3 Branches 0 Tags
ae838f8cee08ddecb4f40e957c043ec2f41948a3
Commit Graph

720 Commits

Author SHA1 Message Date
Anusha Godavarthy Surya ae838f8cee merge from master 2019-10-25 15:52:09 +05:30
Anusha Godavarthy Surya c0fc5e718c Merge branch 'master' into tex_unbind_issue_fix 2019-10-25 15:36:55 +05:30
satyanveshd 6c5fbf9b4a Fix occupany APIs (#1560) 
Addresses SWDEV-205006
 2019-10-24 17:44:47 +05:30
Vladislav Sytchenko 432380aa5d Remove extra #endif. 2019-10-18 16:40:29 -04:00
Vladislav Sytchenko f4440817cb _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 a21fe1443b Merge pull request #1544 from vsytch/master 
QoL changes to the hipMemset family
 2019-10-16 18:54:20 -07:00
Vladislav Sytchenko 86d0c5fa5a hipMemset2D and hipMemset3D tests should be passing by default. 2019-10-16 11:02:38 -04:00
vsytch c2aadd4d12 Update hipMathFunctions, hipTestHalf and hipTestNativeHalf tests to support Navi10 and Navi14. (#1545) 2019-10-16 10:51:48 +05:30
Vladislav Sytchenko cc5abec092 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 f402b6d01a Update indentation in the hipMemset3D test. Replace all tabs with four spaces. 2019-10-15 15:29:14 -04:00
Vladislav Sytchenko c83b6adb33 Add async subtest to hipMemSet3D 2019-10-15 14:24:04 -04:00
Vladislav Sytchenko 39e42d4056 hipMemset2D test should pass only if both async and sync subtests pass. 2019-10-15 14:20:14 -04:00
Anusha Godavarthy Surya 20cfe17805 Added unbind texture to samples and tests 2019-10-15 11:34:15 +05:30
Jatin Chaudhary 444177ffac Re enable test RTC (#1516) 
Adding target resolution in hiprtc tests and reenable them.
 2019-10-10 19:59:55 +05:30
ansurya 9bb22c4e0f 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
Anusha Godavarthy Surya a5d9f56bef Fix undefine ref to hipUbindTexture for texture types 2019-10-09 16:26:06 +05:30
ansurya 96890792b0 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
Sarbojit2019 6c06fb5f0a [dtests] Separated C macros from CPP header file (#1429) 
* Separated C macros from CPP header file

* Updated review comment
 2019-10-01 12:38:32 +05:30
Yaxun (Sam) Liu 7b3b82bd0d Fix cast of __half for HIP-clang (#1475) 2019-09-30 10:40:42 +05:30
AlexBinXie cda068edd5 [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
AlexBinXie 313726a457 [hip]Skip test when hipHostMallocCoherent is not supported by implementation (#1380) 2019-09-16 08:31:43 +00:00
ansurya e2a934f377 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
Aryan Salmanpour 51c7fedd36 [hip][tests] add a unit test for testing hipLaunchCooperativeKernel (#1361) 
* [hip][tests] add a unit test for testing hipLaunchCooperativeKernel

* use __ockl_grid_sync function

* remove already defined __ockl_grid_sync function

* use sync function for grid synchronization
 2019-09-16 08:31:09 +00:00
Sameer Sahasrabuddhe 68c133bd78 remove obsolete test for OCKL Asynchronous Streams 
The implementation for OCKL AS was recently removed from the device
library since that feature is now superseded by hostcall.
 2019-08-30 20:41:29 +05:30
Sarbojit2019 1ae43cbeba [HIP] Reclaiming hipLaunchKernel API (#1353) 
* [HIP] Reclaiming hipLaunchKernel API

* Reclaiming hipLaunchKernel : Incorporated review comments

* Incorporated review comments

* Removed hipLaunchKernel Macro from nvcc path
 2019-08-29 01:02:41 +00:00
Rahul Garg c741ad3c80 [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
 2019-08-16 02:13:00 +00:00
amd-lthakur 19ad365834 [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.
 2019-08-09 11:53:16 +00:00
amd-lthakur 93f5940ef8 [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.
 2019-08-09 11:52:46 +00:00
ansurya fc60f3a95b [dtests[ Fix build issues with hipEnvVar*.cpp on windows (#1299) 
* replace getopt with clara based command line options

* Removed header getopt.h
 2019-08-09 11:52:10 +00:00
amd-lthakur 36977dc276 [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
amd-lthakur c212c484af [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
 2019-08-09 11:49:31 +00:00
lthakur 80acd13ba7 Resubmitting the fix so as to address the changed format in the last submission 2019-08-08 11:26:26 +05:30
lthakur c4f6d58354 Fixed compilation errors being observed on windows 2019-08-07 15:54:46 +05:30
Sarbojit2019 f23c1a1499 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
 2019-08-05 09:51:36 +00:00
wkwchau ed04e96e2d Added CooperativeLaunch and CooperativeMultiDeviceLaunch flag and property for hipDeviceGetAttribute() and hipGetDeviceProperties() (#1247) 2019-08-02 10:00:25 +00:00
wkwchau abe6776677 Added query of hipDeviceAttributeHdpMemFlushCntl and hipDeviceAttribu… (#1238) 
* Added query of hipDeviceAttributeHdpMemFlushCntl and hipDeviceAttributeHdpRegFlushCntl

* Added NVCC blocker for the hip*FlushCntl test cases
 2019-08-01 16:03:35 +00:00
Maneesh Gupta 6ee5fcc07c Merge pull request #1276 from vsytch/SWDEV-197675 
[hip][tests] Don't use a hardcoded warp size, since it can be dynamically changed.…
 2019-08-01 08:59:43 +00:00
wkwchau 7b9801fe9a 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()
 2019-08-01 08:58:48 +00:00
Vladislav Sytchenko 9a1835ddc3 Don't use a hardcoded warp size, since it can be dynamically changed. Query it from the runtime instead. 2019-07-31 17:04:31 -04:00
Rahul Garg c610159b85 Add HIP init in hipFuncGetAttributes (#1262) 
* Add HIP init in hipFuncGetAttributes

* [dtest]Remove explicit hip init call in hipFuncGetAttributes dtest
 2019-07-31 15:42:08 +00:00
ansurya 440c5f1677 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
 2019-07-31 05:02:35 +00:00
Aryan Salmanpour 571af6d85b [hip][tests] add a unit test for using hipExtLaunchMultiKernelMultiDevice API (#1250) 2019-07-24 07:57:39 +00:00
Aaron Enye Shi 8c82f9db77 Add GFX908 specific changes to HIP (#1229) 
* Add GFX908 specific for HIP

* Fix missing __halfTest in hipTestNativeHalf
 2019-07-24 07:51:17 +00:00
Maneesh Gupta 7feda764b6 [dtests] Fix complex_loading_behavior.cpp build issues on nvcc path (#1242) 2019-07-24 07:49:39 +00:00
Aaron Enye Shi c56876cc19 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
 2019-07-24 07:49:20 +00:00
ansurya f566bec546 [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
 2019-07-19 04:45:20 +00:00
ansurya 00aa42e05f 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
 2019-07-18 03:18:50 +00:00
Maneesh Gupta d206d66dfe [dtests] Fix typo in hipAPIStreamDisable.cpp (#1227) 
Change-Id: Ib88a6be49ba192578129bb88ad09817839981398
 2019-07-17 07:28:38 +00:00
Maneesh Gupta 4d2f2396aa [dtests] Temporarily disable failing tests (#1218) 
Change-Id: I7bb36a964c635bfbdf67484f3454d8fff7168eb2
 2019-07-17 07:28:21 +00:00
kpyzhov 728ce926d9 Added gfx906 kernel binary to the HIPFB file for hipModule test. (#1215) 2019-07-12 03:13:45 +00:00