[yocto] liblzma: memory allocation failed

[Peter Bergin]

On 2018-09-24 00:06, Andrea Adami wrote:
> On Fri, Sep 21, 2018 at 1:04 AM Andrea Adami <andrea.adami at gmail.com> wrote:
>> On Thu, Sep 20, 2018 at 1:03 PM Peter Bergin <peter at berginkonsult.se> wrote:
>>> On 2018-09-17 10:27, Burton, Ross wrote:
>>>
>>> On Mon, 17 Sep 2018 at 08:13, Peter Bergin <peter at berginkonsult.se> wrote:
>>>
>>> I'm pretty sure I have narrowed down the root cause to the restriction
>>> of virtual memory and that liblzma base its memory calculations on
>>> physical RAM.
>>>
>>> To prove this I added a printout in rpm-native/rpmio/rpmio.c and the
>>> function lzopen_internal.
>>>
>>>           uint64_t memory_usage = lzma_stream_encoder_mt_memusage(&mt_options);
>>>          rpmlog(RPMLOG_NOTICE, "DBG: memory_usage %lu\n", memory_usage);
>>>
>>>
>>> The value of memory_usage is the same regardless of which 'ulimit -v'
>>> value I set. On the host with 256GB of physical RAM and 32GB of virtual
>>> memory, memory_usage is ~5.1GB. On another host with 16GB of physical
>>> RAM I get memory_usage of ~660MB.
>>>
>>> I guess you have not seen this kind of failure if you not have
>>> restricted virutal memory on your host. If you want to try to reproduce
>>> this set 'ulimit -v 8388608' (8GB) in your shell and then 'bitbake
>>> glibc-locale -c package_write_rpm -f'.
>>>
>>> Wouldn't a solution be to change lzma to look at free memory, not
>>> total physical memory?
>>>
>>> Ross
>>>
>>> I have been in contact with the maintainer of liblzma. There is currently no way to restrict the memory usage in liblzma during multi threaded compression. He recommended to adjust the number of threads used during compression. This kind of check is done for 32-bits but not when running 64-bits (in rpmio/rpmio.c lzopen_internal). To rewrite liblzma is another option but I took an easier way out.
>>>
>>> I have come up with a patch (https://patchwork.openembedded.org/patch/155017/) that solves my problem and do a restriction of memory usage when the 'ulimit -v' is set. The calculation is based on the assumption that lzopen_internal is run in parallel with as many instances as cpu threads as '#pragma omp parallel' is used in build/pack.c.
>>>
>>> When running test on my machine with 4 cores 16GB of physical RAM and 'ulimit -v 2097152' (2GB). It works good and the log shows:
>>>
>>> XZ: virtual memory restricted to 2147483648 and per CPU thread 536870912
>>> XZ: Adjusted the number of threads from 4 to 3 to not exceed the memory usage limit of 2147483648 bytes
>>>
>>> Didn't get a clear answer if this is something Yocto/OE should support but I hope my patch solves the issue and it will not affect the normal environments where 'ulimit -v' is not set.
>>>
>>> /Peter
>>> --
>> Peter,
>> first of all sorry for butting-in again. My bad I misunderstood the point,
>>
>> Looking properly at it, I see the sources do restrict only #if __WORDSIZE == 32.
>>
>> Again, there is the other way to reduce total memory footprint just
>> using lower preset in mt_options.
>> As far as I see default is  #define LZMA_PRESET_DEFAULT     UINT32_C(6)
>> so you could tr to modify   mt_options.preset to your needs.
>> I think more threads is normally  better.
>>
>> Cheers
>> Andrea
>>
>>> _______________________________________________
>>> yocto mailing list
>>> yocto at yoctoproject.org
>>> https://lists.yoctoproject.org/listinfo/yocto
>
> Well,
> call it luck, I now get similar problems with
> -  opkg-utils: use multithreaded xz when building packages
>     369c43cca4f0
>
> I build in tmpfs (8GB) and have 8 cores.
> Strange enough, it does happen with only one machine of our bsp (akita).
>
> Build Configuration:
> BB_VERSION           = "1.39.1"
> BUILD_SYS            = "x86_64-linux"
> NATIVELSBSTRING      = "ubuntu-16.04"
> TARGET_SYS           = "arm-oe-linux-gnueabi"
> MACHINE              = "akita"
> DISTRO               = "nodistro"
> DISTRO_VERSION       = "nodistro.0"
> TUNE_FEATURES        = "arm armv5 thumb dsp"
> TARGET_FPU           = "soft"
> meta                 = "master:8cc08e44cf3e969c124456d459c6c06a76cad018"
> meta-handheld        = "master:61e16e253ea870b87592075efd87727e8b5c574d"
> meta-initramfs
> meta-oe              = "master:7ac8d82fec470a8c8e66cfc4216381e2364cb4b2"
>
> ...
> Installing kernel-module-nls-cp1251-4.14.62-handheld (4.14) on root
> Downloading file:/tmp/build/tmp-glibc/work/akita-oe-linux-gnueabi/core-image-base/1.0-r0/oe-rootfs-repo/akita/kernel-module-nls-cp1251-4.14.62-handheld_4.14-r0_akita.ipk.
> Installing kernel-mo
> ERROR: core-image-base-1.0-r0 do_rootfs: Function failed: do_rootfs
> ERROR: Logfile of failure stored in:
> /tmp/build/tmp-glibc/work/akita-oe-linux-gnueabi/core-image-base/1.0-r0/temp/log.do_rootfs.28481
> ERROR: Task (/oe/oe-core/meta/recipes-core/images/core-image-base.bb:do_rootfs)
> failed with exit code '1'
> ...
>
> and in dmesg you see opkg segfaulting and OOM kicking in.
> It is the same issue...unnoticed building for other similar devices
> (spitz). Maybe it did not happen using musl as TC_LIBC.
>
> Reverting the patch fixes that.
> Ross, worth opening a bug?
>
> Cheers
> Andrea
Andrea,

do you have any virtual memory restrictions (ulimit -v) or overcommit 
settings (vm.overcommit_memory)  on your build host?

Regarding my problem with rpm and liblzma when virtual memory is 
restricted I have supplied a patch to oe-core 
https://patchwork.openembedded.org/patch/155017/ with a suggested solution.

Regards,
/Peter