search for: __s1

...morg-8.0.0 -b llvm8.0 cmake -G "Unix Makefiles" ../llvm-project/llvm -DCMAKE_BUILD_TYPE=Debug -DLLVM_ENABLE_PROJECTS="clang;lld" -DLLVM_TARGETS_TO_BUILD="X86;NVPTX;AMDGPU;ARM;AArch64" [arm.cpp] #define vst4_lane_f16(__p0, __p1, __p2) __extension__ ({ \ float16x4x4_t __s1 = __p1; \ __builtin_neon_vst4_lane_v(__p0, __s1.val[0], __s1.val[1], __s1.val[2], __s1.val[3], __p2, 8); \ }) typedef __fp16 float16_t; typedef __attribute__((neon_vector_type(4))) float16_t float16x4_t; typedef struct float16x4x4_t { float16x4_t val[4]; } float16x4x4_t; void test_vst4_lane_f16...

...d, and we'd be golden. But we don't have a C library - we use whatever is provided by the system we're running on, so that's not really an option. For my testing, I changed libc++'s <cstring> header: -using ::memcpy; +inline _LIBCPP_INLINE_VISIBILITY +void* memcpy(void* __s1, const void* __s2, size_t __n) __attribute__((nonnull(1, 2))) +{ return ::memcpy(__s1, __s2, __n); } (similarly for memmove and memcmp), and I found several cases of simple code that now UBSAN fires off on: such as: std::vector<int> v; v.push_back(1); and : int *p = NULL; std:...

...e-pointer-types]     vst1q_s64( corr_QC + offset + 0, corr_QC_s64x2[ 0 ] );                ^~~~~~~~~~~~~~~~~~~~ /Users/andrewl/android/toolchain-r16b-arm64-v8a/lib64/clang/5.0.300080/include/arm_neon.h:25122:26: note: expanded from macro 'vst1q_s64'   __builtin_neon_vst1q_v(__p0, (int8x16_t)__s1, 35); \                          ^~~~ silk/fixed/arm/warped_autocorrelation_FIX_neon_intr.c:50:16: warning: incompatible pointer types assigning to 'long *' from 'long long *' [-Wincompatible-pointer-types]     vst1q_s64( corr_QC + offset + 2, corr_QC_s64x2[ 1 ] );                ^~...

....c:1775: warning: data definition has no type or storage class client/clitar.c:1775: error: parse error before '}' token client/clitar.c:1775: error: conflicting declarations of `__result' client/clitar.c:1775: error: `__result' previously declared here client/clitar.c:1775: error: `__s1' undeclared here (not in a function) client/clitar.c:1775: error: parse error before "if" client/clitar.c:1775: error: conflicting declarations of `__result' client/clitar.c:1775: error: `__result' previously defined here client/clitar.c:1775: warning: data definition has no t...

New architectures only define the renameat2() system call, which was added in Linux 3.15. Define rename() and renameat() as wrappers for it if necessary. Signed-off-by: Ben Hutchings <ben at decadent.org.uk> --- --- a/usr/klibc/Kbuild +++ b/usr/klibc/Kbuild @@ -59,7 +59,8 @@ klib-y += vsnprintf.o snprintf.o vsprint inet/inet_ntoa.o inet/inet_aton.o inet/inet_addr.o \

...ibc/archsetjmp.h @@ -0,0 +1,26 @@ +/* + * include/arch/loongarch64/klibc/archsetjmp.h + */ + +#ifndef _KLIBC_ARCHSETJMP_H +#define _KLIBC_ARCHSETJMP_H + +struct __jmp_buf { + unsigned long __ra; + unsigned long __sp; + unsigned long __r21; + unsigned long __fp; + unsigned long __s0; + unsigned long __s1; + unsigned long __s2; + unsigned long __s3; + unsigned long __s4; + unsigned long __s5; + unsigned long __s6; + unsigned long __s7; + unsigned long __s8; +}; + +typedef struct __jmp_buf jmp_buf[1]; + +#endif /* _SETJMP_H */ diff --git a/usr/include/arch/loongarch64/klibc/archsignal.h b/usr/incl...

...bc/archsetjmp.h + * include/arch/loongarch64/klibc/archsetjmp.h */ #ifndef _KLIBC_ARCHSETJMP_H #define _KLIBC_ARCHSETJMP_H struct __jmp_buf { - unsigned long __pc; + unsigned long __ra; + unsigned long __sp; + unsigned long __r21; + unsigned long __fp; unsigned long __s0; unsigned long __s1; unsigned long __s2; @@ -16,10 +19,6 @@ struct __jmp_buf { unsigned long __s6; unsigned long __s7; unsigned long __s8; - unsigned long __s9; - unsigned long __s10; - unsigned long __s11; - unsigned long __sp; }; typedef struct __jmp_buf jmp_buf[1]; diff --git a/usr/include/arch/ppc/klib...

