Magic-Mirror/llvm-capstone
1
0
Fork 0
mirror of https://github.com/capstone-engine/llvm-capstone.git synced 2025-04-02 05:02:15 +00:00
Code Issues Actions 5 Packages Projects Releases Wiki Activity
275,352 Commits 13 Branches 0 Tags
Commit Graph

413 Commits

Author SHA1 Message Date
Jan Vesely
4cb612e140 exp2: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317245
 2017-11-02 19:48:33 +00:00
Jan Vesely
e99ba9a23d cospi: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317244
 2017-11-02 19:48:31 +00:00
Jan Vesely
c708278f13 cosh: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317243
 2017-11-02 19:48:30 +00:00
Jan Vesely
f76371d948 cos: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317242
 2017-11-02 19:48:27 +00:00
Jan Vesely
50a3cccdbe cbrt: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317241
 2017-11-02 19:48:25 +00:00
Jan Vesely
a4df39bcad atanpi: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317240
 2017-11-02 19:48:23 +00:00
Jan Vesely
1bd2ac257a atanh: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317239
 2017-11-02 19:48:22 +00:00
Jan Vesely
0942b5e1bf atan: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317238
 2017-11-02 19:48:20 +00:00
Jan Vesely
d3d5e322e3 asinpi: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317237
 2017-11-02 19:48:18 +00:00
Jan Vesely
48bda32986 asinh: Use unary_dec instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317236
 2017-11-02 19:48:16 +00:00
Jan Vesely
ba4b98c691 asin: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317235
 2017-11-02 19:48:15 +00:00
Jan Vesely
61171847b7 acospi: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317234
 2017-11-02 19:48:13 +00:00
Jan Vesely
720783d9f5 acosh: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317233
 2017-11-02 19:48:11 +00:00
Jan Vesely
caca914218 acos: Use unary_decl instead of custom inc file 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-By: Aaron Watry <awatry@gmail.com>
llvm-svn: 317232
 2017-11-02 19:48:06 +00:00
Jan Vesely
47e093da9b math: Implement native_log10 
Use llvm instrinsic by default
Provide amdgpu workaround

v2: drop old amd copyrights

Reviewer: Aaron Watry
Reviewed-by: Vedran Miletić <vedran@miletic.net>
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 316588
 2017-10-25 16:49:22 +00:00
Jan Vesely
9fedbb9d8e amdgpu/math: Don't use llvm instrinsic for native_log 
AMDGPU targets don't have insturction for it,
so it'll be expanded to C * log2 anyway.

v2: use native_log2 instead of the more precise sw implementation
v3: move to amdgpu
v4: drop old AMD copyright

Reviewer: Aaron Watry
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 316587
 2017-10-25 16:49:17 +00:00
Jan Vesely
7ab2d0bdcd shared: Implement aligned vector stores (vstorea_half) 
Float version passes newly posted piglit tests on turks, float and double pass on carrizo.
v2: scalar vstorea_half
v3: fix typo

Reviewer: Aaron Watry
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 316291
 2017-10-22 14:21:59 +00:00
Jan Vesely
12061c7125 shared: Implement aligned vector loads (vloada_half) 
Passes newly posted piglits on turks and carrizo
v2: add scalar vloada_half
v3: fix typo

Reviewer: Aaron Watry
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 316290
 2017-10-22 14:21:56 +00:00
Jan Vesely
c420b61b26 amdgcn: Add missing datalayout info to .ll files 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Acked-by: Aaron Watry <awatry@gmail.com>
llvm-svn: 316239
 2017-10-20 21:10:18 +00:00
Jan Vesely
66b32ad9ad r600: Add missing datalayout to .ll files 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Acked-by: Aaron Watry <awatry@gmail.com>
llvm-svn: 316238
 2017-10-20 21:00:31 +00:00
Jan Vesely
577c52b9c7 travis: enable checks of nvptx libraries 
Reviewer: Jeroen Ketema
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315343
 2017-10-10 18:10:25 +00:00
Jan Vesely
2601429bac travis: Enable external function call checks on llvm-{4,5} 
Reviewer: Aaron Watry
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315342
 2017-10-10 18:10:24 +00:00
Jan Vesely
3d349ea98e Make image builtins r600/llvm-3.9 only 
The implementation uses r600 sepcific intrinsics
LLVM-4 switched to _ro_t and _rw_t image types
Portions of the code can be moved back as more targets/llvm versions add image support

Reviewer: Aaron Watry
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315341
 2017-10-10 18:10:21 +00:00
Jeroen Ketema
1364d268a4 Implement mem_fence on ptx 
PTX does not differentiate between read and write fences. Hence, these a
lowered to a mem_fence call. The mem_fence function compiles to the
“member.cta” instruction, which commits all outstanding reads and writes
of a thread such that these become visible to all other threads in the same
CTA (i.e., work-group). The instruction does not differentiate between
global and local memory. Hence, the flags parameter is ignored, except
for deciding whether a “member.cta” instruction should be issued at all.

Reviewed-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315235
 2017-10-09 19:43:04 +00:00
Jeroen Ketema
4f5a3d5d6f Make ptx barrier work irrespective of the cl_mem_fence_flags 
This generates a "bar.sync 0” instruction, which not only causes the
threads to wait, but does acts as a memory fence, as required by
OpenCL. The fence does not differentiate between local and global
memory. Unfortunately, there is no similar instruction which does
not include a memory fence. Hence, we cannot optimize the case
where neither CLK_LOCAL_MEM_FENCE nor CLK_GLOBAL_MEM_FENCE is
passed.

llvm-svn: 315228
 2017-10-09 18:36:48 +00:00
