AI/rocm-systems
2
0
フォーク 0
コード イシュー プルリクエスト Actions パッケージ プロジェクト リリース Wiki アクティビティ
1,782 コミット 3 ブランチ 0 タグ
67afe0ec04c41b7d47029c544508bbdc3eeb9f4c
コミットグラフ

61 コミット

作成者 SHA1 メッセージ 日付
Maneesh Gupta 1d986efecf [dt] temporarily disable broken tests 
Change-Id: I3ce23e410dc36e06d460263d768412f8368a6699


[ROCm/clr commit: 814eddcd96]
 2017-07-18 11:17:02 +05:30
Ben Sander f1bed37a34 Clean up old USE_* and RELEASE.md notes. 
[ROCm/clr commit: 42882ddf9c]
 2017-06-23 18:05:30 -05:00
Rahul Garg 942fc5de3f Update P2P test for using memcpy and kernel tests 
Change-Id: Ib0f8fc9425e6e85fd11d7d02395c52bc713dcb37


[ROCm/clr commit: ce6e455677]
 2017-06-12 11:53:25 +05:30
Maneesh Gupta 57bfd56a0d hipMemcpy-size test: reduce max size to make it work correctly on nvcc path 
Change-Id: I9ce9f5a9e141ffd8ddf961269010b33358e02771


[ROCm/clr commit: ff8ade59aa]
 2017-06-07 15:25:54 +05:30
Maneesh Gupta e23be58d91 p2p_copy_coherency test: gracefully handle single gpu case 
Change-Id: I216663f67ef58c673136332635dab8b57079b909


[ROCm/clr commit: a7dc938ec0]
 2017-06-07 15:23:37 +05:30
Ben Sander 7237ed04f3 Fix HIP_SYNC_NULL_STREAM=0 mode. 
- Fix null-stream sync
- hipStreamDestroy of null stream returns hipErrorInvalidResourceHandle
- Update documentation.
- Add tests for null stream sync, hipEventElapsedTime.
- Rename internal enum hipEventStatusRecorded to hipEventStatusComplete
- refactor hipStreamWaitEvent to streamline control-flow


[ROCm/clr commit: 823281dcba]
 2017-06-05 08:50:22 -05:00
Ben Sander be21cd1a91 Update tests. 
Fix some NVCC issues.
Add hipStreamSync2, record_event tests.


[ROCm/clr commit: 863b7c3f56]
 2017-06-04 20:18:37 -05:00
Ben Sander 6aaeed821d Update tests, add p2p coherency test. 
[ROCm/clr commit: 15f54fb943]
 2017-06-03 17:11:34 -05:00
Maneesh Gupta 0e4e17db27 Fix hipMemoryAllocate test for single GPU 
Change-Id: If121c18ab490ba125dc689ffc08a8839fd280c38


[ROCm/clr commit: 06ee0d3704]
 2017-05-31 10:16:57 +05:30
Ben Sander 0ca3262f0a Add event controls for release fences. 
Env var : HIP_EVENT_SYS_RELEASE
Event allocation flags : hipEventReleaseToDevice, hipEventReleaseToSystem
   (remove hipEventDisableSystemRelease)

Update test for new functionality.


[ROCm/clr commit: 942ec0eff8]
 2017-05-27 16:02:34 -05:00
Ben Sander d6e8f5bbdc Cleanup hipEvent. (Intermediate checkpoint) 
Support hipEventDisableSystemRelease flag.
Update test.
Remove stray printf


[ROCm/clr commit: c8178c6838]
 2017-05-27 16:02:34 -05:00
Ben Sander 9442c6dd2d Updates so hip compiles on CUDA. 
[ROCm/clr commit: 8dc968f036]
 2017-05-27 15:55:07 -05:00
Ben Sander d302498787 Add hipHostMallocCoherent, hipHostMallocNonCoherent 
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.


[ROCm/clr commit: dda70ae514]
 2017-05-24 00:48:10 -05:00
Ben Sander 59e07db865 Expand test to cover copy followed by event sync 
[ROCm/clr commit: 92bd54d7b3]
 2017-05-23 23:15:45 -05:00
Ben Sander 33cfd1a35e Make hipMultiThreadStreams1 test a little harsher. 
Fail faster if synchronization rules are violated.
Run vectorAddRevers to read last elements of array first - if the
vector add kernel starts before preceding copy finishes we
will read stale data and flag the error.

Increase default array sizes, so synchronization errors more easily
exposed.


[ROCm/clr commit: 848d77ebb5]
 2017-05-16 19:04:25 -05:00
