AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
74,770 Commits 3 Branches 0 Tags
48a4cda75c888bea344085a5feff6cf2c19e1924
Commit Graph

74770 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
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 9941ba0bc6 fix nvcc compiler 
- MallocHost and FreeHost deprecation.
- Change tests to call new hipHost* equivs.
- Add missing StreamSynchronize.
 2016-03-19 04:20:15 -05:00
Ben Sander 194d02ac5a Refactor copy - place common code in resolveMemoryKind. 2016-03-19 22:56:10 -05:00
Ben Sander cea37c3e91 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)
 2016-03-19 22:53:59 -05:00
Ben Sander 52cc2bb75a 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.
 2016-03-19 05:42:19 -05:00
Ben Sander d41836a4a1 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/clr commit: 4c6fd4e7ec]
 2016-03-19 04:11:39 -05:00
Ben Sander 4c6fd4e7ec 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.
 2016-03-19 04:11:39 -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 95e1c8eb32 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.
 2016-03-19 04:11:39 -05:00
Ben Sander cf95ea5468 Swap in corrected hipHostAlloc (bad merge) 
[ROCm/clr commit: aaa2429feb]
 2016-03-19 04:11:08 -05:00
Ben Sander aaa2429feb Swap in corrected hipHostAlloc (bad merge) 2016-03-19 04:11:08 -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 d898997c65 Swap in corrected hipHostAlloc (bad merge) 2016-03-19 04:11:08 -05:00
Ben Sander c7d2605a37 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 
Conflicts:
	src/hip_hcc.cpp


[ROCm/hip-tests commit: 221973404f]
 2016-03-19 03:22:09 -05:00
Ben Sander 221973404f Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 
Conflicts:
	src/hip_hcc.cpp
 2016-03-19 03:22:09 -05:00
Ben Sander 3305c49949 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 
Conflicts:
	src/hip_hcc.cpp


[ROCm/clr commit: 90ad8ddc5d]
 2016-03-19 03:22:09 -05:00
Ben Sander 90ad8ddc5d Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 
Conflicts:
	src/hip_hcc.cpp
 2016-03-19 03:22:09 -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 1de63bfeea Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 
Conflicts:
	src/hip_hcc.cpp
 2016-03-19 03:22:09 -05:00
Ben Sander 3323d2005c disable mt streams tests (for now) 
[ROCm/clr commit: efc9df8805]
 2016-03-19 03:10:31 -05:00
Ben Sander efc9df8805 disable mt streams tests (for now) 2016-03-19 03:10:31 -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 dfca4faf27 disable mt streams tests (for now) 2016-03-19 03:10:31 -05:00
Ben Sander 57c08b7fce Describe HIP env vars 
[ROCm/clr commit: c39b0f9660]
 2016-03-19 03:09:57 -05:00
Ben Sander c39b0f9660 Describe HIP env vars 2016-03-19 03:09:57 -05:00
Ben Sander 8204d20644 Describe HIP env vars 
[ROCm/hip commit: 2dc7e9ccfa]
 2016-03-19 03:09:57 -05:00
Ben Sander 2dc7e9ccfa Describe HIP env vars 2016-03-19 03:09:57 -05:00
Ben Sander 1abdd6602f 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/clr commit: 44522eb607]
 2016-03-19 02:44:26 -05:00
Ben Sander 44522eb607 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.
 2016-03-19 02:44:26 -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 6472c8b915 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.
 2016-03-19 02:44:26 -05:00
Ben Sander 3097de0b0e Add beastperiteration and onesize for testing. 
onesize allows running tests at one specific size.


[ROCm/hip-tests commit: d011d7cf6e]
 2016-03-19 02:43:04 -05:00
Ben Sander d011d7cf6e Add beastperiteration and onesize for testing. 
onesize allows running tests at one specific size.
 2016-03-19 02:43:04 -05:00
Ben Sander d207f3bc26 Add beastperiteration and onesize for testing. 
onesize allows running tests at one specific size.


[ROCm/clr commit: 5197cf250d]
 2016-03-19 02:43:04 -05:00
Ben Sander 5197cf250d Add beastperiteration and onesize for testing. 
onesize allows running tests at one specific size.
 2016-03-19 02:43:04 -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 7ff5b16d2a Add beastperiteration and onesize for testing. 
