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

253 Commits

Author SHA1 Message Date
Payam fabe62e31f removing oocupancy tests from hip-vdi for now 
Change-Id: I06e966d07021af87fa2c195e4bbaf6bcc336658d
 2020-02-13 21:40:06 -05:00
Satyanvesh Dittakavi 3fb4135946 Add c++11 option for nvcc 2020-02-13 19:48:26 +05:30
Satyanvesh Dittakavi ead254cdd5 updated test for nvidia path 2020-02-13 16:34:05 +05:30
Laurent Morichetti 2cf3257795 Merge branch 'master' into amd-master-next 
Change-Id: Ibb7775e7acd263d2ece40a241517bbd15976fdd4
 2020-02-12 00:14:07 -08:00
Paul 26bb6a97a7 Revert "Try to initialize the primary context on cuda" 
This reverts commit fd98514113.
 2020-02-11 12:34:11 -06:00
Paul e82e3c2339 Revert "Push ctx to the stack as current" 
This reverts commit bff8cbe950.
 2020-02-11 12:34:10 -06:00
Paul bff8cbe950 Push ctx to the stack as current 2020-02-11 11:46:29 -06:00
Paul fd98514113 Try to initialize the primary context on cuda 2020-02-11 11:26:24 -06:00
Paul b9f97ec3fe Skip test on cuda 2020-02-10 17:23:58 -06:00
Paul 30e8dfdd86 Reduce threads on cuda 2020-02-10 16:37:34 -06:00
Paul 2d9a2d866c Set context on each thread 2020-02-10 16:01:53 -06:00
Paul e5d077f70e Create context for cuda 2020-02-10 15:52:34 -06:00
Paul 29a257d79b Add setDevice to try and initialize the context on cuda 2020-02-10 13:37:45 -06:00
Maneesh Gupta f8e1c01900 Revert "Match Occupancy APIs syntax with CUDA (#1625)" (#1857) 
Reverting this for now till we figure out how to avoid the build
breakage.

This reverts commit fa98798b63.
 2020-02-10 10:45:28 +05:30
Payam e4e8c4b74b Excluding vdi platform for now from the following tests so we can build 
Change-Id: I651255c2515a62c8bdfdd17a3ac85c3d66a5761b
 2020-02-07 02:16:05 -05:00
Paul 8e494cfce8 Make threads a multiple of hardware concurrency 2020-02-06 16:23:29 -06:00
Paul 5361424702 Add multithreaded test 2020-02-06 16:21:40 -06:00
lthakur 4d472b777f [dtest] Update hipLaunchCoopMultiKernel.cpp (#1844) 
used reinterpret_cast<uint32_t*> for numBlocks, as expected by hipOccupancyMaxActiveBlocksPerMultiprocessor() api.
 2020-02-04 19:37:38 +05:30
gandryey 48d1f766d5 [dtest] RCCL multi device launch test (#1731) 
Simple test for hipLaunchCooperativeKernelMultiDevice API.
 2020-02-04 08:53:43 +05:30
satyanveshd fa98798b63 Match Occupancy APIs syntax with CUDA (#1625) 
* Match Occupancy APIs syntax with CUDA and fix tests using these APIs
 2020-01-29 13:05:53 -08:00
Evgeny Mankov 0dadb23327 Merge pull request #1759 from emankov/master 
[HIP] Unify hipError_t (Step 2)
 2019-12-30 19:21:09 +03:00
Evgeny Mankov 4921678b6c [HIP] Clean-up deprecated HIP error codes 
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle
 2019-12-23 17:01:35 +03:00
Alex Voicu 75a11330aa Fix late-coming issues. (#1724) 
Implementation for hipMemcpyWithStream.
 2019-12-23 19:11:24 +05:30
Vladislav Sytchenko bf3df9d7c0 Add comments explaining choice on the cap for system memory on Windows. 2019-12-13 21:38:27 -05:00
Vladislav Sytchenko 12634879e2 Add explicit cast when computing the available amount of system memory. 2019-12-13 21:37:30 -05:00
Vladislav Sytchenko b12c53cceb Reduce the amount of free host memory to 40% of what is reported on Windows, otherwise we can run into OOM situations. 2019-12-11 20:21:12 -05:00
Rahul Garg e53fc316f1 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.
 2019-12-06 09:51:53 +05:30
Rahul Garg 892d2a562e Fix hipMemcpyWithStream (#1707) 
* Fix hipMemcpyWithStream
* Add a dtest for the same.
 2019-12-04 11:56:23 +05:30
Sarbojit2019 153a959280 Revert [HIP] Fixed hipStreamAddCallback (#1674) 
This reverts commit 45613311d7.
Addresses SWDEV#212675.
 2019-11-20 11:55:46 +05:30
Rahul Garg 188752b2cb [dtest] Rename hipExtLaunchMultiKernelMultiDevice dtest (#1671) 2019-11-19 09:41:13 -08:00
Alex Voicu 69e74c3e96 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
 2019-11-16 22:24:07 -08:00
Sarbojit2019 45613311d7 [HIP] Fixed hipStreamAddCallback [SWDEV#165185] (#1425) 
Fixed hipStreamAddCallback() as requested in SWDEV#165185
Added unit test to test the behavior
 2019-11-07 13:18:12 +05:30
Rahul Garg 579a4f36fa 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
 2019-11-07 13:17:10 +05:30
Aryan Salmanpour cf92fae9e6 [hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel (#1613) 2019-11-05 12:32:46 +05:30
Rahul Garg 4739e68bbe Merge pull request #1582 from amd-lthakur/hipExtMLK 
Adding a directed test case for hipExtModuleLaunchKernel() api.
 2019-10-31 17:13:26 -07:00
Rahul Garg 55f2a38120 Formatting changes 2019-10-30 18:12:51 -07:00
Rahul Garg 4ab71216b4 Formatting changes ,variable name and check update 2019-10-30 18:09:21 -07:00
Rahul Garg e4a1e44162 Revert "Fix occupany APIs (#1560)" 
This reverts commit af351d7e1b.
 2019-10-29 11:41:08 -07:00
amd-lthakur 4239c94fe5 Excluded the test case for nvcc platform 2019-10-25 15:52:11 +05:30
Rahul Garg 12e1a86ec1 [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.
 2019-10-25 15:44:05 +05:30
amd-lthakur 564418c308 Refactored the file as suggested 2019-10-25 10:44:38 +05:30
amd-lthakur 318df5c36b Update matmul.cpp 2019-10-25 09:22:07 +05:30
amd-lthakur cd25149225 Update hipExtModuleLaunchKernel.cpp 2019-10-25 09:19:49 +05:30
satyanveshd af351d7e1b Fix occupany APIs (#1560) 
Addresses SWDEV-205006
 2019-10-24 17:44:47 +05:30
amd-lthakur 8b496e4715 Adding a directed test case for hipExtModuleLaunchKernel() api. 2019-10-24 15:06:28 +05:30
Vladislav Sytchenko 8f0a226660 _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
Vladislav Sytchenko c747b77ac1 hipMemset2D and hipMemset3D tests should be passing by default. 2019-10-16 11:02:38 -04:00
Vladislav Sytchenko f5af263aba 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 346bfa90d6 Update indentation in the hipMemset3D test. Replace all tabs with four spaces. 2019-10-15 15:29:14 -04:00
Vladislav Sytchenko 00425bdf3d Add async subtest to hipMemSet3D 2019-10-15 14:24:04 -04:00