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

247 Commits

Author SHA1 Message Date
Paul c1b707ff63 Push ctx to the stack as current 
[ROCm/clr commit: e8a7cc6957]
 2020-02-11 11:46:29 -06:00
Paul d9cbd5a143 Try to initialize the primary context on cuda 
[ROCm/clr commit: 86cdb30195]
 2020-02-11 11:26:24 -06:00
Paul 5e16db1f16 Skip test on cuda 
[ROCm/clr commit: accdd882dc]
 2020-02-10 17:23:58 -06:00
Paul e6663a7c23 Reduce threads on cuda 
[ROCm/clr commit: 5d24a2beef]
 2020-02-10 16:37:34 -06:00
Paul 44c4b72f83 Set context on each thread 
[ROCm/clr commit: 7a6e88480b]
 2020-02-10 16:01:53 -06:00
Paul 8fb4e25cf1 Create context for cuda 
[ROCm/clr commit: bb145e77ae]
 2020-02-10 15:52:34 -06:00
Paul 218994969f Add setDevice to try and initialize the context on cuda 
[ROCm/clr commit: 9494d0e3c9]
 2020-02-10 13:37:45 -06:00
Maneesh Gupta a21b1f84cb 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 2c6e880e05.

[ROCm/clr commit: d032637934]
 2020-02-10 10:45:28 +05:30
Payam a5fdb0c135 Excluding vdi platform for now from the following tests so we can build 
Change-Id: I651255c2515a62c8bdfdd17a3ac85c3d66a5761b


[ROCm/clr commit: 141aa8e5dc]
 2020-02-07 02:16:05 -05:00
Paul daaa1ebb80 Make threads a multiple of hardware concurrency 
[ROCm/clr commit: fb8c7cb3ec]
 2020-02-06 16:23:29 -06:00
Paul b29fe7e893 Add multithreaded test 
[ROCm/clr commit: bf69c7ae32]
 2020-02-06 16:21:40 -06:00
