Commit Graph

16 Commits

Author SHA1 Message Date
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
Ben Sander 1c7e71e1b3 Add option to deny peer access.
Also fix test.

Change-Id: I1b247f6c4271442b008e560669bca4daf8eb94c7


[ROCm/hip commit: 1e5515ee9f]
2016-11-10 23:12:48 -06:00
Ben Sander 56cd9ce82f Improve Peer support and testing.
Change-Id: Icadc65988aaf145a265587ab0357c5bf4d26f3eb


[ROCm/hip commit: d728819d17]
2016-11-06 03:22:36 -06:00
Ben Sander 5741930acb Expand hipP2PSimple testing.
Cover cases where P2P is used for H2D copies, where host is pinned
but not accessible to the copy agent.

Change-Id: I9464b787228b40f93473708c3fde9726e1986365


[ROCm/hip commit: ff3298f40e]
2016-11-04 16:13:32 -05:00
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
Maneesh Gupta c76800372a directed tests: Enabled top-level uncategorized tests in HIT
Change-Id: If37cbd00244ebfa0e5bff8362820aa68aaa163f1


[ROCm/hip commit: 8e55fc7b42]
2016-09-23 16:15:31 +05:30
Ben Sander a6f28e1708 Peer-to-Peer improvements.
- Bug fix for peer visibility.  Now contexts correctly detect when they can use SDMA for P2P vs staging buffers.
- Interface to new HCC copy_ext function.
- Improve context and peer print /debug options.
- Add comments and usage to hipPeerToPeer_simple test.


[ROCm/hip commit: c769abcbeb]
2016-09-22 14:21:19 -05:00
Ben Sander 32f9d67741 Fixes for P2P and hipDeviceReset
- devicereset would lose track of default stream and thus subsequent
  synchronization calls might not actually sychronize.
- Also deviceReset now correctly frees streams.
- fix waits in P2P staging copy - first phase (Device0-to-Staging) must
  wait for second phase (Staging to Device1) to finish draining the
  buffer.


[ROCm/hip commit: e020d68309]
2016-04-18 20:49:33 -05:00
Ben Sander 3817725dad test update
[ROCm/hip commit: 8ec1aad95d]
2016-04-17 07:54:39 -05:00
Ben Sander d4f449a95e P2P Update.
- add P2P staging buffer copy.
- If copy device does not have sufficient access permissions, fall back
  to staging buffer.
- improve docs for which copy device is used.


[ROCm/hip commit: dcabc9dbf7]
2016-04-16 10:18:56 -05:00
Ben Sander c8c269136c add simple negative P2P tests
[ROCm/hip commit: 4a0c0479d4]
2016-04-11 07:58:59 -05:00
Ben Sander c964e3c75a P2p checkpoint.
- set USE_PEER_TO_PEER=3 (requires HCC "am_memtracker_update_peers")
- when enabling peer, turn it on for previously allocated memory.
- hipDeviceCanAccessPeer is no longer self-ware (self does not qualify
  as a peer)
- device peerlist always includes self, so when we call allow_access
  we never remove self access.
- hipDeviceReset() removes old peer mappings.


[ROCm/hip commit: 83f0de7806]
2016-04-11 07:58:59 -05:00
Ben Sander a563ec9700 Improve P2P test.
- Ensure proper device is set before each command.

- Add command line switches:
    +bool p_memcpyWithPeer = false; // use the peer device for the P2P copy
    +bool p_mirrorPeers = false; // in addition to mapping current to peer
            space, map peer to current space.
    +int  p_peerDevice = -1;  // explicly specify which peer to use, else
use p_gpuDevice + 1.


[ROCm/hip commit: c2d37b4bbd]
2016-04-11 07:58:58 -05:00
Ben Sander 07de649833 Improve P2P test.
Add option to select which device does the copy.


[ROCm/hip commit: 40d24f67f5]
2016-04-11 07:58:58 -05:00
Ben Sander fc4af30e16 Fix simple P2P test, had device ptrs swapped
[ROCm/hip commit: eeb41955e4]
2016-04-11 07:58:58 -05:00
Ben Sander 00c7d8dbbc Add simple P2P test
[ROCm/hip commit: 71dac8e37c]
2016-04-11 07:58:58 -05:00