AI/rocm-systems
2
0
Bifurcation 0
Code Tickets Demandes d'ajout Actions Paquets Projets Publications Wiki Activité
287 Révisions 3 Branches 0 Étiquette
ee280265ea0a557f9813ef3cd41e40c7e97b0366
Graphe des révisions

287 Révisions

Cette branche
Cette branche
Toutes les branches
Auteur SHA1 Message Date
Aditya Atluri ee280265ea Update README.md 
[ROCm/hip commit: 3bece3798b]
 2016-03-23 18:16:11 -05:00
Aditya Atluri 6841aa084c reverted back to old infra with cmake added 
[ROCm/hip commit: 5637bde4b3]
 2016-03-23 11:13:02 -05:00
Aditya Atluri c667d9c170 Update README.md 
[ROCm/hip commit: de91445e20]
 2016-03-23 15:05:50 -05:00
Aditya Atluri 4ca4cae3fa WIP added modular feature for device apis 
[ROCm/hip commit: 89bfc0e375]
 2016-03-23 07:54:01 -05:00
Aditya Atluri 459a8c2104 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 
[ROCm/hip commit: dc429aade6]
 2016-03-23 11:40:18 -05:00
Aditya Atluri ad91545586 Logging dispatch latency through database util 
[ROCm/hip commit: 78407ea40a]
 2016-03-23 11:39:57 -05:00
Siu Chi Chan e964f00377 Merge pull request #18 from AMDComputeLibraries/grid_launch_index 
Grid launch index fix

[ROCm/hip commit: 1d3860a8eb]
 2016-03-23 11:26:28 -05:00
Ben Sander 7632b769a0 Update docs: 
- Some comments in hip_hcc.cpp
 - document hipHostRegister* flags.
 - expand docs on hipHostRegister/Unregister. Use "register" rather than
   "pin" to describe action these take.
 - change required CUDA version to 6 (require unified memory)
 - remake doxygen.


[ROCm/hip commit: eced013ae4]
 2016-03-23 23:11:15 -05:00
scchan 22c79027a5 add compiler version guard to the grid launch fix 
[ROCm/hip commit: 0eead76d4e]
 2016-03-23 11:24:37 -05:00
scchan 2b25f5c1ff fix builtins mapping for IDs and Dims 
[ROCm/hip commit: 56a1863c74]
 2016-03-23 11:08:28 -05:00
Aditya Atluri 5b597511b6 fixed hipHostGetFlags test 
[ROCm/hip commit: 362867d325]
 2016-03-23 02:45:21 -05:00
Aditya Atluri 5f343cb38b Remove redundant hpiHostGetDevicePointer 
[ROCm/hip commit: 36d0da99c1]
 2016-03-23 09:21:02 -05:00