lthakur a5409a5556 [dtest] Update hipLaunchCoopMultiKernel.cpp (#1844) 
used reinterpret_cast<uint32_t*> for numBlocks, as expected by hipOccupancyMaxActiveBlocksPerMultiprocessor() api.

[ROCm/clr commit: 2ef4dead24]
 2020-02-04 19:37:38 +05:30
gandryey f33fa4ab31 [dtest] RCCL multi device launch test (#1731) 
Simple test for hipLaunchCooperativeKernelMultiDevice API.


[ROCm/clr commit: 3c718ebe15]
 2020-02-04 08:53:43 +05:30
satyanveshd 2c6e880e05 Match Occupancy APIs syntax with CUDA (#1625) 
* Match Occupancy APIs syntax with CUDA and fix tests using these APIs


[ROCm/clr commit: 262ad13dd5]
 2020-01-29 13:05:53 -08:00
Evgeny Mankov 8c58286a9b Merge pull request #1759 from emankov/master 
[HIP] Unify hipError_t (Step 2)

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


[ROCm/clr commit: 4aaa2336a8]
 2019-12-23 17:01:35 +03:00
Alex Voicu 1f762e3970 Fix late-coming issues. (#1724) 
Implementation for hipMemcpyWithStream.


[ROCm/clr commit: 150e690a3a]
 2019-12-23 19:11:24 +05:30
Vladislav Sytchenko dc12f8017e Add comments explaining choice on the cap for system memory on Windows. 
[ROCm/clr commit: a91bafca40]
 2019-12-13 21:38:27 -05:00
Vladislav Sytchenko 014f068e2f Add explicit cast when computing the available amount of system memory. 
[ROCm/clr commit: 4c21eed68b]
 2019-12-13 21:37:30 -05:00
Vladislav Sytchenko d2be30f0e0 Reduce the amount of free host memory to 40% of what is reported on Windows, otherwise we can run into OOM situations. 
[ROCm/clr commit: 282367ed6d]
 2019-12-11 20:21:12 -05:00
Rahul Garg 48faf7423a 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/clr commit: a369bd4418]
 2019-12-06 09:51:53 +05:30
Rahul Garg 6c7a338471 Fix hipMemcpyWithStream (#1707) 
* Fix hipMemcpyWithStream
* Add a dtest for the same.


[ROCm/clr commit: 261a04580f]
 2019-12-04 11:56:23 +05:30
Sarbojit2019 2c00d66995 Revert [HIP] Fixed hipStreamAddCallback (#1674) 
This reverts commit 4d0b7e65bb.
Addresses SWDEV#212675.

[ROCm/clr commit: 8a3c36a424]
 2019-11-20 11:55:46 +05:30
Rahul Garg 6813f0436c [dtest] Rename hipExtLaunchMultiKernelMultiDevice dtest (#1671) 
[ROCm/clr commit: fa1335f419]
 2019-11-19 09:41:13 -08:00
Alex Voicu f48b38b0ed 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/clr commit: 355d0bdf95]
 2019-11-16 22:24:07 -08:00
Sarbojit2019 4d0b7e65bb [HIP] Fixed hipStreamAddCallback [SWDEV#165185] (#1425) 
Fixed hipStreamAddCallback() as requested in SWDEV#165185
Added unit test to test the behavior


[ROCm/clr commit: 97fca3439d]
 2019-11-07 13:18:12 +05:30
Rahul Garg cf648f7dbe 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/clr commit: dfee3ae279]
 2019-11-07 13:17:10 +05:30
Aryan Salmanpour 92a06b531d [hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel (#1613) 
[ROCm/clr commit: 7a3d592ed0]
 2019-11-05 12:32:46 +05:30
Rahul Garg 2cf205bc7b Merge pull request #1582 from amd-lthakur/hipExtMLK 
Adding a directed test case for hipExtModuleLaunchKernel() api.

[ROCm/clr commit: 1bec1445bb]
 2019-10-31 17:13:26 -07:00
Rahul Garg 31fc374120 Formatting changes 
[ROCm/clr commit: 07f4431de8]
 2019-10-30 18:12:51 -07:00
Rahul Garg 5bcc1f66c5 Formatting changes ,variable name and check update 
[ROCm/clr commit: cd1435cbc7]
 2019-10-30 18:09:21 -07:00
Rahul Garg 72c686ed67 Revert "Fix occupany APIs (#1560)" 
This reverts commit ad1e409a24.


[ROCm/clr commit: 27221bc823]
 2019-10-29 11:41:08 -07:00
amd-lthakur 6bb2cba965 Excluded the test case for nvcc platform 
[ROCm/clr commit: 626cd5d07a]
 2019-10-25 15:52:11 +05:30
Rahul Garg 9c599a3581 [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/clr commit: 66a3c874c8]
 2019-10-25 15:44:05 +05:30
amd-lthakur 796566f156 Refactored the file as suggested 
[ROCm/clr commit: b2238bacd4]
 2019-10-25 10:44:38 +05:30
amd-lthakur 40c7970293 Update matmul.cpp 
[ROCm/clr commit: 84fb936dfe]
 2019-10-25 09:22:07 +05:30
amd-lthakur 42fe3f5247 Update hipExtModuleLaunchKernel.cpp 
[ROCm/clr commit: 9a860e6766]
 2019-10-25 09:19:49 +05:30
satyanveshd ad1e409a24 Fix occupany APIs (#1560) 
Addresses SWDEV-205006 

[ROCm/clr commit: 6c5fbf9b4a]
 2019-10-24 17:44:47 +05:30
amd-lthakur 5189d287eb Adding a directed test case for hipExtModuleLaunchKernel() api. 
[ROCm/clr commit: 0adcc890b0]
 2019-10-24 15:06:28 +05:30
Vladislav Sytchenko 54eddfc8f0 _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/clr commit: f4440817cb]
 2019-10-17 18:58:32 -04:00
Vladislav Sytchenko 577bac5de8 hipMemset2D and hipMemset3D tests should be passing by default. 
[ROCm/clr commit: 86d0c5fa5a]
 2019-10-16 11:02:38 -04:00
Vladislav Sytchenko 2bc49fb55c In the hipMemset2D and hipMemset3D tests synchronize with the default stream after performing an async memset. 
[ROCm/clr commit: cc5abec092]
 2019-10-15 17:15:49 -04:00
Vladislav Sytchenko 91ceb7dd2b Update indentation in the hipMemset3D test. Replace all tabs with four spaces. 
[ROCm/clr commit: f402b6d01a]
 2019-10-15 15:29:14 -04:00
Vladislav Sytchenko d20c5251b1 Add async subtest to hipMemSet3D 
[ROCm/clr commit: c83b6adb33]
 2019-10-15 14:24:04 -04:00
Vladislav Sytchenko e6f426dee3 hipMemset2D test should pass only if both async and sync subtests pass. 
[ROCm/clr commit: 39e42d4056]
 2019-10-15 14:20:14 -04:00
ansurya 0abb25a2fe 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/clr commit: 9bb22c4e0f]
 2019-10-10 19:58:41 +05:30
ansurya efc64a4f8a Added new Memory API's (#1399) 
Added new memory API's hipMemAllocPitch, hipMemAllocHost, hipMemsetD16, hipMemsetD16Async, hipMemsetD8Async
Modified to support all scenarios hipMemcpyParam2DAsync, hipMemcpyParam2D.


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

[ROCm/clr commit: cda068edd5]
 2019-09-30 10:38:37 +05:30
AlexBinXie cc921b35be [hip]Skip test when hipHostMallocCoherent is not supported by implementation (#1380) 
[ROCm/clr commit: 313726a457]
 2019-09-16 08:31:43 +00:00
ansurya 4436a38e65 Added new device attributes (#1377) 
* Added new device attributes

* updated comment

* updated with new device attributes supported


[ROCm/clr commit: e2a934f377]
 2019-09-16 08:31:30 +00:00