Commit graph

172 Commits

Autor SHA1 Nachricht Datum
Maneesh Gupta aab655ff01 Force stdlib=libc++ on UB14.04
Change-Id: I7f24d663e57fbbee56afde12a0e61fc8bfc1e9b6


[ROCm/clr commit: 3df134971b]
2017-04-03 15:09:31 +05:30
Sun, Peng b323510002 Fix hip Module APIs by disabling GGL when hipcc takes -genco option
Change-Id: I0a79e9c8e750f92c3d0be336d6ff709a2d1afd63


[ROCm/clr commit: f9c8ac5435]
2017-04-02 11:56:15 -05:00
emankov 0cab597d16 [HIPIFY] set execute mode for bash scripts
[ROCm/clr commit: fee6eeed51]
2017-03-29 17:23:41 +03:00
Evgeny Mankov c48fd0b6eb [HIPIFY] Rename bash scripts.
[ROCm/clr commit: 941adfc4c5]
2017-03-29 16:36:46 +03:00
Aditya Atluri bdaf6a3aaa disabled metadata apis
Change-Id: Ifb8839c581644cccc2afcd18c38a866f649a4144


[ROCm/clr commit: 4e5861df7a]
2017-03-28 10:46:31 -05:00
Aditya Atluri c3f1a37c28 Re-enabled metadata parsing in HIP
Change-Id: If8caa844571cb8581450df9ffdb76e2445c75f13


[ROCm/clr commit: abf369049b]
2017-03-27 11:00:39 -05:00
Aditya Atluri 620bbbc583 removed LLVM_HOME from hipcc
Change-Id: Ic3dfdde9d28f08bf54b12dfc38ab1f25884bcfab


[ROCm/clr commit: 9aef93f03e]
2017-03-23 11:08:19 -05:00
Aditya Atluri 478eb4e350 removed llvm dependency and metadata functionality
Change-Id: Ib9783b75d326559ed29c5aa2218aed40d20ad0fb


[ROCm/clr commit: 5a0685c137]
2017-03-23 10:16:37 -05:00
Aditya Atluri fa70da22ed fixed paths to find llvm
Change-Id: I0a4af8cea2f44fea011d09fc300e382984746d17


[ROCm/clr commit: a19bce16e4]
2017-03-21 14:22:49 -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
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 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 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 928832a432 FindHIP: better handling for custom HCC_HOME
Change-Id: Ica267de11cde58d1e759cd1fd053b699649ea76a


[ROCm/clr commit: 90478d90d4]
2017-03-07 14:40:04 +05:30
Siu Chi Chan f005cea396 fix hcc version detection in hipcc
Change-Id: I880be03ad67e99280a259369bfe25488bf53f0bd


[ROCm/clr commit: f9db1690c3]
2017-03-06 15:34:30 +05:30
pensun 077e789db5 Define __HIPCC__ flag at compile time when using HIPCC on HCC path
Change-Id: I5e967e0e2327264d5d3b0ca705c2504fcd33d75e


[ROCm/clr commit: be95cc914f]
2017-02-28 16:20:48 -06:00
Siu Chi Chan 652f3e01bb Squashed commit of the following:
commit 931d3de6c1c903cfd47842bc5026a9294ac492b4
Author: Siu Chi Chan <siuchi.chan@amd.com>
Date:   Mon Feb 13 10:54:06 2017 -0500

    only force to libstdc++ if the g++ is older than version 5 since hcc already defaults to libstdc++ with newer g++

commit 1ef8d71aa788de7b9eead4906fe56186f06d7d3f
Author: scchan <siuchi.chan@amd.com>
Date:   Sun Feb 12 14:44:11 2017 -0500

    remove hardcoded -lc++ in tests

commit 5d99ef338eb3a66523cc9ddd139e86c6fd707b9c
Author: scchan <siuchi.chan@amd.com>
Date:   Sun Feb 12 14:35:46 2017 -0500

    force include libstdc++ headers and stdc++ only if g++ version < 5 since hcc uses libstdc++ by default if g++ > 5 is present

commit a2bc21b24d100feefe91cd3cb2271238bda0738a
Author: scchan <siuchi.chan@amd.com>
Date:   Fri Feb 10 04:36:27 2017 -0500

    use hcc-config to generate compiler and linker flags

Change-Id: I13a79629c0adfd75439a47d0488ff4fd619c55ba
(cherry picked from commit 866e744e40cf1378af8a679b54959bf5226c340f)


[ROCm/clr commit: ca8045e6e4]
2017-02-16 13:12:32 +05:30
Maneesh Gupta 2b6171816d Fix arch specific hcc extra libs env var
Change-Id: I7429da2f1cb98750d6a9601e7e5bde844a098487


[ROCm/clr commit: 71363810dd]
2017-02-09 14:38:39 +05:30
Aditya Atluri ba45e02007 added architecture specific macros
1. Added __HIP_ARCH_GFXNUM__
2. Usage, -D__HIP_ARCH_GFX803__=1

