Grafik Komit

57 Melakukan

Penulis SHA1 Pesan Tanggal
Maneesh Gupta 7213c7a1ad p2p_copy_coherency test: gracefully handle single gpu case
Change-Id: I216663f67ef58c673136332635dab8b57079b909


[ROCm/hip commit: 1efb6ce994]
2017-06-07 15:23:37 +05:30
Ben Sander 445042f916 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/hip commit: 39c18e5e5f]
2017-06-05 08:50:22 -05:00
Ben Sander f3950e0748 Update tests.
Fix some NVCC issues.
Add hipStreamSync2, record_event tests.


[ROCm/hip commit: 8ce6d17983]
2017-06-04 20:18:37 -05:00
Ben Sander a1bdd5f585 Update tests, add p2p coherency test.
[ROCm/hip commit: d5c1616324]
2017-06-03 17:11:34 -05:00
Maneesh Gupta 404c3f6751 Fix hipMemoryAllocate test for single GPU
Change-Id: If121c18ab490ba125dc689ffc08a8839fd280c38


[ROCm/hip commit: 502a74fcd6]
2017-05-31 10:16:57 +05:30
Ben Sander b3e01ed74f 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/hip commit: ec7102f461]
2017-05-27 16:02:34 -05:00
Ben Sander e24627aa80 Cleanup hipEvent. (Intermediate checkpoint)
Support hipEventDisableSystemRelease flag.
Update test.
Remove stray printf


[ROCm/hip commit: 620eb30691]
2017-05-27 16:02:34 -05:00
Ben Sander c88190d698 Updates so hip compiles on CUDA.
[ROCm/hip commit: be8d0ba644]
2017-05-27 15:55:07 -05:00
Ben Sander 5b9ce41633 Add hipHostMallocCoherent, hipHostMallocNonCoherent
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.


[ROCm/hip commit: 75f691ec2f]
2017-05-24 00:48:10 -05:00
Ben Sander 247c34195f Expand test to cover copy followed by event sync
[ROCm/hip commit: 236ce70e94]
2017-05-23 23:15:45 -05:00
Ben Sander bd7a374f20 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/hip commit: 2e1fec47ab]
2017-05-16 19:04:25 -05:00
Ben Sander a55ce5bee4 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/hip commit: 27877f8854]
2017-05-16 19:04:25 -05:00
Ben Sander 7d07d804d8 split debugging into separate .md file
[ROCm/hip commit: db097ab392]
2017-05-16 19:04:25 -05:00
Ben Sander ff72a701b7 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/hip commit: c3ccaa01e5]
2017-05-10 17:34:36 -05:00
Ben Sander 5d558861c2 Fix hipStreamWaitEvent for single GPU.
[ROCm/hip commit: e0c3ea15b2]
2017-05-10 13:23:49 -05:00
Ben Sander 639d152ff8 Refactor hipHostRegister test.
Run all tests in one command.
Run 128 offsets.


[ROCm/hip commit: 6437f5d2b2]
2017-05-05 17:29:04 -05:00
Ben Sander 2e2c773643 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/hip commit: 2d0f509de5]
2017-05-05 17:29:04 -05:00
wsttiger 3bf30acbd7 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/hip commit: 2a253680da]
2017-05-05 17:29:04 -05:00
Aditya Atluri a2c405c265 added hipFuncSetCacheConfig API for nvcc path
Change-Id: I87fae35bc0e10a0dca5ae1c5015fe5d9e52a1d0d


[ROCm/hip commit: fc6248ce82]
2017-04-26 18:56:57 -05:00
Ben Sander 0e14f7f58e Add host offset checking
[ROCm/hip commit: cd93a2f229]
2017-04-24 22:30:54 -05:00
Ben Sander e0bd60a22f Refactor hipHostRegister test.
- Add more testing for offsets.
- Parse cmdline options and use --tests.


[ROCm/hip commit: b7b17c3841]
2017-04-24 22:30:54 -05:00
Ben Sander 244e79d54d Refactor hipHostRegister to cover misaligned cases.
[ROCm/hip commit: 8ba993e36c]
2017-04-24 22:30:54 -05:00
Ben Sander ed7b16786a Add test for non-page-aligned mem copies.
[ROCm/hip commit: ab410add5c]
2017-04-24 22:30:54 -05:00
Ben Sander 70ed508153 Add corrected test for offsets
[ROCm/hip commit: c5d89d9e7f]
2017-04-24 22:30:54 -05:00
Ben Sander 9699bcc3da Refactor hipMemcpy test to share mem alloc for multiple copies.
[ROCm/hip commit: 2bc0a6030e]
2017-04-24 22:30:54 -05:00
Ben Sander 3ef01532b9 Add negative testing for memory full condition.
[ROCm/hip commit: dc001ef9b4]
2017-04-24 22:30:54 -05:00
Maneesh Gupta 86e2a5d11d Disable broken tests on hcc path
Change-Id: Id6234da576566faa32d5fdf42dca6d6267596823


[ROCm/hip commit: 65bb22eefc]
2017-03-15 12:03:44 +05:30
Ben Sander 3b768fb36c Update hiphostregister test.
Move check to correct place.


