/*
* The ManaPlus Client
* Copyright (C) 2011-2016 The ManaPlus Developers
*
* This file is part of The ManaPlus Client.
*
* This program is free software; you can redistribute it and/or modify
* it under the terms of the GNU General Public License as published by
* the Free Software Foundation; either version 2 of the License, or
* any later version.
*
* This program is distributed in the hope that it will be useful,
* but WITHOUT ANY WARRANTY; without even the implied warranty of
* MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the
* GNU General Public License for more details.
*
* You should have received a copy of the GNU General Public License
* along with this program. If not, see .
*/
#include "resources/dye/dyepalette.h"
#include "logger.h"
#ifndef SDL_BIG_ENDIAN
#include
#endif // SDL_BYTEORDER
#ifdef __x86_64__
// avx2
#include "immintrin.h"
#if SDL_BYTEORDER == SDL_BIG_ENDIAN
#define buildHex(a, b, c, d) \
(d) * 16777216U + (c) * 65536U + (b) * 256U + CAST_U32(a)
#else // SDL_BYTEORDER == SDL_BIG_ENDIAN
#define buildHex(a, b, c, d) \
(a) * 16777216U + (b) * 65536U + (c) * 256U + CAST_U32(d)
#endif // SDL_BYTEORDER == SDL_BIG_ENDIAN
#endif // __x86_64__
#include "debug.h"
void DyePalette::replaceSOGLColor(uint32_t *restrict pixels,
const int bufSize) const restrict2
{
#ifdef SIMD_SUPPORTED
if (bufSize >= 8)
replaceSOGLColorSimd(pixels, bufSize);
else
replaceSOGLColorDefault(pixels, bufSize);
#else // SIMD_SUPPORTED
replaceSOGLColorDefault(pixels, bufSize);
#endif // SIMD_SUPPORTED
}
void DyePalette::replaceSOGLColorDefault(uint32_t *restrict pixels,
const int bufSize) const restrict2
{
std::vector::const_iterator it_end = mColors.end();
const size_t sz = mColors.size();
if (!sz || !pixels)
return;
if (sz % 2)
-- it_end;
#ifdef ENABLE_CILKPLUS
cilk_for (int ptr = 0; ptr < bufSize; ptr ++)
{
uint8_t *const p = reinterpret_cast(&pixels[ptr]);
#if SDL_BYTEORDER == SDL_BIG_ENDIAN
const unsigned int data = (pixels[ptr]) & 0xffffff00;
#else // SDL_BYTEORDER == SDL_BIG_ENDIAN
const unsigned int data = (pixels[ptr]) & 0x00ffffff;
#endif // SDL_BYTEORDER == SDL_BIG_ENDIAN
std::vector::const_iterator it = mColors.begin();
while (it != it_end)
{
const DyeColor &col = *it;
++ it;
const DyeColor &col2 = *it;
#if SDL_BYTEORDER == SDL_BIG_ENDIAN
const unsigned int coldata = (col.value[0] << 24)
| (col.value[1] << 16) | (col.value[2] << 8);
#else // SDL_BYTEORDER == SDL_BIG_ENDIAN
const unsigned int coldata = (col.value[0])
| (col.value[1] << 8) | (col.value[2] << 16);
#endif // SDL_BYTEORDER == SDL_BIG_ENDIAN
if (data == coldata)
{
p[0] = col2.value[0];
p[1] = col2.value[1];
p[2] = col2.value[2];
break;
}
++ it;
}
}
#else // ENABLE_CILKPLUS
for (const uint32_t *const p_end = pixels + CAST_SIZE(bufSize);
pixels != p_end;
++pixels)
{
uint8_t *const p = reinterpret_cast(pixels);
#if SDL_BYTEORDER == SDL_BIG_ENDIAN
const unsigned int data = (*pixels) & 0xffffff00;
#else // SDL_BYTEORDER == SDL_BIG_ENDIAN
const unsigned int data = (*pixels) & 0x00ffffff;
#endif // SDL_BYTEORDER == SDL_BIG_ENDIAN
std::vector::const_iterator it = mColors.begin();
while (it != it_end)
{
const DyeColor &col = *it;
++ it;
const DyeColor &col2 = *it;
#if SDL_BYTEORDER == SDL_BIG_ENDIAN
const unsigned int coldata = (col.value[0] << 24)
| (col.value[1] << 16) | (col.value[2] << 8);
#else // SDL_BYTEORDER == SDL_BIG_ENDIAN
const unsigned int coldata = (col.value[0])
| (col.value[1] << 8) | (col.value[2] << 16);
#endif // SDL_BYTEORDER == SDL_BIG_ENDIAN
if (data == coldata)
{
p[0] = col2.value[0];
p[1] = col2.value[1];
p[2] = col2.value[2];
break;
}
++ it;
}
}
#endif // ENABLE_CILKPLUS
}
#ifdef SIMD_SUPPORTED
static void print256(const char *const text, const __m256i &val);
static void print256(const char *const text, const __m256i &val)
{
printf("%s 0x%016llx%016llx%016llx%016llx\n", text, val[0], val[1], val[2], val[3]);
}
__attribute__ ((target ("avx2")))
void DyePalette::replaceSOGLColorSimd(uint32_t *restrict pixels,
const int bufSize) const restrict2
{
std::vector::const_iterator it_end = mColors.end();
const size_t sz = mColors.size();
if (!sz || !pixels)
return;
if (sz % 2)
-- it_end;
for (const uint32_t *const p_end = pixels + CAST_SIZE(bufSize);
pixels != p_end;
pixels += 8)
{
__m256i mask = _mm256_set1_epi32(0x00ffffff);
//__m256i base = _mm256_load_si256(reinterpret_cast<__m256i*>(pixels));
__m256i base = _mm256_loadu_si256(reinterpret_cast<__m256i*>(pixels));
//print256("mask ", mask);
std::vector::const_iterator it = mColors.begin();
while (it != it_end)
{
//print256("base ", base);
const DyeColor &col = *it;
++ it;
const DyeColor &col2 = *it;
__m256i base2 = _mm256_and_si256(mask, base);
//print256("base2 ", base2);
__m256i newMask = _mm256_set1_epi32(buildHex(0, col2.value[2], col2.value[1], col2.value[0]));
//print256("newMask ", newMask);
__m256i cmpMask = _mm256_set1_epi32(buildHex(0, col.value[2], col.value[1], col.value[0]));
//print256("cmpMask ", cmpMask);
__m256i cmpRes = _mm256_cmpeq_epi32(base2, cmpMask);
//print256("cmpRes ", cmpRes);
cmpRes = _mm256_and_si256(mask, cmpRes);
//print256("cmpRes ", cmpRes);
__m256i srcAnd = _mm256_andnot_si256(cmpRes, base);
//print256("srcAnd ", srcAnd);
__m256i dstAnd = _mm256_and_si256(cmpRes, newMask);
//print256("dstAnd ", dstAnd);
base = _mm256_or_si256(srcAnd, dstAnd);
++ it;
}
//print256("res ", base);
//_mm256_store_si256(reinterpret_cast<__m256i*>(pixels), base);
_mm256_storeu_si256(reinterpret_cast<__m256i*>(pixels), base);
}
}
#endif // SIMD_SUPPORTED
FUNCTION_SIMD_DEFAULT
void DyePalette::replaceSOGLColorSimd(uint32_t *restrict pixels,
const int bufSize) const restrict2
{
replaceSOGLColorDefault(pixels, bufSize);
}