AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
12,234 Commits 3 Branches 0 Tags
7aba1cf4cd3f4e9ac3d1551e7fdb5dea8ea6e464
Commit Graph

12234 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Rahul Garg 017f668a72 Added another variant of bindtextoarray for direct porting 2018-07-05 23:41:31 +05:30
Rahul Garg b15b08d0db Corrected enum type 2018-07-05 23:11:39 +05:30
Rahul Garg f080abe5a5 Added tex2dlayered mapping for HIP/NVCC 2018-07-05 23:00:41 +05:30
foreman e2b18eda3e P4 to Git Change 1576542 by jatang@jatang-opencl-hsa-stg5 on 2018/07/05 09:29:34 
SWDEV-126897 - Remove un-necessary synchronize() for Device Enqueue in LC/ROCm path.

	We don't need it since we have a hsa_signal_wait_acquire() to wait for the scheduler to finish. Moreover, synchronize() sends a barrier packet that could get stuck for some reason.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#25 edit
 2018-07-05 09:39:08 -04:00
foreman 5d025cb8bb P4 to Git Change 1576407 by johtaylo@johtaylo-jtincrementor2-increment on 2018/07/05 03:00:04 
SWDEV-2 - Change OpenCL version number from 2687 to 2688.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2435 edit
 2018-07-05 03:06:54 -04:00
Aaron Enye Shi 96ab7c7b25 Implement Memory Fence Functions in header 
Enabled __llvm_fence_* functions for seq_cst.
 2018-07-04 23:35:24 +00:00
foreman 7e185b873e P4 to Git Change 1576247 by gandryey@gera-w8 on 2018/07/04 16:55:54 
SWDEV-158017 - CL_DEVICE_GLOBAL_FREE_MEMORY_AMD doesn't work correctly on PAL backend
	- Change the free memory detection to account possible memory allocation with oversubscription.
	- Make sure resource cache isn't counted as allocated memory

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#593 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.cpp#244 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuresource.hpp#88 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#94 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#31 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#68 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.hpp#25 edit
 2018-07-04 17:04:53 -04:00
Aaron Enye Shi ce9ca744dc Workaround cast warning of smaller integer type for __to_local 
For now, guard the __to_local function for device compile only since a local pointer should be same size as unsigned int on GPU compile. Also change to void* instead of char*.
 2018-07-04 20:52:55 +00:00
foreman efc584a4b9 P4 to Git Change 1576209 by vsytchen@vsytchen-win10 on 2018/07/04 15:37:58 
SWDEV-79445 - OCL generic changes and code clean-up

	1. Purge redundant AllocMapTarget function

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/15346/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_memobj.cpp#84 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#223 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#309 edit
 2018-07-04 15:50:23 -04:00
foreman 6e589b7de6 P4 to Git Change 1576209 by vsytchen@vsytchen-win10 on 2018/07/04 15:37:58 
SWDEV-79445 - OCL generic changes and code clean-up

	1. Purge redundant AllocMapTarget function

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/15346/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_memobj.cpp#84 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.cpp#223 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/device.hpp#309 edit
 2018-07-04 15:50:23 -04:00
foreman 0bc34b7062 P4 to Git Change 1576208 by vsytchen@vsytchen-win10 on 2018/07/04 15:36:47 
SWDEV-154903 - [Vega10][PAL] clSVMAlloc is failing to create allocations greater than 2GB

	1. Uncommit coarse grain SVM from system memory when calling clEnqueueSVMUnmap

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/15336/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpumemory.cpp#133 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.cpp#133 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/memory.hpp#106 edit
 2018-07-04 15:45:29 -04:00
Aaron Enye Shi f8109c5b06 Merge branch 'master' into hipclang-add-amdgcn-funcs 2018-07-04 17:36:08 +00:00
foreman 2402a28a4d P4 to Git Change 1575903 by johtaylo@johtaylo-jtincrementor2-increment on 2018/07/04 03:00:04 
SWDEV-2 - Change OpenCL version number from 2686 to 2687.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2434 edit
 2018-07-04 03:09:29 -04:00
