Gráfico de commits

153 Commits

Autor SHA1 Mensaje Fecha
Maneesh Gupta 4e9f1e8a66 Fix arch specific hcc extra libs env var
Change-Id: I7429da2f1cb98750d6a9601e7e5bde844a098487


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

Change-Id: I68b3a85d62cfab3a45d2b7a70cb3518ab2565236


[ROCm/hip commit: 9a1989193a]
2017-02-08 19:45:32 -06:00
Aditya Atluri 8794954411 fixed hipcc for new compiler flags
Change-Id: I49ec059be20ff26b7482c84d91ab7a43826c6a8d


[ROCm/hip commit: 55d92833fb]
2017-02-08 14:06:01 -06:00
Aditya Atluri c692cd5d4a include arch specific ir on fallback path
Change-Id: Ib04996aae2c21eb73ef2a9f6305915e0caccd704


[ROCm/hip commit: 27d2fc99ca]
2017-02-08 12:19:06 -06:00
Aditya Atluri 82c0dcb03f 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/hip commit: 01b66dd998]
2017-02-08 12:04:05 -06:00
Aditya Atluri 08a67a522d fixed arch compiler flag
Change-Id: I19f7a0ea513d6b8059f0c10cd0e7a5ead510e246


[ROCm/hip commit: b37422d30b]
2017-01-27 08:51:48 -06:00
Aditya Atluri a13cb5af4f fixed kernel only compilation for module api
Change-Id: I567992fa9b87125318edba41fd82d2f7bc5504a1


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


[ROCm/hip commit: 138cf36547]
2017-01-23 22:34:41 -06:00
Aditya Atluri 7f00c120a7 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/hip commit: d180fdaae0]
2017-01-12 11:30:20 -06:00
Ben Sander 72f6afab45 tolerate spaces in hip args
[ROCm/hip commit: 3a42a7642a]
2017-01-09 20:57:13 -06:00
Maneesh Gupta 977cd8fcb6 hipcc: Link to shared HIP runtime by default
Change-Id: I5030e3245e4afb6863b401656ca5d1ad9ae84310


[ROCm/hip commit: a42da10c44]
2017-01-04 12:39:09 +05:30
Evgeny Mankov db5b0439de [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/hip commit: bcbbc32fa6]
2016-12-23 22:06:20 +03:00
Maneesh Gupta 5d44da9e46 hipcc: link to hip runtime using absolute path
Change-Id: I714b3e9da0bc1d49665b079d9c4cec1c1a2efa80


[ROCm/hip commit: f6e9f6f0bf]
2016-12-23 11:49:00 +05:30
Maneesh Gupta eaf16d02f2 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/hip commit: ef046c7098]
2016-12-01 15:33:12 +05:30
Maneesh Gupta dead181892 hipcc: HCC workaround no longer needs env var
Change-Id: I81f4eafddbda5e9e2f1082932dd502ab451cfc24


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


[ROCm/hip commit: 8a8c7a6b4d]
2016-11-23 14:36:30 -06:00
pensun 16ff329c51 Add several missing APIs in hipify
Change-Id: I58912871cb0b10128f221ef26a11b0d69fb7873c


[ROCm/hip commit: a836395350]
2016-11-23 14:06:18 -06:00
Aditya Atluri 3b1150f0b7 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/hip commit: 043da795f6]
2016-11-23 11:19:15 -06:00
Ben Sander 1cbb76ba24 Improve docs in some places
Change-Id: If31e84fbf0c8595ca72edb842dce7ce47783579b


[ROCm/hip commit: dec59d9909]
2016-11-23 08:16:18 -06:00
Maneesh Gupta 2234b57513 Refactor for building HIP as dynamic library
Change-Id: I65a3d9d589c4fdbbdcf1611e5427224253be8260