Change-Id: I68b3a85d62cfab3a45d2b7a70cb3518ab2565236


[ROCm/clr commit: c6c90f6f5a]
2017-02-08 19:45:32 -06:00
Aditya Atluri 76a58521f5 fixed hipcc for new compiler flags
Change-Id: I49ec059be20ff26b7482c84d91ab7a43826c6a8d


[ROCm/clr commit: 400d0d4f78]
2017-02-08 14:06:01 -06:00
Aditya Atluri 248b42d3e3 include arch specific ir on fallback path
Change-Id: Ib04996aae2c21eb73ef2a9f6305915e0caccd704


[ROCm/clr commit: 26b5e57cfd]
2017-02-08 12:19:06 -06:00
Aditya Atluri 14dcdff8f4 Fixed Hawaii link issues
1. Split hip_ir.ll to hip_hc.ll and hip_hc_gfx803.ll
 a. hip_hc.ll contains arch generic ir implementations
 b. hip_hc_gfx803.ll contains gfx803 (fiji, polaris) specific ir
2. HIPCC can now parse --amdgpu-target=*.
 a. Usage: hipcc --amdgpu-target=gfx803 --amdgpu-target=gfx701
 b. TODO: Convert to --amdgpu-target=gfx803,gfx701
3. With LLC in HCC able to generate native f16 isa, removed inline half asm math ops
4. Fixed threadfence and threadfence_block to use functions in rocdl

Change-Id: Ic9a9e3e04139b0d75d2c2a263c030ca77adc1019


[ROCm/clr commit: 60ec83c683]
2017-02-08 12:04:05 -06:00
Aditya Atluri ebb51a54b9 fixed arch compiler flag
Change-Id: I19f7a0ea513d6b8059f0c10cd0e7a5ead510e246


[ROCm/clr commit: a8c51b822b]
2017-01-27 08:51:48 -06:00
Aditya Atluri 4b732551bb fixed kernel only compilation for module api
Change-Id: I567992fa9b87125318edba41fd82d2f7bc5504a1


[ROCm/clr commit: 33d89d06aa]
2017-01-27 08:41:42 -06:00
Ben Sander 6f2a8bf97b Add HIP_IGNORE_HCC_VERSION.
Ignores strict checking of HCC and HIP version.
Can be useful when developing new HCC code.


[ROCm/clr commit: df74158d1c]
2017-01-23 22:34:41 -06:00
Aditya Atluri 5317ffa9ec Started adding native half math library support
1. Removed HIP_EXPERIMENTAL env variable so that device code will be accessed from LLVM IR
2. Removed soft support from headers and moved to hip_fp16.cpp
3. Added LLVM IR + inline asm to hip_ir.ll
4. Added test for fp16
5. Added barriers for hcc 3.5 and hcc 4.0 for half support
a. Which means, hcc 4.0 can parse __fp16 but hcc 3.5 cant
b. HCC 4.0 code is implemented now, hcc 3.5 will be added later

Change-Id: Ic37859b2688ebb02e168bab643d1882bf4727952


[ROCm/clr commit: c286bf6f8a]
2017-01-12 11:30:20 -06:00
Ben Sander 9d22c4f727 tolerate spaces in hip args
[ROCm/clr commit: 49d1477b9d]
2017-01-09 20:57:13 -06:00
Maneesh Gupta ac59859a25 hipcc: Link to shared HIP runtime by default
Change-Id: I5030e3245e4afb6863b401656ca5d1ad9ae84310


[ROCm/clr commit: 9b02f0d7e5]
2017-01-04 12:39:09 +05:30
Evgeny Mankov 5702fd5fc2 [HIPIFY] Add hipconvertinplace2.sh and hipexamine2.sh scripts for hipify-clang.
The differences from the similar scripts for hipify.pl:
1. CSV file with extended statistics is produced.
2. scripts' arguments are changed a bit:
DIRNAME [hipify options] [--] [clang options]

where -- is a delimiter; all the arguments are optional, except DIRNAME.

Usage example:
./hipexamine2.sh ./tmp -o-stats ./tmp/stats.csv -- -I/usr/local/cuda-7.5/include -I/usr/local/hipify-clang/hipblas/include 2>&1 | tee log


[ROCm/clr commit: f6aa3ddb0e]
2016-12-23 22:06:20 +03:00
Maneesh Gupta 272d6fdfaa hipcc: link to hip runtime using absolute path
Change-Id: I714b3e9da0bc1d49665b079d9c4cec1c1a2efa80


[ROCm/clr commit: 16b705d912]
2016-12-23 11:49:00 +05:30
Maneesh Gupta 5e38114363 Improve shared and static library support
hipcc accepts new parameter -use-staticlib and -use-sharedlib to
control linking behavior. Default is still static library.

Change-Id: I28fb9a939f8177c75abefd8b77d8118a6666d1f4


