Граф коммитов

16 Коммитов

Автор SHA1 Сообщение Дата
Aditya Atluri f009f3533d changed __global__ attribute
1. Moved around tests and added them to HIT

Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b
2017-02-03 10:53:36 -06:00
Ben Sander d666fbaafe Add option to deny peer access.
Also fix test.

Change-Id: I1b247f6c4271442b008e560669bca4daf8eb94c7
2016-11-10 23:12:48 -06:00
Ben Sander f3d38c2615 Improve Peer support and testing.
Change-Id: Icadc65988aaf145a265587ab0357c5bf4d26f3eb
2016-11-06 03:22:36 -06:00
Ben Sander 60a8a5405d 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
2016-11-04 16:13:32 -05:00
Maneesh Gupta 5947878247 directed tests: Updated to use new hip include path
Change-Id: Iab1aee638b7158eb9674a19625dedf6471947e51
2016-10-04 22:20:50 +05:30
Maneesh Gupta 9216464861 directed tests: Enabled top-level uncategorized tests in HIT
Change-Id: If37cbd00244ebfa0e5bff8362820aa68aaa163f1
2016-09-23 16:15:31 +05:30
Ben Sander 944d4eaa18 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.
2016-09-22 14:21:19 -05:00
Ben Sander 6abfa13c34 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.
2016-04-18 20:49:33 -05:00
Ben Sander 3301deb07c test update 2016-04-17 07:54:39 -05:00
Ben Sander c3bd85595d 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.
2016-04-16 10:18:56 -05:00
Ben Sander 1acd16eb5d add simple negative P2P tests 2016-04-11 07:58:59 -05:00
Ben Sander 9e7efd7c65 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.
2016-04-11 07:58:59 -05:00
Ben Sander b039292a8c 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.
2016-04-11 07:58:58 -05:00
Ben Sander b8e17d52dd Improve P2P test.
Add option to select which device does the copy.
2016-04-11 07:58:58 -05:00
Ben Sander fcd1d37ff7 Fix simple P2P test, had device ptrs swapped 2016-04-11 07:58:58 -05:00
Ben Sander e14b2cd9c3 Add simple P2P test 2016-04-11 07:58:58 -05:00