[ROCm/hip commit: c0419cc749]
2016-11-18 14:33:20 +05:30
Ben Sander d35f12558c tweak hcc demangler
[ROCm/hip commit: 0c624c009b]
2016-11-14 15:26:27 -07:00
Maneesh Gupta 3b85d1aec1 Revert "hipcc: Turn back linking hip_ir.ll by default"
This reverts commit b602b3d168.


[ROCm/hip commit: fd1483ce35]
2016-11-14 06:05:31 +05:30
Ben Sander 3ce663c5ae Add &nbsp to demangler
Change-Id: I89586c7c17f5152b7a6850d0d6c2aa1d3ebc8190


[ROCm/hip commit: c9401cb95f]
2016-11-11 16:50:56 -06:00
Maneesh Gupta 8aaa4d6744 hipcc: Default to HIP_LIB_TYPE=1
Change-Id: I83b05accd76f7bc94bd724c66ae060fa0095bc8d


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

Change-Id: I990a7d008da9e8dcc68250cebbc8ee6e723c7e01


[ROCm/hip commit: 72c722c3d6]
2016-11-10 08:56:38 +05:30
Ben Sander 6444dddaa7 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/hip commit: f0bb817c11]
2016-11-04 06:06:04 -05:00
Maneesh Gupta d1a803e5f2 hipdemangleatp: Try handling HC kernels as well
Change-Id: Ie438ddd28e5bc6067fcd682df849d3183046b40a


[ROCm/hip commit: c39ddad215]
2016-10-28 15:46:59 +05:30
Maneesh Gupta 6aa40b6f21 hipcc: Update flags for Fedora support
Change-Id: I90be7768410e491b4f11c3b0f08470246d781d80


[ROCm/hip commit: 6fa9bc3b61]
2016-10-28 14:12:13 +05:30
Ben Sander 22b87992cf Print short hipLaunchKernel correctly.
Change-Id: I6ca03d7c707cd03d6982199830213953d5855f17


[ROCm/hip commit: 024d9ab090]
2016-10-27 23:09:32 -05:00
Ben Sander cd3db22eb6 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/hip commit: e5ef8a2fd7]
2016-10-27 23:09:31 -05:00
Ben Sander ed022118bb Add new hipdemangleatp and snapshot sample update for new functionality
Change-Id: Ie19c683b2b0bdfeb0c3fcf89444c2e21b7f606e7


[ROCm/hip commit: f95482c7c5]
2016-10-27 23:09:31 -05:00
Ben Sander a357a07982 Update docs and improve hipcc error message.
Change-Id: I25636d06959d02cc46c8c476d3948e91ff83ea47


[ROCm/hip commit: bff88d0f63]
2016-10-27 23:09:31 -05:00
Maneesh Gupta b602b3d168 hipcc: Turn back linking hip_ir.ll by default
Change-Id: I9cec5a1a5a4791eddf6ef3e3332143ffc3ceadb6


[ROCm/hip commit: 528b257004]
2016-10-25 12:27:24 +05:30
Maneesh Gupta 0e36aae349 hipcc: Turn back linking hip_ir.ll by default
Change-Id: I9cec5a1a5a4791eddf6ef3e3332143ffc3ceadb6


[ROCm/hip commit: f1a4303b04]
2016-10-25 12:26:54 +05:30
Maneesh Gupta da78bf853f bin/hipcc: Simplify HIP_HCC_SYS_INCLUDES_WA logic
Change-Id: I2d20d6edc1b5c0d065ba6ce6179441fa98712a87


[ROCm/hip commit: df1d6fcff2]
2016-10-19 12:57:33 +05:30
Ben Sander 21cbfecf84 Make HIP_HCC_SYS_INCLUDES_WA disable unless explicitly set =1
Change-Id: Ibfd1e049d51e420bd514b71e3652bc7029dfd4ba


[ROCm/hip commit: baeb966cff]
2016-10-18 22:45:45 -05:00
Evgeny Mankov e621f550bc [hipcc] A workaround for [SWDEV-105366] HCC's omitting of system includes while compiling kernel code leads to 'file not found' error.
Missing includes are set explicitly.
Workaround is switched on by default, to disable it set HCC_SYS_INCLUDES_WA=0.