[ROCm/hip commit: e7d6a34327]
2017-03-12 09:51:33 -05:00
Ben Sander a735ffa947 Update hipHostRegister debug and pointerTracker debug and notes
[ROCm/hip commit: 0a554f4dc1]
2017-03-11 09:18:27 -06:00
Ben Sander 3297a65b8f Fix copying of registered memory.
Set device properly so copying can recover context.
Enhance test to catch this case.


[ROCm/hip commit: 94c85fd4fc]
2017-03-11 09:18:27 -06:00
Maneesh Gupta a1ecc551aa Disable hipMemPtrGetInfo test on nvcc path
Change-Id: I864e571314abfe5ae614e6792c86d7b457c920ee


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

Change-Id: I87976d817b5a6ca5530336c09e7cb0420601cb2c


[ROCm/hip commit: 1546732604]
2017-03-07 13:46:29 -06:00
Maneesh Gupta 2799863a54 Fix compilation of some broken tests on nvcc path
Change-Id: I92406af00c2de09d728e9b7f661c1f3873470560


[ROCm/hip commit: f1c3dd0dff]
2017-02-27 13:17:51 +05:30
Aditya Atluri 37e317ddb4 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/hip commit: 378eb3fa55]
2017-02-10 13:32:13 -06:00
Aditya Atluri 76f30e96e8 fixed hipFunction memory management
Change-Id: I7ebb323419bcd220ebd6466a8eb38e7bfdb1520a


[ROCm/hip commit: 6fd3daed30]
2017-02-09 17:22:55 -06:00
Aditya Atluri 6d5992d445 changed __global__ attribute
1. Moved around tests and added them to HIT

Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b


[ROCm/hip commit: 5e3d63c0a3]
2017-02-03 10:53:36 -06:00
Aditya Atluri 77401c9b64 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/hip commit: b723169ee9]
2017-01-17 14:57:51 -06:00
Ben Sander 77bbf9c832 Fix delete[]
[ROCm/hip commit: a15d236de3]
2017-01-09 21:03:11 -06:00
pensun a446102fcc Add direct test case for threadfence_system workaround
Change-Id: I5b21b590e957c901044741ac94e816cd8b1426f9


[ROCm/hip commit: 50867efa10]
2016-11-11 15:09:43 -06:00
pensun 5b80757b00 Modify hipStreamAddCallback test case to consider both NULL stream and stream
Change-Id: I8468c988f0f01c7d3f3176a01469d69bf7a68237


[ROCm/hip commit: 28aad46674]
2016-10-23 12:36:02 -05:00
pensun ae0143e390 Add direct test for hipStreamAddCallback workaround
Change-Id: I890574eb30a76922888846882986edd0dc345309


[ROCm/hip commit: a7438ac3ee]
2016-10-23 12:18:09 -05:00
Ben Sander f7e9300d4e Several fixes/improvements to directed tests.
Change-Id: Ieb32569ddbf5795d2ab3392165a7ddc22693dc62


[ROCm/hip commit: c4b602a0b9]
2016-10-18 22:27:16 -05:00
Maneesh Gupta 70b6885995 Remove deprecated make and cmake files
Change-Id: I8cac0ec9cb997214559627425af207bbb9be0ddf


[ROCm/hip commit: 66f810ebaa]
2016-10-07 11:44:26 +05:30
Maneesh Gupta 724a024bb6 directed tests: Updated to use new hip include path
Change-Id: Iab1aee638b7158eb9674a19625dedf6471947e51


[ROCm/hip commit: 7e04884d0f]
2016-10-04 22:20:50 +05:30
Ben Sander c3034c06df fix test args
Change-Id: If18eb2a5e504accb72a25716aafb6867002fefb2


[ROCm/hip commit: 3bda7532cf]
2016-10-01 14:39:22 -05:00
Ben Sander 1b24a93b79 Add iterations option to MT test.
Change-Id: I945706a75601006ee55a408f965483dd263190ef


[ROCm/hip commit: c36ba0ea58]
2016-09-27 15:45:40 -05:00
Maneesh Gupta a826689145 directed tests: Enable remaining tests in HIT infrastructure
Change-Id: I800ee00d6f7d339bb5d2ed898a16362a8541ed3a


[ROCm/hip commit: 4807279988]
2016-09-27 17:24:33 +05:30
Ben Sander 6445921e03 Add hipStreamQuery
Change-Id: Ib0813b1065feba4fe9ae861d24cfc6f9c5f580be


[ROCm/hip commit: 4e994a3025]
2016-09-07 15:18:34 -05:00
Ben Sander 4746d3002d refactor ihipPreLaunchKernel phase#1
- Fix calls to HIP_INIT_API to pass all function arguments.
- Change ihipFunction to follow coding convention:
    - leading underscore for member fields,
    - camelCase for member fields.
- move kernel print function inside ihipPreLaunchKernel.
- add HIP_TRACE_API_COLOR, control color of messages.
- add ihipLogStatus wrapper to hipDeviceSynchronize()

Change-Id: I20bbb644da213f821404648945197254e3648fc9


[ROCm/hip commit: 48b1f7a6ea]
2016-09-07 15:18:34 -05:00
Ben Sander 85e7d1799b add hipStreamQuery on nvcc, fix hipStreamWaitEvent for nvcc
[ROCm/hip commit: 1f40a73ae1]
2016-09-02 17:26:16 -05:00