AI/rocm-systems
2
0
Forka 0
Codice Problemi Pull Request Actions Pacchetti Progetti Rilasci Wiki Attività
1.074 Commit 3 Rami (Branch) 0 Tag
d06509f680d83e86c32fc17fbea101302adebcf2
Grafico dei commit

351 Commit

Autore SHA1 Messaggio Data
Aditya Atluri d06509f680 added compiler flag for polaris 
Change-Id: Ib14c14c0618982ac7b48f5bc704c04b54ff40ed9


[ROCm/hip commit: 90a71c4be4]
 2016-10-13 14:16:48 -05:00
Ben Sander a20ed98897 Remove hipblas.h header - this is now hosted in the hcBlas repot. 
Change-Id: I5b3350c900741cb1aee75faf4547f2682a9ec385


[ROCm/hip commit: 586bcdc8dc]
 2016-10-13 11:51:25 -05:00
Aditya Atluri a4c5402bf4 Added HIP_SYMBOL macro to act as a wrapper between HCC and NVCC symbol name parameters 
Change-Id: I008d028b1e29d5a00d0e449af388216396ad2f75


[ROCm/hip commit: 36b73ed8d9]
 2016-10-13 10:31:56 -05:00
Aditya Atluri 50db853e0b added limit api support for nvcc 
Change-Id: Ib6c939e44343158a70e0de7f107d21afc0d0efba


[ROCm/hip commit: ecf347a942]
 2016-10-12 21:06:30 -05:00
Aditya Atluri ef0cb7d619 Added hipDeviceGetLimit api 
1. hipDeviceGetLimit API for HCC path is added
2. Test for hipDeviceGetLimit API is added
3. The feature added only supports querying heap size
4. Corrected indents for malloc and free device functions
5. Removed redundant data structures
6. Added g_heap_malloc_size to store the heap size

Change-Id: If48d1b0ce9270e994f1c542cc283ddbb14746bbb


[ROCm/hip commit: 62ec53740c]
 2016-10-12 19:58:48 -05:00
Aditya Atluri 218b4034bc Added copyright for headers 
Change-Id: I35843d8d3b6acd9553ce00150868e15e2baee1da


[ROCm/hip commit: 7cf8ea5c64]
 2016-10-12 19:12:35 -05:00
Aditya Atluri 6591712299 added malloc and free device functions 
1. Added malloc and free device functions
2. Added test which check malloc and free functions
TODO: Need to add support for multiple device. Works only on one device (multi device support id NOT available).

Change-Id: Id11fc36463915d6ad46c264d5a20c8feb2d2c17c


[ROCm/hip commit: d24a7ef12b]
 2016-10-12 19:08:34 -05:00
Aditya Atluri 0c2d2a4945 changed memcpy and memset device functions 
Change-Id: Ia7f450536a75fad4fe13c7fcf5e9e7a9b5450f52


[ROCm/hip commit: 288f024d00]
 2016-10-11 17:43:15 -05:00
Aditya Atluri a8a315ff80 changed hipTestDeviceSymbol test to compile for both nvcc and hcc path 
Change-Id: I041770ad59d4f88d0c8d27d90cdc8a799935ada1


[ROCm/hip commit: d71c0d10de]
 2016-10-11 13:50:31 -05:00
Aditya Atluri 25dddf5a9b added hipMemcpySymbol feature to nvcc path 
Change-Id: I78d45036083fba62d2b2e4e58f9c72cb4e6eb54f


[ROCm/hip commit: e3712197ca]
 2016-10-11 13:34:54 -05:00
Aditya Atluri 62e25cc961 added more changes to memcpytosymbol 
1. Refactored code to use HCC internal APIs rather than HCC copy APIs
2. Added hipMemcpyToSymbolAsync
3. Added test for hipMemcpyToSymbolAsync
4. Added new error hipErrorInvalidSymbol

Change-Id: I0e359b2d0ff5d682bbccdf9c2923e16b35e39497


[ROCm/hip commit: 3c4af7c371]
 2016-10-11 13:29:46 -05:00
