AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
41,017 Commits 3 Branches 0 Tags
83971da05ef9946e193a86dc400a68ccfb3b1d3f
Commit Graph

41017 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Ben Sander bf83b949f6 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 2016-03-22 01:17:17 -05:00
Ben Sander 8087bc0401 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 2016-03-22 01:17:17 -05:00
Aditya Atluri a8a255b6bc Update CUDA_Runtime_API_functions_supported_by_HIP.md 2016-03-21 18:33:50 -05:00
Aditya Atluri 59324930b5 Update CUDA_Runtime_API_functions_supported_by_HIP.md 2016-03-21 18:33:50 -05:00
foreman c2b98ee500 P4 to Git Change 1249491 by gandryey@gera-w8 on 2016/03/21 17:37:48 
SWDEV-90408 - OpenCL runtime crashes when querying CL_PROGRAM_NUM_KERNELS on a program built with clCompileProgram
	- The app attempts to get query before build/link call. Make sure symbols are available.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_program.cpp#40 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.hpp#39 edit
 2016-03-21 17:51:06 -04:00
foreman 769ff6d3f8 P4 to Git Change 1249491 by gandryey@gera-w8 on 2016/03/21 17:37:48 
SWDEV-90408 - OpenCL runtime crashes when querying CL_PROGRAM_NUM_KERNELS on a program built with clCompileProgram
	- The app attempts to get query before build/link call. Make sure symbols are available.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_program.cpp#40 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/program.hpp#39 edit
 2016-03-21 17:51:06 -04:00