onesize allows running tests at one specific size.
 2016-03-19 02:43:04 -05:00
foreman 666951f151 P4 to Git Change 1249106 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/19 03:00:11 
SWDEV-2 - Change OpenCL version number from 2067 to 2068.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#1814 edit


[ROCm/clr commit: ef7612cfb3]
 2016-03-19 03:12:35 -04:00
foreman ef7612cfb3 P4 to Git Change 1249106 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/19 03:00:11 
SWDEV-2 - Change OpenCL version number from 2067 to 2068.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#1814 edit
 2016-03-19 03:12:35 -04:00
foreman f7347666d7 P4 to Git Change 1249103 by smekhano@stas-rampitec-hsa on 2016/03/19 00:35:23 
SWDEV-77584 - HSA HLC: constant fold get_local_size() with reqd_work_group_size attribute

	Testing: smoke, precheckin, conformance non_uniform_work_group
	Reviewed by Valery Pykhtin

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/backends/common/optimizer.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/AMDUtils.h#5 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/Transforms/AMDIntrinsic.h#5 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/Transforms/AMDMetadataUtils.h#4 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/Transforms/Utils/AMDLibCalls.h#37 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAILKernelManager.cpp#53 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/IntrinsicUtils/AMDIntrinsic.src_cpp#8 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/SPIR/AMDMetadataUtils.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/Utils/AMDLibCalls.cpp#61 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/Utils/AMDUtils.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/tests/hsa/src/ocl/features/metadata/local_size_reqd.cl#1 add
... //depot/stg/opencl/drivers/opencl/tests/hsa/src/ocl/features/metadata/local_size_reqd_intr.cl#1 add
... //depot/stg/opencl/drivers/opencl/tests/hsa/tlst/llc_opt.tlst#87 edit
... //depot/stg/opencl/drivers/opencl/tests/hsa/tlst/ocl_features.tlst#53 edit


[ROCm/clr commit: 80cdbed438]
 2016-03-19 00:43:22 -04:00
foreman 80cdbed438 P4 to Git Change 1249103 by smekhano@stas-rampitec-hsa on 2016/03/19 00:35:23 
SWDEV-77584 - HSA HLC: constant fold get_local_size() with reqd_work_group_size attribute

	Testing: smoke, precheckin, conformance non_uniform_work_group
	Reviewed by Valery Pykhtin

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/lib/backends/common/optimizer.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/AMDUtils.h#5 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/Transforms/AMDIntrinsic.h#5 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/Transforms/AMDMetadataUtils.h#4 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/include/llvm/Transforms/Utils/AMDLibCalls.h#37 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Target/HSAIL/HSAILKernelManager.cpp#53 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/IntrinsicUtils/AMDIntrinsic.src_cpp#8 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/SPIR/AMDMetadataUtils.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/Utils/AMDLibCalls.cpp#61 edit
... //depot/stg/opencl/drivers/opencl/compiler/llvm/lib/Transforms/Utils/AMDUtils.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/tests/hsa/src/ocl/features/metadata/local_size_reqd.cl#1 add
... //depot/stg/opencl/drivers/opencl/tests/hsa/src/ocl/features/metadata/local_size_reqd_intr.cl#1 add
... //depot/stg/opencl/drivers/opencl/tests/hsa/tlst/llc_opt.tlst#87 edit
... //depot/stg/opencl/drivers/opencl/tests/hsa/tlst/ocl_features.tlst#53 edit
 2016-03-19 00:43:22 -04:00
Ben Sander 99b2af44ae Improve formatting - line up cols 
[ROCm/hip-tests commit: f7e2c254df]
 2016-03-18 23:43:04 -05:00
Ben Sander f7e2c254df Improve formatting - line up cols 2016-03-18 23:43:04 -05:00
Ben Sander d3a3e0ba63 Improve formatting - line up cols 
[ROCm/clr commit: c5d0813f03]
 2016-03-18 23:43:04 -05:00
Ben Sander c5d0813f03 Improve formatting - line up cols 2016-03-18 23:43:04 -05:00
Ben Sander 79d0d442d3 Improve formatting - line up cols 
[ROCm/hip commit: 85fce5f21e]
 2016-03-18 23:43:04 -05:00
Ben Sander 85fce5f21e Improve formatting - line up cols 2016-03-18 23:43:04 -05:00