BitMagic-C++
Namespaces | Macros | Functions
bmsse4.h File Reference

Compute functions for SSE4.2 SIMD instruction set (internal). More...

#include <mmintrin.h>
#include <emmintrin.h>
#include <smmintrin.h>
#include <nmmintrin.h>
#include <immintrin.h>
#include "bmdef.h"
#include "bmutil.h"
#include "bmsse_util.h"
Include dependency graph for bmsse4.h:

Go to the source code of this file.

Namespaces

namespace  bm

Macros

#define BM_BSF32   bm::bsf_asm32
#define VECT_XOR_ARR_2_MASK(dst, src, src_end, mask)
#define VECT_ANDNOT_ARR_2_MASK(dst, src, src_end, mask)
#define VECT_BITCOUNT(first, last)
#define VECT_BITCOUNT_AND(first, last, mask)
#define VECT_BITCOUNT_OR(first, last, mask)
#define VECT_BITCOUNT_XOR(first, last, mask)
#define VECT_BITCOUNT_SUB(first, last, mask)
#define VECT_INVERT_BLOCK(first)
#define VECT_AND_BLOCK(dst, src)
#define VECT_AND_DIGEST(dst, src)
#define VECT_AND_OR_DIGEST_2WAY(dst, src1, src2)
#define VECT_AND_DIGEST_5WAY(dst, src1, src2, src3, src4)
#define VECT_AND_DIGEST_3WAY(dst, src1, src2)
#define VECT_AND_DIGEST_2WAY(dst, src1, src2)
#define VECT_OR_BLOCK(dst, src)
#define VECT_OR_BLOCK_2WAY(dst, src1, src2)
#define VECT_OR_BLOCK_3WAY(dst, src1, src2)
#define VECT_OR_BLOCK_5WAY(dst, src1, src2, src3, src4)
#define VECT_SUB_BLOCK(dst, src)
#define VECT_SUB_DIGEST(dst, src)
#define VECT_SUB_DIGEST_2WAY(dst, src1, src2)
#define VECT_SUB_DIGEST_5WAY(dst, src1, src2, src3, src4)
#define VECT_SUB_DIGEST_3WAY(dst, src1, src2)
#define VECT_XOR_BLOCK(dst, src)
#define VECT_XOR_BLOCK_2WAY(dst, src1, src2)
#define VECT_COPY_BLOCK(dst, src)
#define VECT_COPY_BLOCK_UNALIGN(dst, src)
#define VECT_STREAM_BLOCK(dst, src)
#define VECT_STREAM_BLOCK_UNALIGN(dst, src)
#define VECT_SET_BLOCK(dst, value)
#define VECT_IS_ZERO_BLOCK(dst)
#define VECT_IS_ONE_BLOCK(dst)
#define VECT_IS_DIGEST_ZERO(start)
#define VECT_BLOCK_SET_DIGEST(dst, val)
#define VECT_LOWER_BOUND_SCAN_U32(arr, target, from, to)
#define VECT_SHIFT_L1(b, acc, co)
#define VECT_SHIFT_R1(b, acc, co)
#define VECT_SHIFT_R1_AND(b, co, m, digest)
#define VECT_ARR_BLOCK_LOOKUP(idx, size, nb, start)
#define VECT_SET_BLOCK_BITS(block, idx, start, stop)
#define VECT_BLOCK_CHANGE(block, size)
#define VECT_BLOCK_XOR_CHANGE(block, xor_block, size, gc, bc)
#define VECT_BLOCK_CHANGE_BC(block, gc, bc)
#define VECT_BIT_FIND_FIRST(src, off, pos)
#define VECT_BIT_FIND_DIFF(src1, src2, pos)
#define VECT_BIT_BLOCK_XOR(t, src, src_xor, d)
#define VECT_BIT_BLOCK_XOR_2WAY(t, src_xor, d)
#define VECT_GAP_BFIND(buf, pos, is_set)
#define VECT_GAP_TEST(buf, pos)

Functions