[ROCm/clr commit: fd8b1c7d41]
2016-12-01 15:33:12 +05:30
Maneesh Gupta ce325da03f hipcc: HCC workaround no longer needs env var
Change-Id: I81f4eafddbda5e9e2f1082932dd502ab451cfc24


[ROCm/clr commit: f14198956f]
2016-12-01 12:51:58 +05:30
pensun 29a69adda7 Add some missing APIs on nv path and hipify
Change-Id: Ic0f4740ab06bf70b1de61b39fedc7a6e7605cb61


[ROCm/clr commit: 69b43ec17c]
2016-11-23 14:36:30 -06:00
pensun bf34811dbe Add several missing APIs in hipify
Change-Id: I58912871cb0b10128f221ef26a11b0d69fb7873c


[ROCm/clr commit: a4b43a6610]
2016-11-23 14:06:18 -06:00
Aditya Atluri a2ecbc2d6e Added fast math flag
1. Use -DHIP_FAST_MATH to make precise math functions compiled to fast math
2. Added double fast math functions for sqrt
3. Changed hipcc to parse -use_fast_math (not working)
4. Added passed tag to hipFloatMath test

Change-Id: I72884b2436b4efe61e9a9297346c1358fee38a2d


[ROCm/clr commit: c2f6ecf264]
2016-11-23 11:19:15 -06:00
Ben Sander e2f024fc55 Improve docs in some places
Change-Id: If31e84fbf0c8595ca72edb842dce7ce47783579b


[ROCm/clr commit: 9db93a1b96]
2016-11-23 08:16:18 -06:00
Maneesh Gupta b13556367d Refactor for building HIP as dynamic library
Change-Id: I65a3d9d589c4fdbbdcf1611e5427224253be8260


[ROCm/clr commit: 2195e3c37d]
2016-11-18 14:33:20 +05:30
Ben Sander ab0362087f tweak hcc demangler
[ROCm/clr commit: 2ea3f8f68e]
2016-11-14 15:26:27 -07:00
Maneesh Gupta d8564db4a5 Revert "hipcc: Turn back linking hip_ir.ll by default"
This reverts commit 5a48591fc5.


[ROCm/clr commit: f9d598d66c]
2016-11-14 06:05:31 +05:30
Ben Sander 603c3a3a38 Add &nbsp to demangler
Change-Id: I89586c7c17f5152b7a6850d0d6c2aa1d3ebc8190


[ROCm/clr commit: d3dbf66ab1]
2016-11-11 16:50:56 -06:00
Maneesh Gupta d55b32b765 hipcc: Default to HIP_LIB_TYPE=1
Change-Id: I83b05accd76f7bc94bd724c66ae060fa0095bc8d


[ROCm/clr commit: 462ffb8117]
2016-11-10 11:34:00 +05:30
Maneesh Gupta 68b4d20b26 Merge branch 'rocm-rel-1.3' into amd-develop
Conflicts:
	include/hip/nvcc_detail/hip_runtime_api.h

Change-Id: I990a7d008da9e8dcc68250cebbc8ee6e723c7e01


[ROCm/clr commit: e3b5eef7c9]
2016-11-10 08:56:38 +05:30
Ben Sander 97d9a5722e Pre-pend HIP_PATH/lib to linker, so we find developer object code
Previously might pick up libs from /opt/rocm/lib.

Change-Id: Ia7adb345defe433d5952aa61706fe03fd7cbcd35


[ROCm/clr commit: d1db786910]
2016-11-04 06:06:04 -05:00
Maneesh Gupta 63ffd01391 hipdemangleatp: Try handling HC kernels as well
Change-Id: Ie438ddd28e5bc6067fcd682df849d3183046b40a


[ROCm/clr commit: c26f5d7d5a]
2016-10-28 15:46:59 +05:30
Maneesh Gupta 6872cb2ceb hipcc: Update flags for Fedora support
Change-Id: I90be7768410e491b4f11c3b0f08470246d781d80


[ROCm/clr commit: 0d8aa10473]
2016-10-28 14:12:13 +05:30
Ben Sander c8aad6ee8e Print short hipLaunchKernel correctly.
Change-Id: I6ca03d7c707cd03d6982199830213953d5855f17


[ROCm/clr commit: 3d0fa30183]
2016-10-27 23:09:32 -05:00
Ben Sander 61c99f912d HIPCC adds paths to profiler include and libs by default.
Users who desire otherwise can set HIP_ATP_MARKER=0.
Also remove old unused hipcc_explicit_lib option.

Change-Id: I2bf07ba880329e7a3b1365dd33a3b2be6794370f


[ROCm/clr commit: e57baf8d95]
2016-10-27 23:09:31 -05:00
Ben Sander 9b2a6652c4 Add new hipdemangleatp and snapshot sample update for new functionality
Change-Id: Ie19c683b2b0bdfeb0c3fcf89444c2e21b7f606e7


[ROCm/clr commit: 5b7da93e61]
2016-10-27 23:09:31 -05:00