Ben Sander 4ac6ac9d1d Add initial HIP_SYNC_NULL_STREAM=0 mode. 
This eliminates host-synchronization for null stream.  Instead, the
null-stream uses GPU-side events to wait for other streams.
Default is OFF pending additional testing.

Add enhanced null-stream test.

Also refine HIP_TRACE_API.


[ROCm/clr commit: 8bc6ee5932]
 2017-05-16 19:04:25 -05:00
Ben Sander a8d917c092 split debugging into separate .md file 
[ROCm/clr commit: 61c8633113]
 2017-05-16 19:04:25 -05:00
Ben Sander 90e5930923 hipHostMalloc allocation are mapped to all devices by default. 
Support hipHostMallocPortable flag.
Default flags are hipHostMallocPortable | hipHostMallocMapped.

Also:
-refactor tests to move addCount and addCountReverse into HipTest
namespace.
-test multi-GPU host memory.


[ROCm/clr commit: ff9bed6535]
 2017-05-10 17:34:36 -05:00
Ben Sander 501d0b3161 Fix hipStreamWaitEvent for single GPU. 
[ROCm/clr commit: ae9fdf9bc1]
 2017-05-10 13:23:49 -05:00
Ben Sander 4afda1720d Refactor hipHostRegister test. 
Run all tests in one command.
Run 128 offsets.


[ROCm/clr commit: e417eb5d35]
 2017-05-05 17:29:04 -05:00
Ben Sander 48fdf2fc93 Update streamEventTEst. 
- add checks for events across devices.
- refactor test to make sure it runs long enough to sensitive sync
  techniques.
- add tests for DeviceSync, streamWaitEvent.


[ROCm/clr commit: 444e4a20ba]
 2017-05-05 17:29:04 -05:00
wsttiger 618f4bf702 Improve hipStreamWaitEvent test. 
- use addOne kernel, use local initializer rather than init_array.
- use addOneReverse test to add from back of array.  Test alternate fwd and backward to stress dependency logic.
- check device-side dependencies.


[ROCm/clr commit: a10d37e5e6]
 2017-05-05 17:29:04 -05:00
Aditya Atluri afec5e075b added hipFuncSetCacheConfig API for nvcc path 
Change-Id: I87fae35bc0e10a0dca5ae1c5015fe5d9e52a1d0d


[ROCm/clr commit: e91c35fde0]
 2017-04-26 18:56:57 -05:00
Ben Sander 579b8e5050 Add host offset checking 
[ROCm/clr commit: fbf28a8728]
 2017-04-24 22:30:54 -05:00
Ben Sander 20315571bd Refactor hipHostRegister test. 
- Add more testing for offsets.
- Parse cmdline options and use --tests.


[ROCm/clr commit: e7af4ef641]
 2017-04-24 22:30:54 -05:00
Ben Sander aa4c89380e Refactor hipHostRegister to cover misaligned cases. 
[ROCm/clr commit: 5ba167b82b]
 2017-04-24 22:30:54 -05:00
Ben Sander 67383ddb5c Add test for non-page-aligned mem copies. 
[ROCm/clr commit: d120b2dd12]
 2017-04-24 22:30:54 -05:00
Ben Sander 37fcb3bd13 Add corrected test for offsets 
[ROCm/clr commit: b44a3eefd1]
 2017-04-24 22:30:54 -05:00
Ben Sander 04082c14a7 Refactor hipMemcpy test to share mem alloc for multiple copies. 
[ROCm/clr commit: 6b16f56f38]
 2017-04-24 22:30:54 -05:00
Ben Sander 88fa748893 Add negative testing for memory full condition. 
[ROCm/clr commit: 693e5abc1c]
 2017-04-24 22:30:54 -05:00
Maneesh Gupta da5548303e Disable broken tests on hcc path 
Change-Id: Id6234da576566faa32d5fdf42dca6d6267596823


[ROCm/clr commit: 8536af7b71]
 2017-03-15 12:03:44 +05:30
Ben Sander 72b420bab4 Update hiphostregister test. 
Move check to correct place.


[ROCm/clr commit: 9adbbd2980]
 2017-03-12 09:51:33 -05:00
Ben Sander a0932fbcc3 Update hipHostRegister debug and pointerTracker debug and notes 
[ROCm/clr commit: e43592721e]
 2017-03-11 09:18:27 -06:00
Ben Sander c8595b0373 Fix copying of registered memory. 
Set device properly so copying can recover context.
Enhance test to catch this case.


[ROCm/clr commit: 23a58775df]
 2017-03-11 09:18:27 -06:00
Maneesh Gupta 27cf10c094 Disable hipMemPtrGetInfo test on nvcc path 
Change-Id: I864e571314abfe5ae614e6792c86d7b457c920ee


[ROCm/clr commit: 8bd20732f9]
 2017-03-08 16:16:08 +05:30