bm::id_t bm::sse4_bit_count (const __m128i *block, const __m128i *block_end) BMNOEXCEPT
bm::id_t bm::sse42_bit_count_digest (const bm::word_t *BMRESTRICT block, bm::id64_t digest) BMNOEXCEPT
BMFORCEINLINE unsigned bm::op_xor (unsigned a, unsigned b) BMNOEXCEPT
BMFORCEINLINE unsigned bm::op_or (unsigned a, unsigned b) BMNOEXCEPT
BMFORCEINLINE unsigned bm::op_and (unsigned a, unsigned b) BMNOEXCEPT
template<class Func>
bm::id_t bm::sse4_bit_count_op (const __m128i *BMRESTRICT block, const __m128i *BMRESTRICT block_end, const __m128i *BMRESTRICT mask_block, Func sse2_func) BMNOEXCEPT
bool bm::sse4_is_all_zero (const __m128i *BMRESTRICT block) BMNOEXCEPT
 check if block is all zero bits
BMFORCEINLINE bool bm::sse4_is_digest_zero (const __m128i *BMRESTRICT block) BMNOEXCEPT
 check if digest stride is all zero bits
BMFORCEINLINE void bm::sse4_block_set_digest (__m128i *dst, unsigned value) BMNOEXCEPT
 set digest stride to 0xFF.. or 0x0 value
unsigned bm::sse4_and_block (__m128i *BMRESTRICT dst, const __m128i *BMRESTRICT src) BMNOEXCEPT
 AND blocks2 dst &= *src.
BMFORCEINLINE bool bm::sse4_and_digest (__m128i *BMRESTRICT dst, const __m128i *BMRESTRICT src) BMNOEXCEPT
 AND block digest stride dst &= *src.
BMFORCEINLINE bool bm::sse4_and_digest_2way (__m128i *BMRESTRICT dst, const __m128i *BMRESTRICT src1, const __m128i *BMRESTRICT src2) BMNOEXCEPT
 AND block digest stride dst = *src1 & src2.
bool bm::sse4_and_or_digest_2way (__m128i *BMRESTRICT dst, const __m128i *BMRESTRICT src1, const __m128i *BMRESTRICT src2) BMNOEXCEPT
 AND-OR block digest stride dst |= *src1 & src2.
bool bm::sse4_and_digest_3way (__m128i *BMRESTRICT dst, const __m128i *BMRESTRICT src1, const __m128i *BMRESTRICT src2) BMNOEXCEPT
 AND block digest stride.
bool bm::sse4_and_digest_5way (__m128i *BMRESTRICT dst, const __m128i *BMRESTRICT src1, const __m128i *BMRESTRICT src2, const __m128i *BMRESTRICT src3, const __m128i *BMRESTRICT src4) BMNOEXCEPT
 AND block digest stride.
BMFORCEINLINE bool bm::sse4_sub_digest (__m128i *BMRESTRICT dst, const __m128i *BMRESTRICT src) BMNOEXCEPT
 SUB (AND NOT) block digest stride dst &= ~*src.
BMFORCEINLINE bool bm::sse4_sub_digest_2way (__m128i *BMRESTRICT dst, const __m128i *BMRESTRICT src1, const __m128i *BMRESTRICT src2) BMNOEXCEPT
 2-operand SUB (AND NOT) block digest stride dst = src1 & ~*src2
bool bm::sse4_sub_digest_5way (__m128i *BMRESTRICT dst, const __m128i *BMRESTRICT src1, const __m128i *BMRESTRICT src2, const __m128i *BMRESTRICT src3, const __m128i *BMRESTRICT src4) BMNOEXCEPT
 SUB block digest stride.
bool bm::sse4_sub_digest_3way (__m128i *BMRESTRICT dst, const __m128i *BMRESTRICT src1, const __m128i *BMRESTRICT src2) BMNOEXCEPT
 SUB block digest stride.
bool bm::sse4_is_all_one (const __m128i *BMRESTRICT block) BMNOEXCEPT
 check if block is all ONE bits
BMFORCEINLINE bool bm::sse42_test_all_one_wave (const void *ptr) BMNOEXCEPT
 check if SSE wave is all oxFFFF...FFF
BMFORCEINLINE bool bm::sse42_test_all_zero_wave (const void *ptr) BMNOEXCEPT
 check if wave of pointers is all NULL
BMFORCEINLINE bool bm::sse42_test_all_zero_wave2 (const void *ptr0, const void *ptr1) BMNOEXCEPT
 check if 2 waves of pointers are all NULL
BMFORCEINLINE bool bm::sse42_test_all_eq_wave2 (const void *ptr0, const void *ptr1) BMNOEXCEPT
 check if wave of 2 pointers are the same (null or FULL)