...usr/include/arch/riscv64/klibc/archsetjmp.h @@ -1,11 +1,12 @@ /* - * arch/mips64/include/klibc/archsetjmp.h + * arch/riscv64/include/klibc/archsetjmp.h */ #ifndef _KLIBC_ARCHSETJMP_H #define _KLIBC_ARCHSETJMP_H struct __jmp_buf { + unsigned long __pc; unsigned long __s0; unsigned long __s1; unsigned long __s2; @@ -14,12 +15,13 @@ struct __jmp_buf { unsigned long __s5; unsigned long __s6; unsigned long __s7; - unsigned long __gp; - unsigned long __sp; unsigned long __s8; - unsigned long __ra; -} __attribute__ ((aligned(8))); + unsigned long __s9; + unsigned long __s10; + uns...

...jmp.h new file mode 100644 index 0000000..1fbe83e --- /dev/null +++ b/usr/include/arch/mips64/klibc/archsetjmp.h @@ -0,0 +1,39 @@ +/* + * arch/mips/include/klibc/archsetjmp.h + */ + +#ifndef _KLIBC_ARCHSETJMP_H +#define _KLIBC_ARCHSETJMP_H + +struct __jmp_buf { + unsigned long __s0; + unsigned long __s1; + unsigned long __s2; + unsigned long __s3; + unsigned long __s4; + unsigned long __s5; + unsigned long __s6; + unsigned long __s7; + unsigned long __gp; + unsigned long __sp; + unsigned long __s8; + unsigned long __ra; + unsigned long __f20; + unsigned long __f21; + unsigned long __f22; + unsigne...

...jmp.h new file mode 100644 index 0000000..47638b3 --- /dev/null +++ b/usr/include/arch/alpha/klibc/archsetjmp.h @@ -0,0 +1,33 @@ +/* + * arch/alpha/include/klibc/archsetjmp.h + */ + +#ifndef _KLIBC_ARCHSETJMP_H +#define _KLIBC_ARCHSETJMP_H + +struct __jmp_buf { + unsigned long __s0; + unsigned long __s1; + unsigned long __s2; + unsigned long __s3; + unsigned long __s4; + unsigned long __s5; + unsigned long __fp; + unsigned long __ra; + unsigned long __gp; + unsigned long __sp; + + unsigned long __f2; + unsigned long __f3; + unsigned long __f4; + unsigned long __f5; + unsigned long __f6; + unsigned...

...etjmp.h new file mode 100644 index 0000000..1fbe83e --- /dev/null +++ b/usr/include/arch/mips/klibc/archsetjmp.h @@ -0,0 +1,39 @@ +/* + * arch/mips/include/klibc/archsetjmp.h + */ + +#ifndef _KLIBC_ARCHSETJMP_H +#define _KLIBC_ARCHSETJMP_H + +struct __jmp_buf { + unsigned long __s0; + unsigned long __s1; + unsigned long __s2; + unsigned long __s3; + unsigned long __s4; + unsigned long __s5; + unsigned long __s6; + unsigned long __s7; + unsigned long __gp; + unsigned long __sp; + unsigned long __s8; + unsigned long __ra; + unsigned long __f20; + unsigned long __f21; + unsigned long __f22; + unsigne...

I have a new problem: Register RBP is used in a function foo. (I am not allocating RBP to any virtual register, the instances of RBP in function foo are in the machine code when my register allocator starts.) Function foo calls function bar. Register RBP is not saved across the call, though it is live after the call. Function bar includes a virtual register. The code that I'm using to

...trict __dest, __const void *__restrict __src, int __c, size_t __n) __attribute__ ((__nothrow__)) __attribute__ ((__nonnull__ (1, 2))); extern void *memset (void *__s, int __c, size_t __n) __attribute__ ((__nothrow__)) __attribute__ ((__nonnull__ (1))); extern int memcmp (__const void *__s1, __const void *__s2, size_t __n) __attribute__ ((__nothrow__)) __attribute__ ((__pure__)) __attribute__ ((__nonnull__ (1, 2))); extern void *memchr (__const void *__s, int __c, size_t __n) __attribute__ ((__nothrow__)) __attribute__ ((__pure__)) __attribute__ ((__nonnull__ (1))); exter...

I have updated the klibc patchset based on feedback received. In particular, the patchset has been reorganized so as not to break git-bisect. Additionally, this updates the patch base to 2.6.17-git12 (d38b69689c349f35502b92e20dafb30c62d49d63) and klibc 1.4.8; the main difference on the klibc side is removal of obsolete code. This is also available as a git tree at: