Home
last modified time | relevance | path

Searched refs:src (Results 1 – 25 of 77) sorted by relevance

1234

/lib/zstd/compress/
Dzstd_lazy.h34 void const* src, size_t srcSize);
37 void const* src, size_t srcSize);
40 void const* src, size_t srcSize);
43 void const* src, size_t srcSize);
46 void const* src, size_t srcSize);
49 void const* src, size_t srcSize);
52 void const* src, size_t srcSize);
56 void const* src, size_t srcSize);
59 void const* src, size_t srcSize);
62 void const* src, size_t srcSize);
[all …]
Dzstd_opt.h22 void const* src, size_t srcSize);
25 void const* src, size_t srcSize);
28 void const* src, size_t srcSize);
33 void const* src, size_t srcSize);
36 void const* src, size_t srcSize);
40 void const* src, size_t srcSize);
43 void const* src, size_t srcSize);
Dzstd_compress_literals.c16 size_t ZSTD_noCompressLiterals (void* dst, size_t dstCapacity, const void* src, size_t srcSize) in ZSTD_noCompressLiterals() argument
38 ZSTD_memcpy(ostart + flSize, src, srcSize); in ZSTD_noCompressLiterals()
43 size_t ZSTD_compressRleLiteralsBlock (void* dst, size_t dstCapacity, const void* src, size_t srcSiz… in ZSTD_compressRleLiteralsBlock() argument
65 ostart[flSize] = *(const BYTE*)src; in ZSTD_compressRleLiteralsBlock()
74 const void* src, size_t srcSize, in ZSTD_compressLiterals() argument
93 return ZSTD_noCompressLiterals(dst, dstCapacity, src, srcSize); in ZSTD_compressLiterals()
98 if (srcSize <= minLitSize) return ZSTD_noCompressLiterals(dst, dstCapacity, src, srcSize); in ZSTD_compressLiterals()
107 ostart+lhSize, dstCapacity-lhSize, src, srcSize, in ZSTD_compressLiterals()
111 ostart+lhSize, dstCapacity-lhSize, src, srcSize, in ZSTD_compressLiterals()
123 return ZSTD_noCompressLiterals(dst, dstCapacity, src, srcSize); in ZSTD_compressLiterals()
[all …]
Dhist.h31 const void* src, size_t srcSize);
47 const void* src, size_t srcSize,
55 const void* src, size_t srcSize);
63 const void* src, size_t srcSize,
75 const void* src, size_t srcSize);
/lib/
Diomap_copy.c23 const u32 *src = from; in __iowrite32_copy() local
24 const u32 *end = src + count; in __iowrite32_copy()
26 while (src < end) in __iowrite32_copy()
27 __raw_writel(*src++, dst++); in __iowrite32_copy()
45 const u32 __iomem *src = from; in __ioread32_copy() local
46 const u32 __iomem *end = src + count; in __ioread32_copy()
48 while (src < end) in __ioread32_copy()
49 *dst++ = __raw_readl(src++); in __ioread32_copy()
68 const u64 *src = from; in __iowrite64_copy() local
69 const u64 *end = src + count; in __iowrite64_copy()
[all …]
Dstrncpy_from_user.c16 #define IS_UNALIGNED(src, dst) 0 argument
18 #define IS_UNALIGNED(src, dst) \ argument
19 (((long) dst | (long) src) & (sizeof(long) - 1))
28 static __always_inline long do_strncpy_from_user(char *dst, const char __user *src, in do_strncpy_from_user() argument
34 if (IS_UNALIGNED(src, dst)) in do_strncpy_from_user()
41 unsafe_get_user(c, (unsigned long __user *)(src+res), byte_at_a_time); in do_strncpy_from_user()
72 unsafe_get_user(c,src+res, efault); in do_strncpy_from_user()
113 long strncpy_from_user(char *dst, const char __user *src, long count) in strncpy_from_user() argument
129 src = masked_user_access_begin(src); in strncpy_from_user()
130 retval = do_strncpy_from_user(dst, src, count, count); in strncpy_from_user()
[all …]
Dstring_helpers.c185 static bool unescape_space(char **src, char **dst) in unescape_space() argument
187 char *p = *dst, *q = *src; in unescape_space()
209 *src += 1; in unescape_space()
213 static bool unescape_octal(char **src, char **dst) in unescape_octal() argument
215 char *p = *dst, *q = *src; in unescape_octal()
222 while (num < 32 && isodigit(*q) && (q - *src < 3)) { in unescape_octal()
228 *src = q; in unescape_octal()
232 static bool unescape_hex(char **src, char **dst) in unescape_hex() argument
234 char *p = *dst, *q = *src; in unescape_hex()
252 *src = q; in unescape_hex()
[all …]
Dstring.c80 char *strcpy(char *dest, const char *src) in strcpy() argument
84 while ((*dest++ = *src++) != '\0') in strcpy()
92 char *strncpy(char *dest, const char *src, size_t count) in strncpy() argument
97 if ((*tmp = *src) != 0) in strncpy()
98 src++; in strncpy()
107 ssize_t sized_strscpy(char *dest, const char *src, size_t count) in sized_strscpy() argument
122 if ((long)src & (sizeof(long) - 1)) { in sized_strscpy()
123 size_t limit = PAGE_SIZE - ((long)src & (PAGE_SIZE - 1)); in sized_strscpy()
129 if (((long) dest | (long) src) & (sizeof(long) - 1)) in sized_strscpy()
147 c = load_unaligned_zeropad(src+res); in sized_strscpy()
[all …]
Diomap.c337 static inline void mmio_outsb(void __iomem *addr, const u8 *src, int count) in mmio_outsb() argument
340 __raw_writeb(*src, addr); in mmio_outsb()
341 src++; in mmio_outsb()
344 static inline void mmio_outsw(void __iomem *addr, const u16 *src, int count) in mmio_outsw() argument
347 __raw_writew(*src, addr); in mmio_outsw()
348 src++; in mmio_outsw()
351 static inline void mmio_outsl(void __iomem *addr, const u32 *src, int count) in mmio_outsl() argument
354 __raw_writel(*src, addr); in mmio_outsl()
355 src++; in mmio_outsl()
382 void iowrite8_rep(void __iomem *addr, const void *src, unsigned long count) in iowrite8_rep() argument
[all …]
Ducs2_string.c52 ssize_t ucs2_strscpy(ucs2_char_t *dst, const ucs2_char_t *src, size_t count) in ucs2_strscpy() argument
70 c = src[res]; in ucs2_strscpy()
107 ucs2_utf8size(const ucs2_char_t *src) in ucs2_utf8size() argument
112 for (i = 0; src[i]; i++) { in ucs2_utf8size()
113 u16 c = src[i]; in ucs2_utf8size()
135 ucs2_as_utf8(u8 *dest, const ucs2_char_t *src, unsigned long maxlength) in ucs2_as_utf8() argument
139 unsigned long limit = ucs2_strnlen(src, maxlength); in ucs2_as_utf8()
142 u16 c = src[i]; in ucs2_as_utf8()
Dbase64.c32 int base64_encode(const u8 *src, int srclen, char *dst) in base64_encode() argument
40 ac = (ac << 8) | src[i]; in base64_encode()
73 int base64_decode(const char *src, int srclen, u8 *dst) in base64_decode() argument
81 const char *p = strchr(base64_table, src[i]); in base64_decode()
83 if (src[i] == '=') { in base64_decode()
90 if (p == NULL || src[i] == 0) in base64_decode()
Dfortify_kunit.c464 char src[sizeof(pad.buf) + 1] = { }; in fortify_test_strcpy() local
468 for (i = 0; i < sizeof(src) - 2; i++) in fortify_test_strcpy()
469 src[i] = i + '0'; in fortify_test_strcpy()
479 KUNIT_ASSERT_TRUE(test, strcpy(pad.buf, src) in fortify_test_strcpy()
488 src[sizeof(src) - 2] = 'A'; in fortify_test_strcpy()
490 KUNIT_ASSERT_TRUE(test, strcpy(pad.buf, src) in fortify_test_strcpy()
501 src[sizeof(src) - 1] = 'A'; in fortify_test_strcpy()
503 KUNIT_ASSERT_TRUE(test, strcpy(pad.buf, src) in fortify_test_strcpy()
522 char src[] = "Copy me fully into a small buffer and I will overflow!"; in fortify_test_strncpy() local
532 KUNIT_ASSERT_TRUE(test, strncpy(pad.buf, src, in fortify_test_strncpy()
[all …]
/lib/lzo/
Dlzodefs.h22 #define COPY4(dst, src) \ argument
23 put_unaligned(get_unaligned((const u32 *)(src)), (u32 *)(dst))
25 #define COPY8(dst, src) \ argument
26 put_unaligned(get_unaligned((const u64 *)(src)), (u64 *)(dst))
28 #define COPY8(dst, src) \ argument
29 COPY4(dst, src); COPY4((dst) + 4, (src) + 4)
/lib/crypto/
Dchacha20poly1305.c57 __chacha20poly1305_encrypt(u8 *dst, const u8 *src, const size_t src_len, in __chacha20poly1305_encrypt() argument
74 chacha20_crypt(chacha_state, dst, src, src_len); in __chacha20poly1305_encrypt()
90 void chacha20poly1305_encrypt(u8 *dst, const u8 *src, const size_t src_len, in chacha20poly1305_encrypt() argument
105 __chacha20poly1305_encrypt(dst, src, src_len, ad, ad_len, chacha_state); in chacha20poly1305_encrypt()
112 void xchacha20poly1305_encrypt(u8 *dst, const u8 *src, const size_t src_len, in xchacha20poly1305_encrypt() argument
120 __chacha20poly1305_encrypt(dst, src, src_len, ad, ad_len, chacha_state); in xchacha20poly1305_encrypt()
125 __chacha20poly1305_decrypt(u8 *dst, const u8 *src, const size_t src_len, in __chacha20poly1305_decrypt() argument
149 poly1305_update(&poly1305_state, src, dst_len); in __chacha20poly1305_decrypt()
159 ret = crypto_memneq(b.mac, src + dst_len, POLY1305_DIGEST_SIZE); in __chacha20poly1305_decrypt()
161 chacha20_crypt(chacha_state, dst, src, dst_len); in __chacha20poly1305_decrypt()
[all …]
Daescfb.c16 const void *src) in aescfb_encrypt_block() argument
29 aes_encrypt(ctx, dst, src); in aescfb_encrypt_block()
42 void aescfb_encrypt(const struct crypto_aes_ctx *ctx, u8 *dst, const u8 *src, in aescfb_encrypt() argument
50 crypto_xor_cpy(dst, src, ks, min(len, AES_BLOCK_SIZE)); in aescfb_encrypt()
54 src += AES_BLOCK_SIZE; in aescfb_encrypt()
71 void aescfb_decrypt(const struct crypto_aes_ctx *ctx, u8 *dst, const u8 *src, in aescfb_decrypt() argument
85 aescfb_encrypt_block(ctx, ks[!i], src); in aescfb_decrypt()
87 crypto_xor_cpy(dst, src, ks[i], min(len, AES_BLOCK_SIZE)); in aescfb_decrypt()
90 src += AES_BLOCK_SIZE; in aescfb_decrypt()
Daesgcm.c17 const void *src) in aesgcm_encrypt_block() argument
30 aes_encrypt(ctx, dst, src); in aesgcm_encrypt_block()
64 static void aesgcm_ghash(be128 *ghash, const be128 *key, const void *src, in aesgcm_ghash() argument
68 crypto_xor((u8 *)ghash, src, min(len, GHASH_BLOCK_SIZE)); in aesgcm_ghash()
71 src += GHASH_BLOCK_SIZE; in aesgcm_ghash()
89 static void aesgcm_mac(const struct aesgcm_ctx *ctx, const u8 *src, int src_len, in aesgcm_mac() argument
97 aesgcm_ghash(&ghash, &ctx->ghash_key, src, src_len); in aesgcm_mac()
108 static void aesgcm_crypt(const struct aesgcm_ctx *ctx, u8 *dst, const u8 *src, in aesgcm_crypt() argument
124 crypto_xor_cpy(dst, src, buf, min(len, AES_BLOCK_SIZE)); in aesgcm_crypt()
127 src += AES_BLOCK_SIZE; in aesgcm_crypt()
[all …]
Dpoly1305.c30 void poly1305_update_generic(struct poly1305_desc_ctx *desc, const u8 *src, in poly1305_update_generic() argument
37 memcpy(desc->buf + desc->buflen, src, bytes); in poly1305_update_generic()
38 src += bytes; in poly1305_update_generic()
50 poly1305_core_blocks(&desc->h, &desc->core_r, src, in poly1305_update_generic()
52 src += nbytes - (nbytes % POLY1305_BLOCK_SIZE); in poly1305_update_generic()
58 memcpy(desc->buf, src, nbytes); in poly1305_update_generic()
/lib/raid6/
DMakefile37 cmd_unroll = $(AWK) -v N=$* -f $(src)/unroll.awk < $< > $@
40 $(obj)/int%.c: $(src)/int.uc $(src)/unroll.awk FORCE
48 $(obj)/altivec%.c: $(src)/altivec.uc $(src)/unroll.awk FORCE
56 $(obj)/vpermxor%.c: $(src)/vpermxor.uc $(src)/unroll.awk FORCE
70 $(obj)/neon%.c: $(src)/neon.uc $(src)/unroll.awk FORCE
74 $(obj)/s390vx%.c: $(src)/s390vx.uc $(src)/unroll.awk FORCE
/lib/zstd/decompress/
Dzstd_decompress.c394 static size_t ZSTD_frameHeaderSize_internal(const void* src, size_t srcSize, ZSTD_format_e format) in ZSTD_frameHeaderSize_internal() argument
399 { BYTE const fhd = ((const BYTE*)src)[minInputSize-1]; in ZSTD_frameHeaderSize_internal()
413 size_t ZSTD_frameHeaderSize(const void* src, size_t srcSize) in ZSTD_frameHeaderSize() argument
415 return ZSTD_frameHeaderSize_internal(src, srcSize, ZSTD_f_zstd1); in ZSTD_frameHeaderSize()
425 size_t ZSTD_getFrameHeader_advanced(ZSTD_frameHeader* zfhPtr, const void* src, size_t srcSize, ZSTD… in ZSTD_getFrameHeader_advanced() argument
427 const BYTE* ip = (const BYTE*)src; in ZSTD_getFrameHeader_advanced()
432 RETURN_ERROR_IF(src==NULL, GENERIC, "invalid parameter"); in ZSTD_getFrameHeader_advanced()
435 && (MEM_readLE32(src) != ZSTD_MAGICNUMBER) ) { in ZSTD_getFrameHeader_advanced()
436 if ((MEM_readLE32(src) & ZSTD_MAGIC_SKIPPABLE_MASK) == ZSTD_MAGIC_SKIPPABLE_START) { in ZSTD_getFrameHeader_advanced()
441 zfhPtr->frameContentSize = MEM_readLE32((const char *)src + ZSTD_FRAMEIDSIZE); in ZSTD_getFrameHeader_advanced()
[all …]
/lib/zstd/common/
Dzstd_internal.h162 static void ZSTD_copy8(void* dst, const void* src) { in ZSTD_copy8() argument
164 vst1_u8((uint8_t*)dst, vld1_u8((const uint8_t*)src)); in ZSTD_copy8()
166 ZSTD_memcpy(dst, src, 8); in ZSTD_copy8()
175 static void ZSTD_copy16(void* dst, const void* src) { in ZSTD_copy16() argument
177 vst1q_u8((uint8_t*)dst, vld1q_u8((const uint8_t*)src)); in ZSTD_copy16()
179 _mm_storeu_si128((__m128i*)dst, _mm_loadu_si128((const __m128i*)src)); in ZSTD_copy16()
181 ZSTD_memmove(dst, src, 16); in ZSTD_copy16()
185 ZSTD_memcpy(copy16_buf, src, 16); in ZSTD_copy16()
208 void ZSTD_wildcopy(void* dst, const void* src, ptrdiff_t length, ZSTD_overlap_e const ovtype) in ZSTD_wildcopy() argument
210 ptrdiff_t diff = (BYTE*)dst - (const BYTE*)src; in ZSTD_wildcopy()
[all …]
Dhuf.h52 const void* src, size_t srcSize);
84 const void* src, size_t srcSize,
93 const void* src, size_t srcSize,
189 size_t HUF_compress4X_usingCTable(void* dst, size_t dstSize, const void* src, size_t srcSize, const…
190 size_t HUF_compress4X_usingCTable_bmi2(void* dst, size_t dstSize, const void* src, size_t srcSize, …
206 const void* src, size_t srcSize,
228 const void* src, size_t srcSize);
239 const void* src, size_t srcSize,
245 size_t HUF_readCTable (HUF_CElt* CTable, unsigned* maxSymbolValuePtr, const void* src, size_t srcSi…
280 size_t HUF_readDTableX1 (HUF_DTable* DTable, const void* src, size_t srcSize);
[all …]
/lib/zstd/
Dzstd_decompress_module.c83 const void *src, size_t src_size) in zstd_decompress_dctx() argument
85 return ZSTD_decompressDCtx(dctx, dst, dst_capacity, src, src_size); in zstd_decompress_dctx()
90 void *dst, size_t dst_capacity, const void* src, size_t src_size, in zstd_decompress_using_ddict() argument
93 return ZSTD_decompress_usingDDict(dctx, dst, dst_capacity, src, in zstd_decompress_using_ddict()
127 size_t zstd_find_frame_compressed_size(const void *src, size_t src_size) in zstd_find_frame_compressed_size() argument
129 return ZSTD_findFrameCompressedSize(src, src_size); in zstd_find_frame_compressed_size()
133 size_t zstd_get_frame_header(zstd_frame_header *header, const void *src, in zstd_get_frame_header() argument
136 return ZSTD_getFrameHeader(header, src, src_size); in zstd_get_frame_header()
/lib/test_fortify/
DMakefile6 cmd_test_fortify = $(CONFIG_SHELL) $(src)/test_fortify.sh \
9 $(obj)/%.log: $(src)/%.c $(src)/test_fortify.sh FORCE
12 logs = $(patsubst $(src)/%.c, %.log, $(wildcard $(src)/*-*.c))
/lib/vdso/
Dgetrandom.c20 #define MEMCPY_AND_ZERO_SRC(type, dst, src, len) do { \ argument
22 __put_unaligned_t(type, __get_unaligned_t(type, src), dst); \
23 __put_unaligned_t(type, 0, src); \
25 src += sizeof(type); \
30 static void memcpy_and_zero_src(void *dst, void *src, size_t len) in memcpy_and_zero_src() argument
34 MEMCPY_AND_ZERO_SRC(u64, dst, src, len); in memcpy_and_zero_src()
35 MEMCPY_AND_ZERO_SRC(u32, dst, src, len); in memcpy_and_zero_src()
36 MEMCPY_AND_ZERO_SRC(u16, dst, src, len); in memcpy_and_zero_src()
38 MEMCPY_AND_ZERO_SRC(u8, dst, src, len); in memcpy_and_zero_src()
/lib/lz4/
Dlz4defs.h150 #define LZ4_memcpy(dst, src, size) __builtin_memcpy(dst, src, size) argument
151 #define LZ4_memmove(dst, src, size) __builtin_memmove(dst, src, size) argument
153 static FORCE_INLINE void LZ4_copy8(void *dst, const void *src) in LZ4_copy8() argument
156 U64 a = get_unaligned((const U64 *)src); in LZ4_copy8()
160 U32 a = get_unaligned((const U32 *)src); in LZ4_copy8()
161 U32 b = get_unaligned((const U32 *)src + 1); in LZ4_copy8()

1234