unsigned bm::sse42_bit_block_calc_change (const __m128i *BMRESTRICT block, unsigned size) BMNOEXCEPT
void bm::sse42_bit_block_calc_xor_change (const __m128i *BMRESTRICT block, const __m128i *BMRESTRICT xor_block, unsigned size, unsigned *BMRESTRICT gc, unsigned *BMRESTRICT bc) BMNOEXCEPT
void bm::sse42_bit_block_calc_change_bc (const __m128i *BMRESTRICT block, unsigned *gc, unsigned *bc) BMNOEXCEPT
bool bm::sse42_bit_find_first_diff (const __m128i *BMRESTRICT block1, const __m128i *BMRESTRICT block2, unsigned *pos) BMNOEXCEPT
 Find first bit which is different between two bit-blocks.
bool bm::sse42_bit_find_first (const __m128i *BMRESTRICT block, unsigned off, unsigned *pos) BMNOEXCEPT
 Find first non-zero bit.
unsigned bm::sse4_gap_find (const bm::gap_word_t *BMRESTRICT pbuf, const bm::gap_word_t pos, const unsigned size) BMNOEXCEPT
unsigned bm::sse42_gap_bfind (const unsigned short *BMRESTRICT buf, unsigned pos, unsigned *BMRESTRICT is_set) BMNOEXCEPT
 Hybrid binary search, starts as binary, then switches to linear scan.
unsigned bm::sse42_gap_test (const unsigned short *BMRESTRICT buf, unsigned pos) BMNOEXCEPT
 Hybrid binary search to test GAP value, starts as binary, then switches to scan.
int bm::sse42_cmpge_u32 (__m128i vect4, unsigned value) BMNOEXCEPT
 Experimental (test) function to do SIMD vector search (lower bound) in sorted, growing array.
unsigned bm::sse42_idx_arr_block_lookup (const unsigned *idx, unsigned size, unsigned nb, unsigned start) BMNOEXCEPT
void bm::sse42_set_block_bits (bm::word_t *BMRESTRICT block, const unsigned *BMRESTRICT idx, unsigned start, unsigned stop) BMNOEXCEPT
void bm::sse4_bit_block_gather_scatter (unsigned *BMRESTRICT arr, const unsigned *BMRESTRICT blk, const unsigned *BMRESTRICT idx, unsigned size, unsigned start, unsigned bit_idx) BMNOEXCEPT
bool bm::sse42_shift_l1 (__m128i *block, unsigned *empty_acc, unsigned co1) BMNOEXCEPT
 block shift left by 1
bool bm::sse42_shift_r1 (__m128i *block, unsigned *empty_acc, unsigned co1) BMNOEXCEPT
 block shift right by 1
bool bm::sse42_shift_r1_and (__m128i *block, bm::word_t co1, const __m128i *BMRESTRICT mask_block, bm::id64_t *digest) BMNOEXCEPT
 block shift right by 1 plus AND
void bm::sse42_bit_block_xor (bm::word_t *target_block, const bm::word_t *block, const bm::word_t *xor_block, bm::id64_t digest) BMNOEXCEPT
 Build partial XOR product of 2 bit-blocks using digest mask.
void bm::sse42_bit_block_xor_2way (bm::word_t *target_block, const bm::word_t *xor_block, bm::id64_t digest) BMNOEXCEPT
 Build partial XOR product of 2 bit-blocks using digest mask.

Detailed Description

Compute functions for SSE4.2 SIMD instruction set (internal).

Aside from SSE4.2 it also compiles in WASM SIMD mode for 128-bit SIMD portable target.

Definition in file bmsse4.h.

Macro Definition Documentation

◆ BM_BSF32

#define BM_BSF32   bm::bsf_asm32

Definition at line 66 of file bmsse4.h.

Referenced by bm::sse42_bit_find_first(), bm::sse42_bit_find_first_diff(), and bm::sse42_cmpge_u32().

◆ VECT_AND_BLOCK

#define VECT_AND_BLOCK ( dst,
src )
Value:
sse4_and_block((__m128i*) dst, (__m128i*) (src))

Definition at line 2135 of file bmsse4.h.

◆ VECT_AND_DIGEST

#define VECT_AND_DIGEST ( dst,
src )
Value:
sse4_and_digest((__m128i*) dst, (const __m128i*) (src))

Definition at line 2138 of file bmsse4.h.

◆ VECT_AND_DIGEST_2WAY

