Sun, Peng
5c284999b2
Add document for switching to GGL in hip_faq.md
...
Change-Id: I83d9fd3e76d21ab572949c3a446ac3898acb3ded
[ROCm/clr commit: 3bd73d6280 ]
2017-03-20 15:44:28 -05:00
Evgeny Mankov
bd348f5248
[HIP] [FIX] Fix GCC build.
...
[ROCm/clr commit: 70ed1014ad ]
2017-03-20 21:03:18 +03:00
foreman
52932f41fc
P4 to Git Change 1387451 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/18 03:00:05
...
SWDEV-2 - Change OpenCL version number from 2384 to 2385.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2131 edit
[ROCm/clr commit: ef0161bbf5 ]
2017-03-18 03:18:47 -04:00
Aditya Atluri
35d829773d
added support for lgammaf and lgamma
...
1. Implementation inside HIP
Change-Id: I657263b7276a57c56081d3336fef816b5f204eff
[ROCm/clr commit: 52859a8a40 ]
2017-03-17 18:26:10 -05:00
foreman
c014d0372b
P4 to Git Change 1387401 by rili@rili-opencl-pal-stg on 2017/03/17 18:35:37
...
SWDEV-97489 - Initialize variable and fix incorrect code of checking if D3D function finish.
Affected files ...
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_d3d10.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_d3d11.cpp#21 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_d3d9.cpp#31 edit
[ROCm/clr commit: 0b51901411 ]
2017-03-17 18:44:15 -04:00
Sun, Peng
d5f632f271
Disable additional debug warning message
...
Change-Id: Ic5c374589bfad387a7c4c5346430a490e2c6e2a7
[ROCm/clr commit: 2585812fba ]
2017-03-17 15:03:03 -05:00
pensun
a8c91ca379
Change the #define of GENERIC_GRID_LAUNCH to take valueat compilation, disable warning messages
...
Change-Id: Ic6c011529e26de359bcda1e7083727e7ee52887b
[ROCm/clr commit: faf0fbebe9 ]
2017-03-17 14:59:34 -05:00
pensun
9c9a9bb330
Initial integration with Alex' Generic Grid Launch
...
Change-Id: I559afb80e9e39ec0d119bb3bf3b85ef9e448caf6
[ROCm/clr commit: ad882222b0 ]
2017-03-17 14:59:34 -05:00
Aditya Atluri
b4b87b8786
Added default module launch api functionality
...
1. As in hipModuleLaunchKernel(..., kernelParams, nullptr); works with this commit
2. Added headers AMDGPUPTNote.h, AMDGPURuntimeMetadata.h to do code object meta data parsing
3. Changed CMake to look at llvm link libraries
4. HIP developer should set env variable LLVM_HOME to remove link errors
5. HIP depends on installed LLVM (not source, not build)
6. Added sample to test out the feature
7. Right now HCC does not support embedding metadata in code object. Use clang opencl
8. Changed HIPCC to read LLVM_HOME env var
9. New argument to CMake should be given -DLLVM_HOME=<where llvm 5.0 is installed>
Change-Id: Iba38194aa872d97cc2c90a8e5ff746c48055c868
[ROCm/clr commit: 9645b0e0dc ]
2017-03-17 13:11:34 -05:00
Ben Sander
7466b4005b
Move USE_PROMOTE_FREE_HCC
...
[ROCm/clr commit: 20ea5e179f ]
2017-03-17 12:04:13 -05:00
Ben Sander
e0171505b4
Add __device__ to needful functions for promote-free.
...
[ROCm/clr commit: 92fd4c8f10 ]
2017-03-17 11:19:48 -05:00
Ben Sander
572be5449d
Add USE_PROMOTE_FREE_HCC for smooth transition to new HCC caps.
...
ADDRESS_SPACE_1 defines
[ROCm/clr commit: f4256cb57c ]
2017-03-17 11:04:39 -05:00
Ben Sander
c81fb24611
Add simple device-side assert macro
...
Currently swallows asserts but will compile.
[ROCm/clr commit: c9f64bbd2d ]
2017-03-17 10:25:56 -05:00
foreman
96ab410afb
P4 to Git Change 1386940 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/17 03:00:05
...
SWDEV-2 - Change OpenCL version number from 2383 to 2384.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2130 edit
[ROCm/clr commit: 1e561f40e5 ]
2017-03-17 03:13:06 -04:00
foreman
6d775d0419
P4 to Git Change 1386753 by gandryey@gera-w8 on 2017/03/16 18:08:37
...
SWDEV-115529 - Interoperability DX11/OGL/OCL
- Make sure displayable tiling property is passed to the aliased memory object
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gslbe/src/rt/GSLDeviceGL.cpp#28 edit
[ROCm/clr commit: 3f0f26193f ]
2017-03-16 18:14:01 -04:00
Evgeny Mankov
151612e184
[HIP] [DOC] Update hip_porting_driver_api.md
...
+ Fix typos, formatting, update CUDA Driver API support.
[ROCm/clr commit: c6de5b92b5 ]
2017-03-16 14:39:28 +03:00
foreman
86d9e0ee94
P4 to Git Change 1386335 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/16 03:00:05
...
SWDEV-2 - Change OpenCL version number from 2382 to 2383.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2129 edit
[ROCm/clr commit: 3da0a50292 ]
2017-03-16 03:11:07 -04:00
Siu Chi Chan
ff4621af4e
replace code names with gfx names
...
Change-Id: I5e0b96a0b474b16cfa92077a30a5b80b7230254b
[ROCm/clr commit: c6efbc1f25 ]
2017-03-15 12:26:13 -04:00
Maneesh Gupta
f1bfcb634c
Merge branch 'amd-develop' into amd-master
...
Change-Id: Ifc503b382fc93491b7d72ba2f5bb3511ceeb8e3d
[ROCm/clr commit: 516866a410 ]
2017-03-15 14:10:43 +05:30
foreman
3d9131ba30
P4 to Git Change 1385795 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/15 03:00:06
...
SWDEV-2 - Change OpenCL version number from 2381 to 2382.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2128 edit
[ROCm/clr commit: 4506b41314 ]
2017-03-15 03:06:32 -04:00
Maneesh Gupta
da5548303e
Disable broken tests on hcc path
...
Change-Id: Id6234da576566faa32d5fdf42dca6d6267596823
[ROCm/clr commit: 8536af7b71 ]
2017-03-15 12:03:44 +05:30
Maneesh Gupta
fe01aec686
hipcc: Fix warning when HCC_AMDGPU_TARGET is not defined
...
Change-Id: I5cc6b0e9fb23ec78152d8bcfe9e7511e2fe91055
[ROCm/clr commit: 42faa4a4fe ]
2017-03-15 12:03:05 +05:30
Maneesh Gupta
d43640c77c
Merge branch 'amd-master' into amd-develop
...
Change-Id: I01a77c34e11b1b02cb20e11b105741f6bd383543
[ROCm/clr commit: e3aa3d7ba6 ]
2017-03-15 09:56:45 +05:30
foreman
9b7e6d6ffb
P4 to Git Change 1385583 by gandryey@gera-w8 on 2017/03/14 16:43:09
...
SWDEV-79445 - OCL generic changes and code clean-up
- replace NULL with nullptr in the ROCm backend
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocappprofile.cpp#5 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#16 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.hpp#7 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccompiler.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/roccompilerlib.cpp#5 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#44 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#18 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#20 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.hpp#14 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.hpp#7 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprintf.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprintf.hpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#59 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.hpp#20 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocsettings.cpp#15 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#33 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.hpp#9 edit
[ROCm/clr commit: 34fc049ad5 ]
2017-03-14 16:47:51 -04:00
foreman
a5aa5566a7
P4 to Git Change 1385569 by wchau@wchau_brahma on 2017/03/14 16:12:25
...
SWDEV-115692 - Remove Lexa and Polaris 22 support from Linux Pro
Affected files ...
... //depot/stg/opencl/drivers/opencl/compiler/legacy-lib/utils/v0_8/target_mappings.h#18 edit
... //depot/stg/opencl/drivers/opencl/compiler/legacy-lib/utils/v0_8/target_mappings_amdil.h#17 edit
... //depot/stg/opencl/drivers/opencl/compiler/legacy-lib/utils/v0_8/target_mappings_amdil64.h#16 edit
... //depot/stg/opencl/drivers/opencl/compiler/legacy-lib/utils/v0_8/target_mappings_hsail.h#17 edit
... //depot/stg/opencl/drivers/opencl/compiler/legacy-lib/utils/v0_8/target_mappings_hsail64.h#17 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings.h#50 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_amdil.h#43 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_amdil64.h#39 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail.h#42 edit
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/v0_8/target_mappings_hsail64.h#37 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudefs.hpp#146 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpudevice.cpp#564 edit
[ROCm/clr commit: 598d635fc4 ]
2017-03-14 16:20:13 -04:00
Rahul Garg
6e4f693cd8
hipMemsetD8 support for HIP/NVCC path
...
Change-Id: I48eee8266afd7b45a12d5ce2c4849b687a006c0f
[ROCm/clr commit: 09d1a46139 ]
2017-03-14 23:49:21 +05:30
foreman
48f33c9888
P4 to Git Change 1385483 by smekhano@stas-mwamba-rocm on 2017/03/14 13:44:00
...
SWDEV-115974 - ROCm OCL RT: pass OpenCL relaxation options to clang
Testing: smoke, precheckin, MLOpen/LC
Reviewed by Evgeny Mankov
Affected files ...
... //depot/stg/opencl/drivers/opencl/compiler/lib/utils/options.cpp#39 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#36 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#58 edit
[ROCm/clr commit: b33adc24e1 ]
2017-03-14 13:53:50 -04:00
Rahul Garg
4443b7520c
Added hipMemsetD8
...
Change-Id: I6a230a036c9c46c72a77d5f93c16ce8a00c3f837
[ROCm/clr commit: dccf9e2aa9 ]
2017-03-14 22:11:34 +05:30
Wen-Heng (Jack) Chung
54f40acc7a
Revert "Changes to HIP to cope with Promote-free HCC"
...
This reverts commit 9591c5a447 .
Change-Id: I20a9bab3883ad09913b320210344d37599cb8fcd
[ROCm/clr commit: 17af837120 ]
2017-03-14 22:59:27 +08:00
Maneesh Gupta
b054a30dec
Merge branch 'amd-develop' into amd-master
...
Change-Id: I8921e67e352e35e4c496e78a797fb309279ab7d0
[ROCm/clr commit: 62870fdc39 ]
2017-03-14 15:57:53 +05:30
Maneesh Gupta
ee45f273fd
4_shfl and 5_2dshfl samples are unsupported on gfx701
...
Change-Id: I81eb880350f25e89573ba14c62b549c6c43f8c91
[ROCm/clr commit: f91583b294 ]
2017-03-14 15:56:18 +05:30
Maneesh Gupta
f400aa48f5
default to gfx803 instead of fatbin if no arch specified
...
Change-Id: I83d56c6ede11c356d383b09d7eb3a5f08c8d8c84
[ROCm/clr commit: f32980847f ]
2017-03-14 14:34:25 +05:30
Maneesh Gupta
59f1401f54
hipcc: Support targets specified via HCC_AMDGPU_TARGET
...
Change-Id: I69fda40d9f666325d377f4b4335e7ee693069214
[ROCm/clr commit: d29a097905 ]
2017-03-14 14:29:30 +05:30
Maneesh Gupta
5cf4c4e440
Add gfx900 support
...
Change-Id: I3be2fbdcb6d3fa776c4fe668586c67245a1323f2
[ROCm/clr commit: 1b92ae9917 ]
2017-03-14 13:51:38 +05:30
Maneesh Gupta
8d526e796e
Merge branch 'amd-master' into amd-develop
...
[ROCm/clr commit: 0853c8ac2e ]
2017-03-14 13:44:41 +05:30
Aditya Atluri
725f20ab1e
make sure the inter-thread intrinsics are working post hawaii
...
Change-Id: I30ea5284c2160276f5bc0f937dfd386ca8640ce8
[ROCm/clr commit: af56898ea0 ]
2017-03-13 11:16:05 -05:00
Ben Sander
72b420bab4
Update hiphostregister test.
...
Move check to correct place.
[ROCm/clr commit: 9adbbd2980 ]
2017-03-12 09:51:33 -05:00
Ben Sander
49d7ea94f5
Refactor registered memory calls.
...
[ROCm/clr commit: b7acb85fa8 ]
2017-03-11 09:18:27 -06:00
Ben Sander
e1c95b083d
Add first step to a "registerd" mode in hipBusBandwidth.
...
[ROCm/clr commit: f23b5a1f90 ]
2017-03-11 09:18:27 -06:00
Ben Sander
a0932fbcc3
Update hipHostRegister debug and pointerTracker debug and notes
...
[ROCm/clr commit: e43592721e ]
2017-03-11 09:18:27 -06:00
Ben Sander
c8595b0373
Fix copying of registered memory.
...
Set device properly so copying can recover context.
Enhance test to catch this case.
[ROCm/clr commit: 23a58775df ]
2017-03-11 09:18:27 -06:00
foreman
7adc1224a7
P4 to Git Change 1384488 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/11 03:00:05
...
SWDEV-2 - Change OpenCL version number from 2380 to 2381.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2127 edit
[ROCm/clr commit: 8eb86b3bda ]
2017-03-11 03:14:08 -05:00
foreman
11db3a12b4
P4 to Git Change 1384479 by kzhuravl@kzhuravl-fiji-cl-on-lc on 2017/03/11 01:30:12
...
SWDEV-94644 - Fix the build after r297498
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#35 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#57 edit
[ROCm/clr commit: d08bdc6603 ]
2017-03-11 01:40:12 -05:00
Aditya Atluri
c8a1b6bc30
fixed warning raised by g++ using hip_vector_types.h
...
Change-Id: I9e7cdfc8b28b03b690eecd068529cf7629296d68
[ROCm/clr commit: a47066153f ]
2017-03-10 15:14:26 -06:00
Rahul Garg
b2b8361763
IPC supported using ROCR APIs
...
Change-Id: I0a353b1240098f4b20fa266a871f5f5826290af9
[ROCm/clr commit: 3af487007b ]
2017-03-10 23:45:28 +05:30
pensun
a49f5c7e1d
update porting guide for updated __HIP_DEVICE_COMPILE__
...
Change-Id: I0f025d354f76e2d728231bf112a77e8c8fcacc8c
[ROCm/clr commit: 1a2844e3a3 ]
2017-03-10 10:01:12 -06:00
Aditya Atluri
a816a9eb54
Added architecture guards around __shfl, dpp and ds_permute device functions
...
Change-Id: I10f9b08618fbf25b61c1932278fc5759e41c0d66
[ROCm/clr commit: 046ec0375b ]
2017-03-10 08:40:59 -06:00
foreman
1fe9a8e490
P4 to Git Change 1384033 by johtaylo@johtaylo-jtincrementor-increment on 2017/03/10 03:00:04
...
SWDEV-2 - Change OpenCL version number from 2379 to 2380.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2126 edit
[ROCm/clr commit: 554e85ee3e ]
2017-03-10 02:07:49 -06:00
Rahul Garg
4dd856eb67
Fix for HCSWAP-128, make 5_2dshfl cookbook sample only for fiji
...
Change-Id: I8869c28151bca1bd47a053a2808e93a801d16d00
[ROCm/clr commit: d48943699d ]
2017-03-10 10:29:52 +05:30
foreman
8bb5fba243
P4 to Git Change 1383787 by skeely@skeely_HSA_linux on 2017/03/09 19:08:12
...
SWDEV-3 - Fix createView for interop images.
Affected files ...
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#13 edit
[ROCm/clr commit: 4a7edb2164 ]
2017-03-09 19:33:44 -05:00