AI/rocm-systems
2
0 Forc 0
Cód Saincheisteanna Iarratais Tarraingthe Gníomhartha Pacáistí Tionscadail Scaoileann Vicí Gníomhaíocht
4,332 Tiomáintí 3 Brainsí 0 Clibeanna
e340a8e921088c47753f1b173b92d5e58e8a93fa
Graf Tiomantas
186 Tiomáintí
Údar SHA1 Teachtaireacht Dáta
lthakur e340a8e921 [dtest] Update hipLaunchCoopMultiKernel.cpp (#1844) 
used reinterpret_cast<uint32_t*> for numBlocks, as expected by hipOccupancyMaxActiveBlocksPerMultiprocessor() api.

[ROCm/hip commit: 4d472b777f]
 2020-02-04 19:37:38 +05:30
gandryey 42bc78d148 [dtest] RCCL multi device launch test (#1731) 
Simple test for hipLaunchCooperativeKernelMultiDevice API.


[ROCm/hip commit: 48d1f766d5]
 2020-02-04 08:53:43 +05:30
satyanveshd e38db9fb6f Match Occupancy APIs syntax with CUDA (#1625) 
* Match Occupancy APIs syntax with CUDA and fix tests using these APIs


[ROCm/hip commit: fa98798b63]
 2020-01-29 13:05:53 -08:00
Evgeny Mankov 6ac4d18753 Merge pull request #1759 from emankov/master 
[HIP] Unify hipError_t (Step 2)

[ROCm/hip commit: 0dadb23327]
 2019-12-30 19:21:09 +03:00
Evgeny Mankov abef353b5b [HIP] Clean-up deprecated HIP error codes 
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle


[ROCm/hip commit: 4921678b6c]
 2019-12-23 17:01:35 +03:00
Alex Voicu 1f5ecc0f6a Fix late-coming issues. (#1724) 
Implementation for hipMemcpyWithStream.


[ROCm/hip commit: 75a11330aa]
 2019-12-23 19:11:24 +05:30
Vladislav Sytchenko 6015efe6f5 Add comments explaining choice on the cap for system memory on Windows. 
[ROCm/hip commit: bf3df9d7c0]
 2019-12-13 21:38:27 -05:00
Vladislav Sytchenko 29ca9f7d53 Add explicit cast when computing the available amount of system memory. 
[ROCm/hip commit: 12634879e2]
 2019-12-13 21:37:30 -05:00
Vladislav Sytchenko 9dade23425 Reduce the amount of free host memory to 40% of what is reported on Windows, otherwise we can run into OOM situations. 
[ROCm/hip commit: b12c53cceb]
 2019-12-11 20:21:12 -05:00
Rahul Garg ebdd811632 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.

[ROCm/hip commit: e53fc316f1]
 2019-12-06 09:51:53 +05:30
Rahul Garg fa87abd58a Fix hipMemcpyWithStream (#1707) 
* Fix hipMemcpyWithStream
* Add a dtest for the same.


[ROCm/hip commit: 892d2a562e]
 2019-12-04 11:56:23 +05:30
Sarbojit2019 6679cd3998 Revert [HIP] Fixed hipStreamAddCallback (#1674) 
This reverts commit fa1e44aa0e.
Addresses SWDEV#212675.

[ROCm/hip commit: 153a959280]
 2019-11-20 11:55:46 +05:30
Rahul Garg f55b1cd6a4 [dtest] Rename hipExtLaunchMultiKernelMultiDevice dtest (#1671) 
[ROCm/hip commit: 188752b2cb]
 2019-11-19 09:41:13 -08:00
Alex Voicu 3ea404a8ba 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


[ROCm/hip commit: 69e74c3e96]
 2019-11-16 22:24:07 -08:00
Sarbojit2019 fa1e44aa0e [HIP] Fixed hipStreamAddCallback [SWDEV#165185] (#1425) 
Fixed hipStreamAddCallback() as requested in SWDEV#165185
Added unit test to test the behavior


[ROCm/hip commit: 45613311d7]
 2019-11-07 13:18:12 +05:30
Rahul Garg 6968362d99 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


[ROCm/hip commit: 579a4f36fa]
 2019-11-07 13:17:10 +05:30
Aryan Salmanpour 2ad99a6326 [hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel (#1613) 
[ROCm/hip commit: cf92fae9e6]
 2019-11-05 12:32:46 +05:30
Rahul Garg 25a5ca94de Merge pull request #1582 from amd-lthakur/hipExtMLK 
Adding a directed test case for hipExtModuleLaunchKernel() api.

[ROCm/hip commit: 4739e68bbe]
 2019-10-31 17:13:26 -07:00
Rahul Garg b68c8d2f60 Formatting changes 
[ROCm/hip commit: 55f2a38120]
 2019-10-30 18:12:51 -07:00
Rahul Garg 8429e15052 Formatting changes ,variable name and check update 
[ROCm/hip commit: 4ab71216b4]
 2019-10-30 18:09:21 -07:00
Rahul Garg 70449cfa92 Revert "Fix occupany APIs (#1560)" 
This reverts commit 4f23f9cb18.


[ROCm/hip commit: e4a1e44162]
 2019-10-29 11:41:08 -07:00
amd-lthakur 5e11495936 Excluded the test case for nvcc platform 
[ROCm/hip commit: 4239c94fe5]
 2019-10-25 15:52:11 +05:30
Rahul Garg 849ae2bff0 [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.

[ROCm/hip commit: 12e1a86ec1]
 2019-10-25 15:44:05 +05:30
amd-lthakur 158cab3bb7 Refactored the file as suggested 
[ROCm/hip commit: 564418c308]
 2019-10-25 10:44:38 +05:30
amd-lthakur 629a933b63 Update matmul.cpp 
[ROCm/hip commit: 318df5c36b]
 2019-10-25 09:22:07 +05:30
amd-lthakur 4b771db194 Update hipExtModuleLaunchKernel.cpp 
[ROCm/hip commit: cd25149225]
 2019-10-25 09:19:49 +05:30
satyanveshd 4f23f9cb18 Fix occupany APIs (#1560) 
Addresses SWDEV-205006 

[ROCm/hip commit: af351d7e1b]
 2019-10-24 17:44:47 +05:30
amd-lthakur 297a20eac7 Adding a directed test case for hipExtModuleLaunchKernel() api. 
[ROCm/hip commit: 8b496e4715]
 2019-10-24 15:06:28 +05:30
Vladislav Sytchenko fd17d3b737 _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.


[ROCm/hip commit: 8f0a226660]
 2019-10-17 18:58:32 -04:00
Vladislav Sytchenko 779d723ac2 hipMemset2D and hipMemset3D tests should be passing by default. 
[ROCm/hip commit: c747b77ac1]
 2019-10-16 11:02:38 -04:00
Vladislav Sytchenko 948dd510eb In the hipMemset2D and hipMemset3D tests synchronize with the default stream after performing an async memset. 
[ROCm/hip commit: f5af263aba]
 2019-10-15 17:15:49 -04:00
Vladislav Sytchenko 6180a9edb3 Update indentation in the hipMemset3D test. Replace all tabs with four spaces. 
[ROCm/hip commit: 346bfa90d6]
 2019-10-15 15:29:14 -04:00
Vladislav Sytchenko 5a29d10dbb Add async subtest to hipMemSet3D 
[ROCm/hip commit: 00425bdf3d]
 2019-10-15 14:24:04 -04:00
Vladislav Sytchenko 28089f61b6 hipMemset2D test should pass only if both async and sync subtests pass. 
[ROCm/hip commit: 3db2ecc52b]
 2019-10-15 14:20:14 -04:00
ansurya b37210badc 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.

[ROCm/hip commit: 87834500b9]
 2019-10-10 19:58:41 +05:30
ansurya 66e94b1b1f Added new Memory API's (#1399) 
Added new memory API's hipMemAllocPitch, hipMemAllocHost, hipMemsetD16, hipMemsetD16Async, hipMemsetD8Async
Modified to support all scenarios hipMemcpyParam2DAsync, hipMemcpyParam2D.


[ROCm/hip commit: ba9c6e13e4]
 2019-10-04 13:36:31 +05:30
AlexBinXie e404049a71 [hip] Added gfx803,gfx1010,gfx1012 kernel binary hipModule test. (#1444) 
This is to address hipModule test seg fault in GFX1010

[ROCm/hip commit: b3e6ba50c3]
 2019-09-30 10:38:37 +05:30
AlexBinXie d86d4d674d [hip]Skip test when hipHostMallocCoherent is not supported by implementation (#1380) 
[ROCm/hip commit: 5ed1f3e2c8]
 2019-09-16 08:31:43 +00:00
ansurya b5549f4397 Added new device attributes (#1377) 
* Added new device attributes

* updated comment

* updated with new device attributes supported


[ROCm/hip commit: ceb734b917]
 2019-09-16 08:31:30 +00:00
Aryan Salmanpour 8e18dee555 [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


[ROCm/hip commit: 48880a017e]
 2019-09-16 08:31:09 +00:00
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
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
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
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
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
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 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
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