#define VECT_AND_DIGEST_2WAY ( dst,
src1,
src2 )
Value:
sse4_and_digest_2way((__m128i*) dst, (const __m128i*) (src1), (const __m128i*) (src2))

Definition at line 2150 of file bmsse4.h.

◆ VECT_AND_DIGEST_3WAY

#define VECT_AND_DIGEST_3WAY ( dst,
src1,
src2 )
Value:
sse4_and_digest_3way((__m128i*) dst, (const __m128i*) (src1), (const __m128i*) (src2))

Definition at line 2147 of file bmsse4.h.

◆ VECT_AND_DIGEST_5WAY

#define VECT_AND_DIGEST_5WAY ( dst,
src1,
src2,
src3,
src4 )
Value:
sse4_and_digest_5way((__m128i*) dst, (const __m128i*) (src1), (const __m128i*) (src2), (const __m128i*) (src3), (const __m128i*) (src4))

Definition at line 2144 of file bmsse4.h.

◆ VECT_AND_OR_DIGEST_2WAY

#define VECT_AND_OR_DIGEST_2WAY ( dst,
src1,
src2 )
Value:
sse4_and_or_digest_2way((__m128i*) dst, (const __m128i*) (src1), (const __m128i*) (src2))

Definition at line 2141 of file bmsse4.h.

◆ VECT_ANDNOT_ARR_2_MASK

#define VECT_ANDNOT_ARR_2_MASK ( dst,
src,
src_end,
mask )
Value:
sse2_andnot_arr_2_mask((__m128i*)(dst), (__m128i*)(src), (__m128i*)(src_end), (bm::word_t)mask)
bm::word_t
unsigned int word_t
Definition bmconst.h:39

Definition at line 2109 of file bmsse4.h.

◆ VECT_ARR_BLOCK_LOOKUP

#define VECT_ARR_BLOCK_LOOKUP ( idx,
size,
nb,
start )
Value:
sse42_idx_arr_block_lookup(idx, size, nb, start)

Definition at line 2225 of file bmsse4.h.

◆ VECT_BIT_BLOCK_XOR

#define VECT_BIT_BLOCK_XOR ( t,
src,
src_xor,
d )
Value:
sse42_bit_block_xor(t, src, src_xor, d)

Definition at line 2248 of file bmsse4.h.

◆ VECT_BIT_BLOCK_XOR_2WAY

#define VECT_BIT_BLOCK_XOR_2WAY ( t,
src_xor,
d )
Value:
sse42_bit_block_xor_2way(t, src_xor, d)

Definition at line 2251 of file bmsse4.h.

◆ VECT_BIT_FIND_DIFF

#define VECT_BIT_FIND_DIFF ( src1,
src2,
pos )
Value:
sse42_bit_find_first_diff((__m128i*) src1, (__m128i*) (src2), pos)

Definition at line 2245 of file bmsse4.h.

◆ VECT_BIT_FIND_FIRST

#define VECT_BIT_FIND_FIRST ( src,
off,
pos )
Value:
sse42_bit_find_first((__m128i*) src, off, pos)

Definition at line 2242 of file bmsse4.h.

◆ VECT_BITCOUNT

#define VECT_BITCOUNT ( first,
last )
Value:
sse4_bit_count((__m128i*) (first), (__m128i*) (last))

Definition at line 2112 of file bmsse4.h.

◆ VECT_BITCOUNT_AND

#define VECT_BITCOUNT_AND ( first,
last,
mask )
Value:
sse4_bit_count_op((__m128i*) (first), (__m128i*) (last), (__m128i*) (mask), sse2_and)

Definition at line 2120 of file bmsse4.h.

◆ VECT_BITCOUNT_OR

#define VECT_BITCOUNT_OR ( first,
last,
mask )
Value:
sse4_bit_count_op((__m128i*) (first), (__m128i*) (last), (__m128i*) (mask), sse2_or)

Definition at line 2123 of file bmsse4.h.

◆ VECT_BITCOUNT_SUB

#define VECT_BITCOUNT_SUB ( first,
last,
mask )
Value:
sse4_bit_count_op((__m128i*) (first), (__m128i*) (last), (__m128i*) (mask), sse2_sub)

Definition at line 2129 of file bmsse4.h.

◆ VECT_BITCOUNT_XOR

#define VECT_BITCOUNT_XOR ( first,
last,
mask )
Value:
sse4_bit_count_op((__m128i*) (first), (__m128i*) (last), (__m128i*) (mask), sse2_xor)

Definition at line 2126 of file bmsse4.h.

◆ VECT_BLOCK_CHANGE

#define VECT_BLOCK_CHANGE ( block,
size )
Value:
sse42_bit_block_calc_change((__m128i*)block, size)

Definition at line 2231 of file bmsse4.h.

◆ VECT_BLOCK_CHANGE_BC

#define VECT_BLOCK_CHANGE_BC ( block,
gc,
bc )
Value:
sse42_bit_block_calc_change_bc((__m128i*)block, gc, bc)

Definition at line 2238 of file bmsse4.h.

◆ VECT_BLOCK_SET_DIGEST

#define VECT_BLOCK_SET_DIGEST ( dst,
val )
Value:
sse4_block_set_digest((__m128i*)dst, val)

Definition at line 2210 of file bmsse4.h.

◆ VECT_BLOCK_XOR_CHANGE

#define VECT_BLOCK_XOR_CHANGE ( block,
xor_block,
size,
gc,
bc )
Value:
sse42_bit_block_calc_xor_change((__m128i*)block, (__m128i*)xor_block, size, gc, bc)

Definition at line 2234 of file bmsse4.h.

◆ VECT_COPY_BLOCK

#define VECT_COPY_BLOCK ( dst,
src )
Value:
sse2_copy_block((__m128i*) dst, (__m128i*) (src))

Definition at line 2186 of file bmsse4.h.

◆ VECT_COPY_BLOCK_UNALIGN

#define VECT_COPY_BLOCK_UNALIGN ( dst,
src )
Value:
sse2_copy_block_unalign((__m128i*) dst, (__m128i*) (src))

Definition at line 2189 of file bmsse4.h.

◆ VECT_GAP_BFIND

#define VECT_GAP_BFIND ( buf,
pos,
is_set )
Value:
sse42_gap_bfind(buf, pos, is_set)

Definition at line 2255 of file bmsse4.h.

◆ VECT_GAP_TEST

#define VECT_GAP_TEST ( buf,
pos )
Value:
sse42_gap_test(buf, pos)

Definition at line 2258 of file bmsse4.h.

◆ VECT_INVERT_BLOCK

#define VECT_INVERT_BLOCK ( first)
Value:
sse2_invert_block((__m128i*)first);

Definition at line 2132 of file bmsse4.h.

◆ VECT_IS_DIGEST_ZERO

#define VECT_IS_DIGEST_ZERO ( start)
Value:
sse4_is_digest_zero((__m128i*)start)

Definition at line 2207 of file bmsse4.h.

◆ VECT_IS_ONE_BLOCK

#define VECT_IS_ONE_BLOCK ( dst)
Value:
sse4_is_all_one((__m128i*) dst)

Definition at line 2204 of file bmsse4.h.

◆ VECT_IS_ZERO_BLOCK

#define VECT_IS_ZERO_BLOCK ( dst)
Value:
sse4_is_all_zero((__m128i*) dst)

Definition at line 2201 of file bmsse4.h.

◆ VECT_LOWER_BOUND_SCAN_U32

#define VECT_LOWER_BOUND_SCAN_U32 ( arr,
target,
from,
to )
Value:
sse2_lower_bound_scan_u32(arr, target, from, to)

Definition at line 2213 of file bmsse4.h.

◆ VECT_OR_BLOCK

#define VECT_OR_BLOCK ( dst,
src )
Value:
sse2_or_block((__m128i*) dst, (__m128i*) (src))

Definition at line 2153 of file bmsse4.h.

◆ VECT_OR_BLOCK_2WAY

#define VECT_OR_BLOCK_2WAY ( dst,
src1,
src2 )
Value:
sse2_or_block_2way((__m128i*) (dst), (const __m128i*) (src1), (const __m128i*) (src2))

Definition at line 2156 of file bmsse4.h.

◆ VECT_OR_BLOCK_3WAY

#define VECT_OR_BLOCK_3WAY ( dst,
src1,
src2 )
Value:
sse2_or_block_3way((__m128i*) (dst), (const __m128i*) (src1), (const __m128i*) (src2))

Definition at line 2159 of file bmsse4.h.

◆ VECT_OR_BLOCK_5WAY

#define VECT_OR_BLOCK_5WAY ( dst,
src1,
src2,
src3,
src4 )
Value:
sse2_or_block_5way((__m128i*) (dst), (__m128i*) (src1), (__m128i*) (src2), (__m128i*) (src3), (__m128i*) (src4))