WA will be removed after fixing [SWDEV-105366].


[ROCm/hip commit: 2027fcd0a2]
2016-10-18 22:38:04 +03:00
Maneesh Gupta ef66a5828a Disable linking hip_ir.ll by default
Change-Id: I4917f0d75c66eee347de41bc16d999fc563a5be2


[ROCm/hip commit: 86c718a668]
2016-10-16 11:14:42 +05:30
Maneesh Gupta 51141f539d Bump HIP version to 1.0
Change-Id: Ie215a1ad4c1bf9b4a0ce94f750ddacce668bbc63


[ROCm/hip commit: 933b8c1dc5]
2016-10-15 22:42:45 +05:30
Ben Sander fc49a6b28f Add LLVM/LC version info
Change-Id: I6d0f49c75777744dbbca255d45681ed663b401c0


[ROCm/hip commit: 165c58c3db]
2016-10-14 23:45:13 -05:00
Aditya Atluri d06509f680 added compiler flag for polaris
Change-Id: Ib14c14c0618982ac7b48f5bc704c04b54ff40ed9


[ROCm/hip commit: 90a71c4be4]
2016-10-13 14:16:48 -05:00
Maneesh Gupta 029d09ea57 .buildInfo -> .hipInfo & .version -> .hipVersion
Change-Id: I8023f4349621fd81c58615737b7e897649e0f7ca


[ROCm/hip commit: 1329be958a]
2016-10-11 11:13:41 +05:30
Aditya Atluri cb75432ac4 added threadfence feature for hcc
1. Added feature for __threadfence and __threadfence_block
2. Added feature for using LLVM IR files directly while compilation
3. Added test for threadfence and threadfence_block

Change-Id: Ib7e5d89b4cca1a135952b317e5809cd05b56a3c9


[ROCm/hip commit: dc1042ce6d]
2016-10-10 15:29:50 -05:00
Maneesh Gupta 38b583d6f0 Set _binary_kernel_* symbol value to 1
Change-Id: I92255a8238a8084010662a3ccf5d624dd2d352c0


[ROCm/hip commit: f5d14382af]
2016-10-06 09:50:35 +05:30
Maneesh Gupta 3ffd026a36 hipcc: Updated to use new include path
Change-Id: I4de6bb6978f2908dbb4d4cfd6e394d21fed90dd5


[ROCm/hip commit: f74e54102f]
2016-10-05 10:54:42 +05:30
pensun a3256a4b73 update hipcc to search for lib using CUDA_PATH on NV path
Change-Id: I7e19d1f82237a8a13f3d8284b313ac049be3f920


[ROCm/hip commit: 6a97ff68a4]
2016-09-29 15:11:57 -05:00
Ben Sander 00f8a4f5a7 Small tool, doc, sample enhancements.
- Expand message when HIP version mismatch detected.
- Doc touchup.
- change sorting of hipBusBandwidth so byte results shown at top.
-

Change-Id: Ifb4e44a5fdfb65d59c4994b11e5f13385705f7e0


[ROCm/hip commit: 7bc1af2776]
2016-09-26 16:36:01 -05:00
pensun cf56754431 fix of HIPCC on libc++ option on HCC path
Change-Id: Ie0d3213a165fa13f033b777b490eb60b980d02da


[ROCm/hip commit: b7fcdc6121]
2016-09-26 14:39:57 -05:00
Rahul Garg ccf9b08949 Removed deprecated hipHostAlloc
Change-Id: Ia592a3545c5d72f37e049ce29f910e404323c01c


[ROCm/hip commit: daef1d2906]
2016-09-26 10:58:46 +05:30
Maneesh Gupta 20a3765fe3 hipcc: Don't try to linking unpinned_copy_engine
Change-Id: Iaa4d8b4f6dbb7940bba553f82c157a2ee9468c9e


[ROCm/hip commit: ede43b3e6e]
2016-09-23 10:43:09 +05:30