foreman 3f6cc5b851 P4 to Git Change 1249484 by kzhuravl@kzhuravl-kaveri-sc on 2016/03/21 17:26:34 
SWDEV-76911 - Fix base/full profile loader issues on SoftCP path [integration of CL 1249449]

	1) Introduce internal API that provides kernel host address given kernel device address
	2) Remove base/full profile loader hacks we have today

	+ runtime changes:
	1) Remove asserts when querying host address of a host address in hsart's loader context

	ReviewBoardURL: http://ocltc.amd.com/reviews/r/10054/
	Testing: precheckin (http://ocltc.amd.com:8111/viewModification.html?modId=68651&personal=true&tab=vcsModificationBuilds)

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/sc/HSAIL/ext/loader/executable.cpp#22 integrate
... //depot/stg/opencl/drivers/opencl/compiler/sc/HSAIL/ext/loader/executable.hpp#11 integrate
... //depot/stg/opencl/drivers/opencl/compiler/sc/HSAIL/include/amd_hsa_kernel_code.h#12 integrate
... //depot/stg/opencl/drivers/opencl/compiler/sc/HSAIL/include/amd_hsa_loader.hpp#10 integrate
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuprogram.hpp#65 edit
 2016-03-21 17:40:05 -04:00
foreman 43f22a686d P4 to Git Change 1249380 by asalmanp@asalmanp-opencl-stg on 2016/03/21 13:17:27 
SWDEV-79278 - [OpenCL][GFX9 Bring up] renaming the Vega10 device name to GFX9_0_0
	ReviewBoardURL = http://ocltc.amd.com/reviews/r/10036/

Affected files ...

... //depot/stg/opencl/drivers/opencl/compiler/legacy-lib/utils/v0_8/target_mappings.h#9 edit
... //depot/stg/opencl/drivers/opencl/compiler/legacy-lib/utils/v0_8/target_mappings_amdil.h#9 edit
... //depot/stg/opencl/drivers/opencl/compiler/legacy-lib/utils/v0_8/target_mappings_amdil64.h#8 edit
... //depot/stg/opencl/drivers/opencl/compiler/legacy-lib/utils/v0_8/target_mappings_hsail.h#8 edit
... //depot/stg/opencl/drivers/opencl/compiler/legacy-lib/utils/v0_8/target_mappings_hsail64.h#8 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/backends/common/linker.cpp#140 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings.h#41 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_amdil.h#36 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_amdil64.h#32 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail.h#31 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail64.h#26 edit
... //depot/stg/opencl/drivers/opencl/compiler/tools/driver/driver.cpp#61 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudefs.hpp#135 edit
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/runtime/OCLDeviceQueries.cpp#35 edit
... //depot/stg/opencl/drivers/opencl/tests/ocltst/module/runtime/OCLPerfCounters.cpp#27 edit
 2016-03-21 13:27:06 -04:00
Aditya Atluri 8af8ee2476 Revert "Revert "fixed memory free apis"" 
This reverts commit 1fa4d0d4b9.
 2016-03-21 10:40:42 -05:00
Aditya Atluri 52cf63472c Revert "Revert "fixed memory free apis"" 
This reverts commit 287ba34aca.
 2016-03-21 10:40:42 -05:00
Aditya Atluri bde1e6182d Revert "Revert "fix nvcc for hipHostMalloc* flags."" 
This reverts commit 83fee90e83.
 2016-03-21 10:39:49 -05:00
Aditya Atluri e5918ce729 Revert "Revert "fix nvcc for hipHostMalloc* flags."" 
This reverts commit 3f5eb20cf0.
 2016-03-21 10:39:49 -05:00
Aditya Atluri 83fee90e83 Revert "fix nvcc for hipHostMalloc* flags." 
This reverts commit d495ffb1d3.
 2016-03-21 10:36:14 -05:00
Aditya Atluri 3f5eb20cf0 Revert "fix nvcc for hipHostMalloc* flags." 
This reverts commit b6962826eb.
 2016-03-21 10:36:14 -05:00
Aditya Atluri 1fa4d0d4b9 Revert "fixed memory free apis" 
This reverts commit 71a6b5cb6c.
 2016-03-21 10:36:11 -05:00
Aditya Atluri 287ba34aca Revert "fixed memory free apis" 
This reverts commit 96a1899df7.
 2016-03-21 10:36:11 -05:00
Aditya Atluri e99179edc8 Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 2016-03-21 10:34:08 -05:00
Aditya Atluri caa80af31b Merge branch 'privatestaging' of https://github.com/AMDComputeLibraries/HIP-privatestaging into privatestaging 2016-03-21 10:34:08 -05:00
Aditya Atluri 71a6b5cb6c fixed memory free apis 2016-03-21 10:32:30 -05:00
Aditya Atluri 93e6362104 Disabling default-stream per-thread tests 2016-03-21 14:42:23 -05:00
Aditya Atluri 96a1899df7 fixed memory free apis 2016-03-21 10:32:30 -05:00
Aditya Atluri 6d1420ab68 Disabling default-stream per-thread tests 2016-03-21 14:42:23 -05:00
Ben Sander d495ffb1d3 fix nvcc for hipHostMalloc* flags. 2016-03-21 09:33:46 -05:00
Ben Sander b6962826eb fix nvcc for hipHostMalloc* flags. 2016-03-21 09:33:46 -05:00
Ben Sander ac1eca47f7 Remove kind (aka direction) for copy commands. 
This is always auto-detected from the src/dest location.
 2016-03-21 05:35:36 -05:00
Ben Sander 04af145d6a Remove kind (aka direction) for copy commands. 
This is always auto-detected from the src/dest location.
 2016-03-21 05:35:36 -05:00
foreman 19564646c7 P4 to Git Change 1249227 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/21 03:00:09 
SWDEV-2 - Change OpenCL version number from 2069 to 2070.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#1816 edit
 2016-03-21 03:15:29 -04:00
James Edwards (xN/A) TX c9ffe0004e Check open source core runtime code into perforce. This includes license and README files. 
[git-p4: depot-paths = "//depot/stg/hsa/drivers/hsa/runtime/": change = 1249136]
 2016-03-20 15:39:40 -05:00
James Edwards (xN/A) TX 67e6064a6a Check open source core runtime code into perforce. This includes license and README files. 
[git-p4: depot-paths = "//depot/stg/hsa/drivers/hsa/runtime/": change = 1249136]


[ROCm/ROCR-Runtime commit: c9ffe0004e]
 2016-03-20 15:39:40 -05:00
Aditya Atluri ea352aba6b suppressed warning in hipFreeHost 2016-03-20 15:31:59 -05:00
Aditya Atluri 6b3821afc7 suppressed warning in hipFreeHost 2016-03-20 15:31:59 -05:00
foreman d58bf7ea73 P4 to Git Change 1249126 by johtaylo@johtaylo-JTBUILDER03-increment on 2016/03/20 03:00:10 
SWDEV-2 - Change OpenCL version number from 2068 to 2069.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#1815 edit
 2016-03-20 15:08:57 -04:00
Aditya Atluri f6b38b18b6 Added feature for --default-streams not working tests and hipcc 2016-03-20 08:08:33 -05:00
Aditya Atluri a232d65db1 Added feature for --default-streams not working tests and hipcc 2016-03-20 08:08:33 -05:00
Ben Sander 80d708846a Implement hipHostFree on HCC path 2016-03-19 23:25:11 -05:00
Ben Sander deb38625ca Implement hipHostFree on HCC path 2016-03-19 23:25:11 -05:00
Ben Sander 6984f24d3d 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 03731020f1 Refactor copy - place common code in resolveMemoryKind. 2016-03-19 22:56:10 -05:00
Ben Sander 57365eb7a3 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 a88c2b1ec9 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 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 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 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 aaa2429feb Swap in corrected hipHostAlloc (bad merge) 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 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 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