Definition at line 2162 of file bmsse4.h.

◆ VECT_SET_BLOCK

#define VECT_SET_BLOCK ( dst,
value )
Value:
sse2_set_block((__m128i*) dst, value)

Definition at line 2198 of file bmsse4.h.

◆ VECT_SET_BLOCK_BITS

#define VECT_SET_BLOCK_BITS ( block,
idx,
start,
stop )
Value:
sse42_set_block_bits(block, idx, start, stop)

Definition at line 2228 of file bmsse4.h.

◆ VECT_SHIFT_L1

#define VECT_SHIFT_L1 ( b,
acc,
co )
Value:
sse42_shift_l1((__m128i*)b, acc, co)

Definition at line 2216 of file bmsse4.h.

◆ VECT_SHIFT_R1

#define VECT_SHIFT_R1 ( b,
acc,
co )
Value:
sse42_shift_r1((__m128i*)b, acc, co)

Definition at line 2219 of file bmsse4.h.

◆ VECT_SHIFT_R1_AND

#define VECT_SHIFT_R1_AND ( b,
co,
m,
digest )
Value:
sse42_shift_r1_and((__m128i*)b, co, (__m128i*)m, digest)

Definition at line 2222 of file bmsse4.h.

◆ VECT_STREAM_BLOCK

#define VECT_STREAM_BLOCK ( dst,
src )
Value:
sse2_stream_block((__m128i*) dst, (__m128i*) (src))

Definition at line 2192 of file bmsse4.h.

◆ VECT_STREAM_BLOCK_UNALIGN

#define VECT_STREAM_BLOCK_UNALIGN ( dst,
src )
Value:
sse2_stream_block_unalign((__m128i*) dst, (__m128i*) (src))

Definition at line 2195 of file bmsse4.h.

◆ VECT_SUB_BLOCK

#define VECT_SUB_BLOCK ( dst,
src )
Value:
sse2_sub_block((__m128i*) dst, (const __m128i*) (src))

Definition at line 2165 of file bmsse4.h.

◆ VECT_SUB_DIGEST

#define VECT_SUB_DIGEST ( dst,
src )
Value:
sse4_sub_digest((__m128i*) dst, (const __m128i*) (src))

Definition at line 2168 of file bmsse4.h.

◆ VECT_SUB_DIGEST_2WAY

#define VECT_SUB_DIGEST_2WAY ( dst,
src1,
src2 )
Value:
sse4_sub_digest_2way((__m128i*) dst, (const __m128i*) (src1), (const __m128i*) (src2))

Definition at line 2171 of file bmsse4.h.

◆ VECT_SUB_DIGEST_3WAY

#define VECT_SUB_DIGEST_3WAY ( dst,
src1,
src2 )
Value:
sse4_sub_digest_3way((__m128i*) dst, (const __m128i*) (src1), (const __m128i*) (src2))

Definition at line 2177 of file bmsse4.h.

◆ VECT_SUB_DIGEST_5WAY

#define VECT_SUB_DIGEST_5WAY ( dst,
src1,
src2,
src3,
src4 )
Value:
sse4_sub_digest_5way((__m128i*) dst, (const __m128i*) (src1), (const __m128i*) (src2), (const __m128i*) (src3), (const __m128i*) (src4))

Definition at line 2174 of file bmsse4.h.

◆ VECT_XOR_ARR_2_MASK

#define VECT_XOR_ARR_2_MASK ( dst,
src,
src_end,
mask )
Value:
sse2_xor_arr_2_mask((__m128i*)(dst), (__m128i*)(src), (__m128i*)(src_end), (bm::word_t)mask)

Definition at line 2106 of file bmsse4.h.

◆ VECT_XOR_BLOCK

#define VECT_XOR_BLOCK ( dst,
src )
Value:
sse2_xor_block((__m128i*) dst, (__m128i*) (src))

Definition at line 2180 of file bmsse4.h.

◆ VECT_XOR_BLOCK_2WAY

#define VECT_XOR_BLOCK_2WAY ( dst,
src1,
src2 )
Value:
sse2_xor_block_2way((__m128i*) (dst), (const __m128i*) (src1), (const __m128i*) (src2))

Definition at line 2183 of file bmsse4.h.

Generated by doxygen 1.15.0