Ben Sander 87830e8cff Add USE_AV_COPY (replaces calls to am_copy with new acc_view::copy 
[ROCm/hip commit: 6ab48d7b90]
 2016-03-23 10:30:53 -05:00
Ben Sander 748180c769 use the CPU_Agent for memory copies to indicate direction. 
[ROCm/hip commit: 0f81c5bcf2]
 2016-03-23 10:29:44 -05:00
Ben Sander 2313b4b7b5 Only include activity logger if CodeXL installed. 
Fix hipHostMalloc in hipBusBandwidth.


[ROCm/hip commit: 3a5f964c4f]
 2016-03-22 09:27:10 -05:00
Ben Sander c31a02348b remove unneeded files 
[ROCm/hip commit: 7715fe424c]
 2016-03-23 03:41:01 -05:00
Ben Sander a7ff86a141 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 
Conflicts:
	src/hip_hcc.cpp


[ROCm/hip commit: d07b347cac]
 2016-03-23 03:22:09 -05:00
Ben Sander 241befc9f6 Add unique stream_id to devices to improve debug 
[ROCm/hip commit: f863c5c6aa]
 2016-03-23 03:17:19 -05:00
Ben Sander 6d5968027c Improve trace API 
- Validate compile-time disables.
- Add README.md section explain how to install/use CodeXL tracing
- Add code docs on trace_helper.h
- fix color on hipLaunchKernel to green.


[ROCm/hip commit: 2569e15375]
 2016-03-23 02:57:52 -05:00
Ben Sander 5c8b743588 HIP_TRACE_API prints function args, and in color 
[ROCm/hip commit: 33bbf1463f]
 2016-03-23 02:19:49 -05:00
Ben Sander 82cda5c087 use codexl marker interface to mark HIP function/begin end. 
- Creates markers in HIP group and they show up in CodeXL trace
- Marker text includes HIP functioin arguments
- (Add trace_helper to convert arguments to strings)
- Still need to add HIP_INIT_API for ~30 HIP functions.


[ROCm/hip commit: b6b3fea05b]
 2016-03-23 01:17:53 -05:00
Ben Sander f9b2f0c840 Describe how to file an issue 
[ROCm/hip commit: 608bb21797]
 2016-03-23 01:15:05 -05:00
Aditya Atluri 01ef054798 Update CUDA_Runtime_API_functions_supported_by_HIP.md 
[ROCm/hip commit: 1d6dcb70ee]
 2016-03-22 10:42:34 -05:00
Ben Sander b319209299 hipHostRegister and hipHostMalloc refactor. 
Note hipHostMalloc (not hipHostAlloc or hipMallocHost).
 -  the hipHost* is used for all HIP APIs dealing with Host memory.
    (including hipHostMalloc, hipHostFree, hipHostRegister,
hipHostUnregister, hipHostGetFlags, hipHostGetDevicePointer).
  - hipMallocHost is consistent with "hipMalloc" for allocating device
    memory.  Enumerations hipHostMalloc* also used as optional
    flags parm to hipHostMalloc.


[ROCm/hip commit: ab910efb96]
 2016-03-22 02:30:10 -05:00
Ben Sander f392d143ff Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 
[ROCm/hip commit: 8087bc0401]
 2016-03-22 01:17:17 -05:00
Aditya Atluri a19d8a0eff Update CUDA_Runtime_API_functions_supported_by_HIP.md 
[ROCm/hip commit: 59324930b5]
 2016-03-21 18:33:50 -05:00
Aditya Atluri 9741873703 Revert "Revert "fixed memory free apis"" 
This reverts commit 9ba9f2a407.


[ROCm/hip commit: 52cf63472c]
 2016-03-21 10:40:42 -05:00
Aditya Atluri 831b55129d Revert "Revert "fix nvcc for hipHostMalloc* flags."" 
This reverts commit 4bebb99566.


[ROCm/hip commit: e5918ce729]
 2016-03-21 10:39:49 -05:00
Aditya Atluri 4bebb99566 Revert "fix nvcc for hipHostMalloc* flags." 
This reverts commit 9f071dde99.


[ROCm/hip commit: 3f5eb20cf0]
 2016-03-21 10:36:14 -05:00
Aditya Atluri 9ba9f2a407 Revert "fixed memory free apis" 
This reverts commit 2a044e3823.


[ROCm/hip commit: 287ba34aca]
 2016-03-21 10:36:11 -05:00
Aditya Atluri 733d085171 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 
[ROCm/hip commit: caa80af31b]
 2016-03-21 10:34:08 -05:00
Aditya Atluri 2a044e3823 fixed memory free apis 
[ROCm/hip commit: 96a1899df7]
 2016-03-21 10:32:30 -05:00
Aditya Atluri 776d201d0e Disabling default-stream per-thread tests 
[ROCm/hip commit: 6d1420ab68]
 2016-03-21 14:42:23 -05:00
Ben Sander 9f071dde99 fix nvcc for hipHostMalloc* flags. 
[ROCm/hip commit: b6962826eb]
 2016-03-21 09:33:46 -05:00
Ben Sander 7891e8baba Remove kind (aka direction) for copy commands. 
This is always auto-detected from the src/dest location.


[ROCm/hip commit: 04af145d6a]
 2016-03-21 05:35:36 -05:00
Aditya Atluri f0d86c6b78 suppressed warning in hipFreeHost 
[ROCm/hip commit: 6b3821afc7]
 2016-03-20 15:31:59 -05:00
Aditya Atluri dd6fc044d6 Added feature for --default-streams not working tests and hipcc 
[ROCm/hip commit: a232d65db1]
 2016-03-20 08:08:33 -05:00
Ben Sander 8c1e55c937 Implement hipHostFree on HCC path 
[ROCm/hip commit: deb38625ca]
 2016-03-19 23:25:11 -05:00
Ben Sander 9c3100894c fix nvcc compiler 
- MallocHost and FreeHost deprecation.
- Change tests to call new hipHost* equivs.
- Add missing StreamSynchronize.


[ROCm/hip commit: 9941ba0bc6]
 2016-03-19 04:20:15 -05:00
Ben Sander b520a34579 Refactor copy - place common code in resolveMemoryKind. 
[ROCm/hip commit: 194d02ac5a]
 2016-03-19 22:56:10 -05:00
Ben Sander 4c77ecef9a Deprecate hipMallocHost and hipFreeHost. 
These will print compiler warnings if used, so we can weed them out
before removing.

Also add a default flags args for hipHostAlloc, in the C++ functioin
headers.  So you can replace hipMallocHost(&ptr, size( with hipHostAlloc(&ptr, size)


[ROCm/hip commit: cea37c3e91]
 2016-03-19 22:53:59 -05:00
Ben Sander 36d2a024c0 Refactor waitALlDevices and async mem copy. 
- move waitAllStreams to device member function.
- create separate stream member function for copyAsync, like copySync.
  hipMemcpyAsync now calls the copyAsync.


[ROCm/hip commit: 52cc2bb75a]
 2016-03-19 05:42:19 -05:00
Ben Sander 11603764be Fix bug: test was allocating host mem instead of device mem. 
Caused assertion when checking free + allocated should
not exceed total.  Bug introduced in hipHostAlloc conversion.


[ROCm/hip commit: 95e1c8eb32]
 2016-03-19 04:11:39 -05:00
Ben Sander 16df30e767 Swap in corrected hipHostAlloc (bad merge) 
[ROCm/hip commit: d898997c65]
 2016-03-19 04:11:08 -05:00
Ben Sander 5297376252 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 
Conflicts:
	src/hip_hcc.cpp


[ROCm/hip commit: 1de63bfeea]
 2016-03-19 03:22:09 -05:00
Ben Sander 013f08418f disable mt streams tests (for now) 
[ROCm/hip commit: dfca4faf27]
 2016-03-19 03:10:31 -05:00
Ben Sander 8204d20644 Describe HIP env vars 
[ROCm/hip commit: 2dc7e9ccfa]
 2016-03-19 03:09:57 -05:00
Ben Sander 662cd0bb30 Fix copy and sync bugs. Remove extra sync in default stream. 
- NULL stream was waiting for itself to be empty before each command.
- Force "blocking" streams to wait for NULL to empty.  This was missing
  before.
- async copy was disabling itself via trueAsync=false for common cases.

Refactor:
- rename _null_stream to _default_stream.
- move some null sync function to defaultSync, move to dev member func.


[ROCm/hip commit: 6472c8b915]
 2016-03-19 02:44:26 -05:00
Ben Sander b6de799f47 Add beastperiteration and onesize for testing. 
onesize allows running tests at one specific size.


[ROCm/hip commit: 7ff5b16d2a]
 2016-03-19 02:43:04 -05:00
Ben Sander 79d0d442d3 Improve formatting - line up cols 
[ROCm/hip commit: 85fce5f21e]
 2016-03-18 23:43:04 -05:00