Maneesh Gupta 874af1bf7d Merge pull request #539 from ROCm-Developer-Tools/fix-tf-link 
Add workaround to hipcc for build failure in tensorflow due to missin…
 2018-07-04 11:08:52 +05:30
Maneesh Gupta e54ffe52a0 Merge pull request #530 from ROCm-Developer-Tools/hipclang-compute-mode 
Add HIP Compute Mode
 2018-07-04 10:55:48 +05:30
Maneesh Gupta 3b157546f9 Merge pull request #517 from ROCm-Developer-Tools/fix-hipcc-link 
Let hipcc handle static library for hip-clang only if it contains bun…
 2018-07-04 10:51:44 +05:30
Maneesh Gupta d372d0eaad Update hip_hcc_internal.h 
Adding missing include for hip_hcc_internal in order to build with HCC
 2018-07-04 09:33:51 +05:30
foreman 1c17b90822 P4 to Git Change 1575517 by gandryey@gera-w8 on 2018/07/03 11:55:33 
SWDEV-133815 - PAL support for Linux Pro w/OpenCL 2.0 support
	- Reenable OCL2.0 support on Linux.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#53 edit
 2018-07-03 12:03:24 -04:00
Jenkins cad8e47d59 Merge 'master' into 'amd-master' 
Change-Id: I27adce1f61a95f244523ad1ffbf8e1c2626b49d8
 2018-07-03 04:09:34 -05:00
Rahul Garg 77cbd4476d Fixed offset null check in bind texture functions 2018-07-03 08:54:17 +05:30
Rahul Garg f554e48db3 Revert "Use memcpy kernel for all pinned memory cases in hipMemcpy2DAsync" 2018-07-02 14:32:11 +05:30
Maneesh Gupta 1978cea4b7 Update hip-targets.cmake for hip::host & hip::device 2018-07-02 10:37:20 +05:30
foreman cfef94d7fb P4 to Git Change 1574721 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/30 03:00:05 
SWDEV-2 - Change OpenCL version number from 2685 to 2686.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2433 edit
 2018-06-30 03:11:58 -04:00
Rahul Garg 805906d2ad Updated heading 2018-06-30 11:42:17 +05:30
Rahul Garg cc14d6440f Updated indentation 2018-06-30 11:40:32 +05:30
Jenkins daaeecaa66 Merge 'master' into 'amd-master' 
Change-Id: I70b2b1a6fc8998d1a0ea0e7532a0a99050784ae1
 2018-06-29 04:09:59 -05:00
foreman bb2d543728 P4 to Git Change 1574275 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/29 03:00:05 
SWDEV-2 - Change OpenCL version number from 2684 to 2685.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2432 edit
 2018-06-29 03:11:17 -04:00
foreman 167d628a49 P4 to Git Change 1574251 by skudchad@skudchad_rocm on 2018/06/29 01:49:57 
SWDEV-145570 - [HIP] Fix hipHostUnregister.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#35 edit
 2018-06-29 01:59:22 -04:00
Alex Voicu f931980a6a Add scalar operands and fix C implementation. 2018-06-29 05:23:49 +01:00
Alex Voicu c061d885f6 Re-sync with upstream. 2018-06-29 00:16:34 +01:00
foreman 13cce36625 P4 to Git Change 1573750 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/28 03:00:05 
SWDEV-2 - Change OpenCL version number from 2683 to 2684.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2431 edit
 2018-06-28 03:13:17 -04:00
Maneesh Gupta 0eeb58b26e Merge pull request #528 from ROCm-Developer-Tools/fix-hipclang-hipcc 
HIPCC - Use clang if clang++ is not compiled
 2018-06-28 12:36:49 +05:30
Maneesh Gupta 1340adce1a Merge pull request #503 from ROCm-Developer-Tools/fix-complex 
Fix hip_complex.h
 2018-06-28 12:15:22 +05:30