Aditya Atluri c861d10d1e Added new API, hipMemPtrGetInfo 
1. This API returns memory allocation size of pointer
2. Added test to check its functionality

Change-Id: I87976d817b5a6ca5530336c09e7cb0420601cb2c


[ROCm/clr commit: 7b7d53f875]
 2017-03-07 13:46:29 -06:00
Maneesh Gupta 26c65c826b Fix compilation of some broken tests on nvcc path 
Change-Id: I92406af00c2de09d728e9b7f661c1f3873470560


[ROCm/clr commit: 40bcf5ed3b]
 2017-02-27 13:17:51 +05:30
Aditya Atluri 3577c19d66 v2: Fixed hipModule memory management 
1. Changed test to assert for same hipFunction values
2. Added better memory management for hipModule

Change-Id: I10d7aef13c215a2211e262f3c79017f26a17d9a7


[ROCm/clr commit: 554fe191e1]
 2017-02-10 13:32:13 -06:00
Aditya Atluri 6c76483ac8 fixed hipFunction memory management 
Change-Id: I7ebb323419bcd220ebd6466a8eb38e7bfdb1520a


[ROCm/clr commit: 6110fcdfb6]
 2017-02-09 17:22:55 -06:00
Aditya Atluri 3937b398e9 changed __global__ attribute 
1. Moved around tests and added them to HIT

Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b


[ROCm/clr commit: f009f3533d]
 2017-02-03 10:53:36 -06:00
Aditya Atluri 42c627fbe8 Moved device code to mimic cuda header behavior 
1. All fp32, fp64 math device/host functions should be in math_functions.h/.cpp
2. All fp32, fp64 fast math intrinsics for device/host functions should be in device_functions.h/.cpp
3. All the device code implementations should be in device_util.h/.cpp
4. Hence, made changes appropriately by moving code and creating new header files
5. Added math_functions.cpp/.h
6. Changed #ifndef signature to make sure no conflicts between headers with same names in hip/hip_runtime.h and hip/hcc_detail/hip_runtime.h
7. Changed tests to fit the code changes, making them to include appropriate headers
8. Added math_functions.cpp to CMakeLists.txt
9. Some of the tests are still broken, mostly host math functions will fix them in next commit
10. TODO: FIX compilation issues for host math functions

Change-Id: I7a17637d7e294a7d224ffba932c1a08668febd26


[ROCm/clr commit: d23b6b8694]
 2017-01-17 14:57:51 -06:00
Ben Sander 9af6545379 Fix delete[] 
[ROCm/clr commit: ff77106399]
 2017-01-09 21:03:11 -06:00
pensun dd1061b874 Add direct test case for threadfence_system workaround 
Change-Id: I5b21b590e957c901044741ac94e816cd8b1426f9


[ROCm/clr commit: 992f94b3a1]
 2016-11-11 15:09:43 -06:00
pensun b98e815865 Modify hipStreamAddCallback test case to consider both NULL stream and stream 
Change-Id: I8468c988f0f01c7d3f3176a01469d69bf7a68237


[ROCm/clr commit: 4a93beb3b0]
 2016-10-23 12:36:02 -05:00
pensun 57fab304c7 Add direct test for hipStreamAddCallback workaround 
Change-Id: I890574eb30a76922888846882986edd0dc345309


[ROCm/clr commit: ad09270d7b]
 2016-10-23 12:18:09 -05:00
Ben Sander 90bc4809b0 Several fixes/improvements to directed tests. 
Change-Id: Ieb32569ddbf5795d2ab3392165a7ddc22693dc62


[ROCm/clr commit: 4acb7dd947]
 2016-10-18 22:27:16 -05:00
Maneesh Gupta 6b41768920 Remove deprecated make and cmake files 
Change-Id: I8cac0ec9cb997214559627425af207bbb9be0ddf


[ROCm/clr commit: c4dd17cce9]
 2016-10-07 11:44:26 +05:30
Maneesh Gupta 43d07079e9 directed tests: Updated to use new hip include path 
Change-Id: Iab1aee638b7158eb9674a19625dedf6471947e51


[ROCm/clr commit: 5947878247]
 2016-10-04 22:20:50 +05:30
Ben Sander f8856acbd1 fix test args 
Change-Id: If18eb2a5e504accb72a25716aafb6867002fefb2


[ROCm/clr commit: bf3ce40fb1]
 2016-10-01 14:39:22 -05:00
Ben Sander 89dd26a07a Add iterations option to MT test. 
Change-Id: I945706a75601006ee55a408f965483dd263190ef


[ROCm/clr commit: c53349a371]
 2016-09-27 15:45:40 -05:00