simd_utils_avx_strings.h

/*
 * Project : SIMD_Utils
 * Version : 0.2.6
 * Author  : JishinMaster
 * Licence : BSD-2
 */

#pragma once
#include <fenv.h>
#include <stdint.h>
#ifndef ARM
#include <immintrin.h>
#else
#include "AVX2neon_wrapper.h"
#endif

#include <math.h>
#include <string.h>

#ifdef __AVX2__
size_t strnlen_s_256(const char *s, size_t maxlen) {
    if (s == NULL)
        return 0;

    size_t stop_len = maxlen / (AVX_LEN_BYTES);
    stop_len *= (AVX_LEN_BYTES);

    if (isAligned((uintptr_t) (s), AVX_LEN_BYTES)) {
        for (size_t i = 0; i < stop_len; i += AVX_LEN_BYTES) {
			__m256i chunk = _mm256_load_si256((const __m256i *)(s + i));
			__m256i cmp = _mm256_cmpeq_epi8(chunk, _mm256_setzero_si256());
			size_t mask = _mm256_movemask_epi8(cmp);
			if (mask != 0) {
				size_t offset = __builtin_ctz(mask);
				return i + offset;
			}
        }
    } else {
		 for (size_t i = 0; i < stop_len; i += AVX_LEN_BYTES) {
			__m256i chunk = _mm256_loadu_si256((const __m256i *)(s + i));
			__m256i cmp = _mm256_cmpeq_epi8(chunk, _mm256_setzero_si256());
			size_t mask = _mm256_movemask_epi8(cmp);
			if (mask != 0) {
				size_t offset = __builtin_ctz(mask);
				return i + offset;
			}
        }
    }

	if((maxlen - stop_len) > 16){
		__m128i chunk = _mm_loadu_si128((const __m128i *)(s + stop_len));
		__m128i cmp = _mm_cmpeq_epi8(chunk, _mm_setzero_si128());
		size_t mask = _mm_movemask_epi8(cmp);
		if (mask != 0) {
			size_t offset = __builtin_ctz(mask);
			return stop_len + offset;
		}
		stop_len+=16;
	}

    for (int i = stop_len; i < maxlen; i++) {
		if (s[i] == '\0') {
            return i;
        }
    }

	return maxlen;
}

#endif