a3e2660669
Create context for cuda
...
[ROCm/hip commit: e5d077f70e
2020-02-10 15:52:34 -06:00
b6e01adc72
Add setDevice to try and initialize the context on cuda
...
[ROCm/hip commit: 29a257d79b
2020-02-10 13:37:45 -06:00
3fa3e99a9a
Make threads a multiple of hardware concurrency
...
[ROCm/hip commit: 8e494cfce8
2020-02-06 16:23:29 -06:00
5cfa3c626a
Add multithreaded test
...
[ROCm/hip commit: 5361424702
2020-02-06 16:21:40 -06:00
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
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
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
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
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
1f5ecc0f6a
Fix late-coming issues. ( #1724 )
...
Implementation for hipMemcpyWithStream.
[ROCm/hip commit: 75a11330aa
2019-12-23 19:11:24 +05:30
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
29ca9f7d53
Add explicit cast when computing the available amount of system memory.
...
[ROCm/hip commit: 12634879e2
2019-12-13 21:37:30 -05:00
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
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
fa87abd58a
Fix hipMemcpyWithStream ( #1707 )
...
* Fix hipMemcpyWithStream
* Add a dtest for the same.
[ROCm/hip commit: 892d2a562e
2019-12-04 11:56:23 +05:30
6679cd3998
Revert [HIP] Fixed hipStreamAddCallback ( #1674 )
...
This reverts commit fa1e44aa0e153a959280
2019-11-20 11:55:46 +05:30
f55b1cd6a4
[dtest] Rename hipExtLaunchMultiKernelMultiDevice dtest ( #1671 )
...
[ROCm/hip commit: 188752b2cb
2019-11-19 09:41:13 -08:00
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
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
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
2ad99a6326
[hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel ( #1613 )
...
[ROCm/hip commit: cf92fae9e6
2019-11-05 12:32:46 +05:30
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
b68c8d2f60
Formatting changes
...
[ROCm/hip commit: 55f2a38120
2019-10-30 18:12:51 -07:00
8429e15052
Formatting changes ,variable name and check update
...
[ROCm/hip commit: 4ab71216b4
2019-10-30 18:09:21 -07:00
70449cfa92
Revert "Fix occupany APIs ( #1560 )"
...
This reverts commit 4f23f9cb18e4a1e44162
2019-10-29 11:41:08 -07:00
5e11495936
Excluded the test case for nvcc platform
...
[ROCm/hip commit: 4239c94fe5
2019-10-25 15:52:11 +05:30
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
158cab3bb7
Refactored the file as suggested
...
[ROCm/hip commit: 564418c308
2019-10-25 10:44:38 +05:30
629a933b63
Update matmul.cpp
...
[ROCm/hip commit: 318df5c36b
2019-10-25 09:22:07 +05:30
4b771db194
Update hipExtModuleLaunchKernel.cpp
...
[ROCm/hip commit: cd25149225
2019-10-25 09:19:49 +05:30
4f23f9cb18
Fix occupany APIs ( #1560 )
...
Addresses SWDEV-205006
[ROCm/hip commit: af351d7e1b
2019-10-24 17:44:47 +05:30
297a20eac7
Adding a directed test case for hipExtModuleLaunchKernel() api.
...
[ROCm/hip commit: 8b496e4715
2019-10-24 15:06:28 +05:30
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
779d723ac2
hipMemset2D and hipMemset3D tests should be passing by default.
...
[ROCm/hip commit: c747b77ac1
2019-10-16 11:02:38 -04:00
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
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
5a29d10dbb
Add async subtest to hipMemSet3D
...
[ROCm/hip commit: 00425bdf3d
2019-10-15 14:24:04 -04:00
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
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
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
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
d86d4d674d
[hip]Skip test when hipHostMallocCoherent is not supported by implementation ( #1380 )
...
[ROCm/hip commit: 5ed1f3e2c8
2019-09-16 08:31:43 +00:00
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
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
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
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
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
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
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
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
Paul
lthakur
gandryey
satyanveshd
Evgeny Mankov
Alex Voicu
Vladislav Sytchenko
Rahul Garg
Sarbojit2019
Aryan Salmanpour
amd-lthakur
amd-lthakur
ansurya
AlexBinXie
wkwchau