Aditya Atluri 3cddc50058 Added feature for memcpy to Symbol 
1. Currently works only for __attribute__((addrspace(1))
2. Need to pass in string for name of the variable
3. Added test to check functionality

Change-Id: I4c3cc1bf151cb5423e4aef59fcc4ad5693b31641


[ROCm/hip commit: 6952b59401]
 2016-10-11 12:09:58 -05:00
Aditya Atluri cb75432ac4 added threadfence feature for hcc 
1. Added feature for __threadfence and __threadfence_block
2. Added feature for using LLVM IR files directly while compilation
3. Added test for threadfence and threadfence_block

Change-Id: Ib7e5d89b4cca1a135952b317e5809cd05b56a3c9


[ROCm/hip commit: dc1042ce6d]
 2016-10-10 15:29:50 -05:00
Maneesh Gupta eebcf24ee0 Add back deprecated hipHostAlloc, hipMallocHost, hipFreeHost 
Change-Id: Ib8494078c852b07e1958c3acc21fa1866542122c


[ROCm/hip commit: 7c943ef20a]
 2016-10-09 16:30:46 +05:30
Elias Konstantinidis 7d0d42712e Added support for __mul24 and __umul24 
[ROCm/hip commit: 2bc541e15f]
 2016-10-06 09:29:36 +05:30
Maneesh Gupta fc58842fcf Move include/* to include/hip/* 
Change-Id: I7a7b2839b4df59c7a4c503550f99fdc9e45c0f54


[ROCm/hip commit: b951cc99ed]
 2016-10-04 22:17:18 +05:30
Ben Sander e99878f5fb Fix hipMemSetAsync compilation, bounds check on name copy 
[ROCm/hip commit: 88fb0efa6d]
 2016-10-03 19:05:19 -05:00
Aditya Atluri dd55ba8b5d Stream fix on nvcc hipMemsetAsync 
Change-Id: Ia0eb81dff0f422af55d93b4635d42e9aa6921377


[ROCm/hip commit: 9f05eca0a0]
 2016-10-03 12:38:41 -05:00
Ben Sander 679b9be947 disable DB_SHOW_TID 
Change-Id: Ia415437e8ba9903de149997380f61f1272488642


[ROCm/hip commit: d4a6010e2d]
 2016-10-02 05:56:38 -05:00
Aditya Atluri 2083f2c29e added vector types for C path 
Change-Id: I4ccd4082f1b2ce4f0f4fd9fb498506234783a803


[ROCm/hip commit: 2835e86e39]
 2016-09-29 19:44:00 -05:00
Aditya Atluri e4e4c54055 Added C guard for math headers 
Change-Id: I0e71819c6436b3e6c99b2deddb2ee2d2a16acedd


[ROCm/hip commit: e04b8d6aa7]
 2016-09-29 13:54:34 -05:00
Aditya Atluri d31206acb8 Fixed issue on git #39 
Change-Id: I5b507fc2b544df0cd3a900a2763c7a3ad6295c13


[ROCm/hip commit: 1e56dead78]
 2016-09-29 10:06:26 -05:00
pensun 04871c910b add hipEvent* macros on NV path 
Change-Id: I28ff0fa24f69560e13366e7cd8d3a485665c67e1


[ROCm/hip commit: 4fa5e980ef]
 2016-09-29 01:22:19 -05:00
Ben Sander 7fc988bc45 Refactor asyncCopy and syncCopy to fix deadlock case. 
- Minimize time that locks are held.
- Eliminate copy code that locked stream and ctx at same time.
    - Stream was locked to ensure thread-safe enqueue to the queue.
    - Devices were locked to query peer-lists.

Change-Id: Ibe8880bb7fb995a3da8f90ff911f212d81525018


[ROCm/hip commit: 4ff6dc8f38]
 2016-09-27 15:45:40 -05:00
Ben Sander 7f7340fb29 Add debug option to print ThreadID with each message. 
Also print messages with single fprintf to prevents threads from
interleaving.

Change-Id: Ib3999fe6b1e67b4a16cd7dcde82f3dfc99dd48ff


[ROCm/hip commit: 6de9136002]
 2016-09-27 15:45:40 -05:00
Ben Sander 0dadf681db Fix signal resource issue. 
Remove memory leak with new hc::completion_future.
Implement HIP_LAUNCH_BLOCKING with queue-level wait.

Change-Id: I45975f81c4d239fdeed7776970988d28449865dc


[ROCm/hip commit: 225e37fdc9]
 2016-09-26 16:47:32 -05:00
Rahul Garg f80ea5aa78 Doxygen documentation changes for hipCtxXXX APIs 
Change-Id: I1e5e3a621b732bd8bdeef1c607c004d6adfdab32


[ROCm/hip commit: 280249918f]
 2016-09-26 23:11:07 +05:30
Rahul Garg bfaf47dcfa Doxygen related document updates for texture/ array related functions 
Change-Id: Iedc5b6512b5ddecb98c0e51a353957f08b955fde


[ROCm/hip commit: f4f12cf50c]
 2016-09-26 16:18:53 +05:30
Rahul Garg ccf9b08949 Removed deprecated hipHostAlloc 
Change-Id: Ia592a3545c5d72f37e049ce29f910e404323c01c


[ROCm/hip commit: daef1d2906]
 2016-09-26 10:58:46 +05:30
Rahul Garg d304ad4e1f Removed deprecated hipMallocHost 
Change-Id: I3141fe05a34b6a306297a30721509965f49ccb97


[ROCm/hip commit: 6790ff6b11]
 2016-09-26 05:52:21 +05:30
Rahul Garg 8f68e34442 Removed deprecated hipFreeHost 
Change-Id: I9747ea3993090e0da6a2e1f5e9ce318762bc03e1


[ROCm/hip commit: 7b87a972cb]
 2016-09-26 05:35:14 +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 c845631845 Add kind translation for hipMemcpyDeviceToDevice 
[ROCm/hip commit: 0d47e62cb0]
 2016-09-22 14:21:19 -05:00
Ben Sander 21d1c29312 Remove unpinned_copy code. Other cleanup. 
Change-Id: Ie3f71439cf1ba729ef223d078917c403d3de879a


[ROCm/hip commit: c645e53fdd]
 2016-09-22 14:21:19 -05:00
Ben Sander b9a0abe32e Cleanup. Remove cfs, ihipSignal_t, staging buffer calls. 
Change-Id: I8bb67c484e3a65be06a03665f059217930da2bed


[ROCm/hip commit: e0ce1d3954]
 2016-09-22 14:21:19 -05:00
Ben Sander 41c4ea49ba Cleanup: Remove HIP signal pool. 
Change-Id: Icebfd0509d12396cc5933d5556d68b53e1be36e0


[ROCm/hip commit: 12cb1d88aa]
 2016-09-22 14:21:19 -05:00
Ben Sander a9e3786e0c Remove HIP command dependency tracking. 
Change-Id: I991c13bc5108193959ba70f9f6f9c692c9ad3a5b


[ROCm/hip commit: 7530fa6dbe]
 2016-09-22 14:21:19 -05:00
Ben Sander f145954a9d Cleanup, remove preCopyCommand. 
Change-Id: I3768d3789a99be8136b43179d4152fa1875665cb


[ROCm/hip commit: 8c4cecf367]
 2016-09-22 14:21:19 -05:00
Ben Sander d71686d4f5 Remove USE_AV_COPY, USE_PEER_TO_PEER fallback paths. 
Change-Id: I9c20173e62029c4caebabc98784c6d7697758e4f


[ROCm/hip commit: e843d8cb51]
 2016-09-22 14:21:19 -05:00
Ben Sander b7dda7be0d Remove HIP_STAGING_BUFFER 
Code simplification/cleanup:
Remove stale fallback paths that uses something besides the unpinned engine.
Remove HIP_STAGING_BUFFER env var - now is const 2, 0 no longer has
special meaning.

Change-Id: I7d24cdd1067dd0c244e87b6a83897cb135d307e7


[ROCm/hip commit: ccc1bbe6b1]
 2016-09-22 14:21:18 -05:00
Ben Sander f7987aaa33 Move isLargeBar to UnpinnedCopyEngine constructor. 
Change-Id: I7a7d3a40b1d4e0c6ec856658a6a70e5e70d287ce


[ROCm/hip commit: 442d74f027]
 2016-09-22 14:21:18 -05:00
Ben Sander 7935c8b929 Refactor Staging Buffer CopyDeviceToHost 
Use copyMode.  Embed algorithm selection inside the unpinned class.

Change-Id: Ic75fd5931717a3160904402794bbed3ccd445112


[ROCm/hip commit: e300cb4405]
 2016-09-22 14:21:18 -05:00
Ben Sander fd5d85ee6b Refactor staging buffer CopyHostToDevice. 
- Move algorithm selection inside Unpinned class.
- Refactor function names.
- Use size_t for size threshholds.

Change-Id: Iac4de652ac9d49acbf527aa0849e388b8ecd8486


[ROCm/hip commit: c532de9f5a]
 2016-09-22 14:21:18 -05:00
Ben Sander f028a2e833 Updates docs for hipHcc* functions, move to header 
[ROCm/hip commit: 83140f8423]
 2016-09-22 13:05:47 -05:00
Aditya Atluri 468565058e added ipc runtime api for nvcc backend 
Change-Id: I3297c4c9db34e7bc3267fec64a6757f9ebf91905


[ROCm/hip commit: 50b78439af]
 2016-09-22 12:55:41 -05:00
Rahul Garg e729fa1dee Added hipRuntimeGetVersion function 
Change-Id: I59ec2beacb5a94439deed0dcc8eb37d6de1cc900


[ROCm/hip commit: bfc033cc3e]
 2016-09-22 15:21:23 +05:30
pensun 85a63c778f doc fix for hipStream 
Change-Id: I618464c8b9ffa0a566434e72d2bc87a152884ca1


[ROCm/hip commit: 751a2cfce5]
 2016-09-21 12:03:01 -05:00
Rahul Garg fbad743243 Added return error code hipErrorInvalidValue in hipMemGetInfo 
Change-Id: If01b012136b655ff8eb4878eb703dfe3e6a36530


[ROCm/hip commit: ffd49cfa37]
 2016-09-17 23:54:20 +05:30
pensun 068e744783 Revert "resolve merge conflict" 
This reverts commit 64f6a4f1b0.


[ROCm/hip commit: d69e56fdc9]
 2016-09-16 16:04:48 -05:00
pensun 64f6a4f1b0 resolve merge conflict 
Change-Id: I041730d4208ae1865820f5df73a67ba60fd4bc3c


[ROCm/hip commit: 575e1f5024]
 2016-09-16 11:13:43 -05:00