Maneesh Gupta b6f5c61a2c Merge pull request #495 from ROCm-Developer-Tools/hip-clang-upstream 
add more device functions for hip-clang
 2018-06-28 11:42:01 +05:30
Maneesh Gupta 22ffc0f1a7 Merge pull request #522 from pradeepisro/cmake_verbose_fix 
added changes to FindHIP.cmake which would allow us to build using ninja #467
 2018-06-28 11:39:03 +05:30
Maneesh Gupta f426491f17 Fix typo 2018-06-28 11:19:22 +05:30
Maneesh Gupta 06c1c93945 Merge pull request #536 from ROCm-Developer-Tools/hotfix_remove_unimplemented_math 
Removes use of unimplemented OCML functionality.
 2018-06-28 11:15:57 +05:30
Maneesh Gupta 18ccab33c3 Merge pull request #538 from ROCm-Developer-Tools/fix-fp16-include 
Include host_defines.h in hip_fp16.h since it uses __host__ __device_…
 2018-06-28 11:14:07 +05:30
foreman a5bf56e9bc P4 to Git Change 1573627 by skudchad@skudchad_test2_win_opencl on 2018/06/27 18:26:38 
SWDEV-145570 - [HIP] Report 64KB LDS for Linux

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/15296/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#52 edit
 2018-06-27 18:36:59 -04:00
foreman 7bb3d41155 P4 to Git Change 1573623 by gandryey@gera-w8 on 2018/06/27 18:23:10 
SWDEV-155433 - Add OpenCL API type for RGP files generated from OpenCL
	- Add API type events to the SQTT

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#93 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#30 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.hpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#112 edit
 2018-06-27 18:32:23 -04:00
Srinivasuluch ef33a0ad4d Update hipLaunchParm.cpp 
Changing macro name
 2018-06-27 22:06:53 +05:30
Srinivasuluch 52e808da4d Update hipLaunchParm.cpp 
wrap up to 80 characters per line
 2018-06-27 22:04:12 +05:30
Srinivasuluch f69d89e79f Update hipLaunchParm.cpp 
changing the condition, a = b, as Sam suggested
 2018-06-27 21:48:37 +05:30
Srinivasuluch 22fd883df8 Update hipLaunchParm.cpp 2018-06-27 20:49:07 +05:30
Srinivasuluch 681ce0182e Update hipLaunchParm.cpp 
Added a macro to disable the alignment test as it's broken
 2018-06-27 19:57:44 +05:30
Srinivasuluch 52f3ec8f26 Update hipLaunchParm.cpp 
pass by value for struct
 2018-06-27 16:45:51 +05:30
foreman 4e22474825 P4 to Git Change 1573154 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/27 03:00:06 
SWDEV-2 - Change OpenCL version number from 2682 to 2683.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2430 edit
 2018-06-27 03:09:59 -04:00
foreman 717c0e3e6c P4 to Git Change 1572945 by jatang@jatang-opencl-hsa-stg5 on 2018/06/26 16:09:41 
SWDEV-155654 - TDR\BSOD observed while running Nuke Performance Benchmark test on Hawaii Asics.

	Need to support the new power-related appprofile parameters for gfx8 ASICs.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuappprofile.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuappprofile.hpp#8 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#592 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gslbe/src/rt/GSLDevice.cpp#183 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gslbe/src/rt/GSLDevice.h#64 edit
 2018-06-26 16:18:18 -04:00
Aaron Enye Shi e44eaa1a1e Implement __shfl_* funcs into HIP headers 2018-06-26 18:32:11 +00:00
foreman a7bd1f9ece P4 to Git Change 1572669 by johtaylo@johtaylo-jtincrementor2-increment on 2018/06/26 03:00:06 
SWDEV-2 - Change OpenCL version number from 2681 to 2682.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2429 edit
 2018-06-26 03:12:55 -04:00