Home
last modified time | relevance | path

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

12345

/lib/
A Diomem_copy.c65 *(u8 *)dst = __raw_readb(src); in memcpy_fromio()
66 src++; in memcpy_fromio()
73 long val = __raw_readq(src); in memcpy_fromio()
75 long val = __raw_readl(src); in memcpy_fromio()
80 src += sizeof(long); in memcpy_fromio()
86 *(u8 *)dst = __raw_readb(src); in memcpy_fromio()
87 src++; in memcpy_fromio()
107 __raw_writeb(*(u8 *)src, dst); in memcpy_toio()
108 src++; in memcpy_toio()
121 src += sizeof(long); in memcpy_toio()
[all …]
A 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
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()
71 while (src < end) in __iowrite64_copy()
[all …]
A 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))
34 if (IS_UNALIGNED(src, dst)) 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()
136 src_addr = (unsigned long)untagged_addr(src); in strncpy_from_user()
148 if (user_read_access_begin(src, max)) { in strncpy_from_user()
[all …]
A Dstring_helpers.c190 char *p = *dst, *q = *src; in unescape_space()
212 *src += 1; in unescape_space()
231 *src = q; in unescape_octal()
255 *src = q; in unescape_hex()
280 *src += 1; in unescape_special()
330 while (*src && --size) { in string_unescape()
331 if (src[0] == '\\' && src[1] != '\0' && size > 1) { in string_unescape()
332 src++; in string_unescape()
353 *out++ = *src++; in string_unescape()
658 if (!src) in kstrdup_quotable()
[all …]
A Dstring.c84 while ((*dest++ = *src++) != '\0') in strcpy()
97 if ((*tmp = *src) != 0) in strncpy()
98 src++; in strncpy()
155 c = read_word_at_a_time(src+res); in sized_strscpy()
177 c = src[res]; in sized_strscpy()
189 return src[res] ? -E2BIG : res; in sized_strscpy()
255 size_t len = strlen(src); in strlcat()
624 const char *s = src; in memcpy()
647 if (dest <= src) { in memmove()
649 s = src; in memmove()
[all …]
A Diomap.c340 __raw_writeb(*src, addr); in mmio_outsb()
341 src++; in mmio_outsb()
347 __raw_writew(*src, addr); in mmio_outsw()
348 src++; in mmio_outsw()
354 __raw_writel(*src, addr); in mmio_outsl()
355 src++; in mmio_outsl()
385 kmsan_check_memory(src, count); in iowrite8_rep()
386 IO_COND(addr, outsb(port, src, count), mmio_outsb(addr, src, count)); in iowrite8_rep()
391 kmsan_check_memory(src, count * 2); in iowrite16_rep()
392 IO_COND(addr, outsw(port, src, count), mmio_outsw(addr, src, count)); in iowrite16_rep()
[all …]
A 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()
A 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()
/lib/crypto/x86/
A Dchacha_glue.c16 u8 *dst, const u8 *src,
19 u8 *dst, const u8 *src,
25 u8 *dst, const u8 *src,
28 u8 *dst, const u8 *src,
31 u8 *dst, const u8 *src,
35 u8 *dst, const u8 *src,
38 u8 *dst, const u8 *src,
41 u8 *dst, const u8 *src,
62 src += CHACHA_BLOCK_SIZE * 8; in chacha_dosimd()
114 src += CHACHA_BLOCK_SIZE * 4; in chacha_dosimd()
[all …]
/lib/zstd/compress/
A Dzstd_lazy.h42 void const* src, size_t srcSize);
45 void const* src, size_t srcSize);
48 void const* src, size_t srcSize);
51 void const* src, size_t srcSize);
54 void const* src, size_t srcSize);
57 void const* src, size_t srcSize);
60 void const* src, size_t srcSize);
63 void const* src, size_t srcSize);
87 void const* src, size_t srcSize);
90 void const* src, size_t srcSize);
[all …]
A Dzstd_compress_literals.c23 static size_t showHexa(const void* src, size_t srcSize) in showHexa() argument
25 const BYTE* const ip = (const BYTE*)src; in showHexa()
64 ZSTD_memcpy(ostart + flSize, src, srcSize); in ZSTD_noCompressLiterals()
69 static int allBytesIdentical(const void* src, size_t srcSize) in allBytesIdentical() argument
72 assert(src != NULL); in allBytesIdentical()
73 { const BYTE b = ((const BYTE*)src)[0]; in allBytesIdentical()
76 if (((const BYTE*)src)[p] != b) return 0; in allBytesIdentical()
88 assert(allBytesIdentical(src, srcSize)); in ZSTD_compressRleLiteralsBlock()
105 ostart[flSize] = *(const BYTE*)src; in ZSTD_compressRleLiteralsBlock()
132 const void* src, size_t srcSize, in ZSTD_compressLiterals() argument
[all …]
A Dhist.h32 const void* src, size_t srcSize);
48 const void* src, size_t srcSize,
56 const void* src, size_t srcSize);
64 const void* src, size_t srcSize,
76 const void* src, size_t srcSize);
83 void HIST_add(unsigned* count, const void* src, size_t srcSize);
A Dzstd_opt.h27 void const* src, size_t srcSize);
30 void const* src, size_t srcSize);
33 void const* src, size_t srcSize);
47 void const* src, size_t srcSize);
50 void const* src, size_t srcSize);
53 void const* src, size_t srcSize);
60 void const* src, size_t srcSize);
/lib/crypto/arm/
A Dchacha-glue.c21 u8 *dst, const u8 *src, int nrounds);
23 u8 *dst, const u8 *src,
30 asmlinkage void chacha_doarm(u8 *dst, const u8 *src, unsigned int bytes,
48 chacha_4block_xor_neon(state, dst, src, nrounds, l); in chacha_doneon()
50 src += l; in chacha_doneon()
55 const u8 *s = src; in chacha_doneon()
59 s = d = memcpy(buf, src, bytes); in chacha_doneon()
80 void chacha_crypt_arch(struct chacha_state *state, u8 *dst, const u8 *src, in chacha_crypt_arch() argument
85 chacha_doarm(dst, src, bytes, state, nrounds); in chacha_crypt_arch()
94 chacha_doneon(state, dst, src, todo, nrounds); in chacha_crypt_arch()
[all …]
A Dpoly1305-glue.c23 const u8 *src, u32 len, u32 hibit);
25 const u8 *src, u32 len, u32 hibit);
33 void poly1305_blocks_arch(struct poly1305_block_state *state, const u8 *src, in poly1305_blocks_arch() argument
43 poly1305_blocks_neon(state, src, todo, padbit); in poly1305_blocks_arch()
47 src += todo; in poly1305_blocks_arch()
50 poly1305_blocks_arm(state, src, len, padbit); in poly1305_blocks_arch()
/lib/zstd/common/
A Dzstd_internal.h164 static void ZSTD_copy8(void* dst, const void* src) { in ZSTD_copy8() argument
166 vst1_u8((uint8_t*)dst, vld1_u8((const uint8_t*)src)); in ZSTD_copy8()
168 ZSTD_memcpy(dst, src, 8); in ZSTD_copy8()
177 static void ZSTD_copy16(void* dst, const void* src) { in ZSTD_copy16() argument
179 vst1q_u8((uint8_t*)dst, vld1q_u8((const uint8_t*)src)); in ZSTD_copy16()
183 ZSTD_memmove(dst, src, 16); in ZSTD_copy16()
187 ZSTD_memcpy(copy16_buf, src, 16); in ZSTD_copy16()
212 ptrdiff_t diff = (BYTE*)dst - (const BYTE*)src; in ZSTD_wildcopy()
213 const BYTE* ip = (const BYTE*)src; in ZSTD_wildcopy()
246 ZSTD_memcpy(dst, src, length); in ZSTD_limitCopy()
[all …]
/lib/crypto/arm64/
A Dchacha-neon-glue.c32 u8 *dst, const u8 *src, int nrounds);
34 u8 *dst, const u8 *src,
41 static void chacha_doneon(struct chacha_state *state, u8 *dst, const u8 *src, in chacha_doneon() argument
50 memcpy(buf, src, l); in chacha_doneon()
56 chacha_4block_xor_neon(state, dst, src, nrounds, l); in chacha_doneon()
58 src += l; in chacha_doneon()
77 void chacha_crypt_arch(struct chacha_state *state, u8 *dst, const u8 *src, in chacha_crypt_arch() argument
82 return chacha_crypt_generic(state, dst, src, bytes, nrounds); in chacha_crypt_arch()
88 chacha_doneon(state, dst, src, todo, nrounds); in chacha_crypt_arch()
92 src += todo; in chacha_crypt_arch()
A Dpoly1305-glue.c23 const u8 *src, u32 len, u32 hibit);
25 const u8 *src, u32 len, u32 hibit);
33 void poly1305_blocks_arch(struct poly1305_block_state *state, const u8 *src, in poly1305_blocks_arch() argument
42 poly1305_blocks_neon(state, src, todo, padbit); in poly1305_blocks_arch()
46 src += todo; in poly1305_blocks_arch()
49 poly1305_blocks(state, src, len, padbit); in poly1305_blocks_arch()
/lib/crypto/powerpc/
A Dchacha-p10-glue.c18 const u8 *src, unsigned int len, int nrounds);
34 static void chacha_p10_do_8x(struct chacha_state *state, u8 *dst, const u8 *src, in chacha_p10_do_8x() argument
40 chacha_p10le_8x(state, dst, src, l, nrounds); in chacha_p10_do_8x()
42 src += l; in chacha_p10_do_8x()
48 chacha_crypt_generic(state, dst, src, bytes, nrounds); in chacha_p10_do_8x()
58 void chacha_crypt_arch(struct chacha_state *state, u8 *dst, const u8 *src, in chacha_crypt_arch() argument
63 return chacha_crypt_generic(state, dst, src, bytes, nrounds); in chacha_crypt_arch()
69 chacha_p10_do_8x(state, dst, src, todo, nrounds); in chacha_crypt_arch()
73 src += todo; in chacha_crypt_arch()
/lib/lzo/
A 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/
A Dchacha20poly1305.c73 chacha20_crypt(chacha_state, dst, src, src_len); in __chacha20poly1305_encrypt()
104 __chacha20poly1305_encrypt(dst, src, src_len, ad, ad_len, in chacha20poly1305_encrypt()
120 __chacha20poly1305_encrypt(dst, src, src_len, ad, ad_len, in xchacha20poly1305_encrypt()
151 poly1305_update(&poly1305_state, src, dst_len); in __chacha20poly1305_decrypt()
161 ret = crypto_memneq(b.mac, src + dst_len, POLY1305_DIGEST_SIZE); in __chacha20poly1305_decrypt()
163 chacha20_crypt(chacha_state, dst, src, dst_len); in __chacha20poly1305_decrypt()
186 ret = __chacha20poly1305_decrypt(dst, src, src_len, ad, ad_len, in chacha20poly1305_decrypt()
210 bool chacha20poly1305_crypt_sg_inplace(struct scatterlist *src, in chacha20poly1305_crypt_sg_inplace() argument
258 sg_miter_start(&miter, src, sg_nents(src), flags); in chacha20poly1305_crypt_sg_inplace()
323 sg_copy_buffer(src, sg_nents(src), b.mac[encrypt], in chacha20poly1305_crypt_sg_inplace()
[all …]
A Daescfb.c15 const void *src) in aescfb_encrypt_block() argument
28 aes_encrypt(ctx, dst, src); in aescfb_encrypt_block()
41 void aescfb_encrypt(const struct crypto_aes_ctx *ctx, u8 *dst, const u8 *src, in aescfb_encrypt() argument
49 crypto_xor_cpy(dst, src, ks, min(len, AES_BLOCK_SIZE)); in aescfb_encrypt()
53 src += AES_BLOCK_SIZE; in aescfb_encrypt()
70 void aescfb_decrypt(const struct crypto_aes_ctx *ctx, u8 *dst, const u8 *src, in aescfb_decrypt() argument
84 aescfb_encrypt_block(ctx, ks[!i], src); in aescfb_decrypt()
86 crypto_xor_cpy(dst, src, ks[i], min(len, AES_BLOCK_SIZE)); in aescfb_decrypt()
89 src += AES_BLOCK_SIZE; in aescfb_decrypt()
/lib/zstd/decompress/
A Dzstd_decompress.c633 src = (const BYTE *)src + skippableSize; in ZSTD_findDecompressedSize()
650 src = (const BYTE *)src + frameSrcSize; in ZSTD_findDecompressedSize()
805 src = (const BYTE*)src + compressedSize; in ZSTD_decompressBound()
845 src = (const BYTE*)src + compressedSize; in ZSTD_decompressionMargin()
1055 src = (const BYTE *)src + skippableSize; in ZSTD_decompressMultiFrame()
1213 assert(src != NULL); in ZSTD_decompressContinue()
1230 assert(src != NULL); in ZSTD_decompressContinue()
2011 const char* const src = (const char*)input->src; in ZSTD_decompressStream() local
2012 const char* const istart = input->pos != 0 ? src + input->pos : src; in ZSTD_decompressStream()
2013 const char* const iend = input->size != 0 ? src + input->size : src; in ZSTD_decompressStream()
[all …]
/lib/raid6/
A DMakefile38 cmd_unroll = $(AWK) -v N=$* -f $(src)/unroll.awk < $< > $@
41 $(obj)/int%.c: $(src)/int.uc $(src)/unroll.awk FORCE
49 $(obj)/altivec%.c: $(src)/altivec.uc $(src)/unroll.awk FORCE
57 $(obj)/vpermxor%.c: $(src)/vpermxor.uc $(src)/unroll.awk FORCE
71 $(obj)/neon%.c: $(src)/neon.uc $(src)/unroll.awk FORCE
75 $(obj)/s390vx%.c: $(src)/s390vx.uc $(src)/unroll.awk FORCE
/lib/zstd/
A 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()

Completed in 46 milliseconds

12345