Jan Vesely
3c51ae5bd9 travis: Make sure we report failure even if only earlier checked files fail 
for loop would only report status of the last command
v2: return '1'
    call test instead of '['

Reviewer: Jeroen Ketema
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315193
 2017-10-08 20:07:58 +00:00
Jan Vesely
136381dc38 check_external_calls.sh: Print number of calls in tested file. 
Reviewer: Jeroen Ketema
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315192
 2017-10-08 20:07:56 +00:00
Jan Vesely
80bb52ae75 ptx: Use __clc_nextafter to implement nextafter 
using clang builtin results in external library call

Reviewer: Jeroen Ketema
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315191
 2017-10-08 19:34:00 +00:00
Jan Vesely
1de1444d62 Do not include clc_nextafter header globally 
Drop unused clc/math/clc_nextafter.h header

Reviewer: Jeroen Ketema
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315190
 2017-10-08 19:33:58 +00:00
Jan Vesely
6a5c8ddb3a math/nextafter: Use custom declaration inc file 
Reviewer: Jeroen Ketema
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315189
 2017-10-08 19:33:55 +00:00
Jan Vesely
72be1cc0be math/binary_decl.inc: Do not declare mixed float/double functions 
fmin/fmax only need vector/scalar mix

Reviewer: Jeroen Ketema
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315188
 2017-10-08 19:33:53 +00:00
Jan Vesely
beb6591753 ldexp: Fix double precision function return type 
Fixes ~1200 external calls from nvtpx library.

Reviewer: Jeroen Ketema
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315170
 2017-10-08 06:56:14 +00:00
Jan Vesely
391305638c configure: Fix handling of directories with compats only source lists 
Reviewer: Jeroen Ketema
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 315018
 2017-10-05 20:16:28 +00:00
Jeroen Ketema
957151bd86 Add vload_half helpers for ptx 
The removes the vload_half unresolved calls from the nvptx libraries.

Reviewed-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 314998
 2017-10-05 18:17:40 +00:00
Jeroen Ketema
feefb0870f Add vstore_half helpers for ptx 
Reviewed-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 314925
 2017-10-04 19:07:48 +00:00
Jan Vesely
a02d0e2c50 integer/sub_sat: Use clang builtin instead of llvm asm 
reviewer: Tom Stellard

Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 314703
 2017-10-02 18:39:03 +00:00
Jan Vesely
1964df8fad integer/add_sat: Use clang builtin instead of llvm asm 
reviewer: Tom Stellard

Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 314702
 2017-10-02 18:39:00 +00:00
Jan Vesely
943057a288 integer/clz: Use clang builtin instead of llvm asm 
The generated llvm IR mostly identical. char/uchar case is a bit worse.

reviewer: Tom Stellard

Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 314701
 2017-10-02 18:38:57 +00:00
Jeroen Ketema
fe9fa89854 Let get_work_dim take exactly 0 arguments 
Reviewed-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 314634
 2017-10-01 20:11:46 +00:00
Jeroen Ketema
17fdf263c5 Do no circularly define NULL 
Reviewed-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 314633
 2017-10-01 20:10:14 +00:00
Jan Vesely
2b7fa1c6f6 Fix amdgcn-amdhsa on llvm-3.9 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Acked-by: Aaron Watry <awatry@gmail.com>
llvm-svn: 314548
 2017-09-29 19:06:52 +00:00
Jan Vesely
aee030f284 travis: Check built libraries on llvm-3.9 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Acked-by: Aaron Watry <awatry@gmail.com>
llvm-svn: 314547
 2017-09-29 19:06:50 +00:00
Jan Vesely
8c8c287adf Add script to check for unresolved function calls 
v2: add shell shebang
    improve error checks and reporting
v3: fix typo

Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-by: Aaron Watry <awatry@gmail.com>
llvm-svn: 314546
 2017-09-29 19:06:48 +00:00
Jan Vesely
41b1500db0 geometric: geometric functions are only supported for vector lengths <=4 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Reviewed-by: Aaron Watry <awatry@gmail.com>
llvm-svn: 314545
 2017-09-29 19:06:47 +00:00
Jan Vesely
8d08f01eff travis: add build using llvm-3.9 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Acked-by: Aaron Watry <awatry@gmail.com>
llvm-svn: 314544
 2017-09-29 19:06:45 +00:00
Jan Vesely
ce29e8cde1 Restore support for llvm-3.9 
Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
Acked-by: Aaron Watry <awatry@gmail.com>
llvm-svn: 314543
 2017-09-29 19:06:41 +00:00
Jan Vesely
3bb50f6f7b Add missing HAVE_LLVM define to fix build with latest llvm 
Broken since r314111

V2: pointed out by Jan Vesely
   - Use format() instead of % formating

Patch-by: Pavel Ondračka <pavel.ondracka@gmail.com>
Signed-off-by: Pavel Ondračka <pavel.ondracka@gmail.com>
Reviewed-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 314261
 2017-09-26 23:15:54 +00:00
Jan Vesely
1fa727d615 Rework atomic ops to use clang builtins rather than llvm asm 
reviewer: Aaron Watry

Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 314112
 2017-09-25 16:07:34 +00:00
Jan Vesely
760052047b prepare_builtins: Fix compile breakage with older LLVM 
Fixes r314050

reviewer: Tom Stellard

Signed-off-by: Jan Vesely <jan.vesely@rutgers.edu>
llvm-svn: 314111
 2017-09-25 16:04:37 +00:00
Reid Kleckner
3fc649cb76 [Support] Rename tool_output_file to ToolOutputFile, NFC 
This class isn't similar to anything from the STL, so it shouldn't use
the STL naming conventions.

llvm-svn: 314050
 2017-09-23 01:03:17 +00:00